intel/compute-runtime
1
0
Fork 0
mirror of https://github.com/intel/compute-runtime.git synced 2025-12-19 06:24:51 +08:00
Code Issues Packages Projects Releases Wiki Activity
11,426 Commits 42 Branches 655 Tags
cdffa8619c8770f950768600e3e7363d314b64ec
Commit Graph

11426 Commits

This Branch
This Branch
All Branches
Author SHA1 Message Date
Mateusz Hoppe
cdffa8619c Fix help in generate_cpp_array tool 
Signed-off-by: Mateusz Hoppe <mateusz.hoppe@intel.com>
 2022-10-10 13:19:07 +02:00
Lukasz Jobczyk
1fedaee18c Wait on timestamps in Event::wait 
Signed-off-by: Lukasz Jobczyk <lukasz.jobczyk@intel.com>
 2022-10-10 13:04:21 +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
Compute-Runtime-Validation
1c73031a9b Revert "Wait on timestamps in Event::wait" 
This reverts commit f91047f2ee.

Signed-off-by: Compute-Runtime-Validation <compute-runtime-validation@intel.com>
 2022-10-08 06:17:33 +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
Brandon Yates
f570cb37be Update to L0 Loader v1.8.8 
Signed-off-by: Brandon Yates <brandon.yates@intel.com>
 2022-10-07 22:09:15 +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
Kacper Nowak
d4cddc7ecd Zebin: fix segfault in zebin decoder 
Current implementation of getIntelGTNotes function causes
segfault in case empty owner name string would be passed.
This commit removes potential out-of-bound array access.
Signed-off-by: Kacper Nowak <kacper.nowak@intel.com>
 2022-10-07 17:32:09 +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
Lukasz Jobczyk
f91047f2ee Wait on timestamps in Event::wait 
Signed-off-by: Lukasz Jobczyk <lukasz.jobczyk@intel.com>
 2022-10-07 12:04:45 +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
Mateusz Hoppe
ff5b6918fd Allow using interface include dir from aubstream 
Signed-off-by: Mateusz Hoppe <mateusz.hoppe@intel.com>
 2022-10-06 12:43:50 +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
Jaime Arteaga
6532cb28bb Fix minor typos 
Signed-off-by: Jaime Arteaga <jaime.a.arteaga.molina@intel.com>
 2022-10-06 11:32:42 +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
Mateusz Jablonski
1808ebd0f9 infra update 
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2022-10-06 10:54:46 +02:00
Dunajski, Bartosz
caaf82bb83 Fix L3 size query 
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2022-10-06 10:46:39 +02:00
Dunajski, Bartosz
9100610b5d Remove test API to disable overdispatch 
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2022-10-06 10:12:47 +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
Compute-Runtime-Validation
f226718fef Revert "Remove test API to disable overdispatch" 
This reverts commit 3b92cef7a1.

Signed-off-by: Compute-Runtime-Validation <compute-runtime-validation@intel.com>
 2022-10-05 23:51:17 +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
Neumann, Marta
1b669f52d8 Embed NEO regkeys in AUB file 
Resolves: NEO-3105

Signed-off-by: Neumann, Marta <marta.neumann@intel.com>
 2022-10-05 14:49:13 +02:00
Szymon Morek
5c26ecf004 Remove duplicated code in command container 
Signed-off-by: Szymon Morek <szymon.morek@intel.com>
 2022-10-05 14:32:52 +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
Mateusz Jablonski
edca8aa6de Add cmake flag to add legacy platforms support 
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2022-10-05 13:28:45 +02:00
Mateusz Hoppe
2f24ef6855 Error from clEnqueueNDRangeKernel() for too big group counts 
Resolves: NEO-6976

Signed-off-by: Mateusz Hoppe <mateusz.hoppe@intel.com>
 2022-10-05 12:35:16 +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
Mateusz Jablonski
06817090bf Correct kernel binary names in case of skipped builtins compilation 
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2022-10-04 18:07:34 +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
Kacper Nowak
65f7ff2027 Ocloc: Add -s to options string for non-spirv input with -g option passed 
Automatically add "-s" (source path) option if -g flag is present.
This applies only to non-spirv input.
- Due to conflict, do not automatically append source path when
CMC compiler is used.
- Minor code refactor: use defined compiler options instead of local
strings; wrap filename in quotes (in case of space-separated filename
string).

Related-To: NEO-7285
Signed-off-by: Kacper Nowak kacper.nowak@intel.com
 2022-10-04 14:49:53 +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