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

333 Commits

Author SHA1 Message Date
Kamil Kopryk 7c23ea3928 Refactor: don't use global ProductHelper getter in ocl files 2/n 
Related-To: NEO-6853
Signed-off-by: Kamil Kopryk <kamil.kopryk@intel.com>
 2022-12-29 09:41:39 +01:00
Compute-Runtime-Validation 8d18a0cd12 Revert "feat(ocl): Generate minimal set of args info" 
This reverts commit ea6c91eccc.

Signed-off-by: Compute-Runtime-Validation <compute-runtime-validation@intel.com>
 2022-12-29 07:07:32 +01:00
Kacper Nowak ea6c91eccc feat(ocl): Generate minimal set of args info 
- Provide minimalistic arg info metada when provided native binary is missing
kernels_misc_info section.
Signed-off-by: Kacper Nowak <kacper.nowak@intel.com>
 2022-12-28 20:24:44 +01:00
Warchulski, Jaroslaw f275eea6ec Cleanup includes 14 
Cleaned up files:
shared/source/device/device.h

Related-To: NEO-5548

Signed-off-by: Warchulski, Jaroslaw <jaroslaw.warchulski@intel.com>
 2022-12-23 10:46:34 +01:00
Kamil Kopryk d35f4249cd Use static isWorkaroundRequired in isOffsetToSkipSetFFIDGPWARequired function 
Related-To: NEO-6853
Signed-off-by: Kamil Kopryk <kamil.kopryk@intel.com>
 2022-12-20 16:40:51 +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
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