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

169 Commits

Author SHA1 Message Date
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
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
Patryk Wrobel 46e0317548 Remove possibility of accessing directly USM device memory in debug logs 
clEnqueueSVMMemFill() is utilized by clEnqueueMemFillINTEL().
The latter may receive USM device pointers. If anyone passed
such pointer then SEGMENTATION_FAULT would occur.

Signed-off-by: Patryk Wrobel <patryk.wrobel@intel.com>
 2022-09-23 17:14:05 +02:00
Kamil Kopryk d4d54f5093 Cleanup includes 
Signed-off-by: Kamil Kopryk <kamil.kopryk@intel.com>
 2022-07-25 09:58:38 +02:00
Milczarek, Slawomir 3e22f30ed5 clEnqueueMigrateMemINTEL with memory prefetch for KMD migrated shared allocation 
Related-To: NEO-6740

Signed-off-by: Milczarek, Slawomir <slawomir.milczarek@intel.com>
 2022-07-14 17:35:22 +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
Mateusz Hoppe 5a3a39a281 Experimental support for OCL debugging with L0 
- initial changes

Related-To: NEO-7075

Signed-off-by: Mateusz Hoppe <mateusz.hoppe@intel.com>
 2022-07-12 12:57:15 +02:00
Naklicki, Mateusz fd867c1621 Update OCL headers 
Update headers to the OpenCL-Headers-2022.05.18 release:
https://github.com/KhronosGroup/OpenCL-Headers/releases/tag/v2022.05.18

Related-to: NEO-7102
Signed-off-by: Naklicki, Mateusz <mateusz.naklicki@intel.com>
 2022-06-23 17:07:16 +02:00
Neumann, Marta 0583413499 Remove error for unused parameter 
Remove error for unused parameter
from clGetKernelMaxConcurrentWorkGroupCountINTEL

Resolves: NEO-7044

Signed-off-by: Neumann, Marta <marta.neumann@intel.com>
 2022-06-15 18:48:22 +02:00
Artur Harasimiuk 6d43e96dee style: configure readability-identifier-naming.ClassCase 
Signed-off-by: Artur Harasimiuk <artur.harasimiuk@intel.com>
 2022-06-13 18:02:39 +02:00
Daniel Chabrowski c303c218be Add missing pragma once in header files 
Signed-off-by: Daniel Chabrowski <daniel.chabrowski@intel.com>
 2022-06-07 16:19:11 +02:00
Daniel Chabrowski 7463e1970b Cleanup headers 
Make TUs and headers self-contained, remove unused headers

Signed-off-by: Daniel Chabrowski <daniel.chabrowski@intel.com>
 2022-05-18 11:42:06 +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
Bartosz Dunajski 83a9037640 Revert async Event destruction 
This reverts f9a5f8a86e and
f89c731a11

Signed-off-by: Bartosz Dunajski <bartosz.dunajski@intel.com>
 2022-05-12 13:33:02 +02:00
Lukasz Jobczyk a31a674c38 L0 support for expose sub devices as API devices 
Signed-off-by: Lukasz Jobczyk <lukasz.jobczyk@intel.com>
 2022-05-11 15:41:53 +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
Lukasz Jobczyk 17aac9d1bf Add debug flag to expose each subdevice as a separate cl device 
Signed-off-by: Lukasz Jobczyk <lukasz.jobczyk@intel.com>
 2022-05-10 14:04:26 +02:00
Bartosz Dunajski f9a5f8a86e Defer Event destruction if command is not completed 
Signed-off-by: Bartosz Dunajski <bartosz.dunajski@intel.com>
 2022-05-10 11:22:58 +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
Bartosz Dunajski 0fd8b850a6 Support for enabling perf counters with clCreateCommandQueueWithProperties 
Signed-off-by: Bartosz Dunajski <bartosz.dunajski@intel.com>
 2022-03-22 10:33:40 +01: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
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 9bc364e7a7 Fix for clSetKernelArgSVMPointer optimization 
Related-To: NEO-6737

Signed-off-by: Dominik Dabek <dominik.dabek@intel.com>
 2022-03-01 12:56:04 +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
Krzysztof Gibala e518a8f3f9 Add debug flag ForceExtendedUSMBufferSize 
Forces extended buffer size by adding pageSize specify by number when
debug flag is >=1 in:
- clHostMemAllocINTEL
- clDeviceMemAllocINTEL
- clSharedMemAllocINTEL

Usage:
ForceExtendedUSMBufferSize=2
size += (2 * pageSize)

Signed-off-by: Krzysztof Gibala <krzysztof.gibala@intel.com>
 2022-02-07 11:44:31 +01:00
Katarzyna Cencelewska 3d0c065183 Remove device enqueue part 16 
-delete old unused flags

Related-To: NEO-6559
Signed-off-by: Katarzyna Cencelewska <katarzyna.cencelewska@intel.com>
 2022-02-03 19:38:41 +01:00
Katarzyna Cencelewska 58055aecdf Remove device enqueue part 12 
remove:
- debug flag ForceDeviceEnqueueSupport
- functions isDeviceEnqueueSupported, supportsDeviceEnqueue

Related-To: NEO-6559
Signed-off-by: Katarzyna Cencelewska <katarzyna.cencelewska@intel.com>
 2022-01-28 13:38:34 +01:00
Katarzyna Cencelewska 3d9e1ea3a5 Remove device enqueue part 11 
- remove templates from queue functions

Related-To: NEO-6559
Signed-off-by: Katarzyna Cencelewska <katarzyna.cencelewska@intel.com>
 2022-01-25 12:40:56 +01:00
Krzysztof Gibala b75f5d4c8b Add debug flag ForceExtendedBufferSize 
Forces extended buffer size by adding pageSize specify by number when
debug flag is >=1 in:
- clCreateBuffer
- clCreateBufferWithProperties
- clCreateBufferWithPropertiesINTEL

Usage:
ForceExtendedBufferSize=2
size += (2 * pageSize)

Signed-off-by: Krzysztof Gibala <krzysztof.gibala@intel.com>
 2022-01-19 18:52:10 +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
Artur Harasimiuk 42115e4a1d fix identifier naming 
Signed-off-by: Artur Harasimiuk <artur.harasimiuk@intel.com>
 2021-10-14 21:10:58 +02:00
Mateusz Jablonski b1df167632 Move enable_product.inl to shared 
extract api agnostic validators to shared
remove not needed opencl includes from neo shared


Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2021-10-12 22:02:16 +02:00
Fabian Zwolinski 332720920a Expose clGetKernelSuggestedLocalWorkSizeKHR func 
Related-to: NEO-2922
Signed-off-by: Fabian Zwolinski <fabian.zwolinski@intel.com>
 2021-10-12 20:06:57 +02:00
Mateusz Jablonski ec1e39bab8 Move OCL specific part of FileLogger to ClFileLogger 
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2021-10-11 23:55:08 +02:00
Mateusz Jablonski 48f01f28f5 Move core part of MemoryPropertiesHelpers to shared 
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2021-10-07 23:14:38 +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
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
Filip Hazubski 3d6d4acda2 Update isCooperativeDispatchSupported 
Signed-off-by: Filip Hazubski <filip.hazubski@intel.com>
 2021-09-02 17:36:58 +02:00
Bartosz Dunajski 0345d9f707 Improve queries with number of SubDevices 
Signed-off-by: Bartosz Dunajski <bartosz.dunajski@intel.com>
 2021-09-01 14:01:57 +02:00
Bartosz Dunajski cb91474b1a Improve getDevice methods 
Signed-off-by: Bartosz Dunajski <bartosz.dunajski@intel.com>
 2021-08-26 14:45:00 +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
Szymon Morek 3c15023871 Add AllowUnrestrictedSize debug flag 
This debug flag allows to allocate memory with size greater than
CL_DEVICE_MAX_MEM_ALLOC_SIZE.

Signed-off-by: Szymon Morek <szymon.morek@intel.com>
 2021-08-05 15:35:26 +02:00
Michal Mrozek d18172c00e Add debug flag to control tryFlushEvent 
Signed-off-by: Michal Mrozek <michal.mrozek@intel.com>
 2021-07-15 11:40:13 +02:00
Szymon Morek 399dc60bf8 Remove processing extra properties 
Related-To: NEO-6024

Signed-off-by: Szymon Morek <szymon.morek@intel.com>
 2021-07-08 16:18:06 +02:00
Kamil Kopryk dbe3ef21c1 Prefer unique_ptr instead of raw pointer nv12 ults 
Signed-off-by: Kamil Kopryk <kamil.kopryk@intel.com>
Related-To: NEO-4692
 2021-06-28 13:54:37 +02:00