intel/compute-runtime
1
0
Fork 0
mirror of https://github.com/intel/compute-runtime.git synced 2025-12-30 01:35:20 +08:00
Code Issues Packages Projects Releases Wiki Activity
8,548 Commits 42 Branches 655 Tags
0d74ab8ae8c4033b3a54953367d55e22be67ea55
Commit Graph

121 Commits

Author SHA1 Message Date
Mateusz Hoppe
10e4b54986 Copy ISA before making it resident 
Signed-off-by: Mateusz Hoppe <mateusz.hoppe@intel.com>
 2021-10-12 21:51:06 +02:00
Raiyan Latif
0859f99d64 Enable zeDeviceCanAccessPeer 
- Propagate return value up from Batch Buffer exec
- Add zeDeviceCanAccessPeer functionality

Signed-off-by: Raiyan Latif <raiyan.latif@intel.com>
 2021-10-12 09:38:22 +02:00
Zbigniew Zdanowicz
96fef37834 Move shared local work size code to shared directory 
Signed-off-by: Zbigniew Zdanowicz <zbigniew.zdanowicz@intel.com>
 2021-10-04 14:04:28 +02:00
Jaime Arteaga
11980db8eb Create L0 list and module with correct NEO device on explicit mode 
When implicit scaling is not used, a root device in L0 defaults to
sub-device 0. In that case, all allocations need to be made against
that sub-device.

For list and module creation, we were passing the root NEO device
instead, and we were allocating their internal allocations using
the least-occupied bank, which meant we were allocating alternately
between the two sub-devices.

This patch makes sure the NEO device used on explicit mode for
the root device is sub-device 0.

Signed-off-by: Jaime Arteaga <jaime.a.arteaga.molina@intel.com>
 2021-10-01 00:43:53 +02:00
Zbigniew Zdanowicz
25c71a6c13 Move kernel info to shared directory 
Signed-off-by: Zbigniew Zdanowicz <zbigniew.zdanowicz@intel.com>
 2021-09-29 23:49:49 +02:00
Mateusz Jablonski
e82c2e4653 Patch printf buffer in implicit args in L0 
Related-To: NEO-5081
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2021-09-16 10:31:40 +02:00
Mateusz Jablonski
5a59a6ad2e Add support for implicit args in L0 
Related-To: NEO-5081
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2021-09-15 11:12:23 +02:00
Mateusz Jablonski
f958b053ab Merge patchWorkDim method's logic into setGroupCount method 
Related-To: NEO-5081
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2021-09-14 08:57:24 +02:00
Mateusz Jablonski
caddc63eec Remove not needed function 
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2021-09-07 12:24:35 +02:00
Bartosz Dunajski
0345d9f707 Improve queries with number of SubDevices 
Signed-off-by: Bartosz Dunajski <bartosz.dunajski@intel.com>
 2021-09-01 14:01:57 +02:00
Filip Hazubski
de1e4e0074 Add adjustMaxWorkGroupCount helper 
Signed-off-by: Filip Hazubski <filip.hazubski@intel.com>
 2021-08-27 15:39:48 +02:00
Jaime Arteaga
0bd41cc3ec Add support for ze_kernel_preferred_group_size_properties_t 
Related-To: LOCI-2313

Signed-off-by: Jaime Arteaga <jaime.a.arteaga.molina@intel.com>
 2021-08-25 00:10:13 +02:00
Compute-Runtime-Validation
c92ff15d59 Revert "Add support for ze_kernel_preferred_group_size_properties_t" 
This reverts commit b193475abb.

Signed-off-by: Compute-Runtime-Validation <compute-runtime-validation@intel.com>
 2021-08-24 04:44:59 +02:00
Jaime Arteaga
b193475abb Add support for ze_kernel_preferred_group_size_properties_t 
Related-To: LOCI-2313

Signed-off-by: Jaime Arteaga <jaime.a.arteaga.molina@intel.com>
 2021-08-23 19:23:40 +02:00
Compute-Runtime-Validation
0ae53851da Revert "Add support for ze_kernel_preferred_group_size_properties_t" 
This reverts commit 4586238c0e.

Signed-off-by: Compute-Runtime-Validation <compute-runtime-validation@intel.com>
 2021-08-17 04:28:15 +02:00
Jaime Arteaga
4586238c0e Add support for ze_kernel_preferred_group_size_properties_t 
Related-To: LOCI-2313

Signed-off-by: Jaime Arteaga <jaime.a.arteaga.molina@intel.com>
 2021-08-16 20:02:42 +02:00
Vinod Tipparaju
37670aeb91 Add support for new thread arbitration policies via zeKernelSchedulingHintExp 
Related-To: LOCI-2319

Signed-off-by: Vinod Tipparaju <vinod.tipparaju@intel.com>
 2021-08-09 21:07:08 +02:00
Krystian Chmielewski
8f72a68440 Use proper private mem allocation 
Related-To: NEO-6063
Signed-off-by: Krystian Chmielewski <krystian.chmielewski@intel.com>
 2021-08-06 13:17:21 +02:00
Jaroslaw Chodor
7c6c45f5b5 Add option to allocate private mem per dispatch 
Signed-off-by: Jaroslaw Chodor <jaroslaw.chodor@intel.com>
Signed-off-by: Krystian Chmielewski <krystian.chmielewski@intel.com>
 2021-07-27 13:34:12 +02:00
Compute-Runtime-Validation
1d1a8473aa Revert "Add support for ze_kernel_preferred_group_size_properties_t" 
This reverts commit aa98c9211d.

Signed-off-by: Compute-Runtime-Validation <compute-runtime-validation@intel.com>
 2021-07-27 05:07:23 +02:00
Jaime Arteaga
aa98c9211d Add support for ze_kernel_preferred_group_size_properties_t 
Related-To: LOCI-2313

Signed-off-by: Jaime Arteaga <jaime.a.arteaga.molina@intel.com>
 2021-07-26 20:31:38 +02:00
Zbigniew Zdanowicz
a869921c2a Remove RMW from gfx allocations 
Signed-off-by: Zbigniew Zdanowicz <zbigniew.zdanowicz@intel.com>
 2021-07-15 11:28:03 +02:00
Dominik Dabek
dc9b2351d5 Change patchGlobalOffset in l0 kernel to void 
Signed-off-by: Dominik Dabek <dominik.dabek@intel.com>
 2021-07-06 11:36:53 +02:00
Dominik Dabek
62f89b174a Add work_dim patching to l0 kernel 
Related-To: NEO-5931

Signed-off-by: Dominik Dabek <dominik.dabek@intel.com>
 2021-07-05 20:09:20 +02:00
Compute-Runtime-Validation
233aab88e7 Revert "Add support for ze_kernel_preferred_group_size_properties_t" 
This reverts commit 6b0b5ef2ff.

Signed-off-by: Compute-Runtime-Validation <compute-runtime-validation@intel.com>
 2021-07-03 11:19:38 +02:00
Jaime Arteaga
6b0b5ef2ff Add support for ze_kernel_preferred_group_size_properties_t 
Signed-off-by: Jaime Arteaga <jaime.a.arteaga.molina@intel.com>
 2021-07-02 12:10:33 +02:00
Jim Snow
2acc0fb3f6 Add memory backed buffer allocation for L0 ray tracing. 
This allocates the buffer on a per-device basis and enables ray
tracing on devices that support it when given a kernel with ray
tracing calls.

Signed-off-by: Jim Snow <jim.m.snow@intel.com>
 2021-07-02 11:56:18 +02:00
Maciej Plewka
4dda709b41 Fix add unaligned part to size in surface state 
Signed-off-by: Maciej Plewka <maciej.plewka@intel.com>
 2021-06-29 13:13:26 +02:00
Compute-Runtime-Validation
20ba56f254 Revert "Add support for ze_kernel_preferred_group_size_properties_t" 
This reverts commit ef07bbd041.

Signed-off-by: Compute-Runtime-Validation <compute-runtime-validation@intel.com>
 2021-06-28 17:21:33 +02:00
Jaime Arteaga
ef07bbd041 Add support for ze_kernel_preferred_group_size_properties_t 
Signed-off-by: Jaime Arteaga <jaime.a.arteaga.molina@intel.com>
 2021-06-28 13:15:50 +02:00
Maciej Plewka
0d973aaaa3 Programm smaller buffer size in SS when offset not patched 
Signed-off-by: Maciej Plewka <maciej.plewka@intel.com>
 2021-06-23 14:20:53 +02:00
Compute-Runtime-Validation
3137e82fca Revert "Remove redundant DualSubSliceCount checks" 
This reverts commit 5e85fe5042.

Signed-off-by: Compute-Runtime-Validation <compute-runtime-validation@intel.com>
 2021-06-17 13:47:49 +02:00
Filip Hazubski
5e85fe5042 Remove redundant DualSubSliceCount checks 
Signed-off-by: Filip Hazubski <filip.hazubski@intel.com>
 2021-06-17 11:11:56 +02:00
Maciej Plewka
689ceacfe6 Fix set allocation adress in SS when offset is patched 
Signed-off-by: Maciej Plewka <maciej.plewka@intel.com>
 2021-06-08 13:05:38 +02:00
Bartlomiej Wolny
b98148fb3f Adjust minWorkGroupSize when EUFusion is enabled 
Related-To: NEO-5260

Co-authored-by: Bartlomiej Wolny <bartlomiej.wolny@intel.com>
Signed-off-by: Maciej Dziuban <maciej.dziuban@intel.com>
 2021-06-08 11:43:26 +02:00
Mateusz Hoppe
32729f6feb Handle VM BIND events - extract ISA allocation info 
Signed-off-by: Mateusz Hoppe <mateusz.hoppe@intel.com>
 2021-05-20 13:19:23 +02:00
lgotszal
3bd4bca911 Copyright header update 
Dates corrected in copyright headers to reflect original publication date
(2018 for OpenCL, 2020 for Level Zero).

Signed-off-by: lgotszal <lukasz.gotszald@intel.com>
 2021-05-17 20:38:19 +02:00
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