intel/compute-runtime
1
0
Fork 0
mirror of https://github.com/intel/compute-runtime.git synced 2025-12-20 00:24:58 +08:00
Code Issues Packages Projects Releases Wiki Activity
15,896 Commits 42 Branches 655 Tags
8342c0ae2ffc25ad1a595ccb3f46fdf8533e7541
Commit Graph

274 Commits

Author SHA1 Message Date
Compute-Runtime-Validation
8342c0ae2f Revert "fix: add cache flush as dependency for bcs ccs synchronization" 
This reverts commit 5e57bb2a32.

Signed-off-by: Compute-Runtime-Validation <compute-runtime-validation@intel.com>
 2024-05-01 03:05:47 +02:00
Maciej Plewka
5e57bb2a32 fix: add cache flush as dependency for bcs ccs synchronization 
Related-to: NEO-9872
Signed-off-by: Maciej Plewka <maciej.plewka@intel.com>
 2024-04-30 11:57:49 +02:00
Andrzej Koska
ae139aeffd refactor: Passing information about the engine 
Extension of the interface with information
about the engine type passed to the function

Related-To: NEO-10678

Signed-off-by: Andrzej Koska <andrzej.koska@intel.com>
 2024-04-22 13:33:56 +02:00
Mrozek, Michal
f71f6d2b72 refactor: remove not needed code 
Signed-off-by: Mrozek, Michal <michal.mrozek@intel.com>
 2024-03-08 18:18:55 +01:00
Kamil Kopryk
168445784e feature: introduce states programming at driver init heapless ocl 
Related-To: NEO-7824
Signed-off-by: Kamil Kopryk <kamil.kopryk@intel.com>
 2024-03-08 12:29:44 +01:00
Zbigniew Zdanowicz
0bf8e8727e refactor: add output buffer argument to store register to memory encoder 
Related-To: NEO-10064

Signed-off-by: Zbigniew Zdanowicz <zbigniew.zdanowicz@intel.com>
 2024-02-27 13:31:55 +01:00
Kamil Kopryk
87d13fcb6e fix: fix scratch programming in heapless mode 
Related-To: NEO-10107

Signed-off-by: Kamil Kopryk <kamil.kopryk@intel.com>
 2024-01-23 15:26:56 +01: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
de93bc6928 refactor: correct naming of enum class constants 10/n 
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2023-12-19 11:30:39 +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
Mateusz Jablonski
432142c574 refactor: correct naming of enum class constants 4/n 
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2023-12-13 08:08:51 +01:00
Milczarek, Slawomir
bec9874487 fix: Improved event profiling setup for bcs split enqueue 
Fixes OpenCL Khronos failures in test profiling with bcs split

Related-To: NEO-8927

Signed-off-by: Milczarek, Slawomir <slawomir.milczarek@intel.com>
 2023-12-07 21:29:55 +01:00
Mateusz Jablonski
da957d1a37 refactor: correct naming of enum class constants 1/n 
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2023-12-05 14:26:42 +01:00
Mateusz Jablonski
c48e57e2de refactor: rename register offsets and constants 
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2023-12-04 18:31:39 +01:00
Mateusz Jablonski
cdcd834712 refactor: correct naming of builtin types 
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2023-12-01 14:08:21 +01:00
Mateusz Jablonski
e57d372608 refactor: correct naming of enum class constants 
EngineGroupType
BlitDirection
PostBlitMode
WaitStatus

Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2023-12-01 11:53:51 +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
Mateusz Jablonski
c9664e6bad refactor: rename global debug manager to debugManager 
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2023-11-30 13:00:59 +01:00
Mateusz Jablonski
aac8686095 fix: correct calculating submit cpu timestamp 
Related-To: NEO-9590, HSD-18035219634
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2023-11-29 17:42:41 +01:00
Kamil Kopryk
ce7298d512 feature: Add heapless mode programming in ocl 
Related-To: NEO-7621
Signed-off-by: Kamil Kopryk <kamil.kopryk@intel.com>
 2023-11-24 12:53:39 +01:00
Lukasz Jobczyk
2fdfc64053 refactor: add const to one time init variables 
Signed-off-by: Lukasz Jobczyk <lukasz.jobczyk@intel.com>
 2023-10-25 06:49:56 +02:00
Mateusz Jablonski
4dfa12c8eb fix: add mechanism to detect gpu timestamp overflows 
unify naming CpuGpu to GpuCpu

Related-To: NEO-8394
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2023-10-19 16:31:06 +02:00
Lukasz Jobczyk
750b5ba89a fix: flush necessary caches when dispatch pipe control 
Signed-off-by: Lukasz Jobczyk <lukasz.jobczyk@intel.com>
 2023-10-19 15:09:31 +02:00
Mateusz Jablonski
c68f7c8fe2 fix: setup both cpu & gpu timestamp when setting timestamp in event 
Related-To: NEO-8394
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2023-10-17 08:51:05 +02:00
Mateusz Jablonski
fc508212de refactor: pass big parameters as reference instead of by value 
Related-To: NEO-9038
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2023-10-04 14:53:13 +02:00
Dominik Dabek
0936fca8cd fix(ocl): set split barrier required correctly 
Fix bug introduced in neo 27314 - splitBarrierRequired was set for all
commands, should be only for cl_command_barrier.

Related-To: NEO-8147

Signed-off-by: Dominik Dabek <dominik.dabek@intel.com>
 2023-09-21 11:32:50 +02:00
Dominik Dabek
1b7e178b25 performance(ocl): program barrier pc in taskStream 
Program barrier to task stream, before next enqueue kernel.
This will reduce the number of batch buffer starts for sequences of
enqueue, barrier, enqueue, ... .

Related-To: NEO-8147

Signed-off-by: Dominik Dabek <dominik.dabek@intel.com>
 2023-09-19 11:48:02 +02:00
Mrozek, Michal
d9f938f3db refactor: remove not needed code 
Signed-off-by: Mrozek, Michal <michal.mrozek@intel.com>
 2023-09-12 14:25:04 +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
Compute-Runtime-Validation
b5e9c10f64 Revert "performance(ocl): program barrier pc in taskStream" 
This reverts commit 839c2d6737.

Signed-off-by: Compute-Runtime-Validation <compute-runtime-validation@intel.com>
 2023-09-12 01:32:28 +02:00
Dominik Dabek
839c2d6737 performance(ocl): program barrier pc in taskStream 
Program barrier immediately to task stream.
This will reduce the number of batch buffer starts.

Related-To: NEO-8147

Signed-off-by: Dominik Dabek <dominik.dabek@intel.com>
 2023-09-11 13:23:26 +02:00
Michal Mrozek
65188fc90b refactor: remove not needed code 
Signed-off-by: Michal Mrozek <michal.mrozek@intel.com>
 2023-09-08 17:22:18 +02:00
Dunajski, Bartosz
a42e88d55b fix: stall RelaxedOrdering scheduler when programming OCL dependencies 
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2023-08-14 10:47:35 +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
6f45574ff9 fix: add proper bcs synchronization when marker 
Related-To: NEO-8105
Signed-off-by: Cencelewska, Katarzyna <katarzyna.cencelewska@intel.com>
 2023-07-24 10:57:41 +02:00
Dominik Dabek
0a4d0917d4 performance(ocl): skip dcFlush on no event 
Skip dcFlush on waitForBarrier without event by default.

Related-To: NEO-8147

Signed-off-by: Dominik Dabek <dominik.dabek@intel.com>
 2023-07-20 14:57:37 +02:00
Dominik Dabek
622a3ed89c performance(ocl): flag to not dcFlush on no event 
If waitForBarrier is not passed outEvent then do
dcFlush on the next synchronize call.

Related-To: NEO-8147

Signed-off-by: Dominik Dabek <dominik.dabek@intel.com>
 2023-07-18 15:38:54 +02:00
Dunajski, Bartosz
d96cf5846a fix: dont allocate TSP for OOQ without Event 
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2023-07-06 15:12:22 +02:00
Dunajski, Bartosz
0372b9410a fix: set correct number of active packets for IOQ barrier 
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2023-05-30 16:02:23 +02:00
Lukasz Jobczyk
0e758e4bb5 performance: Add debug flag to set BCS split minimal size 
Signed-off-by: Lukasz Jobczyk <lukasz.jobczyk@intel.com>
 2023-05-17 08:07:43 +02:00
Lukasz Jobczyk
9f755b54ad performance: Bidirectional BCS split implementation for OCL 
Related-To: NEO-7877

Signed-off-by: Lukasz Jobczyk <lukasz.jobczyk@intel.com>
 2023-05-16 13:34:18 +02:00
Fabian Zwolinski
cbce863dc2 refactor: Rename member variables to camelCase 3/n 
Additionally enable clang-tidy check for member variables

Signed-off-by: Fabian Zwolinski <fabian.zwolinski@intel.com>
 2023-04-28 16:01:14 +02:00
Maciej Plewka
464c67789f fix: Deffer timestamp packet after failed submission 
Related-To: NEO-7835

Signed-off-by: Maciej Plewka <maciej.plewka@intel.com>
 2023-04-28 12:25:32 +02:00
Maciej Plewka
bac02071e7 refactor: Remove template param from enqueueNonBlocked 
Signed-off-by: Maciej Plewka <maciej.plewka@intel.com>
 2023-04-28 09:34:12 +02:00
Fabian Zwolinski
e351a90f81 refactor: Rename member variables to camelCase 2/n 
Signed-off-by: Fabian Zwolinski <fabian.zwolinski@intel.com>
 2023-04-27 20:39:22 +02:00
Cencelewska, Katarzyna
ac8ac62c92 fix: add bcs engine type only if engine exist 
- check bcs availability before insert to bcsEnginesTypes

Resolves: NEO-7886
Signed-off-by: Cencelewska, Katarzyna <katarzyna.cencelewska@intel.com>
 2023-04-20 09:02:38 +02:00
Milczarek, Slawomir
01d03aa5b6 Extended regkey to force prefetch of shared memory in enqueue commands 
Extended the regkey ForceMemoryPrefetchForKmdMigratedSharedAllocations
to force meory prefetch of kmd-migrated shared allocation
in clEnqueueNDRangeKernel(), clEnqueueMemFillINTEL, ...

Related-To: NEO-7841

Signed-off-by: Milczarek, Slawomir <slawomir.milczarek@intel.com>
 2023-04-11 11:23:48 +02:00