intel/compute-runtime
1
0
Fork 0
mirror of https://github.com/intel/compute-runtime.git synced 2026-01-01 12:33:12 +08:00
Code Issues Packages Projects Releases Wiki Activity
12,121 Commits 43 Branches 655 Tags
14d524fe269e784cf8aba34bdbb0030c97bf5db0
Commit Graph

280 Commits

Author SHA1 Message Date
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