intel/compute-runtime
1
0
Fork 0
mirror of https://github.com/intel/compute-runtime.git synced 2025-12-24 12:23:05 +08:00
Code Issues Packages Projects Releases Wiki Activity
16,170 Commits 42 Branches 655 Tags
01c36a38c678bca20308c13a1b96ad1d1849b3f1
Commit Graph

684 Commits

Author SHA1 Message Date
Dunajski, Bartosz
815b37bf3a performance: allow waiting for OOQ timestamps in clEnqueueWaitForEvents 
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2023-07-14 11:33:10 +02:00
Dunajski, Bartosz
712e059ace performance: check completion alloc only once when waiting for Event 
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2023-07-14 08:32:50 +02:00
Dunajski, Bartosz
40c7b2842f fix: check engines completion before releasing deferred TSP nodes 
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>

Related-To: NEO-8146
 2023-07-11 16:11:51 +02:00
Cencelewska, Katarzyna
aa0beb8191 fix: Unify logic calculating threads per work group part 4 
- also use helper when checking that is simd1 to have same flow

Related-To: NEO-8087
Signed-off-by: Cencelewska, Katarzyna <katarzyna.cencelewska@intel.com>
 2023-07-07 15:34:59 +02:00
Dunajski, Bartosz
00bae2c827 fix: add missing nullptr check 
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2023-07-07 11:34:49 +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
2b5e475db9 refactor: use hex values to print TSP usage 
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2023-06-23 11:22:10 +02:00
Dunajski, Bartosz
b004a27e4e refactor: Debug flag to print TSP usage 
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2023-06-22 14:47:39 +02:00
Dominik Dabek
60d5e22f3b fix(ocl): reduce busy waiting in clFinish 
Use flushStamp=taskCount when passed flushStamp==0.
This will cause driver to busy wait for a short while before falling
back to use kmd notify.

Related-To: GSD-3612

Signed-off-by: Dominik Dabek <dominik.dabek@intel.com>
 2023-06-14 13:56:40 +02:00
Cencelewska, Katarzyna
7cb3278eb3 fix: add function to calculate number of threads per tg 
Signed-off-by: Cencelewska, Katarzyna <katarzyna.cencelewska@intel.com>
 2023-06-13 14:02:24 +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
Fabian Zwolinski
c441e9e971 refactor: Rename member variables to camelCase 
Signed-off-by: Fabian Zwolinski <fabian.zwolinski@intel.com>
 2023-04-26 16:05:07 +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
477448c097 RelaxedOrdering dispatch for OCL 2/n 
Related-To: NEO-7458

Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2023-03-14 15:48:06 +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
Zhenjie Pan
00b675643e fix: missed error handler of SubmissionStatus::FAILED 
Related-To: NEO-7802

Signed-off-by: Pan Zhenjie <zhenjie.pan@intel.com>
 2023-03-13 16:08:27 +01:00
Cencelewska, Katarzyna
398c7b2d29 refactor, remove typo in struct name 
change name of EncodeSempahore to EncodeSemaphore
Signed-off-by: Cencelewska, Katarzyna <katarzyna.cencelewska@intel.com>
 2023-03-10 15:44:25 +01:00
Kamil Kopryk
fa8579602f refactor: rename product helper files n/n 
Related-To: NEO-7703
Signed-off-by: Kamil Kopryk <kamil.kopryk@intel.com>
 2023-03-10 13:24:38 +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
Cencelewska, Katarzyna
3e116ea378 refactor: use same paths when add command mi_semaphore_wait 
Signed-off-by: Cencelewska, Katarzyna <katarzyna.cencelewska@intel.com>
 2023-03-07 10:35:26 +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
Dunajski, Bartosz
72ada8b41f Add missing pollForCompletion on clEnqueueVerifyMemoryINTEL 
Related-To: NEO-7618

Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2023-03-03 10:55:33 +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
51887af219 refactor OCL: cleanup after moving multi root device buffers to local mem 
remove debug flag AllocateBuffersInLocalMemoryForMultiRootDeviceContexts

Related-To: NEO-5735
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2023-02-15 09:41:20 +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
Lukasz Jobczyk
7eb91e3b04 Split the L0 BCS split into D2H and H2D 
-use separate pair of engines for D2H and H2D transfers

Related-To: NEO-7716

Signed-off-by: Lukasz Jobczyk <lukasz.jobczyk@intel.com>
 2023-02-13 14:17:39 +01:00
Warchulski, Jaroslaw
d1b2311207 Cleanup includes 49 
Cleaned up files:
opencl/source/command_queue/command_queue_hw.h
opencl/source/gtpin/gtpin_defs.h
opencl/source/mem_obj/mem_obj_helper.h
opencl/source/memory_manager/mem_obj_surface.h
opencl/source/sharings/unified/unified_sharing.h
opencl/test/unit_test/api/cl_enqueue_migrate_mem_objects_tests.inl
opencl/test/unit_test/aub_tests/fixtures/unified_memory_fixture.h
opencl/test/unit_test/command_queue/command_queue_fixture.h

Related-To: NEO-5548

Signed-off-by: Warchulski, Jaroslaw <jaroslaw.warchulski@intel.com>
 2023-02-10 17:26:49 +01:00
Warchulski, Jaroslaw
64f735481d Cleanup includes 48 
Cleaned up files:
shared/source/command_container/command_encoder.inl
shared/source/os_interface/hw_info_config.h

Related-To: NEO-5548
Signed-off-by: Warchulski, Jaroslaw <jaroslaw.warchulski@intel.com>
 2023-02-10 17:23:02 +01:00
Mateusz Jablonski
24c5352350 refactor: remove redundant including of compiler_cache.h 
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2023-02-03 11:16:31 +01:00