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

154 Commits

Author SHA1 Message Date
Fabian Zwoliński
a2f60af5c6 fix: change global Var/Const Buffer type to SharedPoolAllocation 
This is prep work for the future implementation of pooling these allocations.

Related-To: NEO-12287
Signed-off-by: Fabian Zwoliński <fabian.zwolinski@intel.com>
 2025-08-19 17:29:34 +02:00
Mateusz Hoppe
757f4774b6 fix: fix unit tests relying on kernels 
Related-To: NEO-15743

Signed-off-by: Mateusz Hoppe <mateusz.hoppe@intel.com>
 2025-08-05 11:15:08 +02:00
Mateusz Jablonski
066447e5eb refactor: remove not needed code 
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2025-07-24 16:33:29 +02:00
Szymon Morek
bbcca97682 fix: flush cache after accessing img from buffer 
Related-To: NEO-15391

Signed-off-by: Szymon Morek <szymon.morek@intel.com>
 2025-07-23 19:17:47 +02:00
Compute-Runtime-Validation
cf89342bf8 Revert "fix: flush cache after accessing img from buffer" 
This reverts commit b90b77e4e3.

Signed-off-by: Compute-Runtime-Validation <compute-runtime-validation@intel.com>
 2025-07-23 05:25:55 +02:00
Naklicki, Mateusz
dade66307e refactor: cleanup header includes 4/n 
cleanup of opencl/source directory

Related-To: NEO-15383
Signed-off-by: Naklicki, Mateusz <mateusz.naklicki@intel.com>
 2025-07-22 19:36:34 +02:00
Szymon Morek
b90b77e4e3 fix: flush cache after accessing img from buffer 
Related-To: NEO-15391

Signed-off-by: Szymon Morek <szymon.morek@intel.com>
 2025-07-22 16:55:04 +02:00
Mateusz Jablonski
8b6aaceab4 refactor: remove not needed code related to cl accelerator 
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2025-07-10 18:08:32 +02:00
Mateusz Jablonski
0a325e09be fix: correct initialization of Kernel::isBuiltIn 
value is used in Kernel::initialize but was set after initialize call

Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2025-06-11 18:29:06 +02:00
Kamil Kopryk
caf1781e73 fix: add L3 flush after post sync for zero copy mem objects 
Related-To: NEO-13163
Signed-off-by: Kamil Kopryk <kamil.kopryk@intel.com>
 2025-05-22 10:23:26 +02:00
Lukasz Jobczyk
62619f9525 refactor: remove unused kernel tunning 
Signed-off-by: Lukasz Jobczyk <lukasz.jobczyk@intel.com>
 2025-05-08 14:18:21 +02:00
Mateusz Hoppe
34dad4d3de refactor: store implicit args version in kernel 
- adjust tests to work with implicitargs v0 and v1

Related-To: NEO-14115

Signed-off-by: Mateusz Hoppe <mateusz.hoppe@intel.com>
 2025-03-10 22:58:57 +01:00
Filip Hazubski
6b2b42972a fix: Add asserts to ensure NonCopyable and NonMovable 1/n 
Signed-off-by: Filip Hazubski <filip.hazubski@intel.com>
 2025-02-18 09:41:20 +01:00
Kamil Kopryk
6926582915 feature: use bindless samplers in heapless ocl 
Related-To: NEO-12741
Signed-off-by: Kamil Kopryk <kamil.kopryk@intel.com>
 2025-01-22 11:49:48 +01:00
Kamil Kopryk
d263fda1ad feature: patch 64bit addresses for bindless images in heapless OCL 
Related-To: NEO-12741
Signed-off-by: Kamil Kopryk <kamil.kopryk@intel.com>
 2025-01-16 15:24:02 +01:00
Damian Tomczak
b859a3b35b refactor: remove usesBindfulAddressingForBuffers function 
Related-to: NEO-12737

Signed-off-by: Damian Tomczak <damian.tomczak@intel.com>
 2025-01-14 10:45:04 +01:00
Mateusz Jablonski
16458ca0ac refactor: remove not used image transforming logic 
image transformer logic was used on gen9 and gen11

Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2024-09-17 16:19:48 +02:00
Bartosz Dunajski
4f1262645b refactor: pass extra walker params 
Signed-off-by: Bartosz Dunajski <bartosz.dunajski@intel.com>
 2024-09-10 15:30:03 +02:00
Mrozek, Michal
3ded04341c refactor: remove not needed code. 
Signed-off-by: Mrozek, Michal <michal.mrozek@intel.com>
 2024-04-30 16:24:21 +02:00
Mrozek, Michal
03dcff1398 refactor: remove not needed code. 
Signed-off-by: Mrozek, Michal <michal.mrozek@intel.com>
 2024-04-30 15:10:34 +02:00
Fabian Zwoliński
ee71157f7f fix: opencl support for bindless kernels 
Related-To: NEO-11156
Signed-off-by: Fabian Zwoliński <fabian.zwolinski@intel.com>
 2024-04-30 12:02:17 +02:00
Mateusz Jablonski
a697a3f718 refactor: create new members for storing spill and private memory in scratch 
rename private scratch space into scratch space slot 1 as it can be generic

Related-To: NEO-9944
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2024-01-23 12:42:25 +01:00
Compute-Runtime-Validation
f9f9035b95 Revert "refactor: create new members for storing spill and private memory in ... 
This reverts commit 87eb5f554a.

Signed-off-by: Compute-Runtime-Validation <compute-runtime-validation@intel.com>
 2024-01-23 09:13:00 +01:00
Mateusz Jablonski
87eb5f554a refactor: create new members for storing spill and private memory in scratch 
rename private scratch space into scratch space slot 1 as it can be generic

Related-To: NEO-9944
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2024-01-22 19:48:48 +01:00
Mateusz Jablonski
a4888b39c6 build: add clang-tidy restriction for Enum case 
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2023-12-21 08:58:51 +01:00
Mateusz Jablonski
a6458433dc refactor: correct naming of enum class constants 9/n 
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2023-12-19 10:36:25 +01:00
Mateusz Jablonski
dd1b9d6abc refactor: correct naming of enum class constants 8/n 
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2023-12-19 08:18:18 +01:00
Dunajski, Bartosz
d99104d5bf refactor: improve ImplicitArg struct handling 
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2023-12-18 15:19:00 +01:00
Mateusz Jablonski
c3ac7b78bd refactor: correct variable naming 
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2023-12-01 02:18:46 +01:00
Mrozek, Michal
15a0bf9d7b refactor: remove not needed code. 
Signed-off-by: Mrozek, Michal <michal.mrozek@intel.com>
 2023-09-12 13:52:47 +02:00
Mrozek, Michal
ae4757711e refactor: remove not needed code 
Signed-off-by: Mrozek, Michal <michal.mrozek@intel.com>
 2023-09-12 09:39:01 +02:00
Mrozek, Michal
cac547946a refactor: remove not needed code 
Signed-off-by: Mrozek, Michal <michal.mrozek@intel.com>
 2023-09-12 08:51:58 +02:00
Fabian Zwolinski
6fca8ee195 refactor: Remove SourceLevelDebugger 
Removed:
- SourceLevelDebugger (with tests)
- DebuggerLibrary
- DebuggerLibraryRestore
- debuggerSupported field from hwInfo.capabilityTable
- HasSourceLevelDebuggerSupport matcher
- ExperimentalEnableSourceLevelDebugger debug var
- EnableMockSourceLevelDebugger debug var
- DebuggerOptDisable debug var
- lib_names.h.in file
- third_party/source_level_debugger/igfx_debug_interchange_types.h

Related-To: NEO-7213
Signed-off-by: Fabian Zwolinski <fabian.zwolinski@intel.com>
 2023-08-10 11:14:02 +02:00
Cencelewska, Katarzyna
2e17c21728 fix: Unify logic calculating threads per work group part 2 
- use calculateNumThreadsPerThreadGroup instead of getThreadsPerWG to
have same flow and proper values of threads per work groups

Related-To: NEO-8087
Signed-off-by: Cencelewska, Katarzyna <katarzyna.cencelewska@intel.com>
 2023-07-04 10:34:02 +02:00
Compute-Runtime-Validation
39740da9d1 Revert "fix: Unify logic calculating threads per work group part 2" 
This reverts commit 1e8a53bd53.

Signed-off-by: Compute-Runtime-Validation <compute-runtime-validation@intel.com>
 2023-07-02 07:09:14 +02:00
Cencelewska, Katarzyna
1e8a53bd53 fix: Unify logic calculating threads per work group part 2 
- use calculateNumThreadsPerThreadGroup instead of getThreadsPerWG to
have same flow and proper values of threads per work groups

Related-To: NEO-8087
Signed-off-by: Cencelewska, Katarzyna <katarzyna.cencelewska@intel.com>
 2023-06-30 14:16:08 +02:00
Kacper Nowak
7be2ac84d3 Refactor(ocl): refactor OCL Kernel and MultiDeviceKernel class 1/n 
- For static create() method for Kernel and MultiDeviceKernel force errcodeRet
parameter to be passed via reference (instead of a pointer)
- Move part of kernel's creation logic to initialize() method

Signed-off-by: Kacper Nowak <kacper.nowak@intel.com>
 2023-04-11 11:43:26 +02:00
Mateusz Jablonski
90cd433766 Fix OCL: don't set multi storage resource for system memory buffers 
respect pointer size when patching surfaces in 32 bit applications

Related-To: NEO-5735
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2023-02-15 14:22:37 +01:00
Warchulski, Jaroslaw
3d59dce80c Cleanup includes 27 
Cleaned up files:
opencl/source/command_queue/command_queue.h
shared/source/built_ins/registry/built_ins_registry.h
shared/source/kernel/kernel_descriptor.h

Related-To: NEO-5548
Signed-off-by: Warchulski, Jaroslaw <jaroslaw.warchulski@intel.com>
 2023-01-11 16:10:28 +01:00
Warchulski, Jaroslaw
5eef40fedd Cleanup includes 22 
Cleaned up files:
opencl/source/built_ins/builtins_dispatch_builder.h
opencl/source/context/context.h
opencl/source/gtpin/gtpin_notify.h
opencl/source/kernel/kernel.h
opencl/source/kernel/multi_device_kernel.h
opencl/source/mem_obj/buffer.h
opencl/source/mem_obj/mem_obj.h
shared/source/built_ins/registry/built_ins_registry.h
shared/source/page_fault_manager/cpu_page_fault_manager.h

Related-To: NEO-5548
Signed-off-by: Warchulski, Jaroslaw <jaroslaw.warchulski@intel.com>
 2023-01-05 16:59:01 +01:00
Warchulski, Jaroslaw
b7ee3486d9 Cleanup includes 21 
Cleaned up files:
opencl/source/kernel/kernel.h

Related-To: NEO-5548
Signed-off-by: Warchulski, Jaroslaw <jaroslaw.warchulski@intel.com>
 2023-01-04 10:40:26 +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
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
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
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