Commit Graph

2656 Commits

Author SHA1 Message Date
Matias Cabral
4affe9907c Update SLM access offset behavior
Related-To: NEO-5998

Signed-off-by: Matias Cabral <matias.a.cabral@intel.com>
2022-10-17 18:07:27 +02:00
Zbigniew Zdanowicz
3d1dba3d10 Update test cmake file
Signed-off-by: Zbigniew Zdanowicz <zbigniew.zdanowicz@intel.com>
2022-10-17 18:00:18 +02:00
Patryk Wrobel
2dd3c11248 Do not copy ze_ipc_mem_handle_t in internal functions of NEO
The size of this type is at least 64 bytes due to
ZE_MAX_IPC_HANDLE_SIZE. This change introduces usage
of const reference instead of copying.

Signed-off-by: Patryk Wrobel <patryk.wrobel@intel.com>
2022-10-17 13:51:03 +02:00
Patryk Wrobel
90597995d2 Do not copy ze_ipc_event_pool_handle_t in internal functions of NEO
The size of this type is at least 64 bytes due to
ZE_MAX_IPC_HANDLE_SIZE. This change introduces usage
of const reference instead of copying.

Signed-off-by: Patryk Wrobel <patryk.wrobel@intel.com>
2022-10-17 13:17:24 +02:00
Joshua Santosh Ranjan
b2c80be6f9 Fix typo and error check when retrieving pci information
Fix
1. typo PhysialDevicePciSpeedInfo to PhysicalDevicePciSpeedInfo
2. error check to verify open() call

Signed-off-by: Joshua Santosh Ranjan <joshua.santosh.ranjan@intel.com>
2022-10-14 14:57:07 +02:00
Mateusz Hoppe
95505d87a5 L0Debug - fix interrupt
- pass deviceIndex based on deviceBitfield
- do not call ioctl again on EBUSY error

Resolves: NEO-7414

Signed-off-by: Mateusz Hoppe <mateusz.hoppe@intel.com>
2022-10-14 13:56:57 +02:00
Joshua Santosh Ranjan
42e58fd301 Fix pNext usage for ZE_STRUCTURE_TYPE_DEVICE_MEMORY_EXT_PROPERTIES
Signed-off-by: Joshua Santosh Ranjan <joshua.santosh.ranjan@intel.com>
2022-10-14 12:41:18 +02:00
Aravind Gopalakrishnan
f9fab3ff49 Update SBA in hybrid immediate and regular commandlist usages
Fix to check and update heap states.

Related-To: LOCI-3379
Signed-off-by: Aravind Gopalakrishnan <aravind.gopalakrishnan@intel.com>
2022-10-14 11:42:06 +02:00
Lukasz Jobczyk
8b640ca00d Obtain thread count only if needed
Signed-off-by: Lukasz Jobczyk <lukasz.jobczyk@intel.com>
2022-10-14 10:52:44 +02:00
Mayank Raghuwanshi
d3ebf4677b Add ults for windows sysman firmware
Related-To: LOCI-3436

Signed-off-by: Mayank Raghuwanshi <mayank.raghuwanshi@intel.com>
2022-10-14 07:29:08 +02:00
Spruit, Neil R
33a587c704 L0 to read Device LUID from the WDDM driver given Debug Variable
- Added Support for reading the Device LUID of the given device used in
Windows WDDM given EnableL0ReadLUIDExtension=1.
- Added inital support for passing back the NodeMask of 1.

Signed-off-by: Spruit, Neil R <neil.r.spruit@intel.com>
2022-10-14 02:46:40 +02:00
Kacper Nowak
2285772c7e Disable zebin on pre-Gen12 platforms when debugger is active
On pre-Gen12 platform we use igfxdcd kernel module for debugging, which
does not support zebinary format.
- When platform is pre-Gen12 an and debugger is
attached, if binary format is zebin and it's not a builtin:
- If SPIR-V is available - force rebuild with zebin disabled
- Otherwise, return an error.
- Minor refactor: extend check for ir presence for each case of
rebuilt in OCL.

Related-To: NEO-7328
Signed-off-by: Kacper Nowak <kacper.nowak@intel.com>
2022-10-13 17:27:48 +02:00
Lukasz Jobczyk
4eeef388e2 Remove double free from bcs split L0
Signed-off-by: Lukasz Jobczyk <lukasz.jobczyk@intel.com>
2022-10-13 15:53:41 +02:00
Yates, Brandon
44894c1fdf L0 Debug- Create generic topologyMap interface
Move Linux DebugSession thread conversion functions up to
DebugSessionImp to allow reuse in windows implementation

Signed-off-by: Yates, Brandon <brandon.yates@intel.com>
2022-10-13 15:12:05 +02:00
Szymon Morek
3f17b26253 Add cmd buffer to container if needed
Command buffers in CommandContainer are removed
through cmdBufferAllocations. This PR ensures
that allocations will be stored there if they
are currently used by given cmd container.

Signed-off-by: Szymon Morek <szymon.morek@intel.com>
2022-10-13 14:23:44 +02:00
Lukasz Jobczyk
5078cc27e0 Disable L0 bcs split for non USM pointers
Signed-off-by: Lukasz Jobczyk <lukasz.jobczyk@intel.com>
2022-10-13 13:25:16 +02:00
Compute-Runtime-Validation
71149b29c5 Revert "Propagate exec buffer error to L0 API level"
This reverts commit 9a95f3c62d.

Signed-off-by: Compute-Runtime-Validation <compute-runtime-validation@intel.com>
2022-10-13 06:21:31 +02:00
Mateusz Jablonski
9a95f3c62d Propagate exec buffer error to L0 API level
This change makes that drm file is opened in nonblocking mode for prelim
kernels. In such case when calling exec buffer ioctl and get
EAGAIN (aka EWOULDBLOCK) we may return error to API level

Related-To: NEO-7144
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
2022-10-12 17:34:35 +02:00
Zbigniew Zdanowicz
4055acaf01 Enable front end tracking on XE platforms
Related-To: NEO-5019

Signed-off-by: Zbigniew Zdanowicz <zbigniew.zdanowicz@intel.com>
2022-10-12 14:47:56 +02:00
Zbigniew Zdanowicz
87822f94e2 Replace virtual method call for DC flush with stored bool value 2/n
Signed-off-by: Zbigniew Zdanowicz <zbigniew.zdanowicz@intel.com>
2022-10-12 09:43:01 +02:00
Compute-Runtime-Validation
7c6783c4a1 Revert "Return error when image arg does not support media block commands"
This reverts commit e56d18b69f.

Signed-off-by: Compute-Runtime-Validation <compute-runtime-validation@intel.com>
2022-10-12 03:58:33 +02:00
Joshua Santosh Ranjan
6944baaca8 Add check to verify UUID platform support
Related-To: LOCI-3495

Signed-off-by: Joshua Santosh Ranjan <joshua.santosh.ranjan@intel.com>
2022-10-12 01:44:57 +02:00
Spruit, Neil R
1995fd9d92 Revert "Support for L0 to read Device LUID from the WDDM driver using EXT Prop"
This reverts commit b5b9c3500f.

Signed-off-by: Spruit, Neil R <neil.r.spruit@intel.com>
2022-10-12 01:00:18 +02:00
Matias Cabral
56109b882f Support debugger SLM write
Resolves: NEO-5998

Signed-off-by: Matias Cabral <matias.a.cabral@intel.com>
2022-10-11 16:37:14 +02:00
Maciej Plewka
e56d18b69f Return error when image arg does not support media block commands
Signed-off-by: Maciej Plewka <maciej.plewka@intel.com>
2022-10-11 15:47:27 +02:00
Zbigniew Zdanowicz
31f97717db Replace virtual method call for DC flush with stored bool value 1/n
Signed-off-by: Zbigniew Zdanowicz <zbigniew.zdanowicz@intel.com>
2022-10-11 13:27:58 +02:00
Zbigniew Zdanowicz
d3c78a5011 enable pipeline select tracking on systolic mode platforms
Related-To: NEO-5019

Signed-off-by: Zbigniew Zdanowicz <zbigniew.zdanowicz@intel.com>
2022-10-11 13:15:30 +02:00
Szymon Morek
3f5ac0b4d0 Reuse heaps for immediate cmd lists
Signed-off-by: Szymon Morek <szymon.morek@intel.com>
2022-10-11 13:02:13 +02:00
Szymon Morek
d3f30b4046 Remove not needed access to atomic variable
Signed-off-by: Szymon Morek <szymon.morek@intel.com>
2022-10-11 09:34:24 +02:00
Joshua Santosh Ranjan
fc0f600fd2 Update zello_timestamp test
This patch updates zello_timestamp for
1. add parameter to choose test
2. Fix testKernelTimestampMapToHostTimescale test to use timestamp
with lower range for calculations

Related-To: LOCI-3360

Signed-off-by: Joshua Santosh Ranjan <joshua.santosh.ranjan@intel.com>
2022-10-10 19:38:44 +02:00
Zbigniew Zdanowicz
63df08664a change interface to enable tracking of other n-p state commands per platform
Related-To: NEO-5019

Signed-off-by: Zbigniew Zdanowicz <zbigniew.zdanowicz@intel.com>
2022-10-10 12:50:40 +02:00
Krystian Chmielewski
73a58aaf9e feat(zebin): inline sampler
Add support for inline samplers in zebin.
Generate required SAMPLER_STATEs in DSH.

Resolves: NEO-7388

Signed-off-by: Krystian Chmielewski <krystian.chmielewski@intel.com>
2022-10-10 12:47:19 +02:00
Lukasz Jobczyk
b21fef96cb Wait for events from host
Signed-off-by: Lukasz Jobczyk <lukasz.jobczyk@intel.com>
2022-10-10 12:12:13 +02:00
Bellekallu Rajkiran
3323deb825 Add support for serial number property
Related-To: LOCI-3396

Signed-off-by: Bellekallu Rajkiran <bellekallu.rajkiran@intel.com>
2022-10-09 19:37:30 +02:00
Compute-Runtime-Validation
668f988e61 Revert "Add support for serial number property"
This reverts commit ba461e565e.

Signed-off-by: Compute-Runtime-Validation <compute-runtime-validation@intel.com>
2022-10-09 06:59:32 +02:00
Jim Snow
8e9242dc92 Support ray tracing memory allocation extension in L0.
Related-To: NEO-5579

Signed-off-by: Jim Snow <jim.m.snow@intel.com>
2022-10-08 01:13:12 +02:00
Jaime A Arteaga Molina
8a6cf4fd4e Add black-box test for import/export APIs
Signed-off-by: Jaime A Arteaga Molina <jaime.a.arteaga.molina@intel.com>
2022-10-08 00:45:35 +02:00
Bellekallu Rajkiran
ba461e565e Add support for serial number property
Related-To: LOCI-3396

Signed-off-by: Bellekallu Rajkiran <bellekallu.rajkiran@intel.com>
2022-10-07 20:08:01 +02:00
Fabian Zwolinski
7953d15826 Print warning when kernel uses too much SLM
Instead of just returning proper error code in case of exceeding
available Shared Local Memory size we also want to print error message
to make debugging easier.

Related-To: NEO-7280
Signed-off-by: Fabian Zwolinski <fabian.zwolinski@intel.com>
2022-10-07 19:06:19 +02:00
Zbigniew Zdanowicz
f0dd62e5a2 enable state compute mode tracking on XE_HPC platforms
Related-To: NEO-5019

Signed-off-by: Zbigniew Zdanowicz <zbigniew.zdanowicz@intel.com>
2022-10-07 13:59:49 +02:00
Mateusz Hoppe
af4e3d510e Refactor DebugApiWindows tests
- copy att bitmask to event in tests, not in mockWddm
- simplifies logic, gets rid of redundant struct, allows
setting different att bitmask for every event

Signed-off-by: Mateusz Hoppe <mateusz.hoppe@intel.com>
2022-10-07 11:45:25 +02:00
Zbigniew Zdanowicz
add47dc79f Add support for cooperative kernels to immediate command lists
Signed-off-by: Zbigniew Zdanowicz <zbigniew.zdanowicz@intel.com>
2022-10-07 10:16:30 +02:00
Zbigniew Zdanowicz
0270e0f8a5 Add interface to enable state compute mode tracking per platform
Related-To: NEO-5019

Signed-off-by: Zbigniew Zdanowicz <zbigniew.zdanowicz@intel.com>
2022-10-07 09:55:03 +02:00
Zbigniew Zdanowicz
55be825dda Rename files to use unique names
Signed-off-by: Zbigniew Zdanowicz <zbigniew.zdanowicz@intel.com>
2022-10-07 09:39:51 +02:00
Jaime Arteaga
dc1e8f7f80 Fix compilation of fabric ULTs
Related-to: LOCI-3376

Signed-off-by: Jaime Arteaga <jaime.a.arteaga.molina@intel.com>
2022-10-07 07:06:59 +02:00
Jaime Arteaga
f349343100 Enable l0_cache in L0
Name is different from the one used by opencl.

Signed-off-by: Jaime Arteaga <jaime.a.arteaga.molina@intel.com>
2022-10-07 07:01:54 +02:00
Fabian Zwolinski
1142404c0c Add error handling when kernel uses too much SLM
API Functions reporting error:
- clCreateKernel
- clEnqueueNDRangeKernel
- zeKernelCreate
- zeCommandListAppendLaunchKernel
- zeKernelSuggestGroupSize

Related-To: NEO-7280
Signed-off-by: Fabian Zwolinski <fabian.zwolinski@intel.com>
2022-10-06 16:45:42 +02:00
Igor Venevtsev
5a0dd8048b L0Debug Win: fix bitmap reading for EU_ATTN_BIT_SET event
Signed-off-by: Igor Venevtsev <igor.venevtsev@intel.com>
2022-10-06 15:41:14 +02:00
Joshua Santosh Ranjan
44a1f4822b Update Fabric Vertex Support to include iaf querying
This patch adds
1. enumeration of connected iaf devices
2. move fabric vertex to driver, to support deviceless
vertices case

Related-To: LOCI-3376

Signed-off-by: Joshua Santosh Ranjan <joshua.santosh.ranjan@intel.com>
2022-10-06 11:45:39 +02:00
Artur Harasimiuk
2cffaa7dbf clang-tidy: remove redundant store operation
Signed-off-by: Artur Harasimiuk <artur.harasimiuk@intel.com>
2022-10-06 11:21:21 +02:00