intel/compute-runtime
1
0
Fork 0
mirror of https://github.com/intel/compute-runtime.git synced 2025-12-27 07:44:16 +08:00
Code Issues Packages Projects Releases Wiki Activity
3,997 Commits 42 Branches 655 Tags
d023d9ff02f3ea2629e7110a085b5d93de71d832
Commit Graph

538 Commits

Author SHA1 Message Date
Filip Hazubski
d023d9ff02 Move core device objects to core 
Change-Id: Iab6f00ea5cf2595cebc34c18286a6900b90aef92
Signed-off-by: Filip Hazubski <filip.hazubski@intel.com>
 2020-02-07 14:35:14 +01:00
Koska
004ea3946d Correct image format reporting for OCL 1.2 
Change-Id: Ia2160248d1cda6c13219598f8962aa3372885b9a
Signed-off-by: Koska <andrzej.koska@intel.com>
Related-To: NEO-3981
 2020-02-07 10:34:29 +01:00
Michal Mrozek
c9db4b85e0 Add brackets. 
Change-Id: I0e6f4b469c6bc63341a18a878f40da4802abb89c
Signed-off-by: Michal Mrozek <michal.mrozek@intel.com>
 2020-02-06 13:25:34 +01:00
Mateusz Hoppe
3682e29ddc Move blit_commands_helper files to core 
Change-Id: I29fb4e6a91e9fc32f5017eb966d478f51b3b3487
Signed-off-by: Mateusz Hoppe <mateusz.hoppe@intel.com>
 2020-02-06 13:02:59 +01:00
Jobczyk, Lukasz
d810067048 Create dedicated engine for internal usage 
Related-To: NEO-4149

Change-Id: I1641866429cfa87b457a808b22917d191c482a7e
Signed-off-by: Jobczyk, Lukasz <lukasz.jobczyk@intel.com>
 2020-02-05 13:48:04 +01:00
Filip Hazubski
8a6cb1e5ca Add ULT helper functions for PIPE_CONTROL command 
Resolves: NEO-4227

Change-Id: I8cca5edc1dd39c22e1f97fc8163f299fd379ad49
Signed-off-by: Filip Hazubski <filip.hazubski@intel.com>
 2020-02-05 12:21:50 +01:00
Michal Mrozek
6cc9b9d125 Add choose max row size parameter for local id generation. 
Change-Id: I77185b6c114092859c742236a4dfef01deb9ea21
 2020-02-05 10:24:40 +01:00
Mateusz Jablonski
66754c4849 Remove platformDevices from runtime 
Related-To: NEO-4207

Change-Id: I70781b44e7d14360a581808049baf8b61fd1b4e4
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2020-02-05 09:59:13 +01:00
Mateusz Jablonski
e77ed5f4fa Make platformImpl a vector 
Related-To: NEO-4207
Change-Id: I85fa2d5a44160e1cf98321f9835a5173e59e479c
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2020-02-04 15:29:19 +01:00
Filip Hazubski
5495a4b458 Add specializedDevice pointer to Device 
Related-To: NEO-3938

Change-Id: Ic3386580a22c41f34c67949ccb7f7c6957c8f60d
Signed-off-by: Filip Hazubski <filip.hazubski@intel.com>
 2020-02-04 12:32:14 +01:00
Mateusz Jablonski
0a0b1ce1d8 Pass platform to ClDevice 
Related-To: NEO-4207
Change-Id: I1c70d209df2b378573a41fa991ab594746691adb
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2020-01-31 14:10:29 +01:00
Pawel Wilma
9cbafe8bdd Add per-DSS backed buffer programming to dispatch flags 
Related-To: NEO-3220

Change-Id: I16711af6d5b2ca51ab2c92b680d253124774534f
Signed-off-by: Pawel Wilma <pawel.wilma@intel.com>
 2020-01-30 08:40:59 +01:00
Mateusz Hoppe
522dedfbd2 Move files to core 
Change-Id: I78bf6a82df3399a2b79143333989bac81e7a392a
Signed-off-by: Mateusz Hoppe <mateusz.hoppe@intel.com>
 2020-01-29 12:21:40 +01:00
Filip Hazubski
07c4682668 Respect KernelExecutionType in enqueue kernel calls 
Change-Id: I9de07f9e3b77c4a44f6a0127e0ae3bd7e1ab97f8
Signed-off-by: Filip Hazubski <filip.hazubski@intel.com>
 2020-01-27 13:51:49 +01:00
Pawel Wilma
315df91d9d Builtin kernels refactoring 
Related-To: NEO-3220
Change-Id: Ib85a1f4fd69b47bc8e819a29cc4adec73bda72e0
Signed-off-by: Pawel Wilma <pawel.wilma@intel.com>
 2020-01-24 11:56:02 +01:00
Mateusz Hoppe
b6825933f8 Replace Event::eventNotReady with CompletionStamp::levelNotReady 
- move some files to core
- remove unnecessary includes

Related-To: NEO-4175

Change-Id: Ib33dff644452c7cfd6fda7e9bb4b68cd6eb3a61c
Signed-off-by: Mateusz Hoppe <mateusz.hoppe@intel.com>
 2020-01-23 16:16:23 +01:00
Filip Hazubski
a60aa092f8 Rename clEnqueueNDRangeKernelINTEL to clEnqueueNDCountKernelINTEL 
Change-Id: Ibe46bd94a93290b0b6cef0c10aa98e024fc17324
Signed-off-by: Filip Hazubski <filip.hazubski@intel.com>
 2020-01-23 15:46:13 +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
Mateusz Hoppe
b5e2f322f6 Move files from runtime/memory_manager to core 
- remove TbxMemoryManager

Change-Id: I554feff51f08e108b2e9ee22ecaa2cb75a1eead7
Signed-off-by: Mateusz Hoppe <mateusz.hoppe@intel.com>
 2020-01-21 15:28:47 +01:00
Maciej Dziuban
3c27e97c43 Extract gl mocks to windows directory 
Change-Id: I963032bfad880e42100f6233b9570cefb607f26c
 2020-01-21 12:07:13 +01:00
Dunajski, Bartosz
054f2b503a Remove not used method 
Change-Id: I6109d4f1521de157f449cad92ecfbab3d133f815
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2020-01-21 11:14:45 +01:00
Misiak
b498fea989 Removed unused atomic latestTaskCountWaited 
Related-To: NEO-3869

Change-Id: If7e9db2645c9c9c38d65a0b200960e387441c9ca
Signed-off-by: Konstanty Misiak <konstanty.misiak@intel.com>
 2020-01-20 11:43:56 +01:00
Maciej Dziuban
9865003cc2 Move GL sharing to windows directory 
Change-Id: I9aeb60d31d5c49c0464b2cd8296dc5d79ec41d63
Signed-off-by: Maciej Dziuban <maciej.dziuban@intel.com>
 2020-01-20 09:34:08 +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
Adam Cetnerowski
f3c7619dc9 ULT renaming: Zero Size Enqueue tests 
Related-To: NEO-2236

Change-Id: I3070b57d0b906e57b524f7729cb723c7f301bbf5
Signed-off-by: Adam Cetnerowski <adam.cetnerowski@intel.com>
 2020-01-16 18:19:10 +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
Adam Cetnerowski
23b83d5b40 ULT renaming: CPU Read/Write tests 
Related-To: NEO-2236

Change-Id: I003049c4f26f722452059585f14f9896ce050b9b
Signed-off-by: Adam Cetnerowski <adam.cetnerowski@intel.com>
 2020-01-13 15:28:35 +01:00
Mateusz Hoppe
fd4ae3b369 Move gmm to core 
Change-Id: I787dfcb3ca3926ce10e2e3c748594713df5fc467
Signed-off-by: Mateusz Hoppe <mateusz.hoppe@intel.com>
 2020-01-10 14:26:17 +01:00
Mateusz Hoppe
81e9591c31 Refactor ImageInfo 2/n 
Change-Id: I5e6081a75b802cc98fd89e384d550a219353728b
Signed-off-by: Mateusz Hoppe <mateusz.hoppe@intel.com>
 2020-01-10 14:20:31 +01:00
Adam Cetnerowski
0a39140284 ULT renaming: OOQ task tests 
Related-To: NEO-2236

Change-Id: I8d1f7b9a94717a8f6ba10c123ef9eb03426f42c0
Signed-off-by: Adam Cetnerowski <adam.cetnerowski@intel.com>
 2020-01-09 09:22:02 -08:00
Adam Cetnerowski
2bc7ca84ac ULT renaming: MultiDispatchInfo test 
Related-To: NEO-2236

Change-Id: I81a55fac8117a874aa1f8d066771493bad0a348d
Signed-off-by: Adam Cetnerowski <adam.cetnerowski@intel.com>
 2020-01-09 15:41:35 +01:00
Katarzyna Cencelewska
a123cce3e8 Add return CL_INVALID_VALUE from clSetKernelExecInfo 
if attempt to set invalid ThreadArbitrationPolicy

Change-Id: I8208f9b6761c4dafb6ef4cbde550314778ab505e
Signed-off-by: Katarzyna Cencelewska <katarzyna.cencelewska@intel.com>
 2020-01-08 16:19:43 +01:00
Adam Cetnerowski
5ca48f7945 ULT renaming: LWS size tests 
Related-To: NEO-2236

Change-Id: I0630635dcfb405f835fa0da983312783bfcf20ac
Signed-off-by: Adam Cetnerowski <adam.cetnerowski@intel.com>
 2020-01-08 15:57:10 +01:00
Dunajski, Bartosz
7d7e606056 Pass correct throttle hint for enqueue without kernel 
Change-Id: Icbd00cd8508f60a58e8aed92253f7070e512f0f3
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2020-01-08 15:36:11 +01:00
Adam Cetnerowski
8e3c5892ac ULT renaming: Local ID tests 
Related-To: NEO-2236

Change-Id: Ib8a9e21387c28d6a8220089deca3b74e727c4d50
Signed-off-by: Adam Cetnerowski <adam.cetnerowski@intel.com>
 2020-01-02 16:52:42 +01:00
Adam Cetnerowski
a6fe6ac312 ULT renaming: IOQ multi-thread tests 
Related-To: NEO-2236

Change-Id: I3de023ab06f872d98a3dc6f27d400081d7b7fea4
Signed-off-by: Adam Cetnerowski <adam.cetnerowski@intel.com>
 2020-01-02 13:17:27 +01:00
Mateusz Jablonski
10d274daa9 Pass GmmClientContext to Gmm and GmmResourceInfo 
Related-To: NEO-3007
Change-Id: Ia590670e93ed93b0941d5a5dc6ac010268cb561e
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2019-12-31 12:19:32 +01:00
Adam Cetnerowski
1021d8c6d2 ULT renaming: IOQ task count tests 
Related-To: NEO-2236

Change-Id: Id6677810e310892ca1eab2caef40779063609077
Signed-off-by: Adam Cetnerowski <adam.cetnerowski@intel.com>
 2019-12-23 12:05:42 +01:00
Adam Cetnerowski
2242b5dd17 ULT renaming: Get Size tests 
Related-To: NEO-2236

Change-Id: I434803d0a39d3f2d7946dbb591c826501aeea9dd
Signed-off-by: Adam Cetnerowski <adam.cetnerowski@intel.com>
 2019-12-18 09:50:53 +01:00
Dunajski, Bartosz
7b18a919e7 Refactor heaps 
- Remove GENERAL_STATE
- Change allocation types
- IOH can be utilized as 4GB heap

Change-Id: I1c2a7bc284217a26d740b504bf92834d39f3ace2
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2019-12-18 09:50:22 +01:00
Maciej Plewka
8803b4cd4e Move grf size to HwInfo 
Change-Id: I65ee879644573586d63092b487f8b5ea0cedf1e3
Signed-off-by: Maciej Plewka <maciej.plewka@intel.com>
 2019-12-17 17:27:21 +01:00
Adam Cetnerowski
3ff5deaae9 ULT renaming: Get Size Required Image tests 
Related-To: NEO-2236

Change-Id: I8667f98d1dac3d41e8405fe90be713ab9276a169
Signed-off-by: Adam Cetnerowski <adam.cetnerowski@intel.com>
 2019-12-17 12:00:10 +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
Adam Cetnerowski
d5ce5018b0 ULT renaming: Get Size Required Buffer tests 
Related-To: NEO-2236

Change-Id: Ifd4059d309a76f160c6d47f78094fa401af19b6f
Signed-off-by: Adam Cetnerowski <adam.cetnerowski@intel.com>
 2019-12-16 18:13:43 +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
Dunajski, Bartosz
ecc54edbb3 Improve pointers passing in SVM enqueue 
Change-Id: Idf46438e8bd17476c3b3997ac35821d24ce0a081
 2019-12-11 14:38:42 +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
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
Filip Hazubski
f14793895e Fix SyncBufferHandler test 
Change-Id: I281d696b2b349c2189caa28e3d8a29a001e514cb
Signed-off-by: Filip Hazubski <filip.hazubski@intel.com>
 2019-12-09 18:18:41 +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