intel/compute-runtime
1
0
Fork 0
mirror of https://github.com/intel/compute-runtime.git synced 2025-12-21 01:04:57 +08:00
Code Issues Packages Projects Releases Wiki Activity
14,161 Commits 42 Branches 655 Tags
b94f58abaa3d8a83a2999d9ffeaf1ddcc1d7c14d
Commit Graph

245 Commits

Author SHA1 Message Date
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
Mateusz Jablonski
d014a731c5 fix multi device ocl: add missing tag update flush after blit 
when memory is migrated then we need to flush tag update

Related-To: NEO-7552
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2023-04-04 11:06:57 +02:00
Lukasz Jobczyk
18e5664c88 Set stalling command for split marker 
Signed-off-by: Lukasz Jobczyk <lukasz.jobczyk@intel.com>
 2023-03-29 15:34:45 +02:00
Dominik Dabek
d7981e153e fix(ocl): tweak resolve deps with pipecontrols 
Keep resolving with semaphores if multiple (>2) queues are submitting to
the same CSR. In such case, semaphores allow concurrent execution while
pipecontrols would serialize it.

Related-To: NEO-7321

Signed-off-by: Dominik Dabek <dominik.dabek@intel.com>
 2023-03-27 17:22:03 +02:00
Dunajski, Bartosz
f522744886 OCL: Allow for RelaxedOrdering barriers in IOQ mode 
Related-To: NEO-7458

Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2023-03-27 12:25:01 +02:00
Dominik Dabek
a634c6a7b1 fix:pass bool to get CS size instead of reevaluate 
Pass resolveDependenciesByPipecontrol bool value to get command stream
methods instead of reevaluating the condition.

Related-To: NEO-7321

Signed-off-by: Dominik Dabek <dominik.dabek@intel.com>
 2023-03-24 15:24:10 +01:00
Dunajski, Bartosz
b3c2fa41c5 OCL: Optimize IOQ barriers handling 
Related-To: NEO-7458

Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2023-03-24 12:52:47 +01:00
Dunajski, Bartosz
73213c961f Enable RelaxedOrdering for OCL on GPGPU engine 
Related-To: NEO-7458

Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2023-03-22 12:39:52 +01:00
Dunajski, Bartosz
43cc747843 Add Unrecoverable to RelaxedOrdering path 
Related-To: NEO-7458

Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2023-03-20 14:42:20 +01:00
Dunajski, Bartosz
686790274d Disable OCL RelaxedOrdering if tag update is required 
Related-To: NEO-7458

Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2023-03-15 14:44:05 +01:00
Lukasz Jobczyk
320deec53b Wait for barrier on every OCL split blitter 
Signed-off-by: Lukasz Jobczyk <lukasz.jobczyk@intel.com>
 2023-03-15 09:34:41 +01:00
Dunajski, Bartosz
15485fb1c8 Register CSR clients for OCL CommandQueues 
Related-To: NEO-7458

Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2023-03-13 18:29:14 +01:00
Dunajski, Bartosz
97a35debde RelaxedOrdering dispatch for OCL 1/n 
Related-To: NEO-7458

Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2023-03-13 17:37:12 +01:00
Maciej Plewka
6ab9037c35 Use FusedEu Dpas W/A only in ACM 
Signed-off-by: Maciej Plewka <maciej.plewka@intel.com>
 2023-03-08 14:14:58 +01:00
Maciej Plewka
52d322e738 Move barrier flush property from csr to cmdQueue 
Related-To: NEO-6982, HSD-15010621906

Signed-off-by: Maciej Plewka <maciej.plewka@intel.com>
 2023-03-03 14:33:53 +01:00
Dominik Dabek
22d7c2ea28 feat(ocl): move dependencies programming 
Move out of csr dependencies programming to queue stream.
Correct method fillCsrDependenciesForTimestampPacketContainer.

Related-To: NEO-7321

Signed-off-by: Dominik Dabek <dominik.dabek@intel.com>
 2023-02-20 13:42:56 +01:00
Warchulski, Jaroslaw
0556d543a3 Cleanup includes 56 
Related-To: NEO-5548
Signed-off-by: Warchulski, Jaroslaw <jaroslaw.warchulski@intel.com>
 2023-02-16 14:42:44 +01:00
Maciej Plewka
75a3f99685 fix(ocl) use correct lws and groupCount to disable eu fusion check 
Signed-off-by: Maciej Plewka <maciej.plewka@intel.com>
 2023-02-15 14:43:36 +01:00
Mateusz Jablonski
5a89a761f5 Fix OCL: always signal usage when migrating memory 
multi storage memory migration needs to wait until memory is no longer used

Related-To: NEO-5735
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2023-02-14 15:10:02 +01:00
Maciej Plewka
429be6b4cb Disable EUFusion for odd work groups with DPAS on DG2 
Related-To: NEO-7495, HSD-14017007475

Signed-off-by: Maciej Plewka <maciej.plewka@intel.com>
 2023-02-13 15:27:49 +01:00
Compute-Runtime-Validation
606a900080 Revert "Disable EUFusion for odd work groups with DPAS on DG2" 
This reverts commit 017d66a469.

Signed-off-by: Compute-Runtime-Validation <compute-runtime-validation@intel.com>
 2023-02-03 02:45:21 +01:00
Maciej Plewka
017d66a469 Disable EUFusion for odd work groups with DPAS on DG2 
Related-To: NEO-7495, HSD-14017007475

Signed-off-by: Maciej Plewka <maciej.plewka@intel.com>
 2023-02-02 13:57:42 +01:00
Kamil Kopryk
b101f9f2f5 refactor: don't use global ProductHelper getter 12/n 
Related-To: NEO-6853
Signed-off-by: Kamil Kopryk <kamil.kopryk@intel.com>
 2023-01-27 12:29:18 +01:00
Kamil Kopryk
0499a72451 refactor: rename cl_gfx_core_helper files 
Related-To: NEO-6853
Signed-off-by: Kamil Kopryk <kamil.kopryk@intel.com>
 2023-01-24 11:16:03 +01:00
Warchulski, Jaroslaw
49837b7bb5 Cleanup includes 39 
Cleaned up files:
shared/source/command_container/command_encoder.h

Related-To: NEO-5548
Signed-off-by: Warchulski, Jaroslaw <jaroslaw.warchulski@intel.com>
 2023-01-23 11:56:42 +01:00
Maciej Plewka
fa4830036a feature(ocl) use tags to synchronize multi root device events 
Signed-off-by: Maciej Plewka <maciej.plewka@intel.com>
 2023-01-23 10:28:01 +01:00
Kamil Kopryk
a4eba996f7 refactor: don't use global ProductHelper getter 4/n 
Related-To: NEO-6853
Signed-off-by: Kamil Kopryk <kamil.kopryk@intel.com>
 2023-01-20 10:27:27 +01:00
Warchulski, Jaroslaw
77501d86ba Cleanup includes 35 
Cleaned up files:
shared/source/command_stream/command_stream_receiver.h

Related-To: NEO-5548
Signed-off-by: Warchulski, Jaroslaw <jaroslaw.warchulski@intel.com>
 2023-01-17 18:51:40 +01:00
Maciej Plewka
1421796541 Revert "feature(ocl) use tags to synchronize multi root device events" 
This reverts commit 353a7510b2bd2d774d0b7ee82ee48eae7f5dc1d3.

Signed-off-by: Maciej Plewka maciej.plewka@intel.com
 2023-01-17 11:29:58 +01:00
Cencelewska, Katarzyna
f94528097a fix: add set stateCacheInvalidationEnable to flush cache 
when blit operation and dcflush needed

resolves problem with corruptions visible when switch ccs with bcs
on platforms without engines coherency

Resolves: NEO-7577
Signed-off-by: Cencelewska, Katarzyna <katarzyna.cencelewska@intel.com>
 2023-01-13 10:35:54 +01:00