intel/compute-runtime
1
0
Fork 0
mirror of https://github.com/intel/compute-runtime.git synced 2025-12-28 00:03:14 +08:00
Code Issues Packages Projects Releases Wiki Activity
4,109 Commits 42 Branches 655 Tags
e8a98b14b3b419baa4fcc6903ea22e997e749ac8
Commit Graph

543 Commits

Author SHA1 Message Date
Milczarek, Slawomir
4420fe34ba Changed class name from PipeControlHelper to MemorySynchronizationCommands 
Related-To: NEO-4227

Change-Id: Iff59ea5b274fbba3af1dab2ac188f7370cc1e44f
Signed-off-by: Milczarek, Slawomir <slawomir.milczarek@intel.com>
 2020-02-17 16:20:27 +01:00
Dunajski, Bartosz
362a63699f Make SVM_GPU allocation OneTimeAubWritable. 
Reset Aub/Tbx writable flags on enqueue SVM unmap

Change-Id: Ib8370fc049bcbf24d787c5d677520afa12135ee5
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2020-02-12 10:56:57 +01:00
Maciej Plewka
df59101dae Create base class for debugger in core 
Resolves: NEO-4176

Change-Id: Iba48676fe145538c8213d21d514be38c702525c9
Signed-off-by: Maciej Plewka <maciej.plewka@intel.com>
 2020-02-11 08:38:48 +01:00
Michal Mrozek
d2df43d169 Fix a bug with cpu copy and simulation mode. 
- if buffer was used on GPU it would be marked as non-updateable from CPU
- if we do CPU data transfer from the host, we however need to deliver data
to the buffer
- in such scenario mark such buffer for update in subsequent submissions.

Change-Id: Id3813c4193aa18917de117c61303fd6f62745abb
Signed-off-by: Michal Mrozek <michal.mrozek@intel.com>
 2020-02-10 15:02:54 +01:00
kamdiedrich
f3fc466f5b Move memory_manager to core folder 
Change-Id: I8d84d6982fea3cd785f1e15af0ee7fa361258a23
 2020-02-08 15:24:13 +01:00
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