intel/compute-runtime
1
0
Fork 0
mirror of https://github.com/intel/compute-runtime.git synced 2025-12-31 20:13:04 +08:00
Code Issues Packages Projects Releases Wiki Activity
11,394 Commits 42 Branches 655 Tags
f226718fef955a4b5e0d99c0ab73783ca6a00a99
Commit Graph

11394 Commits

This Branch
This Branch
All Branches
Author SHA1 Message Date
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
Maciej Bielski
11eb0aa769 Do not bind command buffer separately 
Improve performance by binding the command buffer together with other
allocations if VM_BIND feature is available. Remove the legacy
flag PassBoundBOToExec from DebugManager to simplify the logic.
Adapt unit tests and reuse handy macros to generate proxy mock-methods.

Related-To: NEO-7348
Signed-off-by: Maciej Bielski <maciej.bielski@intel.com>
 2022-09-30 18:46:16 +02:00
Michal Mrozek
e6daa207ad sizeUsed doesn't have to be atomic. 
Linear stream is always being updated under mutex.
Massive improvement for whole zeCommandListAppendLaunchKernel +20%.

Signed-off-by: Michal Mrozek <michal.mrozek@intel.com>
 2022-09-30 17:07:21 +02:00
Michal Mrozek
2cb4cc3278 Optimize getSpace method for size 0. 
Add early return for this case.
+32% performance gain.

Signed-off-by: Michal Mrozek <michal.mrozek@intel.com>
 2022-09-30 16:04:34 +02:00
Szymon Morek
a91e41ec41 Remove unused struct 
Signed-off-by: Szymon Morek <szymon.morek@intel.com>
 2022-09-30 14:06:10 +02:00
Mateusz Hoppe
ec4d0dd0a6 L0Debug - ignore unknown VM BIND events - do not push to pending 
Related-To: NEO-7366

Signed-off-by: Mateusz Hoppe <mateusz.hoppe@intel.com>
 2022-09-30 13:31:30 +02:00
Compute-Runtime-Validation
ab8579a6c2 Revert "Ocloc: Add -s to options string for non-spirv input with -g option pa... 
This reverts commit 963930925a.

Signed-off-by: Compute-Runtime-Validation <compute-runtime-validation@intel.com>
 2022-09-30 13:11:46 +02:00
Mateusz Jablonski
9d18df63a9 Prevent auto-enabling gen flags for pre-gen12 devices on Windows 
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2022-09-30 13:01:11 +02:00
Mateusz Jablonski
23eff82d0a OCL: optimize creating printf buffer 
Dont create printf buffer when kernel doesnt require it

Related-To: HSD-18023825570
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2022-09-30 12:25:57 +02:00
Dunajski, Bartosz
48824acab2 Improve SBA programming 
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2022-09-30 12:07:16 +02:00
Baj, Tomasz
0eab93501c Add cl_cache mechanism to ocloc 
Related-To: NEO-6476

Signed-off-by: Baj, Tomasz <tomasz.baj@intel.com>
 2022-09-30 12:03:02 +02:00
Mateusz Hoppe
4292a47c53 Add Unit test for deferred deleter 
- test run() function

Signed-off-by: Mateusz Hoppe <mateusz.hoppe@intel.com>
 2022-09-30 11:37:45 +02:00
Matias Cabral
c012034c19 Debugger access to SLM 
Resolves: NEO-5998

Signed-off-by: Matias Cabral <matias.a.cabral@intel.com>
 2022-09-30 11:31:19 +02:00
Mateusz Hoppe
6811b1079f L0Debug - support for out of order debug events 
Related-To: NEO-7366
- if VM BIND comes with VM that cannot be mapped to tile,
push the event to pending events and process next events
until context params event with comes
- when pending event is handled - remove it from queue

Signed-off-by: Mateusz Hoppe <mateusz.hoppe@intel.com>
 2022-09-30 11:26:24 +02:00
sairamud
0d6ad522cb Update zesPowerGetEnergyCounter to return 64BitEnergyCounter in micro joules 
Signed-off-by: sairamud <sairam.udaya.janardhana.muttavarapu@intel.com>
 2022-09-30 11:15:43 +02:00
Jaime Arteaga
a3b3f3e86e Add support for PRELIM_I915_PARAM_SET_PAIR 
This extension allows pairing two buffer objects so they can be
exported using a single dma-buf handle. When imported, a single
buffer object is created with a total size of the two buffer
objects.

Related-To: LOCI-3355

Sync to
https://github.com/intel-gpu/drm-uapi-helper/releases/tag/v2.0-rc15

Signed-off-by: Jaime Arteaga <jaime.a.arteaga.molina@intel.com>
 2022-09-29 23:41:39 +02:00