intel/compute-runtime
1
0
Fork 0
mirror of https://github.com/intel/compute-runtime.git synced 2025-12-31 20:13:04 +08:00
Code Issues Packages Projects Releases Wiki Activity
7,148 Commits 42 Branches 655 Tags
da7aef49e679cc3fd9ad54f8e9c819eab1e5475e
Commit Graph

501 Commits

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