intel/compute-runtime
1
0
Fork 0
mirror of https://github.com/intel/compute-runtime.git synced 2025-12-18 22:08:53 +08:00
Code Issues Packages Projects Releases Wiki Activity
11,409 Commits 42 Branches 655 Tags
add47dc79f451777ce39682462ce23ef2de1d92f
Commit Graph

11409 Commits

This Branch
This Branch
All Branches
Author SHA1 Message Date
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
Jaime Arteaga
a4f13e1984 Add support for PRELIM_I915_PARAM_SET_PAIR (3) 
Add some ULTs.

Signed-off-by: Jaime Arteaga <jaime.a.arteaga.molina@intel.com>
 2022-10-03 19:15:25 +02:00
Zbigniew Zdanowicz
3d92186362 Add heap sharing to immediate command lists 
This change is intended to be used in immediate command lists that are
using flush task functionality.
With this change all immediate command list using the same csr will consume
shared allocations for dsh and ssh heaps. This will decrease number of SBA
commands dispatched when multiple command lists coexists and dispatch kernels.
With this change new SBA command should be dispatched only when current heap
allocation is exhausted.
Functionality is currently disabled and available under debug key.
Functionality will be enabled by default for all immediate command lists
with flush task functionality enabled.

Related-To: NEO-7142

Signed-off-by: Zbigniew Zdanowicz <zbigniew.zdanowicz@intel.com>
 2022-10-03 18:50:10 +02:00
Yates, Brandon
71bef6094d Use max enabled slice in debugger thread mapping 
Signed-off-by: Yates, Brandon <brandon.yates@intel.com>
 2022-10-03 18:11:50 +02:00
Artur Harasimiuk
81845d3781 infra update 
Signed-off-by: Artur Harasimiuk <artur.harasimiuk@intel.com>
 2022-10-03 17:56:38 +02:00
Szymon Morek
67c0378a63 set Event::csr for immediate cmdlists 
Currently Event::csr is set during
initialization and never changes.
This PR is to associate Event::csr with the one
that was used to dispatch task in cmdlist

Signed-off-by: Szymon Morek <szymon.morek@intel.com>
 2022-10-03 11:54:11 +02:00
Compute-Runtime-Validation
95434f446f Revert "Retry in loop when exec or bind fails with ENXIO" 
This reverts commit ec13b185a3.

Signed-off-by: Compute-Runtime-Validation <compute-runtime-validation@intel.com>
 2022-10-01 12:13:35 +02:00
Joshua Santosh Ranjan
8240f65434 Remove Sysman dependency from Iaf nl interfaces 
This patch makes iaf nl interfaces in sysman be usable
by other modules.
1.change Iaf_nl interfaces to remove sysman dependencies
2.move iaf specific interfaces(getPorts()) to iaf specific file
3.move iaf_nl files to sysman/linux

Related-To: LOCI-3357

Signed-off-by: Joshua Santosh Ranjan <joshua.santosh.ranjan@intel.com>
 2022-10-01 01:46:14 +02:00
Jaime Arteaga
aab24e6552 Add support for PRELIM_I915_PARAM_SET_PAIR (2) 
Fix query for SET_PAIR.

Signed-off-by: Jaime Arteaga <jaime.a.arteaga.molina@intel.com>
 2022-09-30 21:20:00 +02:00