Commit Graph

977 Commits

Author SHA1 Message Date
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
Jitendra Sharma
46c51cb8a9 Sysman device reset stability fix
Close PMT, and PMU fds created during Sysman's init before calling
device reset.

Signed-off-by: Jitendra Sharma <jitendra.sharma@intel.com>
2021-04-15 11:53:10 +02:00
vinod krishna
7b974f0ecb Metrics ULT for Metric Groups activate, deactivate & WaitForReports functions.
Resolves: LOCI-2190

Signed-off-by: vinod krishna <vinod.krishna@intel.com>
2021-04-14 23:00:20 +02:00
Bartosz Dunajski
45b005161a Dont create VM IDs if not supported
Signed-off-by: Bartosz Dunajski <bartosz.dunajski@intel.com>
2021-04-14 10:51:56 +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
William Jordan
d2b6d7f241 Fix blackbox zello_sysman output for fabric ports
Code was outputing 1 byte fields as characters instead of numbers.

Signed-off-by: William Jordan <bill.jordan@intel.com>
2021-04-10 02:58:25 +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
Piotr Maciejewski
08210f8be5 Fix for Metric Api test that attempts OS (fstat) function.
Signed-off-by: Piotr Maciejewski <piotr.maciejewski@intel.com>
2021-04-09 17:29:23 +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
Daniel Enriquez
b604ce4da5 Sysman for Windows: Adding break from Listen.
Breaking from the Listen call via registerEvents(0).

Signed-off-by: Daniel Enriquez <daniel.enriquez.montanez@intel.com>
2021-04-09 02:28:47 +02:00
Mateusz Hoppe
a24735b4fd Revert "sysman: add basic steps for IFR status"
Signed-off-by: Mateusz Hoppe <mateusz.hoppe@intel.com>
2021-04-08 20:35:15 +02:00
Bartosz Dunajski
9cf7651643 Simplify Device classes
Signed-off-by: Bartosz Dunajski <bartosz.dunajski@intel.com>
2021-04-08 19:00:59 +02:00
Mateusz Hoppe
a2cbb4f859 Add readEvent method to DebugSession
Related-To: NEO-4556

Signed-off-by: Mateusz Hoppe <mateusz.hoppe@intel.com>
2021-04-08 17:55:54 +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
Vilvaraj, T J Vivek
b56b204f3e sysman: add basic steps for IFR status.
In field repair status information is needed as part of Device
reset status

Signed-off-by: Vilvaraj, T J Vivek <t.j.vivek.vilvaraj@intel.com>
2021-04-07 16:21:26 +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
Kanhaiya Singh
33ba9f45b1 Fix the sysman code by replacing "Unknown" with "unknown"
Signed-off-by: Kanhaiya Singh <kanhaiya.singh@intel.com>
2021-04-06 09:41:43 +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
Jaime Arteaga
1a35b0a8c9 Add Release Notes for L0 v1.1
Signed-off-by: Jaime Arteaga <jaime.a.arteaga.molina@intel.com>
2021-04-02 23:31:19 +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
Jitendra Sharma
b0f2c76434 In Sysman PMT Fix telemetry node sort logic
Signed-off-by: Jitendra Sharma <jitendra.sharma@intel.com>
2021-04-02 07:21:07 +02:00