intel/compute-runtime
1
0
Fork 0
mirror of https://github.com/intel/compute-runtime.git synced 2025-12-28 16:48:45 +08:00
Code Issues Packages Projects Releases Wiki Activity
7,215 Commits 42 Branches 655 Tags
ef5174f3fc7f708cc6a568e93d8cb34fe451e46f
Commit Graph

522 Commits

Author SHA1 Message Date
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
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
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
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
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
Aravind Gopalakrishnan
9b2399019c Add fence ULTs (2) 
Signed-off-by: Aravind Gopalakrishnan <aravind.gopalakrishnan@intel.com>
 2021-04-03 09:02:54 +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
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 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
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