intel/compute-runtime
1
0
Fork 0
mirror of https://github.com/intel/compute-runtime.git synced 2026-01-26 06:42:33 +08:00
Code Issues Packages Projects Releases Wiki Activity
11,510 Commits 43 Branches 658 Tags
510ba12cbc1dfcc9cd096feff40081b7366cd9f9
Commit Graph

647 Commits

Author SHA1 Message Date
Zbigniew Zdanowicz
565d820933 Replace virtual method call for DC flush with stored bool value 3/n 
Signed-off-by: Zbigniew Zdanowicz <zbigniew.zdanowicz@intel.com>
 2022-10-18 15:04:02 +02:00
Krystian Chmielewski
c224fd0666 Require LWS to be in ascending format X >= Y >= Z 
This change fixes problem with memory locality.
When calculating work group size do not take into account
work group sizes where there's bigger number of elements in
higher dimensions namely: Y>X or Z>Y.

Related-To: NEO-5719

Signed-off-by: Krystian Chmielewski <krystian.chmielewski@intel.com>
 2022-10-18 13:23:57 +02:00
Compute-Runtime-Validation
945897cf55 Revert "Replace virtual method call for DC flush with stored bool value 3/n" 
This reverts commit 9d94089a95.

Signed-off-by: Compute-Runtime-Validation <compute-runtime-validation@intel.com>
 2022-10-13 04:46:10 +02:00
Zbigniew Zdanowicz
9d94089a95 Replace virtual method call for DC flush with stored bool value 3/n 
Signed-off-by: Zbigniew Zdanowicz <zbigniew.zdanowicz@intel.com>
 2022-10-12 14:38:47 +02:00
Lukasz Jobczyk
1fedaee18c Wait on timestamps in Event::wait 
Signed-off-by: Lukasz Jobczyk <lukasz.jobczyk@intel.com>
 2022-10-10 13:04:21 +02:00
Mateusz Hoppe
2f24ef6855 Error from clEnqueueNDRangeKernel() for too big group counts 
Resolves: NEO-6976

Signed-off-by: Mateusz Hoppe <mateusz.hoppe@intel.com>
 2022-10-05 12:35:16 +02:00
Mateusz Jablonski
23eff82d0a OCL: optimize creating printf buffer 
Dont create printf buffer when kernel doesnt require it

Related-To: HSD-18023825570
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2022-09-30 12:25:57 +02:00
Zbigniew Zdanowicz
5986a7199a Share front end state updates between regular and immediate command lists 
Related-To: NEO-5019

Signed-off-by: Zbigniew Zdanowicz <zbigniew.zdanowicz@intel.com>
 2022-09-23 09:46:35 +02:00
Lukasz Jobczyk
efac290ba3 Do not use selector copy engine 
Signed-off-by: Lukasz Jobczyk <lukasz.jobczyk@intel.com>
 2022-09-20 21:49:00 +02:00
Lukasz Jobczyk
e00a5e0a1e Release main copy engine from device and sub device 
Signed-off-by: Lukasz Jobczyk <lukasz.jobczyk@intel.com>
 2022-09-20 17:12:34 +02:00
Michal Mrozek
3d5e34f727 Reduce the size of masks to 4. 
32 is not required.

Signed-off-by: Michal Mrozek <michal.mrozek@intel.com>
 2022-09-19 21:53:40 +02:00
Milczarek, Slawomir
0192e8038f Check for GPU hang in path with wait for timestamps 
Related-To: NEO-6868

Signed-off-by: Milczarek, Slawomir <slawomir.milczarek@intel.com>
 2022-09-19 15:01:46 +02:00
Lukasz Jobczyk
3a7f266d66 Enable BCS split in OCL 
Signed-off-by: Lukasz Jobczyk <lukasz.jobczyk@intel.com>
 2022-09-08 15:56:30 +02:00
Lukasz Jobczyk
f65d2aeb87 Split copy along single dimension 
Signed-off-by: Lukasz Jobczyk <lukasz.jobczyk@intel.com>
 2022-09-08 12:39:06 +02:00
Compute-Runtime-Validation
c0ce477f85 Revert "Enable BCS split WA in OCL" 
This reverts commit abfcaf1265.

Signed-off-by: Compute-Runtime-Validation <compute-runtime-validation@intel.com>
 2022-09-06 20:42:57 +02:00
Dunajski, Bartosz
16d9000429 Add option to change GRF mode 
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2022-09-06 13:00:17 +02:00
Lukasz Jobczyk
abfcaf1265 Enable BCS split WA in OCL 
Signed-off-by: Lukasz Jobczyk <lukasz.jobczyk@intel.com>
 2022-09-05 13:34:11 +02:00
Lukasz Jobczyk
0d6bef0753 Add BCS split to api specific config 
Signed-off-by: Lukasz Jobczyk <lukasz.jobczyk@intel.com>
 2022-09-05 11:13:10 +02:00
Compute-Runtime-Validation
20f49481f2 Revert "Enable BCS split WA in OCL" 
This reverts commit d672920121.

Signed-off-by: Compute-Runtime-Validation <compute-runtime-validation@intel.com>
 2022-09-03 20:25:10 +02:00
Cencelewska, Katarzyna
fa6bccdb30 Add new mt test for scenario with blitter 
also change in other EnqueueKernelTest to use a proper
retValue per thread
Signed-off-by: Cencelewska, Katarzyna <katarzyna.cencelewska@intel.com>
 2022-09-02 17:31:48 +02:00
Lukasz Jobczyk
01dc470d26 Fix BCS split ULTs on 32 bit 
Signed-off-by: Lukasz Jobczyk <lukasz.jobczyk@intel.com>
 2022-09-02 09:56:21 +02:00
Lukasz Jobczyk
d672920121 Enable BCS split WA in OCL 
Signed-off-by: Lukasz Jobczyk <lukasz.jobczyk@intel.com>
 2022-09-01 16:26:00 +02:00
Lukasz Jobczyk
399758ef17 Change default engines for BCS split 
Signed-off-by: Lukasz Jobczyk <lukasz.jobczyk@intel.com>
 2022-08-31 21:34:36 +02:00
Lukasz Jobczyk
a3dedcc7ee Add minimal transfer size for BCS split 
Signed-off-by: Lukasz Jobczyk <lukasz.jobczyk@intel.com>
 2022-08-31 21:28:40 +02:00
Zbigniew Zdanowicz
f656707fc0 Use hardware support flags for state compute mode state changes 
Related-To: NEO-5019

Signed-off-by: Zbigniew Zdanowicz <zbigniew.zdanowicz@intel.com>
 2022-08-25 18:46:37 +02:00
Jaime Arteaga
f7b3b20f81 Add warning when SLM is not enough for kernel 
Signed-off-by: Jaime Arteaga <jaime.a.arteaga.molina@intel.com>
 2022-08-24 01:56:41 +02:00
Dunajski, Bartosz
595cfebaef Refactor PIPE_CONTROL programming 
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2022-08-23 13:55:25 +02:00
Lukasz Jobczyk
82e29fd048 Add bcs split control mask 
Introduce debug variable to control which engines
the tranfser will be split into

Related-To: NEO-7173

Signed-off-by: Lukasz Jobczyk <lukasz.jobczyk@intel.com>
 2022-08-19 13:21:10 +02:00
Kamil Kopryk
67d7846974 Prepare ults for patch tokens cleanup 
Signed-off-by: Kamil Kopryk <kamil.kopryk@intel.com>

Related-To: IGC-5606
 2022-08-18 20:14:27 +02:00
Lukasz Jobczyk
b10b3ed9dd Add initial enqueue bcs split infrastructure 
Signed-off-by: Lukasz Jobczyk <lukasz.jobczyk@intel.com>
 2022-08-18 15:02:08 +02:00
Cencelewska, Katarzyna
5bdf758049 Add multi thread test for enqueue NDRange and WriteBuffer with queue per thread 
Signed-off-by: Cencelewska, Katarzyna <katarzyna.cencelewska@intel.com>
 2022-08-17 16:24:42 +02:00
Warchulski, Jaroslaw
260a324a6f Move files between shared/test/common and /unit_test (xe_*_core, page_fault...) 
common/xe_hpc_core/test_preemption_xe_hpc_core -> unit_test/xe_hpc_core
common/xe_hpg_core/excludes_xe_hpg_core -> unit_test/xe_hpg_core
common/xe_hpg_core/dg2/excludes_dg2 -> unit_test/xe_hpg_core/dg2
common/xe_hpg_core/test_preemption_xe_hpg_core -> unit_test/xe_hpg_core
unit_test/base_ult_config_listener.cpp -> common
unit_test/base_ult_config_listener.h -> common
unit_test/test_stats.h -> common
unit_test/test_configuration.h -> common
unit_test/page_fault_manager/cpu_page_fault_manager_tests.h -> common/fixtures
unit_test/page_fault_manager/mock_cpu_page_fault_manager.h -> common/mocks

Related-To: NEO-6524

Signed-off-by: Warchulski, Jaroslaw <jaroslaw.warchulski@intel.com>
 2022-08-17 16:17:00 +02:00
Warchulski, Jaroslaw
d795182eae Move files from shared/test/unit_test to /common (preamble, utilities) 
unit_test/preamble/preamble_fixture.h -> common/fixtures
unit_test/source_level_debugger -> common/
unit_test/utilities/base_object_utils.h -> common/utilities
unit_test/utilities/destructor_counted.h -> common/utilities
unit_test/utilities/logger_tests.h -> common/utilities

Related-To: NEO-6524
Signed-off-by: Warchulski, Jaroslaw <jaroslaw.warchulski@intel.com>
 2022-08-17 11:24:58 +02:00
Mateusz Jablonski
bca852617c Remove usage of TestLegacy from opencl tests 
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2022-08-16 22:16:48 +02:00
Mateusz Jablonski
bfc0919999 Remove usage of TestLegacy from shared tests 
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2022-08-16 14:36:33 +02:00
Mateusz Jablonski
5ffeac44c5 Correct shared fixture methods name to meet clang-tidy requirements 
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2022-08-16 12:52:49 +02:00
Katarzyna Cencelewska
fea9c9aca7 Add test to detect potential race 
also add lock inside initialGpgpu

Signed-off-by: Katarzyna Cencelewska <katarzyna.cencelewska@intel.com>
 2022-08-12 09:42:58 +02:00
Mateusz Jablonski
e6fc458d4b Add a struct for test fixtures with correct method naming convention 
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2022-08-11 12:55:52 +02:00
Warchulski, Jaroslaw
aed890a219 Move files between shared/test/unit_test and /common (fixtures, helpers, mocks) 
unit_test/fixtures/mock_aub_center_fixture.h -> common/fixtures
unit_test/helpers/raii_hw_helper.h -> common/helpers
unit_test/helpers/static_size3.h -> common/helpers
unit_test/helpers/ult_limits.h -> common/helpers
unit_test/memory_manager/mock_prefetch_manager.h -> common/memory_manager
common/mocks/mock_aub_stream.h -> unit_test/mocks
common/mocks/mock_csr_simulated_common_hw.h -> unit_test/mocks
common/mocks/mock_direct_submission_diagnostic_collector.h -> unit_test/mocks
common/mocks/mock_lrca_helper.h -> unit_test/mocks
common/mocks/mock_tbx_stream.h -> unit_test/mocks
common/mocks/linux/mock_os_context_linux.h -> unit_test/mocks/linux
common/mocks/windows/mock_wddm_direct_submission.h -> unit_test/mocks/windows

Related-To: NEO-6524
Signed-off-by: Warchulski, Jaroslaw <jaroslaw.warchulski@intel.com>
 2022-08-11 12:53:19 +02:00
Warchulski, Jaroslaw
a6c1d9578e Move files between shared/test/common/helpers and shared/test/unit_test/helpersi 
unit_test/helpers/cmd_buffer_validator.h -> common/helpers
unit_test/helpers/gtest_helpers.h -> common/helpers
common/helpers/blit_commands_helper_tests.inl -> unit_test/helpers
common/helpers/simd_helper_tests.inl -> unit_test/helpers
common/helpers/simd_helper_tests_pvc_and_later.inl -> unit_test/helpers
common/helpers/state_base_address_tests.h -> unit_test/helpers

Related-To: NEO-6524
Signed-off-by: Warchulski, Jaroslaw <jaroslaw.warchulski@intel.com>
 2022-08-10 15:23:12 +02:00
Warchulski, Jaroslaw
e7cca25894 CMake: don't include shared/test/unit_test when shared tests are skipped 1/n 
Related-To: NEO-6524
Signed-off-by: Warchulski, Jaroslaw <jaroslaw.warchulski@intel.com>
 2022-08-09 11:41:09 +02:00
Compute-Runtime-Validation
b38c750cc4 Revert "Add finish before command queue is released" 
This reverts commit 50fae92ea2.

Signed-off-by: Compute-Runtime-Validation <compute-runtime-validation@intel.com>
 2022-08-05 19:25:23 +02:00
Cencelewska, Katarzyna
61510e9a92 Revert optimization of gpgpu csr's mutex lock in the enqueue blit 
optimization available under flag
ForceCsrLockInBcsEnqueueOnlyForGpgpuSubmission

Related-To: NEO-7011
Signed-off-by: Cencelewska, Katarzyna <katarzyna.cencelewska@intel.com>
 2022-08-04 16:42:50 +02:00
Dunajski, Bartosz
98d776867f Add initial support for KernelArgsBuffer allocation 
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2022-08-03 20:28:21 +02:00
Dunajski, Bartosz
53a3cd2cdd Add method to merge LSH pipelined state during cmd list execution 
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2022-07-28 17:32:53 +02:00
Dunajski, Bartosz
a3903c385e Remove HW types from synchronization interface 
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2022-07-25 13:59:26 +02:00
Kamil Kopryk
d4d54f5093 Cleanup includes 
Signed-off-by: Kamil Kopryk <kamil.kopryk@intel.com>
 2022-07-25 09:58:38 +02:00
Dominik Dabek
e88b24eb37 Remove flush on svmmap 
No longer needed, problem was with reusing mem obj allocation.

Related-To: NEO-6948

Signed-off-by: Dominik Dabek <dominik.dabek@intel.com>
 2022-07-20 17:26:15 +02:00
Mateusz Hoppe
50fae92ea2 Add finish before command queue is released 
Related-To: NEO-5279

Signed-off-by: Mateusz Hoppe <mateusz.hoppe@intel.com>
 2022-07-20 12:16:27 +02:00
Zbigniew Zdanowicz
3f8c19eec9 Limit system memory flag in builtin kernels to destination argument 
Related-To: NEO-6959

Signed-off-by: Zbigniew Zdanowicz <zbigniew.zdanowicz@intel.com>
 2022-07-19 10:58:51 +02:00