intel/compute-runtime
1
0
Fork 0
mirror of https://github.com/intel/compute-runtime.git synced 2025-12-30 09:58:55 +08:00
Code Issues Packages Projects Releases Wiki Activity
7,152 Commits 42 Branches 655 Tags
d4823a463ae165fdedda331fb50312745f7b47b5
Commit Graph

655 Commits

Author SHA1 Message Date
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