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

802 Commits

Author SHA1 Message Date
Mateusz Hoppe 8fd65cc6bf Do not append debugKernelEnable internal option 
- module compilation does not need it when L0 debugger used

Signed-off-by: Mateusz Hoppe <mateusz.hoppe@intel.com>
 2021-05-11 08:20:22 +02:00
Compute-Runtime-Validation dd6653892e Revert "Move SVM allocs memory manager to L0::Context (1/N)" 
This reverts commit 9080e2ee5b.

Signed-off-by: Compute-Runtime-Validation <compute-runtime-validation@intel.com>
 2021-05-09 12:37:44 +02:00
Jim Snow ea516527ea Add zello_image L0 black box test 
Signed-off-by: Jim Snow <jim.m.snow@intel.com>
 2021-05-08 01:16:08 +02:00
Jaime Arteaga 9080e2ee5b Move SVM allocs memory manager to L0::Context (1/N) 
Signed-off-by: Jaime Arteaga <jaime.a.arteaga.molina@intel.com>
 2021-05-07 22:17:10 +02:00
Dominik Dabek 47256642c3 Enable Level Zero on ADLS, RKL 
Signed-off-by: Dominik Dabek <dominik.dabek@intel.com>
 2021-05-07 22:08:50 +02:00
Young Jin Yoon 71f777c170 Add append_launch_kernel ULTs for cmdlist_imm 
Related-To: LOCI-2183
Signed-off-by: Young Jin Yoon <young.jin.yoon@intel.com>
 2021-05-07 21:09:13 +02:00
Jaime Arteaga 5f0e4f8e2a Revert "Move memory managers to L0::Context (1/N)" 
This reverts commit 9ce887b8b53a787a7e0a0d808c96e295655ae57b.


Signed-off-by: Jaime Arteaga <jaime.a.arteaga.molina@intel.com>
 2021-05-06 04:56:09 +02:00
Young Jin Yoon 47529148ee Move cache_flush_test to gen12lp directory 
Related-To: LOCI-1877
Signed-off-by: Young Jin Yoon <young.jin.yoon@intel.com>
 2021-05-06 01:52:12 +02:00
Jaime Arteaga 1f1fbb193b Move memory managers to L0::Context (1/N) 
Signed-off-by: Jaime Arteaga <jaime.a.arteaga.molina@intel.com>
 2021-05-05 23:01:42 +02:00
Bartosz Dunajski 9458638718 Affinity mask helper 
Signed-off-by: Bartosz Dunajski <bartosz.dunajski@intel.com>
 2021-05-05 13:59:12 +02:00
Jaime Arteaga d66f855e22 Correctly report ZE_DEVICE_FP_FLAG_ROUNDED_DIVIDE_SQRT if available 
Signed-off-by: Jaime Arteaga <jaime.a.arteaga.molina@intel.com>
 2021-05-05 00:28:51 +02:00
Young Jin Yoon 6f555d6258 Use L3_CONTROL only for DG1 
Related-To: LOCI-1877
Signed-off-by: Young Jin Yoon <young.jin.yoon@intel.com>
 2021-05-04 10:42:06 +02:00
Mateusz Hoppe a79f67958e Report max subslices count in L0 device properties 
Related-To: LOCI-2080

Signed-off-by: Mateusz Hoppe <mateusz.hoppe@intel.com>
 2021-05-04 10:17:21 +02:00
Jaroslaw Chodor 83143c4318 Changing win dev discovery to DXCoreAdapterFactory 
Signed-off-by: Jaroslaw Chodor <jaroslaw.chodor@intel.com>
 2021-04-30 15:57:35 +02:00
Mateusz Hoppe 352254416f Use all registered engines when initializing SBA tracking buffers 
Related-To: NEO-5803

Signed-off-by: Mateusz Hoppe <mateusz.hoppe@intel.com>
 2021-04-29 17:29:59 +02:00
Filip Hazubski 785be7ffd9 Update programFrontEnd function 
Use properties required by command list when VFE_STATE is programmed by
command queue.

Related-To: NEO-4940, NEO-4574

Signed-off-by: Filip Hazubski <filip.hazubski@intel.com>
 2021-04-29 16:37:23 +02:00
Filip Hazubski 3a2281bf77 Program additional VFE_STATE instructions when needed 
Additonal VFE_STATEs may be programmed when appending kernels to a
command list and when the command list is executed.

Related-To: NEO-4940, NEO-4574

Signed-off-by: Filip Hazubski <filip.hazubski@intel.com>
 2021-04-28 16:07:55 +02:00
Zbigniew Zdanowicz edc0a93927 Add preemption synchronization flag to command queue 
Related-To: NEO-5778

Signed-off-by: Zbigniew Zdanowicz <zbigniew.zdanowicz@intel.com>
 2021-04-28 13:14:18 +02:00
Zbigniew Zdanowicz c0b0013bfc Fix offset calculations for imported host pointer allocations 
Related-To: NEO-5126

Signed-off-by: Zbigniew Zdanowicz <zbigniew.zdanowicz@intel.com>
 2021-04-28 10:08:05 +02:00
Jaime Arteaga b48192bcfe Use uint64_t for sizes to support large sizes 
Signed-off-by: Jaime Arteaga <jaime.a.arteaga.molina@intel.com>
 2021-04-27 20:41:41 +02:00
Dominik Dabek bb9d902899 Add padding for ISA allocations 
Related-To: NEO-5771
Signed-off-by: Dominik Dabek <dominik.dabek@intel.com>
 2021-04-27 11:03:58 +02:00
Krystian Chmielewski ef71915c71 Remove KernelArgInfo and use KernelDescriptor's args instead 
Related-To: NEO-4729
Signed-off-by: Krystian Chmielewski <krystian.chmielewski@intel.com>
 2021-04-23 15:12:09 +02:00
Zbigniew Zdanowicz 902cce597a Add new functionality to load SIP from file 
Related-To: NEO-5718

Signed-off-by: Zbigniew Zdanowicz <zbigniew.zdanowicz@intel.com>
 2021-04-23 13:48:26 +02:00
Bartosz Dunajski 176270114b Simplify RootDevice class 
Signed-off-by: Bartosz Dunajski <bartosz.dunajski@intel.com>
 2021-04-22 17:41:52 +02:00
Daria Hinz 53104e0830 Add a parameter to the encode function 
Signed-off-by: Daria Hinz <daria.hinz@intel.com>
 2021-04-22 12:07:16 +02:00
Konstanty Misiak 62d52ba2e9 Fix DG1 tests fail 
Related-To: NEO-5679

Signed-off-by: Konstanty Misiak <konstanty.misiak@intel.com>
 2021-04-21 18:47:22 +02:00
Jaime Arteaga ef5174f3fc Eliminate wrappers in L0::Context class for driverHandle calls 
Signed-off-by: Jaime Arteaga <jaime.a.arteaga.molina@intel.com>
 2021-04-20 23:50:23 +02:00
Jaime Arteaga 5259428647 Add UNRECOVERABLE_IF to getPeerAllocation() 
Signed-off-by: Jaime Arteaga <jaime.a.arteaga.molina@intel.com>
 2021-04-20 15:18:49 +02:00
Maciej Dziuban a367476558 Disable deferred OsContext creation by default 
Related-To: NEO-5610
Signed-off-by: Maciej Dziuban <maciej.dziuban@intel.com>
 2021-04-20 10:50:54 +02:00
Jaime Arteaga 128cd8a31c Add support for non-IPC P2P access to L0 
Signed-off-by: Jaime Arteaga <jaime.a.arteaga.molina@intel.com>
 2021-04-20 01:05:40 +02:00
Jaime Arteaga b95198bac5 Add relaxed memory support to L0 host allocations 
Signed-off-by: Jaime Arteaga <jaime.a.arteaga.molina@intel.com>
 2021-04-20 00:15:38 +02:00
Jitendra Sharma 8a6247d82d Implement ze_device_memory_properties_t.maxClockRate 
Signed-off-by: Jitendra Sharma <jitendra.sharma@intel.com>
 2021-04-19 22:36:26 +02:00
Vinod Tipparaju b5d2d7fc52 Use flushTask() for non-kernel opertaions. Enabled for following APIs 
appendSignalEvent, appendWaitOnEvent, appendResetEvent and appendBarrier
except for TimeStamp events.

Related-To: LOCI-1987

Signed-off-by: Vinod Tipparaju <vinod.tipparaju@intel.com>
 2021-04-19 22:24:47 +02:00
Mateusz Hoppe ffc310858a Add DebugVariable to control opt-disable when debugger is used 
Resolves: NEO-5760

Signed-off-by: Mateusz Hoppe <mateusz.hoppe@intel.com>
 2021-04-19 16:41:14 +02:00
Maciej Dziuban 5318ff1872 Defer OsContext initialization 
Signed-off-by: Maciej Dziuban <maciej.dziuban@intel.com>
Related-To: NEO-5610
 2021-04-19 11:54:34 +02:00
Daria Hinz b18b4e8ad7 Event: Extending the number of timestamp packets 
Signed-off-by: Daria Hinz <daria.hinz@intel.com>
 2021-04-17 20:13:15 +02:00
Compute-Runtime-Validation b5545c2a50 Revert "Implement ze_device_memory_properties_t.maxClockRate" 
This reverts commit c3b63bd8a2.

Signed-off-by: Compute-Runtime-Validation <compute-runtime-validation@intel.com>
 2021-04-17 10:21:25 +02:00
Mayank Raghuwanshi 61c08c052f Implement zesDriverEventListenEx 
Signed-off-by: Mayank Raghuwanshi <mayank.raghuwanshi@intel.com>
 2021-04-17 04:25:35 +02:00
Jaime Arteaga ebb1474210 Isolate shared allocations with respect to context 
Related-To: LOCI-1996

Signed-off-by: Jaime Arteaga <jaime.a.arteaga.molina@intel.com>
 2021-04-17 03:38:46 +02:00
Jitendra Sharma c3b63bd8a2 Implement ze_device_memory_properties_t.maxClockRate 
Current implementation of ze_device_memory_properties_t.maxClockRate
is providing max dynamic frequency of GPU not the max memory frequency.
This change fixes that issue.

Signed-off-by: Jitendra Sharma <jitendra.sharma@intel.com>
 2021-04-16 09:12:29 +02:00
Jaime Arteaga c540af8e5f Fix multidevice support for events 
Signed-off-by: Jaime Arteaga <jaime.a.arteaga.molina@intel.com>
 2021-04-15 22:12:07 +02:00
Maciej Plewka a51ee31500 Add method for unknown kernel arg 
Signed-off-by: Maciej Plewka <maciej.plewka@intel.com>
 2021-04-15 16:39:39 +02:00
Filip Hazubski 77b39ea3df Introduce StreamProperties 
Split programVfeState function.

Related-To: NEO-4940, NEO-4574


Signed-off-by: Filip Hazubski <filip.hazubski@intel.com>
 2021-04-15 16:00:44 +02:00
Milczarek, Slawomir 9839b3049d Move unit test helper to shared code 
Related-To: NEO-5161

Signed-off-by: Milczarek, Slawomir <slawomir.milczarek@intel.com>
 2021-04-13 20:06:08 +02:00
Milczarek, Slawomir e5eba8be53 Add setters and getters for coherency type in render surface state 
Signed-off-by: Milczarek, Slawomir <slawomir.milczarek@intel.com>
 2021-04-13 16:12:46 +02:00
Zbigniew Zdanowicz 3909bd0fea Add setter function to event class 
Related-To: NEO-5244

Signed-off-by: Zbigniew Zdanowicz <zbigniew.zdanowicz@intel.com>
 2021-04-12 10:44:24 +02:00
Jaime Arteaga a56b413392 Improve support for L0 uncached device allocations (2) 
Make sure UNCACHED flags are used in stateful paths.

Related-To: NEO-5500

Signed-off-by: Jaime Arteaga <jaime.a.arteaga.molina@intel.com>
 2021-04-12 09:47:30 +02:00
Young Jin Yoon d4823a463a Add programL3 ULTs for Gen9 
Related-To: LOCI-2076
Signed-off-by: Young Jin Yoon <young.jin.yoon@intel.com>
 2021-04-10 03:44:10 +02:00
Jaime Arteaga b05be25349 Add sub-devices to the list of devices in a context 
Signed-off-by: Jaime Arteaga <jaime.a.arteaga.molina@intel.com>
 2021-04-10 03:36:03 +02:00
Matias Cabral e35ffb0601 Retrieve state save area header from IGC 
Signed-off-by: Matias Cabral <matias.a.cabral@intel.com>
 2021-04-10 03:28:51 +02:00
Jaime Arteaga da7aef49e6 Isolate device allocations with respect to context 
Related-To: LOCI-1996

Signed-off-by: Jaime Arteaga <jaime.a.arteaga.molina@intel.com>
 2021-04-09 17:47:47 +02:00
Jaime Arteaga b510923e25 Fix error code for non-found kernel on zeKernelCreate() 
Signed-off-by: Jaime Arteaga <jaime.a.arteaga.molina@intel.com>
 2021-04-09 10:30:56 +02:00
Jaime Arteaga ddca333045 Improve support for L0 uncached device allocations 
Make sure UNCACHED flags are translated into setting the MOCS index
for uncaching L3.

Related-To: NEO-5500

Signed-off-by: Jaime Arteaga <jaime.a.arteaga.molina@intel.com>
 2021-04-08 13:00:03 +02:00
Kamil Diedrich fabd834941 Fix support for planar images 
Signed-off-by: Kamil Diedrich <kamil.diedrich@intel.com>
 2021-04-07 15:14:30 +02:00
Mateusz Hoppe 223a42c3c7 Refactor DebugSession creation 
Signed-off-by: Mateusz Hoppe <mateusz.hoppe@intel.com>
 2021-04-07 14:40:02 +02:00
Filip Hazubski 31b7fcf653 Update programVFEState function 
Related-To: NEO-4940, NEO-4574

Signed-off-by: Filip Hazubski <filip.hazubski@intel.com>
 2021-04-07 09:45:13 +02:00
Spruit, Neil R 3169b32917 Update test_cmdqueue_gen9 ULT Setup to use mock compiler 
Signed-off-by: Spruit, Neil R <neil.r.spruit@intel.com>
 2021-04-06 20:30:00 +02:00
Lukasz Jobczyk 402082182c Check BCS ULLS availability on copy command queue 
Signed-off-by: Lukasz Jobczyk <lukasz.jobczyk@intel.com>
 2021-04-06 13:53:18 +02:00
Compute-Runtime-Validation 73910d5287 Revert "Update test_cmdqueue_gen9 ULT to use mock compiler" 
This reverts commit 35312d4126.

Signed-off-by: Compute-Runtime-Validation <compute-runtime-validation@intel.com>
 2021-04-06 12:25:46 +02:00
Jim Snow 3e4fb34bba Remove unreachable branch from L0 sampler initialization 
Signed-off-by: Jim Snow <jim.m.snow@intel.com>
 2021-04-06 09:49:46 +02:00
Spruit, Neil R 35312d4126 Update test_cmdqueue_gen9 ULT to use mock compiler 
Signed-off-by: Spruit, Neil R <neil.r.spruit@intel.com>
 2021-04-06 09:33:15 +02:00
Compute-Runtime-Validation ee94cf4a42 Revert "Update test_cmdqueue_gen9 ULT to use mock compiler" 
This reverts commit 893be028c6.

Signed-off-by: Compute-Runtime-Validation <compute-runtime-validation@intel.com>
 2021-04-04 13:30:05 +02:00
Aravind Gopalakrishnan 9b2399019c Add fence ULTs (2) 
Signed-off-by: Aravind Gopalakrishnan <aravind.gopalakrishnan@intel.com>
 2021-04-03 09:02:54 +02:00
Spruit, Neil R 893be028c6 Update test_cmdqueue_gen9 ULT to use mock compiler 
Signed-off-by: Spruit, Neil R <neil.r.spruit@intel.com>
 2021-04-02 21:50:35 +02:00
Bartosz Dunajski 5c15a65b62 Remove not used method 
Signed-off-by: Bartosz Dunajski <bartosz.dunajski@intel.com>
 2021-04-02 16:34:58 +02:00
Mateusz Hoppe 671d916c70 Add Debugger specific log print macros 
- use DebuggerLogBitmask while printing logs for SBA tracking

Signed-off-by: Mateusz Hoppe <mateusz.hoppe@intel.com>
 2021-04-02 15:00:55 +02:00
Spruit, Neil R 7a3095c273 Report failure given Compiler Library Load failed for L0 
- Return ZE_RESULT_ERROR_DEPENDENCY_UNAVAILABLE given the Compiler
  cannot be loaded.
- Print dlopen and LoadLibrary error strings given Debug Print Messages
  are enabled.

Related-To: LOCI-1313

Signed-off-by: Spruit, Neil R <neil.r.spruit@intel.com>
 2021-04-01 23:01:38 +02:00
Maciej Dziuban 2258836b86 Return proper ze_device_image_properties_t when images are not supported 
Signed-off-by: Maciej Dziuban <maciej.dziuban@intel.com>
 2021-04-01 14:01:16 +02:00
Jaime Arteaga d6496f959a Add support for floating point atomics properties extension 
Signed-off-by: Jaime Arteaga <jaime.a.arteaga.molina@intel.com>
 2021-03-31 20:32:55 +02:00
Mateusz Hoppe dc9b856628 Add ults for kernel with printf buffer 
Signed-off-by: Mateusz Hoppe <mateusz.hoppe@intel.com>
 2021-03-31 18:58:33 +02:00
Jaime Arteaga 0561ec183d Add ULT for changeMemoryOperationStatusToL0ResultType 
Signed-off-by: Jaime Arteaga <jaime.a.arteaga.molina@intel.com>
 2021-03-31 17:26:43 +02:00
Igor Venevtsev bd32518d31 Add extra parameters to EncodeComputeMode::adjustComputeMode() method 
Signed-off-by: Igor Venevtsev <igor.venevtsev@intel.com>
 2021-03-31 16:51:55 +02:00
Bartosz Dunajski b6e3817f31 Dont program dcFlush when not allowed 
Signed-off-by: Bartosz Dunajski <bartosz.dunajski@intel.com>
 2021-03-31 16:13:19 +02:00
Zbigniew Zdanowicz b9ed7de40a Parametrize wait operation 
Related-To: NEO-4759


Signed-off-by: Zbigniew Zdanowicz <zbigniew.zdanowicz@intel.com>
 2021-03-31 15:12:59 +02:00
Mateusz Hoppe f51b1f00f5 Add printf L0 blackbox test 
- add printf allocation test


Signed-off-by: Mateusz Hoppe <mateusz.hoppe@intel.com>
 2021-03-31 09:08:29 +02:00
Mateusz Jablonski 8215395401 Simplify Context method 
return if context has multiple sub devices related to a given root device

Related-To: NEO-3691
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2021-03-30 10:22:15 +02:00
Mateusz Hoppe 21e89b121a Optimize preemption programming 
Signed-off-by: Mateusz Hoppe <mateusz.hoppe@intel.com>
 2021-03-30 09:48:57 +02:00
Jaime Arteaga 40ecee5733 Add environment variable to select L0 timer resolution 
Signed-off-by: Jaime Arteaga <jaime.a.arteaga.molina@intel.com>
 2021-03-30 02:56:59 +02:00
Kamil Diedrich 7d64d8e00e Unify reading pci paths 
Signed-off-by: Kamil Diedrich <kamil.diedrich@intel.com>
 2021-03-29 15:59:09 +02:00
Bartosz Dunajski 0bc04f3c31 Refactor TimestampPackets class 
Signed-off-by: Bartosz Dunajski <bartosz.dunajski@intel.com>
 2021-03-29 10:26:32 +02:00
John Falkowski 218387dd47 Apply timerResolution mod for L0 V1.1 
Signed-off-by: John Falkowski <john.falkowski@intel.com>
 2021-03-27 11:43:03 +01:00
Jaime Arteaga c7e65a90d8 Free IPC memory on closeIpcMemHandle() call 
Signed-off-by: Jaime Arteaga <jaime.a.arteaga.molina@intel.com>
 2021-03-27 11:25:57 +01:00
Bartosz Dunajski 5a50ad098c Refactor TagAllocator 
Signed-off-by: Bartosz Dunajski <bartosz.dunajski@intel.com>
 2021-03-26 15:16:56 +01:00
Jaime Arteaga 0dc73ad686 Isolate host allocations with respect to context 
Related-To: LOCI-1996

Signed-off-by: Jaime Arteaga <jaime.a.arteaga.molina@intel.com>
 2021-03-25 06:15:59 +01:00
Jaime Arteaga bf90fabcd2 Expand zello_ipc_copy_dma_buf to spawn several child processes 
Signed-off-by: Jaime Arteaga <jaime.a.arteaga.molina@intel.com>
 2021-03-25 05:54:25 +01:00
Aravind Gopalakrishnan e977de564c Add L0 event ULTs (2) 
Signed-off-by: Aravind Gopalakrishnan <aravind.gopalakrishnan@intel.com>
 2021-03-24 17:11:15 +01:00
Bartosz Dunajski f9197d4e0d Improve memoryPrefetch method 
Signed-off-by: Bartosz Dunajski <bartosz.dunajski@intel.com>
 2021-03-24 15:12:05 +01:00
Mateusz Jablonski 35ff284944 Cleanup Kernel class 
move deviceVector to MultiDeviceKernel class
remove Device arg from Kernel's methods

Related-To: NEO-5001
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2021-03-24 09:17:41 +01:00
Compute-Runtime-Validation 46a971de81 Revert "Free IPC memory on closeIpcMemHandle() call" 
This reverts commit cda914f7d0.

Signed-off-by: Compute-Runtime-Validation <compute-runtime-validation@intel.com>
 2021-03-24 06:58:47 +01:00
Jaime Arteaga cda914f7d0 Free IPC memory on closeIpcMemHandle() call 
Signed-off-by: Jaime Arteaga <jaime.a.arteaga.molina@intel.com>
 2021-03-23 19:09:12 +01:00
Jim Snow 39d450bc84 Refactor L0 sampler error path and add ULTs 
Signed-off-by: Jim Snow <jim.m.snow@intel.com>
 2021-03-23 06:52:08 +01:00
Jaime Arteaga 47bdcce4c6 Add ULTs for missing branches in driverHandleGet() 
Signed-off-by: Jaime Arteaga <jaime.a.arteaga.molina@intel.com>
 2021-03-22 20:31:42 +01:00
Filip Hazubski 8d55bfe21d Implement zeCommandListAppendLaunchCooperativeKernel 
Resolves: NEO-4725


Signed-off-by: Filip Hazubski <filip.hazubski@intel.com>
 2021-03-22 19:26:41 +01:00
Bartosz Dunajski 3dc3ad36f8 Refactor TimestampPacket class 
Signed-off-by: Bartosz Dunajski <bartosz.dunajski@intel.com>
 2021-03-22 17:42:41 +01:00
Jaime Arteaga 689028992a Add ULT for ZE_DEVICE_PROPERTY_FLAG_ONDEMANDPAGING 
Signed-off-by: Jaime Arteaga <jaime.a.arteaga.molina@intel.com>
 2021-03-22 16:31:35 +01:00
Jaime Arteaga 673198ab34 Add ULT for missing branches in getCsrForOrdinalAndIndex() 
Signed-off-by: Jaime Arteaga <jaime.a.arteaga.molina@intel.com>
 2021-03-22 16:27:19 +01:00
Daria Hinz 9ac7f1d370 Adding a parameter to a encode function 
Signed-off-by: Daria Hinz <daria.hinz@intel.com>
 2021-03-19 17:54:46 +01:00
Mateusz Hoppe 1544c6d001 Split getDebugSession and createDebugSession logic 
Related-To: NEO-4554

Signed-off-by: Mateusz Hoppe <mateusz.hoppe@intel.com>
 2021-03-19 15:38:36 +01:00
Zbigniew Zdanowicz d6dde3df33 Add internal argument to encode method 
Related-To: NEO-5244

Signed-off-by: Zbigniew Zdanowicz <zbigniew.zdanowicz@intel.com>
 2021-03-19 09:37:05 +01:00
Jaime Arteaga 521cc56096 Add support for zeContextCreateEx 
Signed-off-by: Jaime Arteaga <jaime.a.arteaga.molina@intel.com>
 2021-03-19 06:14:53 +01:00
Mateusz Hoppe d264dc858f Return all devices from helper function in bbox tests 
Signed-off-by: Mateusz Hoppe <mateusz.hoppe@intel.com>
 2021-03-19 04:58:36 +01:00
Aravind Gopalakrishnan 279349bfab Add ULTs for L0 events 
Signed-off-by: Aravind Gopalakrishnan <aravind.gopalakrishnan@intel.com>
 2021-03-18 22:04:48 +01:00
Slawomir Milczarek 693f2ff384 Ensure shared handle be closed once on Linux 
Related-To: NEO-5644

Signed-off-by: Slawomir Milczarek <slawomir.milczarek@intel.com>
 2021-03-18 18:38:01 +01:00
Mateusz Hoppe 232faf1bd8 Fix test_memory.cpp 
- expect correct result

Signed-off-by: Mateusz Hoppe <mateusz.hoppe@intel.com>
 2021-03-18 17:43:16 +01:00
Mateusz Hoppe 0897f997d6 Fix zeModuleGetGlobalPointer() 
- return size correctly
- check if pSize and pPtr is != nullptr

Resolves: NEO-5641

Signed-off-by: Mateusz Hoppe <mateusz.hoppe@intel.com>
 2021-03-18 17:29:41 +01:00
Jaime Arteaga 5b10cdd5d5 Correct variable misusage in ULT 
Signed-off-by: Jaime Arteaga <jaime.a.arteaga.molina@intel.com>
 2021-03-18 06:17:17 +01:00
Aravind Gopalakrishnan 7764ac44ae Implement support for zeDeviceGetGlobalTimestamps 
Related-To: LOCI-1933

Signed-off-by: Aravind Gopalakrishnan <aravind.gopalakrishnan@intel.com>
 2021-03-17 20:29:07 +01:00
Aravind Gopalakrishnan 3c6d026d7b Add ULTs for fence 
Signed-off-by: Aravind Gopalakrishnan <aravind.gopalakrishnan@intel.com>
 2021-03-17 20:20:41 +01:00
Maciej Dziuban 8df7128901 Make work partition allocation resident in LevelZero 
Related-To: NEO-5546
Signed-off-by: Maciej Dziuban <maciej.dziuban@intel.com>
 2021-03-17 13:27:10 +01:00
Jaime Arteaga 6156fb2673 Add ULTs for L0 context interfaces 
Signed-off-by: Jaime Arteaga <jaime.a.arteaga.molina@intel.com>
 2021-03-16 21:03:25 +01:00
Mateusz Hoppe 3bbbe9facb Print debug string with error when legacy debugger used with env 
Signed-off-by: Mateusz Hoppe <mateusz.hoppe@intel.com>
 2021-03-16 17:08:15 +01:00
Maciej Dziuban 3f5b9df122 Pass EngineUsage to getEngine 
Signed-off-by: Maciej Dziuban <maciej.dziuban@intel.com>
Related-To: NEO-5610
 2021-03-16 16:31:44 +01:00
Daria Hinz bd35d2b3bd Use only first event packet when PC 
If PIPE_CONTROL is used to collect timestamps, only the first event packet is
used and overwritten

Signed-off-by: Daria Hinz <daria.hinz@intel.com>
Related-To: NEO-5611
 2021-03-16 13:13:49 +01:00
Bartosz Dunajski 43d5397de6 Set correct L0 CommandQueue type 
Signed-off-by: Bartosz Dunajski <bartosz.dunajski@intel.com>
 2021-03-16 12:09:47 +01:00
Maciej Dziuban 264f20ea00 Pass EngineTypeUsage to OsContext creation 
Signed-off-by: Maciej Dziuban <maciej.dziuban@intel.com>
Related-To: NEO-5610
 2021-03-16 10:21:18 +01:00
Igor Venevtsev 52e118fe49 Add extra parameters to Buffer::setSurfaceState() method 
Signed-off-by: Igor Venevtsev <igor.venevtsev@intel.com>
 2021-03-16 10:17:59 +01:00
Jaime Arteaga 6a81edfbe1 Add support for ZE_RELAXED_ALLOCATION_LIMITS_EXP_FLAG_MAX_SIZE 
Signed-off-by: Jaime Arteaga <jaime.a.arteaga.molina@intel.com>
 2021-03-15 16:20:10 +01:00
Konstanty Misiak 88a1593913 Add software tags 
Related-To: NEO-344

Signed-off-by: Konstanty Misiak <konstanty.misiak@intel.com>
 2021-03-15 15:51:08 +01:00
Jaime Arteaga 71940061b8 Make sure IPC handles are correctly copied 
Signed-off-by: Jaime Arteaga <jaime.a.arteaga.molina@intel.com>
 2021-03-13 18:22:56 +01:00
Filip Hazubski 6a4ed40a16 Correct Host Mem Capabilities values 
Related-To: NEO-5054

Signed-off-by: Filip Hazubski <filip.hazubski@intel.com>
 2021-03-11 08:54:59 +01:00
Jitendra Sharma 4fd3ac6399 Add device memory name 
Signed-off-by: Jitendra Sharma <jitendra.sharma@intel.com>
 2021-03-10 18:44:10 +01:00
Krzysztof Gibala 4abe4a96b8 Add multiGraphicsAllocation to CSR 
Related-To: NEO-5508
Signed-off-by: Krzysztof Gibala <krzysztof.gibala@intel.com>
 2021-03-10 12:42:01 +01:00
Zbigniew Zdanowicz 779253c49c Add new flag to USM memory manager 
Related-To: NEO-5498

Signed-off-by: Zbigniew Zdanowicz <zbigniew.zdanowicz@intel.com>
 2021-03-10 11:47:34 +01:00
Krystian Chmielewski 41f3bd00ff Remove PatchTokens from KernelInfo 
Use KernelDescriptor instead of patchTokens stored in KernelInfo's
patchInfo.
Removed: SPatchMediaInterfaceDescriptorLoad, SPatchAllocateLocalSurface,
SPatchMediaVFEState(slot 0), SPatchMediaVFEState(slot 1),
SPatchInterfaceDescriptorData, SPatchSamplerStateArray,
SPatchBindingTableState, SPatchDataParameterBuffer,
SPatchDataParameterStream, SPatchThreadPayload,
SPatchKernelAttributesInfo, SPatchAllocateStatelessPrivateSurface,
SPatchAllocateSyncBuffer,
SPatchAllocateStatelessConstantMemorySurfaceWithInitialization,
SPatchAllocateStatelessGlobalMemorySurfaceWithInitialization,
SPatchAllocateSystemThreadSurface.

Related-To: NEO-4729
Signed-off-by: Krystian Chmielewski <krystian.chmielewski@intel.com>
 2021-03-09 17:09:13 +01:00
Jim Snow 142fe1efdb Add sampler ULT to increase branch coverage, remove a sampler branch 
Signed-off-by: Jim Snow <jim.m.snow@intel.com>
 2021-03-09 00:31:18 +01:00
Adam Cetnerowski 07eb59d400 ULT renaming: Level Zero Misc tests 
Related-To: NEO-2236

Signed-off-by: Adam Cetnerowski <adam.cetnerowski@intel.com>
 2021-03-08 19:14:22 +01:00
Mateusz Hoppe 9f3218775d Fix version-script for ze_intel_gpu 
Related-To: NEO-5509
-make only ze* functions globally exported

Signed-off-by: Mateusz Hoppe <mateusz.hoppe@intel.com>
 2021-03-08 09:55:38 +01:00
Maciej Plewka 72b13e9bbd Use copy only command queue in zello_copy_only 
Signed-off-by: Maciej Plewka <maciej.plewka@intel.com>
 2021-03-07 12:38:23 +01:00
Mateusz Hoppe 7d808bd560 Optimize preemption programming 
- limit number of LRI cmds

Signed-off-by: Mateusz Hoppe <mateusz.hoppe@intel.com>
 2021-03-05 13:37:14 +01:00
Maciej Dziuban 1350aa52fb Pass DispatchInfo to estimation functions 
Related-To: NEO-5546

Signed-off-by: Maciej Dziuban <maciej.dziuban@intel.com>
 2021-03-05 12:47:55 +01:00
Aravind Gopalakrishnan db892eaa95 Revert "Use device allocation for events if host visibility not set" 
This reverts commit b204a4f135.

Signed-off-by: Aravind Gopalakrishnan <aravind.gopalakrishnan@intel.com>
 2021-03-05 03:31:17 +01:00
Jaime Arteaga 76db4ce59a Add ULT for openIpcMemHandle 
Signed-off-by: Jaime Arteaga <jaime.a.arteaga.molina@intel.com>
 2021-03-04 22:30:53 +01:00
Compute-Runtime-Validation cac1b5465b Revert "Updating L0 loader to 1.2.3 in manifest" 
This reverts commit 76666662c4.

Signed-off-by: Compute-Runtime-Validation <compute-runtime-validation@intel.com>
 2021-03-04 14:16:39 +01:00
Mateusz Hoppe 6356de6511 Add debug api handlers 2 
Related-To: NEO-4554

Signed-off-by: Mateusz Hoppe <mateusz.hoppe@intel.com>
 2021-03-04 12:45:40 +01:00
Jaime Arteaga 5adfe0704b Add ULTs for checkMemoryAccessFromDevice 
Signed-off-by: Jaime Arteaga <jaime.a.arteaga.molina@intel.com>
 2021-03-03 02:26:39 +01:00
Brandon Yates 76666662c4 Updating L0 loader to 1.2.3 in manifest 
Signed-off-by: Brandon Yates <brandon.yates@intel.com>
 2021-03-03 02:13:41 +01:00
Zbigniew Zdanowicz 24b928303b Rename fields in AllocationProperties 
Related-To: NEO-5498

Signed-off-by: Zbigniew Zdanowicz <zbigniew.zdanowicz@intel.com>
 2021-03-02 18:32:37 +01:00
Maciej Plewka c1cabb505a Fix Get ConstSpecSize based on correlated ConstSpecID 
Signed-off-by: Maciej Plewka <maciej.plewka@intel.com>
 2021-03-02 12:11:08 +01:00
Jaime Arteaga 102de8ffd5 Add option to zello_ipc_copy_dma_buf_p2p to select copy engine 
Signed-off-by: Jaime Arteaga <jaime.a.arteaga.molina@intel.com>
 2021-03-02 09:36:43 +01:00
vinod krishna 22f40d9a8e Adding zello_fence blackbox testcase 
Signed-off-by: vinod krishna <vinod.krishna@intel.com>
 2021-03-02 08:22:22 +01:00
Mateusz Hoppe 8f87dfaf0c Add Debug API handlers 
Related-To: NEO-4554


Signed-off-by: Mateusz Hoppe <mateusz.hoppe@intel.com>
 2021-03-01 15:26:43 +01:00
davidoli 8fdd1931a9 improve stub for zetKernelGetProfileInfo with ULT 
Signed-off-by: davidoli <david.olien@intel.com>
 2021-03-01 00:17:58 +01:00
Compute-Runtime-Validation c0268abc26 Revert "Take spec const value sizes from compiler" 
This reverts commit da3805880b.

Signed-off-by: Compute-Runtime-Validation <compute-runtime-validation@intel.com>
 2021-02-26 16:22:10 +01:00
Zbigniew Zdanowicz 3e4be8d78e Add new allocation type 
Related-To: NEO-5244

Signed-off-by: Zbigniew Zdanowicz <zbigniew.zdanowicz@intel.com>
 2021-02-26 12:57:12 +01:00
Jaime Arteaga 722a80079b Add experimental_properties for indirect access (2) 
Add support to OpenCL to also make use of indirect access properties
provided by IGC and to make use of DisableIndirectAccess debug key.

Signed-off-by: Jaime Arteaga <jaime.a.arteaga.molina@intel.com>
 2021-02-25 11:41:24 +01:00
Maciej Plewka da3805880b Take spec const value sizes from compiler 
Signed-off-by: Maciej Plewka <maciej.plewka@intel.com>
 2021-02-25 10:42:21 +01:00
Jaime Arteaga 0417f5ba12 Add ULT for getIpcMemHandle 
Signed-off-by: Jaime Arteaga <jaime.a.arteaga.molina@intel.com>
 2021-02-25 08:32:32 +01:00
vinod krishna b38642ab6b Adding zello_copy_only, zello_copy_fence & zello_copy_image blackbox testcases 
Signed-off-by: vinod krishna <vinod.krishna@intel.com>
 2021-02-24 17:15:32 +01:00
Mateusz Hoppe c44fff1379 Enable device discovery from test_files in L0 ults 
Signed-off-by: Mateusz Hoppe <mateusz.hoppe@intel.com>
 2021-02-24 10:18:20 +01:00
Daria Hinz 13fe8ed7f1 Revert "Correct POST_SYNC for L0 Events" 
This reverts commit 04d1a3255357a7778a530f054700e211d94f3b6d.

Signed-off-by: Daria Hinz <daria.hinz@intel.com>
 2021-02-24 10:16:22 +01:00