Media
/
compute-runtime
mirror of https://github.com/intel/compute-runtime.git
1
0
Fork 0
Code Issues Packages Projects Releases Wiki Activity
17,779 Commits 36 Branches 607 Tags 169 MiB
Commit Graph

377 Commits

Author SHA1 Message Date
Mateusz Jablonski 10dbfc0d19 Reduce usage of global gfx core helper getter [3/n] 
Related-To: NEO-6853
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2022-12-13 11:13:11 +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
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
Warchulski, Jaroslaw 1fa5710dff Cleanup includes 10 
Related-To: NEO-5548
Signed-off-by: Warchulski, Jaroslaw <jaroslaw.warchulski@intel.com>
 2022-12-05 12:39:33 +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
Andrzej Koska 90034d4173 Added scratch size check 
Related-To: NEO-7508
Signed-off-by: Andrzej Koska <andrzej.koska@intel.com>
 2022-11-22 14:14:33 +01:00
Fabian Zwolinski f6eb2e753a Error check total SLM size not only inline 
Related-To: NEO-7280
Signed-off-by: Fabian Zwolinski <fabian.zwolinski@intel.com>
 2022-11-21 15:30:25 +01:00
Warchulski, Jaroslaw 1c03361273 Cleanup includes 6 
Related-To: NEO-5548
Signed-off-by: Warchulski, Jaroslaw <jaroslaw.warchulski@intel.com>
 2022-11-21 12:02:14 +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
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
Kamil Kopryk 4aa1697e3c Move hwInfoConfig ownership to RootDeviceEnvironment 2/n 
Related-To: NEO-6853
Signed-off-by: Kamil Kopryk <kamil.kopryk@intel.com>

Use RootDeviceEnvironment getHelper<ProductHelper> for
- adjustSamplerState
- adjustPlatformForProductFamily.
 2022-11-14 13:04:31 +01:00
Kamil Kopryk 002a90c717 Move hwHelper ownership to RootDeviceEnvironment 2/n 
Related-To: NEO-6853
Signed-off-by: Kamil Kopryk <kamil.kopryk@intel.com>

UseRootDeviceEnvironment getHelper<CoreHelper> for:
- getMaxBarrierRegisterPerSlice
- getPaddingForISAAllocation
 2022-11-10 16:39:39 +01:00
Warchulski, Jaroslaw ef95bfb45e Cleanup includes 
Related-To: NEO-5548
Signed-off-by: Warchulski, Jaroslaw <jaroslaw.warchulski@intel.com>
 2022-11-04 18:04:13 +01:00
Kacper Nowak 709e322a4a feat(zebin): get extended args metadata on clGetKernelArgInfo API call 
This commit adds support for retrieving extended args metadata passed in
.kernel_misc_info zeInfo's section on clGetKernelArgInfo call.

Related-To: NEO-7372
Signed-off-by: Kacper Nowak <kacper.nowak@intel.com>
 2022-11-03 13:15:09 +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
Maciej Plewka 7f38c5e633 Revert "Return error code for unsuported image arg in gen12lp" 
This reverts commit bbc31e6aac


Signed-off-by: Maciej Plewka maciej.plewka@intel.com
 2022-11-02 12:57:16 +01:00
Maciej Plewka ff01b9361e Return error code when there is no space for scratch/private 
Signed-off-by: Maciej Plewka <maciej.plewka@intel.com>
 2022-11-02 11:55:18 +01:00
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
Compute-Runtime-Validation 052164c559 Revert "Use total SLM instead of inline in error checking" 
This reverts commit e1c49d0f23.

Signed-off-by: Compute-Runtime-Validation <compute-runtime-validation@intel.com>
 2022-10-22 09:41:36 +02:00
Fabian Zwolinski e1c49d0f23 Use total SLM instead of inline in error checking 
Related-To: NEO-7280
Signed-off-by: Fabian Zwolinski <fabian.zwolinski@intel.com>
 2022-10-21 12:39:48 +02:00
Kacper Nowak f06df021b5 feat(zebin): Add support for indirect stateless count 
Add support for newly added indirect statelss count check;
populate related field in kernelInfo.
- Move hasIndirectStatelessAccess check from KernelInfo to
KernelDescriptor.

Related-To: NEO-7428
Signed-off-by: Kacper Nowak <kacper.nowak@intel.com>
 2022-10-19 07:58:02 +02:00
Compute-Runtime-Validation c2ce19ff36 Revert "Include dynamic SLM in clGetKernelWorkGroupInfo" 
This reverts commit 320b020dd6.

Signed-off-by: Compute-Runtime-Validation <compute-runtime-validation@intel.com>
 2022-10-12 22:58:58 +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
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
Fabian Zwolinski 320b020dd6 Include dynamic SLM in clGetKernelWorkGroupInfo 
Current implementation only takes static slmInlineSize into account.
With this change we also include dynamic SLM passed as a kernel arguments.

Related-To: NEO-5761
Signed-off-by: Fabian Zwolinski <fabian.zwolinski@intel.com>
 2022-10-11 09:59:05 +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
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
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
Dunajski, Bartosz 9100610b5d Remove test API to disable overdispatch 
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2022-10-06 10:12:47 +02:00
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 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>
 2022-10-03 19:27:21 +02:00
Fabian Zwolinski ccdb5aaa2a Include dynamic SLM in clGetKernelWorkGroupInfo 
Current implementation only takes static slmInlineSize into account.
With this change we also include dynamic SLM passed as a kernel arguments.

Related-To: NEO-5761
Signed-off-by: Fabian Zwolinski <fabian.zwolinski@intel.com>
 2022-09-29 17:38:44 +02:00
Dunajski, Bartosz f2ce393fc2 Capability to set overdispatch param for Kernel 
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2022-09-27 18:29:04 +02:00
Zbigniew Zdanowicz c3f7e40a8d Rename special pipeline select mode to systolic 
Signed-off-by: Zbigniew Zdanowicz <zbigniew.zdanowicz@intel.com>
 2022-08-31 22:16:26 +02:00
Dunajski, Bartosz 1a28c2a154 Add threads count queries 
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2022-08-24 13:18:20 +02:00
Compute-Runtime-Validation a5b4a13452 Revert "Return error when image arg does not support media block commands" 
This reverts commit 8388e6cf4a.

Signed-off-by: Compute-Runtime-Validation <compute-runtime-validation@intel.com>
 2022-08-24 06:23:22 +02:00
Maciej Plewka 8388e6cf4a Return error when image arg does not support media block commands 
Related-To: NEO-7168

Signed-off-by: Maciej Plewka <maciej.plewka@intel.com>
 2022-08-23 12:07:29 +02:00
Krystian Chmielewski 18adbed233 feat(zebin): add thread scheduling mode support 
Resolves: NEO-7197

Signed-off-by: Krystian Chmielewski <krystian.chmielewski@intel.com>
 2022-08-18 16:10:18 +02:00
Rafal Maziejuk af91f94098 Improve calculateAvailableThreadCount implementation 
Signed-off-by: Rafal Maziejuk <rafal.maziejuk@intel.com>
 2022-07-28 11:43:14 +02:00
Kamil Kopryk d4d54f5093 Cleanup includes 
Signed-off-by: Kamil Kopryk <kamil.kopryk@intel.com>
 2022-07-25 09:58:38 +02:00
Compute-Runtime-Validation 0eb2001d8f Revert "Check indirect access from igc" 
This reverts commit e5d63cd303.

Signed-off-by: Compute-Runtime-Validation <compute-runtime-validation@intel.com>
 2022-07-22 04:39:16 +02:00
Dominik Dabek e5d63cd303 Check indirect access from igc 
Also add workaround for app passing svm pointers by value

Related-To: NEO-7182

Signed-off-by: Dominik Dabek <dominik.dabek@intel.com>
 2022-07-21 12:25:24 +02:00
Zbigniew Zdanowicz 3f8c19eec9 Limit system memory flag in builtin kernels to destination argument 
Related-To: NEO-6959

Signed-off-by: Zbigniew Zdanowicz <zbigniew.zdanowicz@intel.com>
 2022-07-19 10:58:51 +02:00
Compute-Runtime-Validation f9888db0fb Revert "Check indirect access from igc" 
This reverts commit e14c91fa6c.

Signed-off-by: Compute-Runtime-Validation <compute-runtime-validation@intel.com>
 2022-07-16 07:36:49 +02:00
Dominik Dabek e14c91fa6c Check indirect access from igc 
Related-To: NEO-7182

Signed-off-by: Dominik Dabek <dominik.dabek@intel.com>
 2022-07-15 15:01:48 +02:00
Kamil Kopryk 7c538b956a Correct typo 
Signed-off-by: Kamil Kopryk <kamil.kopryk@intel.com>
 2022-07-14 10:13:12 +02:00
Zbigniew Zdanowicz e07f9f0698 Add kernel algorithm to check any argument is using system memory 
Related-To: NEO-6959

Signed-off-by: Zbigniew Zdanowicz <zbigniew.zdanowicz@intel.com>
 2022-07-12 13:08:49 +02:00
Katarzyna Cencelewska 25ce4d0c04 Clean unused code 
remove parts with device queue

Signed-off-by: Katarzyna Cencelewska <katarzyna.cencelewska@intel.com>
 2022-07-07 14:52:26 +02:00
Bartosz Dunajski 4fb4a1d77b Add LogicalStateHelper getter for CommandQueue. 
Refactor Kernel handling

Signed-off-by: Bartosz Dunajski <bartosz.dunajski@intel.com>
 2022-07-04 13:21:15 +02:00
Maciej Plewka 6ab6e1abff Fix mutex order for event task and move args to gpu 
This commit fixes problem with untransfered shared usm memory to gpu
when there is submit to gpu trigerred by user event. Also there is a fix
for dead lock problem caused by mixed orders of locking mutexes in csr
and in direct submission controller.

Related-To: NEO-6762

Signed-off-by: Maciej Plewka <maciej.plewka@intel.com>
 2022-06-21 11:28:25 +02:00
Artur Harasimiuk 3f04769f07 style: configure readability-identifier-naming.FunctionCase 
Signed-off-by: Artur Harasimiuk <artur.harasimiuk@intel.com>
 2022-05-17 20:55:56 +02:00
Katarzyna Cencelewska 96e1eb7467 Move variables baseDieRev and baseDieA0Masked from xe_hpc to pvc 
Pvc specific variables should be located in pvc struct

Related-To: NEO-6738
Signed-off-by: Katarzyna Cencelewska <katarzyna.cencelewska@intel.com>
 2022-05-17 12:19:16 +02:00
Artur Harasimiuk 819e0f5515 style: configure readability-identifier-naming.LocalVariableCase 
Signed-off-by: Artur Harasimiuk <artur.harasimiuk@intel.com>
 2022-05-16 12:39:44 +02:00
Artur Harasimiuk e9be9b64c6 clang-tidy configuration cleanup 
Define single .clang-tidy configuration with all used checks and use
NOLINT to selectively silence tool. That way cleanup should be easier.
third_part/ has its own configuration that disables clang-tidy for this
folder.

Signed-off-by: Artur Harasimiuk <artur.harasimiuk@intel.com>
 2022-05-11 14:02:04 +02:00
Krzysztof Gibala 2fcda0a528 Refactor: Change decanonize method accessing point 
Accessing decanonize method as a member of GmmHelper class object

Signed-off-by: Krzysztof Gibala <krzysztof.gibala@intel.com>
 2022-05-11 12:57:02 +02:00
Dominik Dabek d0a32b1437 Fix: svm pointer caching 
Given a following sequence of setting kernel arg svm pointers: A, nullptr, A
the kernel arg was not being set to A

Related-To: NEO-6895

Signed-off-by: Dominik Dabek <dominik.dabek@intel.com>
 2022-04-25 07:59:47 +02:00
Krystian Chmielewski 2c1bfbb5b2 Encode number barriers 
When programming number of barriers use BARRIER_SIZE enumeration.
Resolves: NEO-6785

Signed-off-by: Krystian Chmielewski <krystian.chmielewski@intel.com>
 2022-04-08 10:32:23 +02:00
Dominik Dabek 76289be8c1 Avoid unnecessary allocation in enqueueHandler 
Related-To: NEO-6837

kernelObjsForAuxTranslation will allocate only if needed

Signed-off-by: Dominik Dabek <dominik.dabek@intel.com>
 2022-04-06 13:03:41 +02:00
Konstanty Misiak 174c27eb31 Fix CFEFusedEUDispatch debug flag 
Signed-off-by: Konstanty Misiak <konstanty.misiak@intel.com>
 2022-03-28 12:32:05 +02:00
Dominik Dabek d5fedf90c5 Fix for svm pointer arg caching 
Previous version could cause segfaults.

Related-To: NEO-6737

Signed-off-by: Dominik Dabek <dominik.dabek@intel.com>
 2022-03-08 12:13:15 +01:00
Filip Hazubski 80b520bc9b Change ThreadArbitrationPolicy enum type to int32_t 
Change ThreadArbitrationPolicy::NotPresent value to -1
Update initial values to ThreadArbitrationPolicy::NotPresent

Related-To: NEO-6728

Signed-off-by: Filip Hazubski <filip.hazubski@intel.com>
 2022-03-07 20:04:24 +01:00
Dominik Dabek 6556d9a510 Improve caching in clSetKernelArgSVMPointer 2/n 
Update allocIdMemoryManagerCounter on cache hit

Related-To: NEO-6737

Signed-off-by: Dominik Dabek <dominik.dabek@intel.com>
 2022-03-02 18:10:52 +01:00
Dominik Dabek 7ab86d44d6 Improve caching in clSetKernelArgSVMPointer 
Check allocId earlier and also reuse if allocationsCounter did not
change from last call.

Related-To: NEO-6737

Co-authored-by: Michal Mrozek <michal.mrozek@intel.com>

Signed-off-by: Dominik Dabek <dominik.dabek@intel.com>
 2022-03-02 15:56:21 +01:00
Dominik Dabek b9d8d8c0fd Optimize setKernelArgSVMPointer 
If same pointer is already set, we don't need to set it again.

Related-To: NEO-6737

Signed-off-by: Dominik Dabek <dominik.dabek@intel.com>
 2022-03-01 09:12:13 +01:00
Konstanty Misiak cf1bc3a2ba Disable EU fusion based on kernel properties from compiler 
Related-To: NEO-6633

Signed-off-by: Konstanty Misiak <konstanty.misiak@intel.com>
 2022-02-28 18:50:38 +01:00
Mateusz Jablonski ea6f089e17 Unify implicit args programming across APIs 
Related-To: NEO-5081
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2022-02-23 11:52:47 +01:00
Katarzyna Cencelewska bd3e296278 Remove unused functions and struct 
getProfilingTimerResolution, getParentObjectCounts,
ObjectCounts

Signed-off-by: Katarzyna Cencelewska <katarzyna.cencelewska@intel.com>
 2022-02-14 09:53:35 +01:00
Bartosz Dunajski 4b0d986876 Move AllocationType enum out of GraphicsAllocation class 
Signed-off-by: Bartosz Dunajski <bartosz.dunajski@intel.com>
 2022-02-04 17:49:09 +01:00
Compute-Runtime-Validation 6f62a784e1 Revert "Check IndirectStatelessCount from igc" 
This reverts commit 5e62df4f8e.

Signed-off-by: Compute-Runtime-Validation <compute-runtime-validation@intel.com>
 2022-02-04 12:15:37 +01:00
Dominik Dabek 5e62df4f8e Check IndirectStatelessCount from igc 
If kernel has no stateless indirect accesses don't set the
kernelHasIndirectAccess flag.
Don't make resident or migrate if kernel has no indirect accesses.
Changed initial values in KernelAttributes.

Related-To: NEO-6597

Signed-off-by: Dominik Dabek <dominik.dabek@intel.com>
 2022-02-02 12:28:30 +01:00
Dominik Dabek 07c75c2de3 Revert "Check IndirectStatelessCount from igc" 
This reverts commit 01f368ac147d99fd0dcb4d71a9a2543cd215adfd.

Signed-off-by: Dominik Dabek <dominik.dabek@intel.com>
 2022-01-27 16:06:13 +01:00
Dominik Dabek 63f406a58c Check IndirectStatelessCount from igc 
If kernel has no stateless indirect accesses don't set the
kernelHasIndirectAccess flag.
Don't make resident or migrate if kernel has no indirect accesses.
Changed initial values in KernelAttributes.

Related-To: NEO-6597

Signed-off-by: Dominik Dabek <dominik.dabek@intel.com>
 2022-01-26 11:10:04 +01:00
Michal Mrozek 27c43b27f3 Remove not needed method. 
Signed-off-by: Michal Mrozek <michal.mrozek@intel.com>
 2022-01-20 15:02:19 +01:00
Katarzyna Cencelewska a06fbd2077 Remove device enqueue part 10 
- remove DeviceQueue

Related-To: NEO-6559
Signed-off-by: Katarzyna Cencelewska <katarzyna.cencelewska@intel.com>
 2022-01-19 17:41:06 +01:00
Katarzyna Cencelewska 97765cd39f Remove device enqueue part 7 
- mainly remove BlockKernelManager and ReflectionSurfaceHelper

Related-To: NEO-6559
Signed-off-by: Katarzyna Cencelewska <katarzyna.cencelewska@intel.com>
 2022-01-19 10:41:57 +01:00
Katarzyna Cencelewska 59683ec491 Remove device enqueue part 6 
- isParentKernel, peekParentKernel, parentKernel
- structs: AUBParentKernelFixture, MockParentKernel,
ParentKernelCommandQueueFixture

Related-To: NEO-6559
Signed-off-by: Katarzyna Cencelewska <katarzyna.cencelewska@intel.com>
 2022-01-17 13:56:29 +01:00
Compute-Runtime-Validation 182042b04d Revert "Update default thread arbitration policy" 
This reverts commit 8c3e9ace69.

Signed-off-by: Compute-Runtime-Validation <compute-runtime-validation@intel.com>
 2022-01-13 21:32:29 +01:00
Bartosz Dunajski 8c3e9ace69 Update default thread arbitration policy 
Signed-off-by: Bartosz Dunajski <bartosz.dunajski@intel.com>
 2022-01-13 16:24:11 +01:00
Katarzyna Cencelewska 45ae4fe881 Remove device enqueue part 3 
- isSchedulerKernel

Related-To: NEO-6559
Signed-off-by: Katarzyna Cencelewska <katarzyna.cencelewska@intel.com>
 2022-01-12 13:50:18 +01:00
Szymon Morek 967d8a56fe Don't reduce LWS if SIMD32 is being used 
Don't divide max kernel work group size by 2
if it's using SIMD 32

Resolves: NEO-6429

Signed-off-by: Szymon Morek <szymon.morek@intel.com>
 2022-01-11 14:03:49 +01:00
Maciej Plewka df7723411f Patch image descriptor fields with dword width 
Signed-off-by: Maciej Plewka <maciej.plewka@intel.com>
 2021-12-27 17:55:42 +01:00
Bartosz Dunajski fe8cb190bc Remove deprecated code 
Signed-off-by: Bartosz Dunajski <bartosz.dunajski@intel.com>
 2021-12-14 11:36:10 +01:00
Bartosz Dunajski 2643eb691a New thread arbitration mode token support 
Signed-off-by: Bartosz Dunajski <bartosz.dunajski@intel.com>
 2021-12-09 16:38:22 +01:00
Bartosz Dunajski 68aea5bf62 Rename compression flags and helpers 
Signed-off-by: Bartosz Dunajski <bartosz.dunajski@intel.com>
 2021-12-03 18:09:02 +01:00
Bartosz Dunajski 5c266f9ab0 Compression refactor [3/n] 
Dont use allocation type for compression preference

Signed-off-by: Bartosz Dunajski <bartosz.dunajski@intel.com>
 2021-12-03 17:20:07 +01:00
Zbigniew Zdanowicz f90932cca7 Use references instead copy ctors 
Signed-off-by: Zbigniew Zdanowicz <zbigniew.zdanowicz@intel.com>
 2021-11-15 14:42:33 +01:00
Krystian Chmielewski f20cdac7d3 Zebin: add support for has_dpas 
Signed-off-by: Krystian Chmielewski <krystian.chmielewski@intel.com>
 2021-10-28 09:59:21 +02:00
Bartosz Dunajski 1f2aa82c5b Remove UNUSED_VARIABLE macro 
Signed-off-by: Bartosz Dunajski <bartosz.dunajski@intel.com>
 2021-10-22 18:56:33 +02:00
Kamil Kopryk 9614d435c5 Simplify code 
Signed-off-by: Kamil Kopryk <kamil.kopryk@intel.com>
 2021-10-20 11:29:49 +02:00
Zbigniew Zdanowicz 279181a384 Remove not needed include header 
Signed-off-by: Zbigniew Zdanowicz <zbigniew.zdanowicz@intel.com>
 2021-10-06 21:32:40 +02:00
Zbigniew Zdanowicz 0363749948 Disjoint local work size code from hw command generation 
Signed-off-by: Zbigniew Zdanowicz <zbigniew.zdanowicz@intel.com>
 2021-10-06 01:09:56 +02:00
Rafal Maziejuk 85a52b7702 Fix typo 
Signed-off-by: Rafal Maziejuk <rafal.maziejuk@intel.com>
 2021-10-05 14:45:24 +02:00
Zbigniew Zdanowicz 1028295a02 Move per thread data to shared directory 
Signed-off-by: Zbigniew Zdanowicz <zbigniew.zdanowicz@intel.com>
 2021-09-30 17:57:41 +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
Milczarek, Slawomir 2abcef2c35 Revert "Disable stateless compression in sba on indirect host access flag" 
Related-To: NEO-5107

This reverts commit 658fa6d85419f4a1f4876b40ef74f77095c29125.

Signed-off-by: Milczarek, Slawomir <slawomir.milczarek@intel.com>
 2021-09-29 13:07:07 +02:00
Artur Harasimiuk a63b9b1273 move common files to shared/ 
Signed-off-by: Artur Harasimiuk <artur.harasimiuk@intel.com>
 2021-09-27 11:10:20 +02:00
Milczarek, Slawomir 5c4c02d2e7 Disable stateless compression in sba on indirect host access flag 
Signed-off-by: Milczarek, Slawomir <slawomir.milczarek@intel.com>
 2021-09-21 16:57:34 +02:00
Maciej Dziuban a4b3dc29e4 Remove unnecessary method 
Signed-off-by: Maciej Dziuban <maciej.dziuban@intel.com>
 2021-09-21 11:34:27 +02:00
Mateusz Jablonski 006afacc95 Reorder Kernel's members 
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2021-09-20 17:19:04 +02:00
Milczarek, Slawomir 0a8b473f3c Add resolves for stateless compression with shared buffer 
Related-To: NEO-5107

Signed-off-by: Milczarek, Slawomir <slawomir.milczarek@intel.com>
 2021-09-17 09:18:45 +02:00
Kamil Kopryk 9ccf43e441 Correct branch_dir_suffix in cmake 
Signed-off-by: Kamil Kopryk <kamil.kopryk@intel.com>
Related-To: NEO-6245
 2021-09-14 16:00:20 +02:00
Mateusz Jablonski e193589582 Add implicit args support for OCL 
Related-To: NEO-5081

Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2021-09-13 10:54:19 +02:00
Milczarek, Slawomir 9d99ee1636 Print driver diagnostics if aux translation of allocation in SVM allocs manager 
Related-To: NEO-5107

Signed-off-by: Milczarek, Slawomir <slawomir.milczarek@intel.com>
 2021-09-13 10:23:32 +02:00
Dominik Dabek a204b11c8f Do not require aux translation on built ins 
Signed-off-by: Dominik Dabek <dominik.dabek@intel.com>
 2021-09-10 14:38:04 +02:00
Rafal Maziejuk bbfbf19a02 Move allowStatelessCompression from HwHelper to HwInfoConfig 
Signed-off-by: Rafal Maziejuk <rafal.maziejuk@intel.com>
Related-To: NEO-4541
 2021-09-09 11:37:47 +02:00
Mateusz Jablonski 7f920139b4 Correct patching private surface in cloned kernel 
Related-To: NEO-5081
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2021-09-07 13:50:22 +02:00
Filip Hazubski 3d6d4acda2 Update isCooperativeDispatchSupported 
Signed-off-by: Filip Hazubski <filip.hazubski@intel.com>
 2021-09-02 17:36:58 +02:00
Maciej Dziuban 3e6b3cd780 Revert "Create single point for selecting engine for builtin ops" 
This reverts commit 6513bd371a69cb821ea45c7c1964ea1f51dd75b2.

Signed-off-by: Maciej Dziuban <maciej.dziuban@intel.com>
 2021-09-02 11:58:46 +02:00
Maciej Dziuban a03b5f8a95 Create single point for selecting engine for builtin ops 
- selectCsrForBuiltinOperation selects proper CSR
- selected CSR is passed to dispatchBcsOrGpgpuEnqueue
- Notifications such as notifyEnqueueReadBuffer are now made on correct engine
- Temporary allocs for hostptrs are now created on gpgpuCsr

Related-To: NEO-6057
Signed-off-by: Maciej Dziuban <maciej.dziuban@intel.com>
 2021-08-31 13:29:17 +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
Filip Hazubski 63f8c9d98b Add new EngineUsage 
Simplify verifying EngineUsage in tryGetEngine function.
Remove unused getGpgpuEnginesCount function.

Related-To: NEO-4940

Signed-off-by: Filip Hazubski <filip.hazubski@intel.com>
 2021-08-23 17:41:13 +02:00
Filip Hazubski 29c64c3dd0 Disable implicit scaling for cooperative kernels 
When implicit scaling is disabled use useSingleSubdeviceValue = true.

Resolves: NEO-5757

Signed-off-by: Filip Hazubski <filip.hazubski@intel.com>
 2021-08-18 14:56:37 +02:00
Filip Hazubski 66ee5bd3c4 Correct typo 
Signed-off-by: Filip Hazubski <filip.hazubski@intel.com>
 2021-08-03 20:08:18 +02:00
Filip Hazubski 2dd0e67e65 Disable overdispatch by default 
When disable overdispatch is available:
- change default value of CFE_STATE::ComputeOverdispatchDisable to true.
- change default value of
INTERFACE_DESCRIPTOR_DATA::ThreadGroupDispatchSize to 3u.

Signed-off-by: Filip Hazubski <filip.hazubski@intel.com>
 2021-08-03 15:28:53 +02:00
Milczarek, Slawomir eb14d8458b Add helper function to enable stateless compression 
Related-To: NEO-5107

Signed-off-by: Milczarek, Slawomir <slawomir.milczarek@intel.com>
 2021-08-02 14:34:33 +02:00
Milczarek, Slawomir f9f5c96ffe Add resolves for USM allocations when aux translation is required 
Related-To: NEO-5107

Signed-off-by: Milczarek, Slawomir <slawomir.milczarek@intel.com>
 2021-07-27 15:10:41 +02:00
Milczarek, Slawomir a18fb402a0 Add resolves for SVM GPU allocations if aux translation is required 
Related-To: NEO-5107

Signed-off-by: Milczarek, Slawomir <slawomir.milczarek@intel.com>
 2021-07-27 10:21:11 +02:00
Milczarek, Slawomir 330856c9e9 Add resolves for unified memory when aux translation is required 
Related-To: NEO-5107

Signed-off-by: Milczarek, Slawomir <slawomir.milczarek@intel.com>
 2021-07-22 14:02:52 +02:00
Mateusz Jablonski 6f3c89decb Add mechanism to migrate multi root device memory 
invalidate TLB cache if kernel requires migration


Related-To: NEO-3691

Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2021-07-19 19:49:22 +02:00
Dominik Dabek bbe599aa95 Selectively enable getMaxThreadsForWorkgroup WA 
Related-To: NEO-6022

Signed-off-by: Dominik Dabek <dominik.dabek@intel.com>
 2021-07-14 17:29:43 +02:00
Maciej Plewka bc121c09fa Use DSS count to callculate max work group size 
This reverts commit 89b7a4c9cc0a69cfd2eb5a0bd138356f34c52f0d.

Signed-off-by: Maciej Plewka <maciej.plewka@intel.com>
 2021-07-05 10:14:20 +02:00
Bartosz Dunajski 64eb82efac Add Kernel restrictions 
Signed-off-by: Bartosz Dunajski <bartosz.dunajski@intel.com>
 2021-07-02 17:41:03 +02:00
Maciej Plewka aed3fada28 Revert "Use Eu per dss to callculate max work group size" 
This reverts commit 86b12dd23979db12e1898013c9162cb7106e40f1.

Signed-off-by: Maciej Plewka <maciej.plewka@intel.com>
 2021-07-02 17:16:06 +02:00
Maciej Plewka bcf93a6aeb Use Eu per dss to callculate max work group size 
Signed-off-by: Maciej Plewka <maciej.plewka@intel.com>
 2021-07-02 12:30:18 +02:00
Bartosz Dunajski e1f42c2ae1 Remove TSP atomic dependency tracking 
This reverts commit d17668f023bee409ee68e766bbc7d5f16ce8d52b.

Signed-off-by: Bartosz Dunajski <bartosz.dunajski@intel.com>
 2021-06-23 16:59:41 +02:00
Krystian Chmielewski 5e8e066541 Bindless support ocl 
Signed-off-by: Krystian Chmielewski <krystian.chmielewski@intel.com>
 2021-06-23 13:56:12 +02:00
Mateusz Jablonski 2ab961be49 Ensure that builtin kernel is patched and can't transform images 
Related-To: NEO-3691
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2021-06-22 16:20:07 +02:00
Maciej Dziuban 843b65bb07 Add usingImages field to the Kernel class 
Signed-off-by: Maciej Dziuban <maciej.dziuban@intel.com>
 2021-06-22 15:25:22 +02:00
Mateusz Jablonski 78e1ea2a68 Don't transform images for builtin kernels 
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2021-06-21 18:30:47 +02:00
Compute-Runtime-Validation 9bc4f02a88 Revert "Ensure that builtin kernel is patched" 
This reverts commit c9c752526e.

Signed-off-by: Compute-Runtime-Validation <compute-runtime-validation@intel.com>
 2021-06-21 12:59:27 +02:00
Bartosz Dunajski 2e97aeccfd Revert TSP changes 
This commit reverts:
a1d2bdc76666059653c79fe39a26113ce47c632a,
71a115129c1698ff15305fd0ea3828cba861be47,
e1a9087a466bfba54d84a64247e6596092034a91.

Signed-off-by: Bartosz Dunajski <bartosz.dunajski@intel.com>
 2021-06-21 12:44:12 +02:00
Mateusz Jablonski c9c752526e Ensure that builtin kernel is patched 
Related-To: NEO-3691
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2021-06-17 17:49:18 +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
Mateusz Jablonski 5770c7b8ea Correct handling device USM arg in multi device kernel 
Related-To: NEO-3691
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2021-06-15 21:02:00 +02:00
Bartosz Dunajski 080b1e2f66 Remove redundant TSP completion tracking logic 
Signed-off-by: Bartosz Dunajski <bartosz.dunajski@intel.com>
 2021-06-15 17:29:19 +02:00
Krystian Chmielewski 6fad8b3100 Refactor ocl kernel 
Removed dispatch traits pointers and added getters. Removed uneeded
tests.

Related-To: NEO-4729
Signed-off-by: Krystian Chmielewski <krystian.chmielewski@intel.com>
 2021-06-11 16:52:09 +02:00
Filip Hazubski b25c0e4fc0 Update StreamProperties 
Signed-off-by: Filip Hazubski <filip.hazubski@intel.com>
 2021-06-08 08:57:55 +02:00
Maciej Plewka 8279567f0e Fix max work group count for esimd kernel 
Signed-off-by: Maciej Plewka <maciej.plewka@intel.com>
 2021-05-27 14:13:51 +02:00
Mateusz Jablonski d2ac316e47 Improve error handling in clCreateKernel 
return nullptr when kernel initialization fails

Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2021-05-20 18:58:08 +02:00
Konstanty Misiak 074fc1d60f Fix clGetKernelSuggestedLocalWorkSizeINTEL 
Related-To: NEO-5456

Signed-off-by: Konstanty Misiak <konstanty.misiak@intel.com>
 2021-05-18 13:35:26 +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
Sebastian Luzynski 95ba83c7e1 Fix ocl program creation on multi device contexts 
Signed-off-by: Sebastian Luzynski <sebastian.jozef.luzynski@intel.com>

Related-To: NEO-5734
 2021-05-10 12:30:09 +02:00
Konstanty Misiak c4502ccf66 Fix OCL MOCS index with UNCACHED flag 
Related-To: NEO-5742

Signed-off-by: Konstanty Misiak <konstanty.misiak@intel.com>
 2021-05-04 10:01:44 +02:00
Dominik Dabek bb9d902899 Add padding for ISA allocations 
Related-To: NEO-5771
Signed-off-by: Dominik Dabek <dominik.dabek@intel.com>
 2021-04-27 11:03:58 +02:00
Milczarek, Slawomir b7883bf838 Add helper to check if non-AUX mode is required 
Signed-off-by: Milczarek, Slawomir <slawomir.milczarek@intel.com>
 2021-04-26 17:51:58 +02:00
Krystian Chmielewski ef71915c71 Remove KernelArgInfo and use KernelDescriptor's args instead 
Related-To: NEO-4729
Signed-off-by: Krystian Chmielewski <krystian.chmielewski@intel.com>
 2021-04-23 15:12:09 +02:00
Adam Cetnerowski 33f05a25cd Fix typo 
Signed-off-by: Adam Cetnerowski <adam.cetnerowski@intel.com>
 2021-04-21 16:25:17 +02:00