intel/compute-runtime
1
0
Fork 0
mirror of https://github.com/intel/compute-runtime.git synced 2025-12-25 21:42:53 +08:00
Code Issues Packages Projects Releases Wiki Activity
3,965 Commits 42 Branches 655 Tags
5c4abe12611caaa326192e279dbbcc2f956f253d
Commit Graph

160 Commits

Author SHA1 Message Date
Mateusz Jablonski
0e3ab96298 Move compiler extensions to cl device 
Related-To: NEO-4207
Change-Id: Ia220085260fbafb062e0e0aedca863eb64b079bd
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2020-01-31 14:11:05 +01:00
Filip Hazubski
f80480de7f Move ClDevice to a separate file 
Related-To: NEO-3938

Change-Id: I275b9285b70dac2c9bc52878f6e517e4f3e083b3
Signed-off-by: Filip Hazubski <filip.hazubski@intel.com>
 2020-01-30 12:46:10 +01:00
Jaroslaw Chodor
33ac782f03 Allow empty kernel arg info 
Change-Id: I0e45e342148dfb4dceca1e7fdba885280e4ab597
 2020-01-29 17:58:22 +01:00
Milczarek, Slawomir
7fe6a2fbed Add oclock option to force stateless to stateful optimization 
Related-To: NEO-2993

Change-Id: I9668053aa749534d09501bfccb1a9b93e69f0e4e
Signed-off-by: Milczarek, Slawomir <slawomir.milczarek@intel.com>
 2020-01-29 10:23:47 +01:00
Jaroslaw Chodor
2e64471f58 Fixing regression in arg_info tests 
Resolves: NEO-4188

Change-Id: I375d0efc084b95d4a93a987b87d9e5635d7ec26b
 2020-01-25 19:09:21 +01:00
Jaroslaw Chodor
b74d502052 Moving patchtokens decoder to core 
Change-Id: I61d9f3ec7a1bca55df5b3b8c1884014acff1a4c0
 2020-01-25 15:16:01 +01:00
Konstanty Misiak
fc5b98970c Moved files from gmm_helper to core 
Related-To: NEO-4138

Change-Id: Ib7aecb1531cebbe34abb5c8e57067464726e9009
Signed-off-by: Konstanty Misiak <konstanty.misiak@intel.com>
 2020-01-25 11:49:17 +01:00
Jaroslaw Chodor
f057712fa7 Program refactor 
* decouple program_info
* move global allocations relocation to linker
* remove obsolete tests
* initial cleanup to kernel_info kernelInfo
* unified patchtoken validation

Change-Id: I0567cd6d607b4f3cf44e6caf33681f6210760f76
 2020-01-25 10:56:30 +01:00
Filip Hazubski
8d34f40aad Add clGetKernelSuggestedLocalWorkSizeINTEL 
This function can be used to query local work size that would be used in
case of querying ND range kernel with local_work_size set to NULL.

Change-Id: I86ac7c97cffb6c3e11b673a28285739edfabb4a6
Signed-off-by: Filip Hazubski <filip.hazubski@intel.com>
 2020-01-23 13:50:37 +01:00
Filip Hazubski
8fcff2241f Add ClDevice 
Decouple cl_device_id from Device class.

Related-To: NEO-3938

Change-Id: I68543a753aea562f3b47ba0d23a059ff3cffa906
Signed-off-by: Filip Hazubski <filip.hazubski@intel.com>
 2020-01-17 12:43:11 +01:00
Mateusz Hoppe
01d8532f52 Move files to core 
- wddm_allocation.h/.cpp
- os_context.h
- residency_container.h

Change-Id: I9f933a09d1142f86550c0d67626f0719b6450303
Signed-off-by: Mateusz Hoppe <mateusz.hoppe@intel.com>
 2020-01-13 18:25:00 +01:00
Jaroslaw Chodor
5cf6d6348e Support mixed program scope ptrs 
Change-Id: Ib2ff6ba2fcd9af66f984f9fcddafa16abfff1bfd
 2020-01-05 21:58:53 +01:00
Pawel Wilma
2ca886b45d Force integer divide emulation for TGLLP A-step 
Related-To: NEO-3661

Change-Id: I305c3cfc14262a832aee749e66f3c426d3ca0343
Signed-off-by: Pawel Wilma <pawel.wilma@intel.com>
 2019-12-20 10:11:41 +01:00
Mateusz Hoppe
f0a6f6b057 Move DebugSettingsManager to core 
- pass registry path in constructor

Change-Id: I2a121da2c9483a0df088989feea490a638c63016
Signed-off-by: Mateusz Hoppe <mateusz.hoppe@intel.com>
 2019-12-17 10:39:53 +01:00
Mateusz Hoppe
5685b285f3 Extract logging logic from DebugSettingsManager 
Change-Id: I0ccc68216c1c3bb23d0389bec17124e09e4f98e1
Signed-off-by: Mateusz Hoppe <mateusz.hoppe@intel.com>
 2019-12-13 15:34:45 +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
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
Jaroslaw Chodor
72a1542140 [2/N] Program refactor - gather compiler options 
Change-Id: I0a614be73fbd87184be2dfea407582a58c27b0bc
 2019-12-06 22:17:19 +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
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
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
Mateusz Jablonski
54f65c0243 Move headers to core 
- hw_info
- hw_cmds
- kmd_notify_properties
- completion_stamp
- bxml_generator_glue

Related-To: NEO-3982
Change-Id: I3ed3ef81f42596f381e60c19250f6eb1296d47a4
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2019-12-02 14:20:45 +01:00
Filip Hazubski
0270ad8015 Add pointer checks 
Change-Id: I37a6898670a4d9e66f0eff404b5282714f293956
Signed-off-by: Filip Hazubski <filip.hazubski@intel.com>
 2019-12-02 12:57:02 +01:00
Jaroslaw Chodor
102bceb4c9 Adding bindless compilation toggles 
Change-Id: I35e37e9319a660fe0e4588f7abdc821557948b18
 2019-11-28 15:23:24 +01:00
Filip Hazubski
5bed747e33 Update Program::extractInternalOptions 
Change-Id: Ie67a8ef7b6f010a44b252666e9d9ef48fdeac9e0
Signed-off-by: Filip Hazubski <filip.hazubski@intel.com>
 2019-11-28 15:04:28 +01:00
Pawel Wilma
472a75912d Return error code from submit() to application. 
Related-To: NEO-3741

Change-Id: I0e0ff6606eb6a8a77673949955c8e799689017b6
Signed-off-by: Pawel Wilma <pawel.wilma@intel.com>
 2019-11-26 12:42:47 +01:00
Jaroslaw Chodor
355e8d3e5a [1/N] Program refactor - decouple from patchokens 
Change-Id: I63bbf6c31a5db9e788124f22b6105e65c16c86d4
 2019-11-25 19:46:21 +01:00
Igor Venevtsev
8ef1466a15 Add UNRECOVERABLE_IF to check device is not a nullptr 
- allocateGlobalsSurface()

Change-Id: Ie6dbcb85228dfd99b65c12d13ad631e2079e79e1
Signed-off-by: Igor Venevtsev <igor.venevtsev@intel.com>
 2019-11-25 14:56:41 +01:00
Mateusz Jablonski
e7ee6daaa0 Remove runtime/gen_common from include paths 
Change-Id: I4d1f9e64e0f4099e7903234e62b070ad4235347a
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2019-11-19 13:37:34 +01:00
Igor Venevtsev
63fd26f6d6 Always specify rootDeviceIndex for graphics memory allocations 
Related-To: NEO-2941

Change-Id: Ia2362fd6b4e72ede02919152475f40b3edbc3658
Signed-off-by: Igor Venevtsev <igor.venevtsev@intel.com>
 2019-11-15 15:14:41 +01:00
Filip Hazubski
5f021afd6d Move HwHelper to core directory 
Change-Id: I2c78a8b737ee8e61b917b4918da37e77bbd9fe34
Signed-off-by: Filip Hazubski <filip.hazubski@intel.com>
 2019-11-15 14:06:40 +01:00
Jaroslaw Chodor
cab8968e1a Fixing regression in rebuildFromIr 
Change-Id: If1604861180d935575cd06fb2978df114453a070
 2019-11-02 21:52:16 +01:00
Maciej Plewka
51dcf2b6d2 add support for packed simd1 dispatch 
Change-Id: I3f2bf8e62e0a38d358fb87f02c88c387c874f6b3
Signed-off-by: Maciej Plewka <maciej.plewka@intel.com>
 2019-10-28 11:58:25 +01:00
Jaroslaw Chodor
28464ab2d4 [N/N] compiler interface refactor - move to core 
Change-Id: I029e3cd7a6adde9df97a0a7760ecbf5d25d8f501
 2019-10-22 19:14:09 +02:00
Jaroslaw Chodor
8ec7e45bff [2/N] compiler interface refactor (spir/spirV fix) 
Fixing regression in spir/spirV scenarios

Resolves: NEO-3854, NEO-3852, NEO-3845, NEO-3851, NEO-3844

Change-Id: Ifee7f1847c7f6598428f96ae2241b3d85e58ad11
 2019-10-20 20:26:10 +02:00
Daria Hinz
2196f7e216 Move ElfLib to core 
Change-Id: I57987e871aac9c72dc786661c1d24f5024dd367b
Signed-off-by: Daria Hinz <daria.hinz@intel.com>
 2019-10-18 08:31:12 +02:00
Jaroslaw Chodor
90e5cf164c Moving hash and file_io to core 
Change-Id: I1e6eece53fadf62a8919aa41e04deee3dac2ce60
 2019-10-17 13:16:20 +02:00
Chodor, Jaroslaw
856e5c6aaf [1/N] compiler interface refactor 
Decouple compiler interface from Program object

Change-Id: Ibd63c6eee01d85527318ccad52e52f5487d3402e
 2019-10-16 16:17:13 +02:00
Artur Harasimiuk
7864c03b0a clang-tidy cleanup 
Related-To: NEO-3676
Change-Id: I538c4ee3a370a71a7e470a441cd101c9ed1b285d
Signed-off-by: Artur Harasimiuk <artur.harasimiuk@intel.com>
 2019-10-15 19:55:43 +02:00
Jobczyk, Lukasz
419916f1b4 Add debug variable to measure processGenBinary execution time 
Related-To: NEO-3773

Change-Id: I79df8e6639ce775329307f4bfb25cbac5606e8c3
Signed-off-by: Jobczyk, Lukasz <lukasz.jobczyk@intel.com>
 2019-10-08 13:07:27 +02:00
Jobczyk, Lukasz
3bd4baeba3 Move a unified memory manager to the core dir 
Related-To: NEO-3677

Change-Id: Ib60dea2bcaaf5feea97d61cb9f54baee4c6b4b64
Signed-off-by: Jobczyk, Lukasz <lukasz.jobczyk@intel.com>
 2019-09-27 10:46:35 +02:00
Kamil Diedrich
115070767c Move graphics_allocation to core folder 
Change-Id: I16b8dbb57c2a40126826a232332c18ba9f563220
 2019-09-18 05:26:55 +02:00
Dunajski, Bartosz
9d6dcd6fff Use Kernels maxKernelWorkGroupSize to compute WG size 
Change-Id: I947b5612f36cd2437e1ead98712c914ffe4b5b15
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2019-09-17 08:39:05 +02:00
Mateusz Jablonski
9c200530c8 Remove not needed inclusions of device.h 
Change-Id: Idfd8122592f58539a569143146443c08a18dace9
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2019-09-09 15:05:29 +02:00
Jobczyk, Lukasz
882a216688 Move Debug helpers to the core dir 
Related-To: NEO-3677

Change-Id: I2c98595190fadfa8ffd9e378e774c0d4485cbf9e
Signed-off-by: Jobczyk, Lukasz <lukasz.jobczyk@intel.com>
 2019-09-05 16:00:35 +02:00
Mrozek, Michal
3f433baf38 Force stateless compilation for builtins path. 
Change-Id: I8ee826fdcc455a3770fa54ee635aaeff62ee35e6
Signed-off-by: Mrozek, Michal <michal.mrozek@intel.com>
 2019-09-05 13:07:21 +02:00
Mrozek, Michal
46b3012eb5 Force stateless compilation when device supports shared system memory 
Change-Id: I8e11ef82baf010a9a400bc9d733b8ec37a9fbb21
Signed-off-by: Mrozek, Michal <michal.mrozek@intel.com>
 2019-09-05 12:34:32 +02:00
Mrozek, Michal
a54dcd98b3 Register cache flushes when ISA allocation is destroyed. 
- when ISA is being destroyed , check what are the users of it and register
instruction cache flushes there.
- For subsequent enqueue commands this would result in properly flushed
instruction cache.

Change-Id: I3791cd77ee42da9f87508c64a65cdc6238950858
Signed-off-by: Mrozek, Michal <michal.mrozek@intel.com>
 2019-08-28 14:15:19 +02:00
Mateusz Jablonski
18982bd016 Move memory for slm window to memory manager 
remove redundant methods from MockDevice

Related-To: NEO-3007

Change-Id: I9cc819b9c9118dbb667f5bf87d1bf15787f9b67f
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2019-08-28 12:09:17 +02:00
Jim Snow
4360aff03c Move runtime/helpers/aligned_memory.h to core/helpers 
Signed-off-by: Jim Snow <jim.m.snow@intel.com>
Change-Id: I15de094c51d4eb18bfff4d17fd34e817b5525fda
 2019-08-06 23:56:24 +02:00