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
12,303 Commits 43 Branches 655 Tags
172ea34fc28e31e3a3942ca2f914ea70355f4d07
Commit Graph

1630 Commits

Author SHA1 Message Date
Maciej Plewka
bbc31e6aac Return error code for unsuported image arg in gen12lp 
Signed-off-by: Maciej Plewka <maciej.plewka@intel.com>
 2022-10-24 16:54:10 +02:00
Jim Snow
f976c7a313 Revert "Allocate RTDispatchGlobals as unboxed array" 
This reverts commit eaa4965ae8.

Signed-off-by: Jim Snow <jim.m.snow@intel.com>
 2022-10-24 05:16:03 +02:00
Compute-Runtime-Validation
d653779098 Revert "L0 debug - Fix thread creation for windows DSS" 
This reverts commit 3724807eed.

Signed-off-by: Compute-Runtime-Validation <compute-runtime-validation@intel.com>
 2022-10-22 14:38:24 +02:00
Yates, Brandon
3724807eed L0 debug - Fix thread creation for windows DSS 
Signed-off-by: Yates, Brandon <brandon.yates@intel.com>
 2022-10-21 18:47:49 +02:00
Zbigniew Zdanowicz
c777f43909 Enable heap sharing for XE_HPG 
Related-To: NEO-7142

Signed-off-by: Zbigniew Zdanowicz <zbigniew.zdanowicz@intel.com>
 2022-10-21 13:43:44 +02:00
Patryk Wrobel
9b26e96b11 Do not copy std::vector of OS handles when it is not needed 
This change replaces unneeded copying of std::vectors
with usage of const references. Furthermore, it adds
reserve() call before filling the container via push_back().

Signed-off-by: Patryk Wrobel <patryk.wrobel@intel.com>
 2022-10-21 10:28:58 +02:00
Jaime Arteaga
1a08240474 Add ze_eu_count_t to get total number of EUs 
Related-To: LOCI-2667

Signed-off-by: Jaime Arteaga <jaime.a.arteaga.molina@intel.com>
 2022-10-20 19:12:16 +02:00
Michal Mrozek
3384b2fed0 Add debug flag to override zeDeviceCanAccessPeer return value. 
Signed-off-by: Michal Mrozek <michal.mrozek@intel.com>
 2022-10-20 14:39:12 +02:00
Joshua Santosh Ranjan
a93edd8620 Support for FabricEdge APIs 
Related-To: LOCI-3377

Signed-off-by: Joshua Santosh Ranjan <joshua.santosh.ranjan@intel.com>
 2022-10-20 10:43:25 +02:00
Compute-Runtime-Validation
4a3862b514 Revert "Add ze_eu_count_t to get total number of EUs" 
This reverts commit 2b963c7359.

Signed-off-by: Compute-Runtime-Validation <compute-runtime-validation@intel.com>
 2022-10-20 06:53:14 +02:00
Jaime Arteaga
2b963c7359 Add ze_eu_count_t to get total number of EUs 
Related-To: LOCI-2667

Signed-off-by: Jaime Arteaga <jaime.a.arteaga.molina@intel.com>
 2022-10-19 07:17:25 +02:00
Compute-Runtime-Validation
fb453f5190 Revert "Enable flush task for immediate command lists" 
This reverts commit a4eb78d524.

Signed-off-by: Compute-Runtime-Validation <compute-runtime-validation@intel.com>
 2022-10-19 03:32:53 +02:00
John Falkowski
0b2491f9e6 createSampler returns error for PVC 
Signed-off-by: John Falkowski <john.falkowski@intel.com>
 2022-10-18 18:13:34 +02:00
Aravind Gopalakrishnan
a4eb78d524 Enable flush task for immediate command lists 
Enabling for all platforms

Related-To: LOCI-3379

Signed-off-by: Aravind Gopalakrishnan <aravind.gopalakrishnan@intel.com>
 2022-10-18 17:17:05 +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
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
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
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
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
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
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
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
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
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
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
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
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