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
11,584 Commits 43 Branches 655 Tags
95c3ef28fcd03b5079fedc8787e85248cc46632b
Commit Graph

2692 Commits

Author SHA1 Message Date
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
Neil R Spruit
8e2fcc9137 Allow init and execution of L0 without IGC unless it is needed 
- Allow usage of L0 with IGC unless Debugger, Mid Thread Premption, or
  SPIRvs need to be compiled from modules. Native Binaries that are
already compiled for GENs will be usable.

Related-To: LOCI-3430

Signed-off-by: Neil R Spruit <neil.r.spruit@intel.com>
 2022-10-06 00:35:21 +02:00
Dunajski, Bartosz
ad2d3d0289 Remove not used method 
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2022-10-05 17:10:51 +02:00
Zbigniew Zdanowicz
88113fbaad enable shared heaps feature on XE_HPC platforms 
Related-To: NEO-7142

Signed-off-by: Zbigniew Zdanowicz <zbigniew.zdanowicz@intel.com>
 2022-10-05 14:50:42 +02:00
Szymon Morek
17655e3ed3 [L0][XE_HPC]Perform memcpy on CPU by default 
Related-To: NEO-7237

Signed-off-by: Szymon Morek <szymon.morek@intel.com>
 2022-10-05 14:12:39 +02:00
Zbigniew Zdanowicz
322719e7a2 prepare tests to enable heap sharing feature 
Related-To: NEO-7142

Signed-off-by: Zbigniew Zdanowicz <zbigniew.zdanowicz@intel.com>
 2022-10-05 11:54:16 +02:00
Mateusz Hoppe
e9a7c990ef L0Debug - log deviceBitfield for ISA event 
- enhancement to logging

Signed-off-by: Mateusz Hoppe <mateusz.hoppe@intel.com>
 2022-10-05 11:44:44 +02:00
Compute-Runtime-Validation
cfd96980a0 Revert "[L0][XE_HPC]Perform memcpy on CPU by default" 
This reverts commit 383f33b482.

Signed-off-by: Compute-Runtime-Validation <compute-runtime-validation@intel.com>
 2022-10-05 08:17:23 +02:00
Zbigniew Zdanowicz
50b9ea2765 Add platform support interface to command list heap sharing 
Related-To: NEO-7142

Signed-off-by: Zbigniew Zdanowicz <zbigniew.zdanowicz@intel.com>
 2022-10-04 16:46:48 +02:00
Dunajski, Bartosz
52b63be026 Remove isCleanLeftoverMemoryRequired() + refactor sampler support path 
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2022-10-04 16:24:03 +02:00
Szymon Morek
6073702941 Reuse command buffer for immediate cmdlist 
Signed-off-by: Szymon Morek <szymon.morek@intel.com>
 2022-10-04 16:02:18 +02:00
Milczarek, Slawomir
e11bcb9882 Fixed offset calculation for blit fill on imported non-usm allocation 
Resolves: NEO-7379

Signed-off-by: Milczarek, Slawomir <slawomir.milczarek@intel.com>
 2022-10-04 15:35:58 +02:00
Igor Venevtsev
66f5af0fec L0Debug: simple code cleanup 
Use dedicated readSystemRoutineIdent() instead of raw readGpuMemory()

Signed-off-by: Igor Venevtsev <igor.venevtsev@intel.com>
 2022-10-04 13:45:18 +02:00
Mateusz Hoppe
fddd1976c1 L0Debug - close connection when releasing Device resources 
- when debugDetach() is not called properly, close connection
in debug session before Device is destroyed

Related-To: NEO-7366

Signed-off-by: Mateusz Hoppe <mateusz.hoppe@intel.com>
 2022-10-04 13:10:12 +02:00
Mateusz Hoppe
cdac54de1d Validate zello_printf output 
Signed-off-by: Mateusz Hoppe <mateusz.hoppe@intel.com>
 2022-10-04 12:06:21 +02:00