intel/compute-runtime
1
0
Fork 0
mirror of https://github.com/intel/compute-runtime.git synced 2026-01-10 15:12:56 +08:00
Code Issues Packages Projects Releases Wiki Activity
3,640 Commits 43 Branches 656 Tags
9f5152e8237bc19b4ad140636c87f3ff64b4d6a5
Commit Graph

3640 Commits

This Branch
This Branch
All Branches
Author SHA1 Message Date
Mateusz Jablonski
9f5152e823 Move linux files to core 
memory_info
engine_info
os_inc

Related-To: NEO-3982
Change-Id: I52ef357f790497fc6efcd590db277ce96ec1e579
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2019-12-13 09:23:33 +01:00
Dunajski, Bartosz
9a1133615e Pass VA while constructing BlitProperties instead of allocation + offset 
Change-Id: Id6f88ff5252cab650ecf103e1e465bf454e6ba4c
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2019-12-12 13:14:46 +01:00
Jacek Danecki
fb8df1a328 fix compilation with clang 9 
ci: add build with clang on Arch

Signed-off-by: Jacek Danecki <jacek.danecki@intel.com>

https://github.com/intel/compute-runtime/pull/241

Change-Id: I1a8620c9f8146e7108098d18e9db75b9ff178f44
 2019-12-12 11:45:08 +01:00
Mateusz Jablonski
c7755c2c48 Move files to core 
engine_node_helper
kmdaf_listener
wddm_engine_mapper
windows_defs

Related-To: NEO-3982
Change-Id: Ia39342059bdeafa97d17f286c167138e5c40553c
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2019-12-11 17:39:14 +01:00
Mateusz Jablonski
495f0e8530 Remove not needed header inclusions 
use full path when include header

Change-Id: I0cae6300b86173aea0f4267282e68aa5107fc1e2
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2019-12-11 16:44:12 +01:00
Mateusz Jablonski
ab2134ae8f Change subDeviceIndex to subDevicesBitfield in allocation properties 
Related-To: NEO-3691
Change-Id: I11d235107bf9b4cee75b910c114795b5df76d9c7
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2019-12-11 15:15:04 +01:00
Dunajski, Bartosz
ecc54edbb3 Improve pointers passing in SVM enqueue 
Change-Id: Idf46438e8bd17476c3b3997ac35821d24ce0a081
 2019-12-11 14:38:42 +01:00
Katarzyna Cencelewska
9aa563ba2b Use MockKernelWithInternals with base initalization 
to test set of default thread arbitration policy

Change-Id: Ife60debf9dd319d5809855e983a71d7c4d128ae2
Signed-off-by: Katarzyna Cencelewska <katarzyna.cencelewska@intel.com>
 2019-12-11 12:38:18 +01:00
Cencelewska
230d808021 Add mechanism to dynamically assign thread arbitration policy by one kernel 
-use clSetKernelExecInfo with param
 CL_KERNEL_EXEC_INFO_THREAD_ARBITRATION_POLICY_INTEL
 to change default value of ThreadArbitrationPolicy

Change-Id: I15d0de0840ed14687c16ae04890b662bc157de76
Signed-off-by: Katarzyna Cencelewska <katarzyna.cencelewska@intel.com>
 2019-12-11 09:30:33 +01:00
Dunajski, Bartosz
3eab5cfe35 Patch flat image params on setKernelArg 
Change-Id: Iae0f37dfcd2ee14a3874835f2e444549d1769074
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2019-12-11 08:18:55 +01:00
Mateusz Hoppe
195f610fa3 Return CL_DEVICE_HOST_UNIFIED_MEMORY cap based on local memory 
Change-Id: Ic896d9aca60a36618b30745db5bd38f98a0bd2e9
Signed-off-by: Mateusz Hoppe <mateusz.hoppe@intel.com>
 2019-12-10 17:43:17 +01:00
Artur Harasimiuk
39b997a276 infrastructure update 
Change-Id: Ibe24fe6a7ebe04bae6fc2984641dde04e7b62201
Signed-off-by: Artur Harasimiuk <artur.harasimiuk@intel.com>
 2019-12-10 16:43:24 +01:00
Zbigniew Zdanowicz
2a50c86945 Use actual MockSip object in ULTs 
Change-Id: I60016a5c2f14f9bf4391df84335856e93bf1e64f
Signed-off-by: Zbigniew Zdanowicz <zbigniew.zdanowicz@intel.com>
 2019-12-10 14:13:17 +01:00
Borzyszkowski, Mateusz
bc4c7fe524 Allow error information in debug mode 
Allow error information in debug mode when starting ocloc 
with the spir-v input attached. Before this change, 
it did not emit an error message, but only stopped running.

Resolves: IGC-2715
Change-Id: I7bfae43b4990f9f09fb7360712c17589bb7d1b07
 2019-12-10 13:56:51 +01:00
Mateusz Jablonski
5fa53f4516 Move headers to core 
- address_patch.h
- options.h
- registered_method_dispatcher.h
- grf_config.h

Rename OCL_RUNTIME_PROFILING -> KMD_PROFILING

Related-To: NEO-3982

Change-Id: I06cf72729e9d7d7d2ff0bd169fcbada00c4b509a
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2019-12-10 12:19:29 +01:00
Dunajski, Bartosz
1856248e7e Dont pass hostPtr for blit operation triggered by SVM enqueue 
Change-Id: I78761f71cb4debe62a41b34e22a614c5245a40ff
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2019-12-10 10:55:39 +01:00
Dunajski, Bartosz
c6a202ab87 Refactor programBindingTableBaseAddress 
Change-Id: I5a1d29ef3551717c7d28617c8af4d5f3bfbe3dbd
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2019-12-10 10:50:32 +01:00
Slawomir Milczarek
9a4e360fc2 AUB file name with suffix to indicate multiple subdevices 
Change-Id: I8a6417e0c1b30c938ce863c15c5cf91da504d330
Signed-off-by: Slawomir Milczarek <slawomir.milczarek@intel.com>
 2019-12-10 09:28:26 +01:00
ocldev
f2e927004c dependencies update 
Change-Id: I22bba83b4414f4be17a475be3f177d019037a9cf
 2019-12-09 23:37:28 +01:00
Artur Harasimiuk
c504040dd7 infrastructure update 
Resolves: NEO-3178
Change-Id: I7ee1934ff2cda0d27367a1f2fe7a62e37bcddeda
Signed-off-by: Artur Harasimiuk <artur.harasimiuk@intel.com>
 2019-12-09 19:19:45 +01:00
Filip Hazubski
f14793895e Fix SyncBufferHandler test 
Change-Id: I281d696b2b349c2189caa28e3d8a29a001e514cb
Signed-off-by: Filip Hazubski <filip.hazubski@intel.com>
19.50.15079 		2019-12-09 18:18:41 +01:00
Jacek Danecki
4cd238d346 doc: Remove obsoleted information about CentOS build 
spec files to build under CentOS are available in:
https://github.com/JacekDanecki/neo-specs/tree/master/specs/centos

Change-Id: I354e63416b9acfce12aed43925c4f2c769bf1b25
Signed-off-by: Jacek Danecki <jacek.danecki@intel.com>
 2019-12-09 17:45:31 +01:00
Mateusz Jablonski
e27c5a9475 Change signature of clAddCommentINTEL function: pass device instead of platform 
Resolves: NEO-3939
Change-Id: I394ef7c2370771569a0ec50ac4644782ce8a384f
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2019-12-09 17:20:04 +01:00
Mateusz Jablonski
16c6d7eb9b Refactor ApiFixture 
- setup number of root devices
- define tested root device

Related-To: NEO-4000

Change-Id: I785d07a7f54932f66fe57637c8d10775743a871c
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2019-12-09 16:32:44 +01:00
Mateusz Jablonski
8ccadbb240 Correct clGetDeviceIDs: return all requested devices 
Related-To: NEO-4000
Change-Id: I2723b5364bf742aa490d88967c19329830f45322
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2019-12-09 15:41:06 +01:00
Gibala
5ac1d1258c Connect UnifiedMemoryProperties with MemoryPropertiesFlags 
-Add support to SvmAllocationData
-Refactor parseMemoryProperties
-Add allocation flags

Related-To: NEO-4011
Change-Id: I3728d2319aeef983dbcc3f8702da9a303a4e2b9c
Signed-off-by: Gibala <krzysztof.gibala@intel.com>
 2019-12-09 14:23:46 +01:00
Jobczyk, Lukasz
ac0471adc5 Remove padding allocation 
Change-Id: I0017640ee22b687af1d85fa10d221d2b3cafed0a
Signed-off-by: Jobczyk, Lukasz <lukasz.jobczyk@intel.com>
 2019-12-09 13:39:39 +01:00
Dunajski, Bartosz
b544b2da60 Remove redundant CommandQueue member 
Change-Id: I2ee338a3134cd81d6de7ecbed47c049dfbbae5aa
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2019-12-09 13:13:45 +01:00
ocldev
063df12af0 igc revision update 
Change-Id: I7c4f3f1885d92d5803ee52e43f0d6c38a1617845
 2019-12-09 11:26:30 +01:00
Dunajski, Bartosz
8c604a6e16 FLAT_IMAGE patch tokens support 
Change-Id: I9f4ea389871113842311de9ef4ac7bf74f7a46fa
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2019-12-09 08:49:04 +01:00
Dunajski, Bartosz
3014b304ca Refactor STATE_BASE_ADDRESS programming 
Change-Id: I977867678ea980f17cbe6ceef51c4f05096c809f
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2019-12-07 19:00:45 +01:00
Jaroslaw Chodor
72a1542140 [2/N] Program refactor - gather compiler options 
Change-Id: I0a614be73fbd87184be2dfea407582a58c27b0bc
19.49.15055 		2019-12-06 22:17:19 +01:00
Jacek Danecki
49ad839818 ci: use IGC from manifest 
Signed-off-by: Jacek Danecki <jacek.danecki@intel.com>

https://github.com/intel/compute-runtime/pull/238

Change-Id: I57316456cbea47bbea19a353475280c0b22baca3
 2019-12-06 21:58:26 +01:00
Dunajski, Bartosz
32d1869d4f Pass svm allocations during SVMMemcpy 
Change-Id: Ief9e5f6b96f870ac9bf152c88f0d21ff4654ac21
 2019-12-06 15:13:32 +01:00
Kamil Kopryk
baba643844 Added support for stateless enqueueSVMMemFill 
Change-Id: Ieaef91def4097c7dce618e24917c4f55cb2b914c
Signed-off-by: Kamil Kopryk <kamil.kopryk@intel.com>
Related-To: NEO-3314
 2019-12-06 15:01:29 +01:00
Dunajski, Bartosz
232dc59cde Make specific SBA heaps programming optional 
Change-Id: I852a9e1d9bcc5d6227b1e8a81ab81ad896d6586f
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2019-12-06 12:52:21 +01:00
Pawel Wilma
632134db30 Disable host ptr tracking for GEN12LP 
Related-To: NEO-3661

Change-Id: I1774aad8ef32f294192a9b679cb9f66e4091198c
Signed-off-by: Pawel Wilma <pawel.wilma@intel.com>
 2019-12-06 11:57:32 +01:00
ocldev
cd198fac0a igc revision update 
Change-Id: I4bb4db57c1e2798f5b6c2492465f9b84de90cda3
 2019-12-06 11:27:08 +01:00
Dunajski, Bartosz
566b845bbc Move state_base_address to core 
Change-Id: I2b64fff4eed31054ae29b7b14ecb9f147914049a
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2019-12-06 09:01:24 +01:00
Pawel Wilma
baeac08662 Remove unused method obtainGpuAddressIfNeeded() 
Change-Id: I0b0ff5c793d31c97f488339dcb75aba617871f88
Signed-off-by: Pawel Wilma <pawel.wilma@intel.com>
 2019-12-04 17:22:43 +01:00
Filip Hazubski
82bc594af0 Add clEnqueueNDRangeKernelINTEL API 
Related-To: NEO-2712

Change-Id: If1d16d9d626871a9dc4b19282f9edc5786ffa398
Signed-off-by: Filip Hazubski <filip.hazubski@intel.com>
 2019-12-04 17:11:28 +01:00
Filip Hazubski
7be937c226 Update clCreateSubDevices implementation 
Make it possible to get SubDevices from given RootDevice.

Resolves: NEO-3977

Change-Id: I9cf06f17b45299009ab6953b9ad7d5cb0bbe848f
Signed-off-by: Filip Hazubski <filip.hazubski@intel.com>
 2019-12-04 16:38:07 +01:00
Mateusz Jablonski
73dad03c66 Fix clSVMAlloc function: use device from context 
Related-To: NEO-4000

Change-Id: Iefad9d7a8908a584b98801bdbe13aa1e0be2e47f
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2019-12-04 16:27:54 +01:00
Dunajski, Bartosz
dfc50f3a75 Move gmm_helper to core 
Change-Id: I31ca317d10697ab884e04f443c8ccfdd6ca9d2ae
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2019-12-04 15:25:32 +01:00
Dunajski, Bartosz
c0cafccacb Fix command container tests cmake generation 
Change-Id: Ie7dcad6aefc375aa0c344764f10683d4b22ace8c
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2019-12-04 15:22:01 +01:00
Pawel Cieslak
2070bd8970 Fix build_spec.py script. 
Change-Id: I0485d6be5f68b3200621de9bcaeaf0289c970a92
Signed-off-by: Pawel Cieslak <pawel.cieslak@intel.com>
 2019-12-04 14:37:38 +01:00
Mateusz Hoppe
dfce56d634 Cleanup headers in print_formatter and move to core 
Change-Id: I2ef5498927b02e0371dc4e484f94b00b4f86721c
Signed-off-by: Mateusz Hoppe <mateusz.hoppe@intel.com>
 2019-12-04 13:37:11 +01:00
ocldev
48f3f10396 dependencies update 
Change-Id: I33b431ba8f10029bb6756db550180fc028e9919d
 2019-12-04 12:59:07 +01:00
Dunajski, Bartosz
c8a34e65f0 Revert "Dont make Surfaces resident on GPGPU CSR for blit enqueue" 
This reverts commit d74edb3d3f.

Change-Id: Idd4fb27afd0b8a30be1dba1630ecd81932963fae
 2019-12-04 12:18:26 +01:00
Mateusz Hoppe
96cc1081c0 Moving print.h/.cpp files to core 
Change-Id: I4972f87a007c7183acdaf79f48ece4ff0a6cf087
Signed-off-by: Mateusz Hoppe <mateusz.hoppe@intel.com>
 2019-12-04 11:05:44 +01:00