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

2695 Commits

Author SHA1 Message Date
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
kamdiedrich 350eb83f02 Move helpers files to core folder 
Change-Id: I7cd2f4afd86adc5296103f61653c6d760b4e80f5
 2019-12-31 10:39:21 +01:00
Jobczyk, Lukasz 44a9ec5c1a Make MemoryOperationsHandler adapter specific 
Change-Id: I978ecaf0fbe3cfc3b645b84d978b7d9234b28bd1
Signed-off-by: Jobczyk, Lukasz <lukasz.jobczyk@intel.com>
 2019-12-30 19:26:19 +01:00
Mateusz Jablonski 84f2185f7c Test non-default root device in api fixture 
Define max number of root devices in ults
Resolves: NEO-4000

Change-Id: Ia8da5c22a36dca3c493a9caf836fc1fb29207ef9
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2019-12-30 15:28:00 +01:00
Mateusz Jablonski be7606388c Make pointer to notifyAubCapture function a non-static variable 
move gmm callbacks to windows subdirectory

Resolves: NEO-3365
Change-Id: I073fef4b527fb5bd0d829eb672bfd71176b0d317
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2019-12-30 13:38:53 +01:00
Mateusz Jablonski 4ed3b46da1 Calculate maxOsContextCount after setting up hardware info 
Change-Id: I98e0275bc84930eea4990ce1c2281f9f82cda66a
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2019-12-30 13:15:43 +01:00
Mateusz Jablonski 14c013f53b Dont create multiple page table managers within single root device 
Resolves: NEO-4090
Change-Id: I148b9a5a2755edbcd15ead5f4a0d5d799ee815e1
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2019-12-27 04:36:51 -08:00
Kamil Kopryk b5dd3abf85 Fix for the IOCTL call to disable persistence on given context 
Change-Id: I6af1ddec3a73300d788c2c59f9f1f272a68924d6
Signed-off-by: Kamil Kopryk <kamil.kopryk@intel.com>
Related-To: NEO-4048
 2019-12-27 09:52:09 +01:00
Kamil Kopryk 07cacd4e70 Add new IOCTL call to disable persistence on given context 
Change-Id: Ia91c8240fe2fac40c067e91ce70867edb2263463
Signed-off-by: Kamil Kopryk <kamil.kopryk@intel.com>
Related-To: NEO-4048
 2019-12-23 16:18:58 +01:00
Mateusz Jablonski 6ba76147d0 Pass proper handle to initContextAuxTableRegister function 
Resolves: NEO-4082, NEO-4080, NEO-4079
Change-Id: If8d0b69126d6442e8a9a102cd21f78944f8551e9
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2019-12-23 14:19:54 +01:00
Mateusz Hoppe aaed434ded Create tested product family list 
Change-Id: I6bdd0a1f03318dec9730a05947f2496f60637623
Signed-off-by: Mateusz Hoppe <mateusz.hoppe@intel.com>
 2019-12-23 13:08:26 +01:00
Jobczyk, Lukasz eac48002ab Calculate a maxOsContextCount variable 
Change-Id: I7b2f7733be74abf4ae299396d616b249b67de58e
Signed-off-by: Jobczyk, Lukasz <lukasz.jobczyk@intel.com>
 2019-12-23 12:24:40 +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
Zbigniew Zdanowicz 6f7d83f7ab Check Windows OsContext is properly initialized 
Related-To: NEO-3639

Change-Id: I9442402a109174bbf9345d8451dba8e7ddb8c1d9
Signed-off-by: Zbigniew Zdanowicz <zbigniew.zdanowicz@intel.com>
 2019-12-20 12:25:43 +01:00
Pawel Wilma 2ca886b45d Force integer divide emulation for TGLLP A-step 
Related-To: NEO-3661

Change-Id: I305c3cfc14262a832aee749e66f3c426d3ca0343
Signed-off-by: Pawel Wilma <pawel.wilma@intel.com>
 2019-12-20 10:11:41 +01:00
Mateusz Jablonski 7ae7ec1dee Pass os interface to gmm helper's constructor 
don't access global platform to obtain os interface
Related-To: NEO-3007

Change-Id: I166023a2c7a531393d6311bf991f31d03c634ca7
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2019-12-20 00:51:32 +01:00
Jobczyk, Lukasz 2ef557bf68 Add support for unrestricted size flag in the USM 
Resolves: NEO-3960

Change-Id: Ie3557de70702b5aee53cc7c08ed602e580282979
Signed-off-by: Jobczyk, Lukasz <lukasz.jobczyk@intel.com>
 2019-12-19 15:46:34 +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
Zbigniew Zdanowicz 58fa5bd347 Add separate methods to Wddm interface to create monitor fence 
Related-To: NEO-3639

Change-Id: Id1216def65c873028eb6a577fa30ad68ebec8f19
Signed-off-by: Zbigniew Zdanowicz <zbigniew.zdanowicz@intel.com>
 2019-12-19 13:38:19 +01:00
Andrzej Swierczynski cc46cdf46c Move PageTableManager to RootDeviceEnvironment 
Related-To: NEO-2285
Change-Id: I77699b5f540b6ac5b73cf1830712a5591326b766
Signed-off-by: Andrzej Swierczynski <andrzej.swierczynski@intel.com>
 2019-12-19 12:26: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
Jobczyk, Lukasz bfa1164675 Make unified memory allocations multistorage resources 
Related-To: NEO-2998

Change-Id: I61e831568a6bbf6e751d7a2ef9c7171c633a128a
Signed-off-by: Jobczyk, Lukasz <lukasz.jobczyk@intel.com>
 2019-12-19 11:06:17 +01:00
Pawel Wilma 2ad089a40b Create MAP_ALLOCATION as non-svm allocation when host ptr tracking is disabled. 
Change-Id: I57c64706e798efa4b23e34b582be5a490d592e87
Signed-off-by: Pawel Wilma <pawel.wilma@intel.com>
 2019-12-19 10:50:07 +01:00
Michal Mrozek 8df7f4e519 Fix casting in GMM constructor. 
Change-Id: Idd5b0388278afb65224a3941c8f156e4c137bfe0
Signed-off-by: Michal Mrozek <michal.mrozek@intel.com>
 2019-12-19 09:25:08 +01:00
Aravind Gopalakrishnan 98c109ea2d Exposing downloadAllocations in base CSR 
Exposing downloadAllocation allows usage from other clients
to perform memory coherency on per allocation basis.

Change-Id: I2314d543a8db534a526a3a844ce91e1bf930c4f4
Signed-off-by: Aravind Gopalakrishnan <Aravind.Gopalakrishnan@intel.com>
 2019-12-18 23:40:26 +01:00
Jaime Arteaga e02162d301 Enable shareable buffer support (1/N) 
Define method to allocate memory in SKL using
DRM_IOCTL_I915_GEM_CREATE.

Change-Id: I3106c690eaa6ce089a21100a1839c4886580f9c0
Signed-off-by: Jaime Arteaga <jaime.a.arteaga.molina@intel.com>
 2019-12-18 22:13:14 +01:00
Mateusz Jablonski d11d3ad27e Move getDeviceIndex method to CommandStreamReceiverSimulatedCommonHw class 
Related-To: NEO-3691
Change-Id: Ie425c035fcdd1467269ead131c4bd063c8b83e08
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2019-12-18 20:43:34 +01:00
Mateusz Hoppe ff30a66624 Use correct macros for enabling tests 
Change-Id: I51f51464918a487001200337b97a542ab4e65f1a
Signed-off-by: Mateusz Hoppe <mateusz.hoppe@intel.com>
 2019-12-18 15:38:51 +01:00
Igor Venevtsev 8a059e636a Add ULTs to check rootDeviceIndex correctness in internal GraphicsAllocations 
Related-To: NEO-2941

Change-Id: I76cfae48ef88fece6fd59453493f499dbf89f43b
Signed-off-by: Igor Venevtsev <igor.venevtsev@intel.com>
 2019-12-18 14:50:10 +01:00
Dunajski, Bartosz 58772f9d20 Use ftrL3IACoherency to set coherency support 
Change-Id: I6cef76869ec90a5b00206a8f640bc77f16603c6f
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2019-12-18 14:15:26 +01:00
Maciej Dziuban 93849d6984 Split updateImgInfoMethod 
Change-Id: Ief0ecd7d0bcca77e02e946c0590674fc82ab3e69
 2019-12-18 13:38:07 +01:00
Pawel Wilma c81f0e5c17 Add check for invalid host ptr when host ptr tracking is disabled. 
Change-Id: I6aa8276c44b0bcb192d13b6a4dc36d55bd1eafb4
Signed-off-by: Pawel Wilma <pawel.wilma@intel.com>
 2019-12-18 13:33:14 +01:00
Mateusz Jablonski 3aa454a771 Move SysCalls to core 
Related-To: NEO-3982
Change-Id: Ie4797e0c83891d689dd8903716bce9292702938d
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2019-12-18 10:02:53 +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
Dunajski, Bartosz 18779537bb Linux: Obtain gpu adress space dynamically 
Change-Id: I86796e5759d81b84a9dce7c6d57e5de7b68400ac
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2019-12-18 09:08:27 +01:00
Slawomir Milczarek 74a38386a4 Switch on a support for multi-storage resources on Linux 
Related-To: NEO-2493

Change-Id: Ieb96ed309d2e1abbe349c372e0b0aabb37dc9c7f
Signed-off-by: Slawomir Milczarek <slawomir.milczarek@intel.com>
 2019-12-17 23:00:05 +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
Zbigniew Zdanowicz 2b0db66c52 Add getter to query Wddm version 
Related-To: NEO-3639

Change-Id: If066f954827982dcc388f3f0ea241dbc98e824ea
Signed-off-by: Zbigniew Zdanowicz <zbigniew.zdanowicz@intel.com>
 2019-12-17 15:27:48 +01:00
Dunajski, Bartosz 73697b7ab4 Add debug flag to override gpu address space 
Change-Id: Ifce09cf2b0f1935ce15f1a718cff36b0c44848ca
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2019-12-17 15:01:35 +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
Maciej Dziuban 72d59aaff6 Unified memory sharing 9/n 
Add support for interleaved images sharing

Change-Id: I98198c8e9870fca653d2d3e2c4e3d6c40cd2659d
Signed-off-by: Maciej Dziuban <maciej.dziuban@intel.com>
Related-To: NEO-3771
 2019-12-17 13:25:58 +01:00
Zbigniew Zdanowicz 9e5b66404d Change WDDM interface to submit command buffer 
Related-To: NEO-3639

Change-Id: Iaad6199372cd374b61a0e288ce52b5cd0d3eef4f
Signed-off-by: Zbigniew Zdanowicz <zbigniew.zdanowicz@intel.com>
 2019-12-17 12:44:45 +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
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
Dunajski, Bartosz 43db1bffed Remove duplicated ULT 
Change-Id: I92c0f55f795935e361767c30555a3a5d24e4abfc
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2019-12-17 09:22:36 +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 a611e4b97d Fix Image patching 
Change-Id: Ibd89ecf18b92ed20972352f2aa39121b4b811d81
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2019-12-16 17:41:20 +01:00
Pawel Wilma 0643a89ff9 Move TGLLP specific workarounds to HwInfo 
Related-To: NEO-3914

Change-Id: I115b28ea6e796dcc69b32105e39a68da0e5af7df
Signed-off-by: Pawel Wilma <pawel.wilma@intel.com>
 2019-12-16 16:25:18 +01:00
Zbigniew Zdanowicz 37a690a185 Destroy WDDM monitor fence during OS Context cleanup 
Change-Id: I654bc28891bcd1ec23fa18a07bef79a98edbce2e
Signed-off-by: Zbigniew Zdanowicz <zbigniew.zdanowicz@intel.com>
 2019-12-16 14:05:07 +01:00
Krzysztof Gibala 03252ee9fe Add support for write combined in unified memory 
Related-To: NEO-3374
Change-Id: I610ad2d71b056f2bc5b8f4bda72e7f08a45cf59d
Signed-off-by: Krzysztof Gibala <krzysztof.gibala@intel.com>
 2019-12-16 08:59:40 +01:00
Kamil Kopryk 2c84c143e6 Add program HDC pipeline flush prior to SBA 
Change-Id: If1223f7dbc07b6a5275a642fac27a44b87a9f97c
Signed-off-by: Kamil Kopryk <kamil.kopryk@intel.com>
Related-To: NEO-3974
 2019-12-16 08:42:45 +01:00
Maciej Dziuban e43e06192f Do not require RenderCompressed or MediaCompressed flags for compression 
Change-Id: I19782bf16b94c34a0af6de62203e2a1b5c25a359
Related-To: NEO-3771
 2019-12-16 07:53:21 +01:00
Dunajski, Bartosz 0aea86d001 Accept CL_MEM_FORCE_LINEAR_STORAGE_INTEL token 
Change-Id: I3574854c133cdab427fd0389ecc464c4e97c7328
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2019-12-13 16:10:15 +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
Andrzej Koska d135944ae0 Improving reporting VME extensions 
Change-Id: Ia7ed2d1587603d8cfed391d8d5f7c1cd1faa1c21
Signed-off-by: Andrzej Koska <andrzej.koska@intel.com>
Related-To: NEO-4047
 2019-12-13 15:34:13 +01:00
Krzysztof Gibala dded0aa3bc Remove unnecessary program of default value for allocation flags 
According to regression, remove setting value
for CL_MEM_ALLOC_DEFAULT_INTEL in MemoryPropertiesFlags

Related-To: NEO-4053
Change-Id: I1761bbf2ed8b977b7e96cebd38040c3977998b63
Signed-off-by: Krzysztof Gibala <krzysztof.gibala@intel.com>
 2019-12-13 14:33:32 +01:00
Dunajski, Bartosz bb248d6742 Rename files with the same name 
Change-Id: I46144a52d755e03587b3b1e41d1883ddf4230889
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2019-12-13 14:17:31 +01:00
Mateusz Jablonski 9f5152e823 Move linux files to core 
memory_info
engine_info
os_inc

Related-To: NEO-3982
Change-Id: I52ef357f790497fc6efcd590db277ce96ec1e579
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2019-12-13 09:23:33 +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
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
Mateusz Jablonski 495f0e8530 Remove not needed header inclusions 
use full path when include header

Change-Id: I0cae6300b86173aea0f4267282e68aa5107fc1e2
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2019-12-11 16:44:12 +01:00
Mateusz Jablonski ab2134ae8f Change subDeviceIndex to subDevicesBitfield in allocation properties 
Related-To: NEO-3691
Change-Id: I11d235107bf9b4cee75b910c114795b5df76d9c7
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2019-12-11 15:15:04 +01:00
Dunajski, Bartosz ecc54edbb3 Improve pointers passing in SVM enqueue 
Change-Id: Idf46438e8bd17476c3b3997ac35821d24ce0a081
 2019-12-11 14:38:42 +01:00
Katarzyna Cencelewska 9aa563ba2b Use MockKernelWithInternals with base initalization 
to test set of default thread arbitration policy

Change-Id: Ife60debf9dd319d5809855e983a71d7c4d128ae2
Signed-off-by: Katarzyna Cencelewska <katarzyna.cencelewska@intel.com>
 2019-12-11 12:38:18 +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
Dunajski, Bartosz 3eab5cfe35 Patch flat image params on setKernelArg 
Change-Id: Iae0f37dfcd2ee14a3874835f2e444549d1769074
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2019-12-11 08:18:55 +01:00
Mateusz Hoppe 195f610fa3 Return CL_DEVICE_HOST_UNIFIED_MEMORY cap based on local memory 
Change-Id: Ic896d9aca60a36618b30745db5bd38f98a0bd2e9
Signed-off-by: Mateusz Hoppe <mateusz.hoppe@intel.com>
 2019-12-10 17:43:17 +01:00
Zbigniew Zdanowicz 2a50c86945 Use actual MockSip object in ULTs 
Change-Id: I60016a5c2f14f9bf4391df84335856e93bf1e64f
Signed-off-by: Zbigniew Zdanowicz <zbigniew.zdanowicz@intel.com>
 2019-12-10 14:13:17 +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 1856248e7e Dont pass hostPtr for blit operation triggered by SVM enqueue 
Change-Id: I78761f71cb4debe62a41b34e22a614c5245a40ff
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2019-12-10 10:55:39 +01:00
Slawomir Milczarek 9a4e360fc2 AUB file name with suffix to indicate multiple subdevices 
Change-Id: I8a6417e0c1b30c938ce863c15c5cf91da504d330
Signed-off-by: Slawomir Milczarek <slawomir.milczarek@intel.com>
 2019-12-10 09:28:26 +01:00
Filip Hazubski f14793895e Fix SyncBufferHandler test 
Change-Id: I281d696b2b349c2189caa28e3d8a29a001e514cb
Signed-off-by: Filip Hazubski <filip.hazubski@intel.com>
 2019-12-09 18:18:41 +01:00
Mateusz Jablonski e27c5a9475 Change signature of clAddCommentINTEL function: pass device instead of platform 
Resolves: NEO-3939
Change-Id: I394ef7c2370771569a0ec50ac4644782ce8a384f
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2019-12-09 17:20:04 +01:00
Mateusz Jablonski 16c6d7eb9b Refactor ApiFixture 
- setup number of root devices
- define tested root device

Related-To: NEO-4000

Change-Id: I785d07a7f54932f66fe57637c8d10775743a871c
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2019-12-09 16:32:44 +01:00
Mateusz Jablonski 8ccadbb240 Correct clGetDeviceIDs: return all requested devices 
Related-To: NEO-4000
Change-Id: I2723b5364bf742aa490d88967c19329830f45322
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2019-12-09 15:41:06 +01:00
Gibala 5ac1d1258c Connect UnifiedMemoryProperties with MemoryPropertiesFlags 
-Add support to SvmAllocationData
-Refactor parseMemoryProperties
-Add allocation flags

Related-To: NEO-4011
Change-Id: I3728d2319aeef983dbcc3f8702da9a303a4e2b9c
Signed-off-by: Gibala <krzysztof.gibala@intel.com>
 2019-12-09 14:23:46 +01:00
Jobczyk, Lukasz ac0471adc5 Remove padding allocation 
Change-Id: I0017640ee22b687af1d85fa10d221d2b3cafed0a
Signed-off-by: Jobczyk, Lukasz <lukasz.jobczyk@intel.com>
 2019-12-09 13:39:39 +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 8c604a6e16 FLAT_IMAGE patch tokens support 
Change-Id: I9f4ea389871113842311de9ef4ac7bf74f7a46fa
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2019-12-09 08:49:04 +01:00
Dunajski, Bartosz 3014b304ca Refactor STATE_BASE_ADDRESS programming 
Change-Id: I977867678ea980f17cbe6ceef51c4f05096c809f
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2019-12-07 19:00:45 +01:00
Jaroslaw Chodor 72a1542140 [2/N] Program refactor - gather compiler options 
Change-Id: I0a614be73fbd87184be2dfea407582a58c27b0bc
 2019-12-06 22:17:19 +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
Dunajski, Bartosz 232dc59cde Make specific SBA heaps programming optional 
Change-Id: I852a9e1d9bcc5d6227b1e8a81ab81ad896d6586f
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2019-12-06 12:52:21 +01:00
Pawel Wilma 632134db30 Disable host ptr tracking for GEN12LP 
Related-To: NEO-3661

Change-Id: I1774aad8ef32f294192a9b679cb9f66e4091198c
Signed-off-by: Pawel Wilma <pawel.wilma@intel.com>
 2019-12-06 11:57:32 +01:00
Dunajski, Bartosz 566b845bbc Move state_base_address to core 
Change-Id: I2b64fff4eed31054ae29b7b14ecb9f147914049a
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2019-12-06 09:01:24 +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
Filip Hazubski 7be937c226 Update clCreateSubDevices implementation 
Make it possible to get SubDevices from given RootDevice.

Resolves: NEO-3977

Change-Id: I9cf06f17b45299009ab6953b9ad7d5cb0bbe848f
Signed-off-by: Filip Hazubski <filip.hazubski@intel.com>
 2019-12-04 16:38:07 +01:00
Mateusz Jablonski 73dad03c66 Fix clSVMAlloc function: use device from context 
Related-To: NEO-4000

Change-Id: Iefad9d7a8908a584b98801bdbe13aa1e0be2e47f
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2019-12-04 16:27:54 +01:00
Dunajski, Bartosz dfc50f3a75 Move gmm_helper to core 
Change-Id: I31ca317d10697ab884e04f443c8ccfdd6ca9d2ae
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2019-12-04 15:25:32 +01:00
Dunajski, Bartosz c0cafccacb Fix command container tests cmake generation 
Change-Id: Ie7dcad6aefc375aa0c344764f10683d4b22ace8c
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2019-12-04 15:22:01 +01:00
Mateusz Hoppe dfce56d634 Cleanup headers in print_formatter and move to core 
Change-Id: I2ef5498927b02e0371dc4e484f94b00b4f86721c
Signed-off-by: Mateusz Hoppe <mateusz.hoppe@intel.com>
 2019-12-04 13:37:11 +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 ec21f06427 Move GMM-OCL types conversions to new helper + includes cleanup 
Change-Id: I13e5917a32a5cd894ee42a848407fe20bf1daa06
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2019-12-04 10:42:49 +01:00
Michal Mrozek 6847893e02 Add support for querying device from usm allocations. 
Change-Id: I8aad69622e3af1ebec74ee9d325340b02ca9a6b2
Signed-off-by: Michal Mrozek <michal.mrozek@intel.com>
 2019-12-04 09:28:06 +01:00
Michal Mrozek e234c89ee4 Change makeResident to be non virtual function. 
- remove wddm version, not a lot of value there as residency is logged
in processResidency anyway.

Change-Id: Icb2814cfce0e8f3cd75445f1fd2e2f8535d476cc
Signed-off-by: Michal Mrozek <michal.mrozek@intel.com>
 2019-12-04 07:29:00 +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
Dunajski, Bartosz b308906999 Return 1 as PreferredTagPoolSize for CSR with aub dump 
Change-Id: I33fbd8131bdd8579cf3e5bbfdc5ea6d66a5c74b6
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2019-12-03 13:42:36 +01:00
Filip Hazubski 2ead0e6910 Update Device::getDeviceBitfield() 
Related-To: NEO-2712

Change-Id: I609f55c9a0ee637dcef7cb176728f2ae65499a58
Signed-off-by: Filip Hazubski <filip.hazubski@intel.com>
 2019-12-03 12:45:23 +01:00
Michal Mrozek 83c0f80431 Avoid casting void* to uint64_t. 
- Add new wrapper that accepts const void *.

Change-Id: I1cea088b563cf704b6673844b533ce44f388e5fc
Signed-off-by: Michal Mrozek <michal.mrozek@intel.com>
 2019-12-03 11:55:26 +01:00
Mateusz Jablonski ee544e2515 Reorder members and methods in Device class 
Related-To: NEO-3938

Change-Id: I18e6ed4b301d5e221263ced5a3213b54dd21745a
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2019-12-03 10:22:31 +01:00
Dunajski, Bartosz 4bcbd476d9 Add missing override 
Change-Id: I8bddaf940b5f7f3920da350cbedb9af9a5cbbd97
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2019-12-03 06:48:50 +01:00
Dunajski, Bartosz 0527c9113c Disable TimestampPacket optimizations in Aub/Tbx mode 
Avoid removing semaphores and reusing returned tags

Change-Id: Ic26167953c5d5a9ccceaae49f4921af11a375fab
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2019-12-02 15:38:13 +01:00
Mateusz Jablonski 54f65c0243 Move headers to core 
- hw_info
- hw_cmds
- kmd_notify_properties
- completion_stamp
- bxml_generator_glue

Related-To: NEO-3982
Change-Id: I3ed3ef81f42596f381e60c19250f6eb1296d47a4
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2019-12-02 14:20:45 +01:00
Marcin Naczk c6354c8741 add output_file_list flag 
Change-Id: I8cec83eaf39db306622ac9d399399ef54397d613
 2019-12-02 13:57:16 +01:00
Filip Hazubski 0270ad8015 Add pointer checks 
Change-Id: I37a6898670a4d9e66f0eff404b5282714f293956
Signed-off-by: Filip Hazubski <filip.hazubski@intel.com>
 2019-12-02 12:57:02 +01:00
Michal Mrozek 04b4198228 Use castToUint64 while casting form void* to uint64_t. 
- Otherwise the uint64_t GPU address may not be proper
- The sign bit is propagated while reinterpret_cast is happening
causing wrong address to be generated.

i.e. in 32 bit application:
void* address = 0xffff0000;
unit64_t gpuAddress = reinterpret_cast<uint64_t>(address);

gpuAddress is equal to 0xffffffffffff0000 instead of 0x00000000ffff0000.

Change-Id: I36665651d615c3ab612b2cea375fa539edc7d08d
 2019-12-02 12:50:33 +01:00
Adam Cetnerowski 8f46761262 ULT renaming: Flush tests 
Related-To: NEO-2236

Change-Id: I86fbac1205dba63d4b8918d4eeec215428bb5949
Signed-off-by: Adam Cetnerowski <adam.cetnerowski@intel.com>
 2019-12-02 09:08:33 +01:00
Gibala 43dd16e1b8 Add unit tests to check value shift 
Related-To: NEO-3962
Change-Id: Ia3ba560201dd495a22742ef9fef767d6aa4c35f9
Signed-off-by: Gibala <krzysztof.gibala@intel.com>
 2019-11-29 15:23:34 +01:00
Dunajski, Bartosz b1fbced81f Fix completion check for TimestampPacketStorage 
Change-Id: If15d2bbc49a1dc2dfb29e3b6cdc3ad1523997cd5
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2019-11-29 14:43:11 +01:00
Mateusz Jablonski 244146c203 Move Device::getProductAbbrev method to MockDevice 
Change-Id: Ia146d0198039b526e563a44d76710ac175ea3b88
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2019-11-29 11:12:08 +01:00
Michal Mrozek b937b54064 Remove 32 bit code. 
- Enable local memory in 32 bit scenarios.

Change-Id: I091570a3d0aa6043febf2721480196425e058978
Signed-off-by: Michal Mrozek <michal.mrozek@intel.com>
 2019-11-28 17:50:42 +01:00
Jaroslaw Chodor 102bceb4c9 Adding bindless compilation toggles 
Change-Id: I35e37e9319a660fe0e4588f7abdc821557948b18
 2019-11-28 15:23:24 +01:00
Dunajski, Bartosz 6dddcbd812 Simplify block copy command interface 
Change-Id: I9c89fdb05bc7734e29678fd396bb6f5bc58e919a
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2019-11-28 15:06:35 +01:00
Filip Hazubski 5bed747e33 Update Program::extractInternalOptions 
Change-Id: Ie67a8ef7b6f010a44b252666e9d9ef48fdeac9e0
Signed-off-by: Filip Hazubski <filip.hazubski@intel.com>
 2019-11-28 15:04:28 +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
Adam Cetnerowski 0ba31a46cb ULT renaming: Write image & buffer tests 
Related-To: NEO-2236

Change-Id: Ida866017f17795140817f9fbdca80def8d00e4c8
Signed-off-by: Adam Cetnerowski <adam.cetnerowski@intel.com>
 2019-11-28 14:27:47 +01:00
Pawel Wilma a08fb12c4c Revert "Disable host ptr tracking for GEN12LP+" 
Related-To: NEO-3661

This reverts commit 8f6a390a2f.

Change-Id: Ib17543e2c2c7e47c92bbc010d376dd53c6116b59
Signed-off-by: Pawel Wilma <pawel.wilma@intel.com>
 2019-11-28 13:02:07 +01:00
Dunajski, Bartosz 1dcc059826 Dont overallocate Tag nodes 
Change-Id: Ia92ed66dbe8d5c0577c612c7e6229e4c12d1426a
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2019-11-28 12:47:00 +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 af47464d89 Expect blitterOperationsSupported if default AuxTranslationMode is Blit 
Change-Id: Ia4338730b23711f09b5f27a8f8d51fd7e0c1400d
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2019-11-28 12:17:55 +01:00
Michal Mrozek a38a0bfe4d Use address above restriction to remove sporadic behavior from test. 
Change-Id: Iea3286ffab078a6762be1cfd3bac468f0a10c356
Signed-off-by: Michal Mrozek <michal.mrozek@intel.com>
 2019-11-28 11:35:41 +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
Zbigniew Zdanowicz 7781650586 Simplify Preemption interface and get device preemption once 
Change-Id: Iaab9b9b60a71651125df27dece1a68e9c9435143
Signed-off-by: Zbigniew Zdanowicz <zbigniew.zdanowicz@intel.com>
 2019-11-27 16:28:45 +01:00
Adam Cetnerowski a0cbc21919 ULT renaming: Finish tests 
Related-To: NEO-2236

Change-Id: I2233ce516b6e8e09191ccdb0733f53fee0a29b6d
Signed-off-by: Adam Cetnerowski <adam.cetnerowski@intel.com>
 2019-11-27 14:54:46 +01:00
Michal Mrozek 0071964138 Do not call malloc for Virtual Alloc mock. 
Change-Id: Ic6689716c4f4cdfa8f18eaccb39e375f9f48b56c
Signed-off-by: Michal Mrozek <michal.mrozek@intel.com>
 2019-11-27 14:44:14 +01:00
Pawel Wilma 8f6a390a2f Disable host ptr tracking for GEN12LP+ 
Related-To: NEO-3661

Change-Id: I969bc70efc65b167996329ea02a29134ffc1ef8c
Signed-off-by: Pawel Wilma <pawel.wilma@intel.com>
 2019-11-27 14:25:55 +01:00
Jaroslaw Chodor fd0d69e144 Fixing race condition in compiler interface 
Change-Id: Iba3e4c3213cff7750260539849c630b3c66d98ca
 2019-11-27 13:29:34 +01:00
Adam Cetnerowski b00a058173 ULT renaming: Unmapping Memory Object tests 
Related-To: NEO-2236

Change-Id: Icf6c3340bef9a7eff2e6715168678ef7ceb2c59d
Signed-off-by: Adam Cetnerowski <adam.cetnerowski@intel.com>
 2019-11-27 12:47:43 +01:00
Michal Mrozek fd17b391c8 Remove 32 bit code paths from allocation schemes. 
Change-Id: I4825ff504abacdd4c08ac49c7d678daa100d23dc
Signed-off-by: Michal Mrozek <michal.mrozek@intel.com>
 2019-11-27 11:19:40 +01:00
Dunajski, Bartosz aafebb2e85 Skip dumping aub allocations on BCS engine 
Change-Id: I7d1cf3b0a0d6e16fd2df2fad1ba5e71dfe04ae23
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2019-11-26 12:52:05 +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
Jaroslaw Chodor f58e9bce8a Add test to ensure tokens decoding 
Change-Id: I3d02de8a539e483d343e0385d00fb64b8c05ab8a
 2019-11-26 12:15:11 +01:00
Adam Cetnerowski b2877d3725 ULT renaming: Enqueue SVM tests 
Related-To: NEO-2236

Change-Id: I9c569846a5a0f16b65566d1d5f52cc98b49b19f7
Signed-off-by: Adam Cetnerowski <adam.cetnerowski@intel.com>
 2019-11-26 08:35:27 +01:00
Jaroslaw Chodor c2bc814ac9 Adding support for new relocation types 
Change-Id: I52e20542b8d7a6ca46e6d8b8ce715cc5b5ace428
 2019-11-25 23:39:59 +01:00
Jaroslaw Chodor 355e8d3e5a [1/N] Program refactor - decouple from patchokens 
Change-Id: I63bbf6c31a5db9e788124f22b6105e65c16c86d4
 2019-11-25 19:46:21 +01:00
Artur Harasimiuk cf8283cc9a clang-tidy improvements and code fixes 
Related-To: NEO-562
Change-Id: Iab9d1ed35e64c9fce849e1b0654ec65f731302e8
Signed-off-by: Artur Harasimiuk <artur.harasimiuk@intel.com>
 2019-11-25 16:06:34 +01:00
Dunajski, Bartosz 61b6d5248d Allocation offset support for BufferToBuffer blit operation 
Change-Id: Ib4a6bd856d123371ea3f667a74a9448953a0b8ca
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2019-11-25 13:13:48 +01:00
Michal Mrozek 0574372efe Merge 2 image tests. 
Change-Id: I537eb18e8feeea4ec1529b903654deed8bd4f252
Signed-off-by: Michal Mrozek <michal.mrozek@intel.com>
 2019-11-25 12:58:55 +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
Pawel Wilma 9b84d8f5ba Use RCS as default engine for TGL LP A0 
Related-To: NEO-3741

Change-Id: Iac79ff5e7142a3ee74990048fcc84565639a2da2
Signed-off-by: Pawel Wilma <pawel.wilma@intel.com>
 2019-11-25 12:24:20 +01:00
Pawel Cieslak f5b2110ac7 Check for limits when setting values from hw config string. 
Related-To: NEO-3841

Change-Id: I80001a1bc25ae839578b9ca92fd7b32ac664ed6e
Signed-off-by: Pawel Cieslak <pawel.cieslak@intel.com>
 2019-11-25 11:37:02 +01:00
Dunajski, Bartosz 7727cb230a Add missing override 
Change-Id: I47bbe57121534cc24b3fb0969a57e5fead498040
 2019-11-25 11:13:28 +01:00
Adam Cetnerowski c5229e9514 ULT renaming: Read image tests 
Related-To: NEO-2236

Change-Id: I426f311702630db48f952d5a265804839db162d2
Signed-off-by: Adam Cetnerowski <adam.cetnerowski@intel.com>
 2019-11-22 20:36:17 -08:00
Adam Cetnerowski c2ab0b1b94 ULT renaming: Write buffer rect tests 
Related-To: NEO-2236

Change-Id: I1ded69858ed6998fe03669383fd697129488a0b7
Signed-off-by: Adam Cetnerowski <adam.cetnerowski@intel.com>
 2019-11-22 16:41:47 +01:00
Maciej Plewka 49cde627c4 Adding Command container implementation 
Change-Id: Ic2c4b9128fa0275fd10db6e37b89a1f36aee60bc
Signed-off-by: Maciej Plewka <maciej.plewka@intel.com>
 2019-11-22 15:52:22 +01:00