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
4,144 Commits 42 Branches 655 Tags
a48b50c554fd368d14908baf8aad8576660df1e5
Commit Graph

554 Commits

Author SHA1 Message Date
Mateusz Jablonski
6ef7fc726b Update copyright headers 
Change-Id: I05eaad34f5af15685c6ad6d5bb3078f21dd1e0af
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2020-02-22 23:44:04 +01:00
kamdiedrich
8f44a95ca0 Changing include paths 
Change-Id: I3b878463289083c956382e68da3473788cf5c15f
 2020-02-22 18:45:39 +01:00
Mateusz Hoppe
daed7cbc00 Move CommandStreamReceiver to core 
Change-Id: Id8ed0e680f77b4dd9614f0096c3e6d9a1d04b3d3
Signed-off-by: Mateusz Hoppe <mateusz.hoppe@intel.com>
 2020-02-21 23:13:38 +01:00
Michal Mrozek
33d5f504c6 Prefer CPU transfer for Local Memory 32 bit applications. 
Change-Id: Icdb1333c0d0123be3d26329088d7ed44df37c84e
Signed-off-by: Michal Mrozek <michal.mrozek@intel.com>
 2020-02-21 15:15:00 +01:00
Maciej Plewka
13e59b26b5 Move dispatch builder to seperate file 
Change-Id: I309986902fda41a389e9facbf186bc8b2740af7a
Signed-off-by: Maciej Plewka <maciej.plewka@intel.com>
 2020-02-21 14:14:21 +01:00
Michal Mrozek
3b2bffc239 [3/n] Refactor CPU transfers. 
- split functions to allowed and preferred versions
- isReadWriteOnCpuAllowed tells if it is possible to do transfer on CPU
- isReadWriteOnCpuPreffered tells about performance preference of doing it

Change-Id: Ibe48d495fc7906dee6382de591baf8447eb6fe95
Signed-off-by: Michal Mrozek <michal.mrozek@intel.com>
 2020-02-21 12:26:03 +01:00
Michal Mrozek
618472c23e [2/n] Refactor CPU copies 
- move blocking flag to command queue function
- refactor buffer function for better readability
- add new method to easily state that buffer is compressed.

Change-Id: I62465b7bc8b109f14d0012b5641d4b822e3cc908
Signed-off-by: Michal Mrozek <michal.mrozek@intel.com>
 2020-02-21 11:05:49 +01:00
Mateusz Hoppe
8cb486e821 Change TimestampPacketHelper method signature 
Change-Id: I0ca375c0ffdeaf572a6649b50d2def57b95c9603
Signed-off-by: Mateusz Hoppe <mateusz.hoppe@intel.com>
 2020-02-21 10:46:39 +01:00
Michal Mrozek
bd1ac55e2c [1/n] Refactor CPU copies. 
- remove waitlist check from buffer
- refactor the flow in CommandQueue::bufferCpuCopyAllowed

Change-Id: I52bb7f886211b05f80118665bb28dfdb5f113fe7
 2020-02-21 09:41:29 +01:00
Maciej Plewka
b218281488 Dont use context in built ins 
Change-Id: Id2af09190edbc1a3bb930210fe340691aa1e4578
Signed-off-by: Maciej Plewka <maciej.plewka@intel.com>
 2020-02-20 17:20:18 +01:00
Jobczyk, Lukasz
a69f393356 Use hwInfo from root device environment [2/N] 
Related-To: NEO-3857

Change-Id: Iad6832f36ae8b0ea218acb6b38fe6ba46599b9d9
Signed-off-by: Jobczyk, Lukasz <lukasz.jobczyk@intel.com>
 2020-02-20 13:06:34 +01:00
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