intel/compute-runtime
1
0
Fork 0
mirror of https://github.com/intel/compute-runtime.git synced 2025-12-25 05:24:02 +08:00
Code Issues Packages Projects Releases Wiki Activity
3,769 Commits 42 Branches 655 Tags
2bc7ca84acedcd72fa66f088171fd817987967ff
Commit Graph

474 Commits

Author SHA1 Message Date
kamdiedrich
9d75828bab move files to core folder 
gdi_interface
os_inc
thk_wrapper
api_intercept
perf_profiler

Change-Id: I943807da06da31244c7c2540dcba2747f4f05b70
 2020-01-09 08:05:43 +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
Mateusz Hoppe
51f7ca1601 Move files to core 
- runtime/gmm_helper files
- engine_control.h
- allocation_properties.h

Change-Id: I108888d639c8fdb298eda00fb1e7961b2ccb26cd
Signed-off-by: Mateusz Hoppe <mateusz.hoppe@intel.com>
 2020-01-02 15:57:05 +01:00
Mateusz Jablonski
142d1f8089 Prevent nullptr dereference in enqueue svm free 
Change-Id: I89ce01be377869c482f68ac19b626baa81f6d0f8
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2019-12-27 09:36:00 +01:00
Dunajski, Bartosz
2c63a956ad Simplify PerfCounter initialization 
Change-Id: Ia393088a80ac7b439efb5e40b70e593e3891cbc5
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2019-12-19 14:25:45 +01:00
Dunajski, Bartosz
8f5e9c8a3a Refactor PerfCounters initialization. Allow only 1 engine type at once 
Change-Id: I14ba28adb1926b0e67e5b147b7391a7284617c29
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2019-12-19 11:50:31 +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
Dunajski, Bartosz
559c67aa7c Execution Model heaps programming cleanup 
Change-Id: I501357f5ad3f7308397364073691b4efd3e7260d
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2019-12-17 14:12:50 +01:00
Dunajski, Bartosz
211ba8adcb Dont call virtual method in CSR destructor 
Change-Id: Idccea2ad8f5bc6ff9933e4f9f1f0549db5ce6a99
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2019-12-17 12:14:38 +01:00
Katarzyna Cencelewska
d60b121735 Remove problems with null pointers in enqueue files 
Change-Id: I751ea4a134deac5a2b87ea258b76f2dfb2c0900d
Signed-off-by: Katarzyna Cencelewska <katarzyna.cencelewska@intel.com>
 2019-12-17 09:19:41 +01:00
Mateusz Hoppe
5685b285f3 Extract logging logic from DebugSettingsManager 
Change-Id: I0ccc68216c1c3bb23d0389bec17124e09e4f98e1
Signed-off-by: Mateusz Hoppe <mateusz.hoppe@intel.com>
 2019-12-13 15:34:45 +01:00
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