intel/compute-runtime
1
0
Fork 0
mirror of https://github.com/intel/compute-runtime.git synced 2025-12-31 03:20:47 +08:00
Code Issues Packages Projects Releases Wiki Activity
12,062 Commits 42 Branches 655 Tags
32bab85f7e06acacf5eace06eb7cdd042a79e9be
Commit Graph

684 Commits

Author SHA1 Message Date
Jaime Arteaga
32bab85f7e Check for context in appendMemoryCopy 
Confirm the allocations used in an appendMemoryCopy operation
belong to the same context as the list.

Related-To: LOCI-1996
Resolves: NEO-6162

Signed-off-by: Jaime Arteaga <jaime.a.arteaga.molina@intel.com>
 2022-12-20 00:13:36 +01:00
Compute-Runtime-Validation
5a29cf8508 Revert "Check for context in appendMemoryCopy" 
This reverts commit afd0784c16.

Signed-off-by: Compute-Runtime-Validation <compute-runtime-validation@intel.com>
 2022-12-16 03:28:06 +01:00
Compute-Runtime-Validation
1894d2da5b Revert "Limit cooperative dispatch support to platforms supporting cooperativ... 
This reverts commit c124bfbc6c.

Signed-off-by: Compute-Runtime-Validation <compute-runtime-validation@intel.com>
 2022-12-16 02:52:59 +01:00
Jaime Arteaga
afd0784c16 Check for context in appendMemoryCopy 
Confirm the allocations used in an appendMemoryCopy operation
belong to the same context as the list.

Related-To: LOCI-1996
Resolves: NEO-6162

Signed-off-by: Jaime Arteaga <jaime.a.arteaga.molina@intel.com>
 2022-12-15 23:42:10 +01:00
Filip Hazubski
c124bfbc6c Limit cooperative dispatch support to platforms supporting cooperative engine 
By default, cooperative dispatch is not supported
for platforms not supporting cooperative engine.

Signed-off-by: Filip Hazubski <filip.hazubski@intel.com>
 2022-12-15 15:12:23 +01:00
Kamil Kopryk
232b886056 Rename HwInfoConfig to ProductHelper 
Related-To: NEO-6853
Signed-off-by: Kamil Kopryk <kamil.kopryk@intel.com>
 2022-12-14 14:39:52 +01:00
Dunajski, Bartosz
bcecd069b4 Add additional kernel flag + capability to pull extra patch tokens 
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2022-12-13 09:04:39 +01:00
Kamil Kopryk
03b687881f Rename HwHelper -> GfxCoreHelper 
Related-To: NEO-6853
Signed-off-by: Kamil Kopryk <kamil.kopryk@intel.com>
 2022-12-09 10:29:06 +01:00
Lukasz Jobczyk
573ac33e1d Enqueue marker before split when OOQ barrier have to be handled 
Signed-off-by: Lukasz Jobczyk <lukasz.jobczyk@intel.com>
 2022-12-07 17:15:41 +01:00
Warchulski, Jaroslaw
be647d42d9 Cleanup includes 12 
Related-To: NEO-5548
Signed-off-by: Warchulski, Jaroslaw <jaroslaw.warchulski@intel.com>
 2022-12-07 13:14:15 +01:00
Dominik Dabek
7d7ecd50b6 DG2, Enable resolving dependecies by pipecontrol 
Enable resolving dependencies by pipecontrol on same CSR, IOQ on DG2 by
default.

Related-To: NEO-7321

Signed-off-by: Dominik Dabek <dominik.dabek@intel.com>
 2022-12-07 12:49:52 +01:00
Dominik Dabek
4adba15dbb Update for resolving dependencies by pipecontrol 
Flag ResolveDependenciesViaPipeControls now removes only same csr
dependencies. Still enables pipe controls.

Works through hwInfoConfig method isResolveDependenciesByPipeControlsSupported

Related-To: NEO-7321

Signed-off-by: Dominik Dabek <dominik.dabek@intel.com>
 2022-12-05 15:48:49 +01:00
Kamil Kopryk
91d39ad5bf Rename ClHwHelper -> ClGfxCoreHelper 
Related-To: NEO-6853
Signed-off-by: Kamil Kopryk <kamil.kopryk@intel.com>
 2022-12-05 11:26:20 +01:00
Kamil Kopryk
785b9eeece Rename CompilerHwInfoConfig -> CompilerProductHelper 
Related-To: NEO-6853
Signed-off-by: Kamil Kopryk <kamil.kopryk@intel.com>
 2022-12-05 11:25:49 +01:00
Maciej Plewka
4b42b066f8 Use dedicated using type for TaskCount 
Related-To: NEO-7155

Signed-off-by: Maciej Plewka <maciej.plewka@intel.com>
 2022-11-28 16:44:44 +01:00
Naklicki, Mateusz
914939c377 Fix execution of cooperative kernels on multi-tile device 
Add flag for forcing execution of kernels on single tile
Force cooperative kernels to use only single tile

Related-to: NEO-6729
Signed-off-by: Naklicki, Mateusz <mateusz.naklicki@intel.com>
 2022-11-28 14:36:21 +01:00
Dunajski, Bartosz
bc619fcbec Queue stall mode for RelaxedOrdering 
Related-To: NEO-7458

Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2022-11-23 12:09:52 +01:00
Mateusz Jablonski
bb308c04ed Refactor aubstream include interface 
set include path to third_party/aub_stream
rename third_party/aub_stream/headers -> third_party/aub_stream/aubstream

Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2022-11-23 10:30:13 +01:00
Mateusz Hoppe
f19abda0e2 Set root device index in OsContext 
- correclty choose default engine context accounting for root device
index and  subdevices bitfield

Related-To: NEO-7516

Signed-off-by: Mateusz Hoppe <mateusz.hoppe@intel.com>
 2022-11-16 23:02:19 +01:00
Mateusz Jablonski
59b3d3fbea Move code from header files to cpp files 
Moved code from:
- shared/test/common/mocks/mock_execution_environment.h
- shared/test/common/fixtures/mock_aub_center_fixture.h

Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2022-11-16 15:06:07 +01:00
Szymon Morek
a66e69abc9 Prealloc cmd buffer for CSR only when being used 
Related-To: NEO-7361

Currently additional command buffer is
preallocated for all CSRs, even for those which
won't be used by application. This PR changes that

Signed-off-by: Szymon Morek <szymon.morek@intel.com>
 2022-11-15 20:06:29 +01:00
Kamil Kopryk
0e47bcde1d Move ClCoreHelper ownership to RootDeviceEnvironment 4/n 
Related-To: NEO-6853
Signed-off-by: Kamil Kopryk <kamil.kopryk@intel.com>

Use RootDeviceEnvironment getHelper<ClCoreHelper> for
- isSupportedKernelThreadArbitrationPolicy
- getSupportedThreadArbitrationPolicies
 2022-11-15 17:24:11 +01:00
Kamil Kopryk
9564af14f5 Move ClCoreHelper ownership to RootDeviceEnvironment 3/n 
Related-To: NEO-6853
Signed-off-by: Kamil Kopryk <kamil.kopryk@intel.com>

Use RootDeviceEnvironment getHelper<ClCoreHelper> for
- getQueueFamilyName
- getKernelPrivateMemSize
- preferBlitterForLocalToLocalTransfers
 2022-11-15 15:45:33 +01:00
Mateusz Jablonski
5f8cc9b99b Remove commented code 
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2022-11-15 14:20:17 +01:00
Kamil Kopryk
1d4240a0c8 Move ClCoreHelper ownership to RootDeviceEnvironment 1/n 
Related-To: NEO-6853
Signed-off-by: Kamil Kopryk <kamil.kopryk@intel.com>

Use RootDeviceEnvironment getHelper<ClCoreHelper> for
- requiresNonAuxMode
- requiresAuxResolves
 2022-11-15 10:35:22 +01:00
Lukasz Jobczyk
0a07ea94c7 Enable bcs split for H2H transfers 
Signed-off-by: Lukasz Jobczyk <lukasz.jobczyk@intel.com>
 2022-11-14 14:23:02 +01:00
Milczarek, Slawomir
25a5ed0dca Allocate buffers in local memory for PVC multi root device platforms (1/n) 
PVC platform with no support for atomic operations on system memory
must always allocate buffers in local memory to avoid atomic access violation.
Note: the feature is being implemented under the new registry key
AllocateBuffersInLocalMemoryForMultiRootDeviceContexts (disabled by default)

Related-To: NEO-7092

Signed-off-by: Milczarek, Slawomir <slawomir.milczarek@intel.com>
 2022-11-14 13:56:50 +01:00
Katarzyna Cencelewska
e75d62af5d Set as default use of device based timestamps 
Related-To: NEO-7042
Signed-off-by: Katarzyna Cencelewska <katarzyna.cencelewska@intel.com>
 2022-11-10 16:39:56 +01:00
Compute-Runtime-Validation
c0ce5f4684 Revert "Set as default use of device based timestamps" 
This reverts commit 2d229f3fea.

Signed-off-by: Compute-Runtime-Validation <compute-runtime-validation@intel.com>
 2022-11-10 11:21:00 +01:00
Mateusz Jablonski
57cea7365e Return submission status from flushTagUpdate method 
Related-To: NEO-7412
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2022-11-09 14:04:16 +01:00
Mateusz Hoppe
f77f47099c OCL: Fix error for too big dimensions 
- cases with null lws should only fail when computed
lws sizes result in too big number of workgroups

Related-To: NEO-6976

Signed-off-by: Mateusz Hoppe <mateusz.hoppe@intel.com>
 2022-11-08 16:11:41 +01:00
Katarzyna Cencelewska
2d229f3fea Set as default use of device based timestamps 
Related-To: NEO-7042
Signed-off-by: Katarzyna Cencelewska <katarzyna.cencelewska@intel.com>
 2022-11-08 13:34:58 +01:00
Kamil Kopryk
68300a9605 Correct typo - createFunc 
Signed-off-by: Kamil Kopryk <kamil.kopryk@intel.com>
 2022-11-08 09:16:43 +01:00
Mateusz Jablonski
1c3d5c3892 Prepare mechanism for returning GPU execution error on OCL API 
translate task count value to OCL error

Related-To: NEO-7412
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2022-11-04 15:54:19 +01:00
Luzynski, Sebastian Jozef
91c69e0fe7 Patch global variables and constants once 
This change replaces mechanism of patching global constants and
variables in kernel per relocation to patching them only once. This
would improve linking time performance for kernels with multiple global
symbols.

Signed-off-by: Luzynski, Sebastian Jozef <sebastian.jozef.luzynski@intel.com>
 2022-11-03 17:45:09 +01:00
Krystian Chmielewski
52b1d92193 Mock debug program instead of using binaries 
Removes usage of precompiled binaries in debug program tests.

Related-To: NEO-7383

Signed-off-by: Krystian Chmielewski <krystian.chmielewski@intel.com>
 2022-11-02 17:50:42 +01:00
Krystian Chmielewski
69bef975f0 OCL cache per thread data 
Add caching mechanism for local ids in OCL.

Signed-off-by: Krystian Chmielewski <krystian.chmielewski@intel.com>
 2022-11-02 17:07:29 +01:00
Zbigniew Zdanowicz
565d820933 Replace virtual method call for DC flush with stored bool value 3/n 
Signed-off-by: Zbigniew Zdanowicz <zbigniew.zdanowicz@intel.com>
 2022-10-18 15:04:02 +02:00
Krystian Chmielewski
c224fd0666 Require LWS to be in ascending format X >= Y >= Z 
This change fixes problem with memory locality.
When calculating work group size do not take into account
work group sizes where there's bigger number of elements in
higher dimensions namely: Y>X or Z>Y.

Related-To: NEO-5719

Signed-off-by: Krystian Chmielewski <krystian.chmielewski@intel.com>
 2022-10-18 13:23:57 +02:00
Compute-Runtime-Validation
945897cf55 Revert "Replace virtual method call for DC flush with stored bool value 3/n" 
This reverts commit 9d94089a95.

Signed-off-by: Compute-Runtime-Validation <compute-runtime-validation@intel.com>
 2022-10-13 04:46:10 +02:00
Zbigniew Zdanowicz
9d94089a95 Replace virtual method call for DC flush with stored bool value 3/n 
Signed-off-by: Zbigniew Zdanowicz <zbigniew.zdanowicz@intel.com>
 2022-10-12 14:38:47 +02:00
Lukasz Jobczyk
1fedaee18c Wait on timestamps in Event::wait 
Signed-off-by: Lukasz Jobczyk <lukasz.jobczyk@intel.com>
 2022-10-10 13:04:21 +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
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
Zbigniew Zdanowicz
5986a7199a Share front end state updates between regular and immediate command lists 
Related-To: NEO-5019

Signed-off-by: Zbigniew Zdanowicz <zbigniew.zdanowicz@intel.com>
 2022-09-23 09:46:35 +02:00
Lukasz Jobczyk
efac290ba3 Do not use selector copy engine 
Signed-off-by: Lukasz Jobczyk <lukasz.jobczyk@intel.com>
 2022-09-20 21:49:00 +02:00
Lukasz Jobczyk
e00a5e0a1e Release main copy engine from device and sub device 
Signed-off-by: Lukasz Jobczyk <lukasz.jobczyk@intel.com>
 2022-09-20 17:12:34 +02:00
Michal Mrozek
3d5e34f727 Reduce the size of masks to 4. 
32 is not required.

Signed-off-by: Michal Mrozek <michal.mrozek@intel.com>
 2022-09-19 21:53:40 +02:00
Milczarek, Slawomir
0192e8038f Check for GPU hang in path with wait for timestamps 
Related-To: NEO-6868

Signed-off-by: Milczarek, Slawomir <slawomir.milczarek@intel.com>
 2022-09-19 15:01:46 +02:00
Lukasz Jobczyk
3a7f266d66 Enable BCS split in OCL 
Signed-off-by: Lukasz Jobczyk <lukasz.jobczyk@intel.com>
 2022-09-08 15:56:30 +02:00