intel/compute-runtime
1
0
Fork 0
mirror of https://github.com/intel/compute-runtime.git synced 2026-01-03 06:49:52 +08:00
Code Issues Packages Projects Releases Wiki Activity
7,762 Commits 43 Branches 655 Tags
4852bca7c391e7f8ca8a583fb95cede0b376d4ef
Commit Graph

822 Commits

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