Media
/
compute-runtime
mirror of https://github.com/intel/compute-runtime.git
1
0
Fork 0
Code Issues Packages Projects Releases Wiki Activity
3,636 Commits 36 Branches 614 Tags 179 MiB
Commit Graph

183 Commits

Author SHA1 Message Date
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
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
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
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
Dunajski, Bartosz d74edb3d3f Dont make Surfaces resident on GPGPU CSR for blit enqueue 
Change-Id: I009e0a9bbbe44287146ba7f5c47dd2c8f3144cfb
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2019-11-28 12:18:27 +01:00
Dunajski, Bartosz 684b3e1774 Improve aux translation restrictions check 
Change-Id: I6e5bd014fef60f89365f536c219ab7d399c51265
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2019-11-25 12:58:12 +01:00
Dunajski, Bartosz 08ceaf432a Enable blit operation on enqueue copy buffer 
Change-Id: Ie9571344a9b1e2a783c59955a68094f2868f36ee
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2019-11-21 20:54:02 +01:00
Pawel Wilma ae0cefc834 Add patchToken OffsetToSkipSetFFIDGP in device execution 
Change-Id: I0634836b787fa371f0b64779732941396a6ba804
Signed-off-by: Pawel Wilma <pawel.wilma@intel.com>
Related-To: NEO-3892
 2019-11-19 17:26:22 +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
Dunajski, Bartosz 2d5169cf65 Setup enqueue dependencies in blocked path 
Change-Id: Ia6d549924e3e557bae74dbdac691987450cbd3b7
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2019-11-19 08:55:55 +01:00
Dunajski, Bartosz 8e945e7919 Improve TimestampPackets handling in blocked path 
Change-Id: Idf381a8750cebec6196eb299661dda892e11144d
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2019-11-18 09:25:56 +01:00
Dunajski, Bartosz 46b5513028 Initial Blit aux translation support 
Change-Id: I67fb71be57cff28a3736d5ffb9e1c39b2498feb8
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2019-11-16 11:42:10 +01:00
Dunajski, Bartosz b6015b5293 Add TimestampPacketDependencies helper 
Change-Id: I3945ac8e495baf442b4f892ba415f939e8d316da
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2019-11-13 16:04:48 +01:00
Dunajski, Bartosz 4102b9cf3d Pass single Node instead of whole Container to BlitProperties 
Change-Id: I7493e836550712633ef95e83b8349a3804df1327
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2019-11-13 09:38:31 +01:00
Dunajski, Bartosz 80407aec15 Program barrierTimestampPacketNodes only on first unblocked command 
Change-Id: I8ebba9f8326e3da2365c001b0c350efb372a3774
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2019-11-12 15:37:51 +01:00
Dunajski, Bartosz af8ce96ab4 Add move logic to TimestampPacketContainer 
Change-Id: Ib666fd57b4ca9123e324a82c3e648b0da49abffc
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2019-11-12 08:50:00 +01:00
Dunajski, Bartosz 0dafcfcce5 Remove not used variable 
Change-Id: I72f696948ca37ed7778fb081afe5f88d3abea4e9
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2019-11-08 17:35:37 +01:00
Dunajski, Bartosz ad2b8a0bbe Allow dispatching multiple blit commands with single flush 
Change-Id: I57ea32dfa8cfd89ec37fc2f1f82ee6f72598c18a
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2019-11-08 14:35:44 +01:00
Dunajski, Bartosz 2368247405 Move blit residency handling to CSR 
Change-Id: If832f9af2e98820986de87b547cc75a4c5d588d0
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2019-11-04 13:10:50 +01:00
Dunajski, Bartosz 0a702ec679 Improve aux translation logic 
- Debug flag to disable aux translation builtin dispatch
- Move MemObjsForAuxTranslation to MultiDispatchInfo

Change-Id: If6f3928440f856a0498e43df388868aa74aa60f2
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2019-10-31 12:30:40 +01:00
Lindong Wu 315d585f99 fix dispatch hints missing in task flush 
Change-Id: Iceec3d28a469a32041e67b7e00b4a02731f3fd0b
Signed-off-by: Lindong Wu <lindong.wu@intel.com>
 2019-10-23 11:31:55 +02:00
Dunajski, Bartosz a046de5689 Improve BCS waiting logic to satisfy AUB/TBX mode 
Change-Id: I52b44959b8bdc1cc66f136a4785233b95870fd0b
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2019-10-22 13:36:43 +02:00
Lindong Wu 9066192dc3 add dispatch hints for more flixable control on workload dispatch 
Change-Id: Iecfe3031172fd108a1ef0d77d2fff8ad3cef22b3
 2019-10-16 15:40:07 +02:00
Dunajski, Bartosz d3e583f7f4 Synchronize blit enqueue after barrier call 
Change-Id: I0349dc5b1581ecb142bdab881877450366bcdb86
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
Related-To: NEO-3020
 2019-10-04 14:56:30 +02:00
Cencelewska 81d587e1f9 Change arguments in creation of DispatchFlags 
Change-Id: I150e0da2bc76a665e82c308ee2094742c13c2aa3
Signed-off-by: Cencelewska <katarzyna.cencelewska@intel.com>
 2019-09-30 13:53:58 +02:00
Katarzyna Cencelewska 260759268a Add logic to change queue slice count 
Change-Id: I4f5ccb4ecb290e1a05e3a312b9fa2a5d9c5c17f7
Signed-off-by: Katarzyna Cencelewska <katarzyna.cencelewska@intel.com>
 2019-09-26 10:21:12 +02:00
Maciej Dziuban a941c53dd8 Allow lack of scheduler_simulation file 
Change-Id: I3a21af165e86983201dda4283543544bf2a09e9c
Signed-off-by: Maciej Dziuban <maciej.dziuban@intel.com>
Related-To: NEO-3545
 2019-09-25 11:29:26 +02:00
Cencelewska 03f910466e Remove default constructor of DispatchFlags 
Resolves: NEO-3394

Change-Id: I6d5d8e389e0680e698423e4e36b4f0d20d173522
Signed-off-by: Cencelewska <katarzyna.cencelewska@intel.com>
 2019-09-24 13:46:34 +02:00
Daria Hinz ae4425351f Preamble Helper Refactor 
Change-Id: Iacd05dcb6d9047fc2814895fa87d1cd9be6df446
Signed-off-by: Daria Hinz <daria.hinz@intel.com>
 2019-09-13 08:29:03 +02:00
Jobczyk, Lukasz 2e8e6bdb18 Move majority of utilities to the core dir 
Related-To: NEO-3677

Change-Id: If2e876028b765ad3ecf5f75db8755623b82955b8
Signed-off-by: Jobczyk, Lukasz <lukasz.jobczyk@intel.com>
 2019-09-12 15:07:02 +02:00
Dunajski, Bartosz 6dae106f07 Improve TimestampPacket residency flow 
- Dont call makeResident in enqueueHandler for blocked path
- Fill csrDeps for blit enqueue only in unblocked path
- Call makeResident on all dependencies during blocked command flush

Change-Id: I6658e4695483bee63eca205f85687ea5f951b099
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2019-09-04 16:33:17 +02:00
Dunajski, Bartosz 47a0c43ad3 Copy EnqueueProperties to KernelOperation in blocked path 
Change-Id: I5b9999901b5b75fc3165f9fa389857732aca2849
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
Related-To: NEO-3020
 2019-09-03 14:11:40 +02:00
Dunajski, Bartosz 712313a3be Remove not used parameter 
Change-Id: I89b8e3f3cd835b6bb3896fb3951941854e804786
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2019-09-02 14:44:32 +02:00
Dunajski, Bartosz 2275f8df0e Rename CommandMarker to CommandWithoutKernel 
Change-Id: Ie19c510465a36ea517a79db9eeac5b5993e44c81
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2019-09-02 12:53:58 +02:00
Dunajski, Bartosz e7e23cd0b4 Remove queueBlocked restriction from blitEnqueueAllowed 
Change-Id: If7fcd15cbbb4e749d16b9d028dac33a8a7b20bde
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
Related-To: NEO-3020
 2019-09-02 12:53:21 +02:00
Dunajski, Bartosz 77e22bd81b Refactor dispatching blit enqueue 
Change-Id: Ibe499e4815a16d5884510c6804221d2b74dbffd4
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
Related-To: NEO-3020
 2019-09-02 07:56:50 +02:00
Mrozek, Michal ae201a47d3 Improve uncached resources handling. 
- Change kernel to properly detect true stateless resources
- do not turn of stateless l3 if arg is used in pure stateful manner
- refactor variable names to better reflect what they do
- improve mock kernel with internal to have setKernelArg capabilties

Change-Id: I2cdde04f2144d9b86dc1486126632db0fd7cad49
Signed-off-by: Mrozek, Michal <michal.mrozek@intel.com>
 2019-08-30 10:51:28 +02:00
Mrozek, Michal cb4e5576cb Pass proper dispatch flags. 
- add new policy to select L1 caching
- this is when kernel doesn't have any stateless writes

Change-Id: I3948e652797420976159bbfec2c2a154eb9e18ee
Signed-off-by: Mrozek, Michal <michal.mrozek@intel.com>
 2019-08-26 18:15:54 +02:00
Dunajski, Bartosz 8135babfc4 Dont use default engine tag address in DeviceQueue 
Change-Id: I84b9ecd9a9e7c1ffe620af8ad54fd5d48532fa5b
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2019-08-26 13:30:18 +02:00
Mrozek, Michal f362739521 Refactor L3 programming. 
- Do not do it via member setting.
- Utilize DispatchFlags

Change-Id: I75d4c8ea6c1e10ca0edeeb0d1c3883a549c1cb1f
Signed-off-by: Mrozek, Michal <michal.mrozek@intel.com>
 2019-08-23 08:46:27 +02:00
Dunajski, Bartosz e88371ceff Minor enqueueHandler cleanup 
Change-Id: I07b2d0571b91b797b7a20ec29bb4cf1496b84f96
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2019-08-05 12:26:37 +02:00
Dunajski, Bartosz 38556cec29 Allow blocked command stream programming for commands without Kernel 
Change-Id: I691a029bd5511c8f710ef1bff8cc5a9feca644f3
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
Related-To: NEO-3433
 2019-07-24 16:01:34 +02:00
Dunajski, Bartosz 4dd3292922 TaskInformation cleanup 
Change-Id: If723f477406ca13e40c77a9471de9b8e35beff1d
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
Related-To: NEO-3433
 2019-07-23 12:04:20 +02:00
Dunajski, Bartosz 95c2dcd8b0 Improve obtaining LinearStream during enqueue call 
- Move logic to enqueueHandler to cover all scenarios
- Create BlockedCommandsData not only for Kernel enqueue
- KernelOperation cleanup

Change-Id: Ie4a673cbbc986c685996a38ab296444d38e7bbd5
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2019-07-22 18:52:14 +02:00
Dunajski, Bartosz 4e98d34471 Update dispatch flags for enqueueCommandWithoutKernel 
Change-Id: I51c8afee84b40db12901f048c03fd92fa3808c0c
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
Related-To: NEO-3020
 2019-07-22 14:50:14 +02:00
Dunajski, Bartosz cc617c0f78 Do implicit flush for blit enqueues 
Change-Id: I872f39a0ea3410b09693b2018c0b86a9a127e5a2
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
Related-To: NEO-3020
 2019-07-19 09:48:52 +02:00
Dunajski, Bartosz dda6e29254 Dont wait for BCS before enqueue completion 
Change-Id: I99fa7834e927049c2faff5dfbf44b3c2a77a1af1
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
Related-To: NEO-3020
 2019-07-17 13:15:06 +02:00
Dunajski, Bartosz 277786d433 Refactor obtaining IndirectHeaps 
Change-Id: I9ad13f35daa18b0ff7ae760749cf4cdc7416b347
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2019-07-17 11:13:49 +02:00
Dunajski, Bartosz 23e9e9e02e Register Blit CSR to CommandQueue 
Change-Id: Ib22ef934492b702990ca549bab576993b0684e98
Related-To: NEO-3020
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2019-07-17 08:04:03 +02:00