intel/compute-runtime
1
0
Fork 0
mirror of https://github.com/intel/compute-runtime.git synced 2025-12-25 21:42:53 +08:00
Code Issues Packages Projects Releases Wiki Activity
7,384 Commits 42 Branches 655 Tags
b415cbae23e54c2175f8685443063fa1e3ccdd67
Commit Graph

84 Commits

Author SHA1 Message Date
Kamil Kopryk
14bc9fb0bf Ignore media block 2d patch token when media block support is disabled 
Signed-off-by: Kamil Kopryk <kamil.kopryk@intel.com>
Related-To: NEO-5820
 2021-05-17 11:38:46 +02:00
Mateusz Hoppe
1414247ed4 Register ELF before transferring ISA to Allocation 
Related-To: NEO-5857

Signed-off-by: Mateusz Hoppe <mateusz.hoppe@intel.com>
 2021-05-14 13:04:54 +02:00
Young Jin Yoon
bb53de1e4e Fix errors for incorrect work group size 
Related-To: LOCI-2084
Signed-off-by: Young Jin Yoon <young.jin.yoon@intel.com>
 2021-05-14 12:05:48 +02:00
Jaime Arteaga
128cd8a31c Add support for non-IPC P2P access to L0 
Signed-off-by: Jaime Arteaga <jaime.a.arteaga.molina@intel.com>
 2021-04-20 01:05:40 +02:00
Maciej Plewka
a51ee31500 Add method for unknown kernel arg 
Signed-off-by: Maciej Plewka <maciej.plewka@intel.com>
 2021-04-15 16:39:39 +02:00
Jaime Arteaga
a56b413392 Improve support for L0 uncached device allocations (2) 
Make sure UNCACHED flags are used in stateful paths.

Related-To: NEO-5500

Signed-off-by: Jaime Arteaga <jaime.a.arteaga.molina@intel.com>
 2021-04-12 09:47:30 +02:00
Jaime Arteaga
b510923e25 Fix error code for non-found kernel on zeKernelCreate() 
Signed-off-by: Jaime Arteaga <jaime.a.arteaga.molina@intel.com>
 2021-04-09 10:30:56 +02:00
Jaime Arteaga
ddca333045 Improve support for L0 uncached device allocations 
Make sure UNCACHED flags are translated into setting the MOCS index
for uncaching L3.

Related-To: NEO-5500

Signed-off-by: Jaime Arteaga <jaime.a.arteaga.molina@intel.com>
 2021-04-08 13:00:03 +02:00
Igor Venevtsev
bd32518d31 Add extra parameters to EncodeComputeMode::adjustComputeMode() method 
Signed-off-by: Igor Venevtsev <igor.venevtsev@intel.com>
 2021-03-31 16:51:55 +02:00
Mateusz Jablonski
8215395401 Simplify Context method 
return if context has multiple sub devices related to a given root device

Related-To: NEO-3691
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2021-03-30 10:22:15 +02:00
Mateusz Jablonski
35ff284944 Cleanup Kernel class 
move deviceVector to MultiDeviceKernel class
remove Device arg from Kernel's methods

Related-To: NEO-5001
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2021-03-24 09:17:41 +01:00
Filip Hazubski
8d55bfe21d Implement zeCommandListAppendLaunchCooperativeKernel 
Resolves: NEO-4725


Signed-off-by: Filip Hazubski <filip.hazubski@intel.com>
 2021-03-22 19:26:41 +01:00
Igor Venevtsev
52e118fe49 Add extra parameters to Buffer::setSurfaceState() method 
Signed-off-by: Igor Venevtsev <igor.venevtsev@intel.com>
 2021-03-16 10:17:59 +01:00
davidoli
8fdd1931a9 improve stub for zetKernelGetProfileInfo with ULT 
Signed-off-by: davidoli <david.olien@intel.com>
 2021-03-01 00:17:58 +01:00
Jaime Arteaga
722a80079b Add experimental_properties for indirect access (2) 
Add support to OpenCL to also make use of indirect access properties
provided by IGC and to make use of DisableIndirectAccess debug key.

Signed-off-by: Jaime Arteaga <jaime.a.arteaga.molina@intel.com>
 2021-02-25 11:41:24 +01:00
Mateusz Hoppe
6dd0f0c728 Relocate debug data 
Related-To: NEO-4769

Signed-off-by: Mateusz Hoppe <mateusz.hoppe@intel.com>
 2021-02-16 14:59:30 +01:00
Jaime Arteaga
1aca16a7ac Add experimental_properties for indirect access 
Read zebin experimental properties indicating whether a kernel has
indirect access and if so, ignore calls to zeKernelSetIndirectAccess.

Signed-off-by: Jaime Arteaga <jaime.a.arteaga.molina@intel.com>
 2021-02-10 14:23:43 +01:00
Igor Venevtsev
3df6110a17 Add extra parameters to setArgStateful() 
Signed-off-by: Igor Venevtsev <igor.venevtsev@intel.com>
 2021-02-05 12:24:27 +01:00
Jaime Arteaga
2fa27ebe73 Move ISA at kernel creation time (2) 
For internal kernels, move ISA only at creation time. For user
kernels, do it a module creation time.

Related-To: LOCI-2009

Signed-off-by: Jaime Arteaga <jaime.a.arteaga.molina@intel.com>
 2021-02-04 21:03:41 +01:00
Mateusz Hoppe
f7613a5827 Program surface state when debugging is enabled 
- surface state for debugSurface should be set when
kernel is compiled for debug

Signed-off-by: Mateusz Hoppe <mateusz.hoppe@intel.com>
 2021-02-02 17:53:12 +01:00
Jaime Arteaga
afffedebb2 Move ISA at kernel creation time 
Instead of moving the ISAs for all kernel in a module when the module
is created, move the ISA when the kernel is created, to avoid
unnecessary memory transfers.

Related-To: LOCI-2009

Signed-off-by: Jaime Arteaga <jaime.a.arteaga.molina@intel.com>
 2021-02-01 13:28:38 +01:00
Young Jin Yoon
4168ee8120 Print output from Kernel dtor to avoid segfault 
Related-to: LOCI-1912
Signed-off-by: Young Jin Yoon <young.jin.yoon@intel.com>
 2021-01-21 23:00:15 +01:00
Jaime Arteaga
05b5ad37ea Initialize kernel private surface when kernel is created 
This instead of when the associated module is created, to avoid
allocating memory for kernels that are never created nor used.

Signed-off-by: Jaime Arteaga <jaime.a.arteaga.molina@intel.com>
 2021-01-13 17:22:40 +01:00
Jaime Arteaga
08655a315c Revert "Initialize kernel private surface when kernel is created" 
This reverts commit be2a87fe98.

Signed-off-by: Jaime Arteaga <jaime.a.arteaga.molina@intel.com>
 2021-01-10 22:56:32 +01:00
Jaime Arteaga
be2a87fe98 Initialize kernel private surface when kernel is created 
This instead of when the associated module is created, to avoid
allocating memory for kernels that are never created nor used.

Signed-off-by: Jaime Arteaga <jaime.a.arteaga.molina@intel.com>
 2021-01-08 19:22:17 +01:00
Slawomir Milczarek
55f3c8f134 Add resolve capability for compressed USM device allocations 
Related-To: NEO-5107

Signed-off-by: Slawomir Milczarek <slawomir.milczarek@intel.com>
 2021-01-08 12:16:26 +01:00
Jaime Arteaga
d7ea713c5f Revert "Initialize kernel immutable data when kernel is created" 
This reverts commit a6ac10088c.

Signed-off-by: Jaime Arteaga <jaime.a.arteaga.molina@intel.com>
 2021-01-04 11:11:39 +01:00
Kamil Diedrich
e0da0e1868 Fix for block load and store 
Signed-off-by: Kamil Diedrich <kamil.diedrich@intel.com>
 2020-12-31 12:28:26 +01:00
Jaime Arteaga
a6ac10088c Initialize kernel immutable data when kernel is created 
This instead of when the associated module is created, to avoid
allocating memory for kernels that are never created nor used.

Signed-off-by: Jaime Arteaga <jaime.a.arteaga.molina@intel.com>
 2020-12-29 19:29:10 +01:00
Krystian Chmielewski
4948c39d39 Remove executionEnvironment from KernelInfo 
Related-To: NEO-3739
 2020-12-16 14:56:57 +01:00
Jim Snow
37cd49330c Implement ZE_CACHE_CONFIG_FLAG_LARGE_DATA for zeKernelSetCacheConfig 
Signed-off-by: Jim Snow <jim.m.snow@intel.com>
 2020-12-16 07:00:13 +01:00
Zbigniew Zdanowicz
b32b5784c2 Fix calculations for offseted addresses 
Signed-off-by: Zbigniew Zdanowicz <zbigniew.zdanowicz@intel.com>
 2020-12-11 20:25:54 +01:00
Jaime Arteaga
beb3c5ed05 Add support for global work offset extension in L0 
Add experimental extension to set global work offest in L0.
Current L0 specification does not have interface to export
experimental function symbols, so for now, applications need
to find the symbol like with dlsym on Linux.

A blackbox test showing functionality is also added.

Signed-off-by: Jaime Arteaga <jaime.a.arteaga.molina@intel.com>
 2020-12-09 07:33:40 +01:00
Zbigniew Zdanowicz
19bea962d0 Use imported host pointers in the driver when available 
Related-To: NEO-5126

Signed-off-by: Zbigniew Zdanowicz <zbigniew.zdanowicz@intel.com>
 2020-12-03 13:52:14 +01:00
Jaime Arteaga
be90b9ff93 Add support for ZE_DEVICE_MEM_ALLOC_FLAG_BIAS_UNCACHED 
Add support for device and shared allocations that use the
ZE_DEVICE_MEM_ALLOC_FLAG_BIAS_UNCACHED flag, whether the
kernel using the memory is stateless or statefull.

Signed-off-by: Jaime Arteaga <jaime.a.arteaga.molina@intel.com>
 2020-12-02 10:43:45 +01:00
macabral
720ba46548 Register kernel Elf for debugging purpose 
Signed-off-by: macabral <matias.a.cabral@intel.com>
 2020-12-01 17:16:14 +01:00
Maciej Plewka
c80353587f Patch bindless offset 
Related-To: NEO-4724

Signed-off-by: Maciej Plewka <maciej.plewka@intel.com>
 2020-11-20 23:02:36 +01:00
Jaroslaw Chodor
451f1e7e0d Fixing residency of global const/var buffers 
Signed-off-by: Jaroslaw Chodor <jaroslaw.chodor@intel.com>
 2020-11-18 13:15:06 +01:00
Mateusz Hoppe
0f42ef1ed7 Differentiate between users ISA and internal ISA allocation 
Related-To: NEO-5240

Signed-off-by: Mateusz Hoppe <mateusz.hoppe@intel.com>
 2020-11-16 13:16:30 +01:00
Jaime Arteaga
b3700370a6 Remove dead-code functions for cache intermediate/last-level config 
Signed-off-by: Jaime Arteaga <jaime.a.arteaga.molina@intel.com>
 2020-11-14 04:23:36 +01:00
Jaroslaw Chodor
d181a2e5a3 Fixing zeKernelGetProperties 
Additionally, adding zell_world_jitc_ocloc BB test

Change-Id: If3b8c7e4bd4a789ec1b4f4de55ab21e91c1e7afa
 2020-11-02 19:38:39 +01:00
Jaroslaw Chodor
345e56a151 Zebin improvements 
* cleaning-up per-thread buffer size calculations
* fixing default slm alignment to 16
* adding scratch space slots
* renaming slm addressing mode
* adding support for zeinfo version

Change-Id: I0450353788b8488a685976d7f1dd26a44360383c
 2020-10-29 16:33:21 +01:00
Filip Hazubski
c3b8727e97 Remove opencl includes from HwHelper 
Resolves: NEO-3964

Change-Id: Ie891ba6a205a89b41ca2cce0fa386dc4c93a0aaa
Signed-off-by: Filip Hazubski <filip.hazubski@intel.com>
 2020-10-23 11:10:52 +02:00
Bartosz Dunajski
1926ef8319 is_simt_thread token support 
Change-Id: I8cee6ff26229f0f492ba0d1e5e61d6e46e0c2486
Signed-off-by: Bartosz Dunajski <bartosz.dunajski@intel.com>
 2020-10-21 14:14:43 +02:00
Krystian Chmielewski
9f08a60a20 KernelInfo Refactor 
Using kernelDescriptor.kernelMetadata.kernelName instead of
kernelInfo.name

Change-Id: I11f5721d8072a3beccb573cec4bea56cf14cf0f9
 2020-10-20 13:18:09 +02:00
Bartosz Dunajski
27f9a95af2 Refactor: Common helper for Blit and CPU memory transfers 
Change-Id: Icc61f82517e75e3066e441494af3bf9a7ffbbeef
Signed-off-by: Bartosz Dunajski <bartosz.dunajski@intel.com>
 2020-10-12 18:29:42 +02:00
Bartosz Dunajski
fb0651521d Linker: Fix incremental patching for local memory allocations 
Change-Id: Ib85e4a2abc8a62477003853aa0c35f8107444f4e
Signed-off-by: Bartosz Dunajski <bartosz.dunajski@intel.com>
 2020-10-09 09:13:42 +02:00
Maciej Dziuban
138f04bdcd Enable L1 cache for Tigerlake 
Change-Id: I33513ed084f9d06ceca11315cac03f1b682db535
Signed-off-by: Maciej Dziuban <maciej.dziuban@intel.com>
Related-To: NEO-4832
 2020-10-06 13:26:54 +02:00
Jaroslaw Chodor
df2e76f526 Fixing residency of extern device functions 
Change-Id: Icad696cbf6fb3fc0276f0d0d488bf92091525d9b
 2020-10-02 12:27:59 +02:00
Spruit, Neil R
7ea864cbd2 Update Kernel Buffer Argument given nullptr value assignment 
- Given a nullptr Arg Buffer value, the argument value in cross thread
data must be updated to be a nullptr value especially given the argument
could have been set previously to a buffer that may not exist or should
not be used during this call to the kernel

Change-Id: Ie3a03ce25a4bb0b5e186863cc912a55863d0fb69
Signed-off-by: Spruit, Neil R <neil.r.spruit@intel.com>
 2020-09-25 00:43:00 +02:00