intel/compute-runtime
1
0
Fork 0
mirror of https://github.com/intel/compute-runtime.git synced 2026-01-13 09:54:06 +08:00
Code Issues Packages Projects Releases Wiki Activity
13,074 Commits 43 Branches 656 Tags
688d958fe80a9e8a9e068f602f637c6aa86ff9ee
Commit Graph

565 Commits

Author SHA1 Message Date
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
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
2484c7ceb2 refactor: rename hw_helper files to gfx_core_helper files 
Related-To: NEO-6853
Signed-off-by: Kamil Kopryk <kamil.kopryk@intel.com>
 2023-02-01 19:37:51 +01:00
Kamil Kopryk
004d3e3416 refactor: don't use global ProductHelper getter 18 
Related-To: NEO-6853
Signed-off-by: Kamil Kopryk <kamil.kopryk@intel.com>
 2023-01-30 08:15:39 +01:00
Kamil Kopryk
5e059d4b30 refactor: don't use global ProductHelper getter 16 
Related-To: NEO-6853
Signed-off-by: Kamil Kopryk <kamil.kopryk@intel.com>
 2023-01-27 17:03:46 +01:00
Kamil Kopryk
445706361d refactor: don't use global ProductHelper 14/n 
Related-To: NEO-6853
Signed-off-by: Kamil Kopryk <kamil.kopryk@intel.com>
 2023-01-27 14:51:12 +01:00
Dunajski, Bartosz
d42ec1ad8a Unify multi regular context selection 
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>

Related-To: NEO-7618
 2023-01-27 14:04:04 +01:00
Kamil Kopryk
026d50c7b9 refactor: don't use global ProductHelper getter 13/n 
Related-To: NEO-6853
Signed-off-by: Kamil Kopryk <kamil.kopryk@intel.com>
 2023-01-27 13:52:36 +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
27393c76ea refactor: don't use global ProductHelper getter 11/n 
Related-To: NEO-6853
Signed-off-by: Kamil Kopryk <kamil.kopryk@intel.com>
 2023-01-26 08:16:52 +01:00
Warchulski, Jaroslaw
e21cf516d3 Cleanup includes 44 
Cleaned up files:
level_zero/tools/source/sysman/windows/os_sysman_imp.h
opencl/source/command_queue/command_queue.h
shared/source/command_container/cmdcontainer.h

Related-To: NEO-5548
Signed-off-by: Warchulski, Jaroslaw <jaroslaw.warchulski@intel.com>
 2023-01-25 16:05:22 +01:00
Warchulski, Jaroslaw
439aa6c87f Cleanup includes 43 
Cleaned up files:
level_zero/core/test/unit_tests/mocks/mock_kernel.h
opencl/source/mem_obj/mem_obj.h

Related-To: NEO-5548
Signed-off-by: Warchulski, Jaroslaw <jaroslaw.warchulski@intel.com>
 2023-01-25 11:33:39 +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
Warchulski, Jaroslaw
8cc4cc1612 Cleanup includes 38 
Cleaned up files:
opencl/source/cl_device/cl_device.h
opencl/source/command_queue/command_queue.h

Related-To: NEO-5548
Signed-off-by: Warchulski, Jaroslaw <jaroslaw.warchulski@intel.com>
 2023-01-20 14:55:17 +01:00
Dunajski, Bartosz
5a5596957a Capability to create multiple Regular BCS contexts per engine. 
Related-To: NEO-7618

Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2023-01-20 13:43:48 +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