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,417 Commits 42 Branches 655 Tags
8a6cf4fd4ed1c0b8f035065f769f37e5c3e264b0
Commit Graph

11417 Commits

This Branch
This Branch
All Branches
Author SHA1 Message Date
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
Mateusz Jablonski
19c4245ae7 infra update 
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2022-10-04 13:35:34 +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
Zbigniew Zdanowicz
9cd47ffeaf Add ownership management when ensuring space for shared heaps 
Related-To: NEO-7142

Signed-off-by: Zbigniew Zdanowicz <zbigniew.zdanowicz@intel.com>
 2022-10-04 12:27:11 +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
Szymon Morek
383f33b482 [L0][XE_HPC]Perform memcpy on CPU by default 
Related-To: NEO-7237

Signed-off-by: Szymon Morek <szymon.morek@intel.com>
 2022-10-04 11:39:30 +02:00
Szymon Morek
c70df154a3 Store EXTERNAL_HOST_PTR as a temporary allocation 
Related-To: NEO-7359

Currently, for copy only async immediate cmdlists
we don't release external host ptr when it's no
longer needed. This is not spec complaint.
This PR fixes this.

Signed-off-by: Szymon Morek <szymon.morek@intel.com>
 2022-10-04 10:41:46 +02:00
Baj, Tomasz
625f88d64d Move API specific logic directly to getDefaultCompilerCacheConfig function 
Signed-off-by: Baj, Tomasz <tomasz.baj@intel.com>
 2022-10-04 10:25:08 +02:00
Dunajski, Bartosz
3b92cef7a1 Remove test API to disable overdispatch 
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2022-10-04 09:54:05 +02:00
Compute-Runtime-Validation
36e17cebef Revert "Include dynamic SLM in clGetKernelWorkGroupInfo" 
This reverts commit ccdb5aaa2a.

Signed-off-by: Compute-Runtime-Validation <compute-runtime-validation@intel.com>
22.41.24420 		2022-10-03 19:27:21 +02:00