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

463 Commits

Author SHA1 Message Date
Mateusz Jablonski c7755c2c48 Move files to core 
engine_node_helper
kmdaf_listener
wddm_engine_mapper
windows_defs

Related-To: NEO-3982
Change-Id: Ia39342059bdeafa97d17f286c167138e5c40553c
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2019-12-11 17:39:14 +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
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
Dunajski, Bartosz 32d1869d4f Pass svm allocations during SVMMemcpy 
Change-Id: Ief9e5f6b96f870ac9bf152c88f0d21ff4654ac21
 2019-12-06 15:13:32 +01:00
Kamil Kopryk baba643844 Added support for stateless enqueueSVMMemFill 
Change-Id: Ieaef91def4097c7dce618e24917c4f55cb2b914c
Signed-off-by: Kamil Kopryk <kamil.kopryk@intel.com>
Related-To: NEO-3314
 2019-12-06 15:01:29 +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
Kamil Kopryk ec63a03337 Added support for stateless enqeueueSVMMemcpy 
Change-Id: I1690735b7888b29572b75756d38698305805b7cb
Signed-off-by: Kamil Kopryk <kamil.kopryk@intel.com>
Related-To: NEO-3314
 2019-12-03 19:00:47 +01:00
Dunajski, Bartosz 1ecad5faed Move IndirectHeap to core and improve unit tests 
Change-Id: If7e329fc12fe934eb0f6b1762d3b0d86aab287e6
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2019-12-03 15:06:27 +01:00
Dunajski, Bartosz 614156dd8b Move cache_policy to core 
Change-Id: I16be70d15f329117539fe6dfcc07c6dc10d54977
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2019-12-03 14:53:49 +01:00
Filip Hazubski 0193b3ea69 Change maxNBitValue to a constexpr function 
Now maxNBitValue can be used with run time variables.

Change-Id: I323071400305e05e6303a33e24e90c521246d73f
Signed-off-by: Filip Hazubski <filip.hazubski@intel.com>
 2019-11-28 14:40:16 +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 3f43224e1b Make EXTERNAL_HOST_PTR one time aub writable 
Change-Id: Ib8ac51ebad8997a0b10431d8c78239dc38beb616
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2019-11-28 09:25:07 +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
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
Gibala Krzysztof de83356b10 Program all semaphores dependencies 
Related-To: NEO-3902
Change-Id: I5d8581cf4d1d50bc63626046972336b92af2a071
Signed-off-by: Gibala Krzysztof <krzysztof.gibala@intel.com>
 2019-11-22 08:53:59 +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
Kamil Kopryk 5ecb9905c9 Add support for stateless copy image to buffer 
Change-Id: I91d1a45d87a5984e0bb7fdb302a716ffcea7bfc8
Signed-off-by: Kamil Kopryk <kamil.kopryk@intel.com>
Related-To: NEO-3314
 2019-11-19 17:17:12 +01:00
Piotr Maciejewski f2d0606301 Performance Counters: gen12 support 
Change-Id: I40ccf4958636fc9ffa9778c7abd9e1663c4bb7e4
 2019-11-19 16:58:04 +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
Zbigniew Zdanowicz b31e25dbb6 Move PreemptionHelper class to core 
Change-Id: I172c4beb8ea2576505d6192585d45cfa3d00da34
Signed-off-by: Zbigniew Zdanowicz <zbigniew.zdanowicz@intel.com>
 2019-11-18 23:59:28 +01:00
Kamil Kopryk 9d705e7905 Add support for stateless copy buffer to image 
Change-Id: I494a64ecea8ff184626eeee3069de16f37e5b24b
Signed-off-by: Kamil Kopryk <kamil.kopryk@intel.com>
Related-To: NEO-3314
 2019-11-18 14:06:06 +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
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
Michal Mrozek e7901775a8 Improve enqueue kernel error handling. 
- Do not allow to enqueue parent kernel if there is no device queue.

Change-Id: I0f06b8ed2387fc87abd652653f2c8bb8c4939a12
Signed-off-by: Michal Mrozek <michal.mrozek@intel.com>
 2019-11-13 19:29:19 +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 50f9674d79 Change HostPtrSurface ownership to target CSR 
Change-Id: I56ab5f7f961f92cf195600b11e836d2f264c9d0d
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2019-11-08 18:11:37 +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
Kamil Kopryk b2fbab7f28 Add support for stateless write buffer rect 
Change-Id: Id10c97ff2b7c07ca828b17d6bcbc36e97fadfb83
Signed-off-by: Kamil Kopryk <kamil.kopryk@intel.com>
Related-To: NEO-3314
 2019-11-07 16:13:04 +01:00
Kamil Kopryk 0ef81b2bc0 Add support for stateless read buffer rect 
Change-Id: I794be4cacaa9de661c0c7e6ec67da85b0d5eed9a
Signed-off-by: Kamil Kopryk <kamil.kopryk@intel.com>
Related-To: NEO-3314
 2019-11-07 16:07:03 +01:00
Kamil Kopryk 011701ee5e Fix for forceStateless check 
Change-Id: Ic1d4787c3d8c7bdd70f13451d703bbc9958af7c7
Signed-off-by: Kamil Kopryk <kamil.kopryk@intel.com>
Related-To: NEO-3314
 2019-11-07 08:28:51 +01:00
Dunajski, Bartosz afb96b0b57 Change temporary allocations cleanup order 
Change-Id: I7c6d52d985da14fb6c7a0bd15e4384c1ddfae622
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2019-11-05 15:36:33 +01:00
Kamil Kopryk 1bfe9f548e Add support for stateless write buffer 
Change-Id: Ie5d5abc9fac268c3467cafed5741828d84b13795
Signed-off-by: Kamil Kopryk <kamil.kopryk@intel.com>
Related-To: NEO-3314
 2019-11-05 12:04:10 +01:00
Kamil Kopryk 2599a712fe Add support for stateless read buffer. 
Change-Id: Iadf46a6d8651de3fd6bb07efc0eda278e04c86f6
Signed-off-by: Kamil Kopryk <kamil.kopryk@intel.com>
Related-To: NEO-3314
 2019-11-05 12:03:29 +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 63f177e9dc Add method and debug flag to obtain aux translation mode 
Change-Id: I86ab1f7847ce61bf653e6be2affd5dafb4f8b211
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2019-10-31 14:47:15 +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
Kamil Kopryk dc0272d86a Add support for stateless fill buffer 
Change-Id: I6dac17090e499f013916b1ba2f2b6d0de47f51a3
Signed-off-by: Kamil Kopryk <kamil.kopryk@intel.com>
Related-To: NEO-3314
 2019-10-30 12:27:04 +01:00
Kamil Kopryk 60237e1f80 Add support for stateless copy buffer rect 
Change-Id: I9781b0d8bd863d8d5087dac6aa6a076005187afb
Signed-off-by: Kamil Kopryk <kamil.kopryk@intel.com>
Related-To: NEO-3314
 2019-10-29 14:15: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