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

684 Commits

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