Media/compute-runtime
1
0
Fork 0
mirror of https://github.com/intel/compute-runtime.git synced 2025-09-15 13:01:45 +08:00
Code Issues Packages Projects Releases Wiki Activity
11,427 Commits 39 Branches 642 Tags
4f0d19628ed5b1f75eff6905fad436fb8b7b3fd5
Commit Graph

310 Commits

Author SHA1 Message Date
Krystian Chmielewski
73a58aaf9e feat(zebin): inline sampler 
Add support for inline samplers in zebin.
Generate required SAMPLER_STATEs in DSH.

Resolves: NEO-7388

Signed-off-by: Krystian Chmielewski <krystian.chmielewski@intel.com>
 2022-10-10 12:47:19 +02:00
Fabian Zwolinski
7953d15826 Print warning when kernel uses too much SLM 
Instead of just returning proper error code in case of exceeding
available Shared Local Memory size we also want to print error message
to make debugging easier.

Related-To: NEO-7280
Signed-off-by: Fabian Zwolinski <fabian.zwolinski@intel.com>
 2022-10-07 19:06:19 +02:00
Fabian Zwolinski
1142404c0c Add error handling when kernel uses too much SLM 
API Functions reporting error:
- clCreateKernel
- clEnqueueNDRangeKernel
- zeKernelCreate
- zeCommandListAppendLaunchKernel
- zeKernelSuggestGroupSize

Related-To: NEO-7280
Signed-off-by: Fabian Zwolinski <fabian.zwolinski@intel.com>
 2022-10-06 16:45:42 +02:00
Compute-Runtime-Validation
36e17cebef Revert "Include dynamic SLM in clGetKernelWorkGroupInfo" 
This reverts commit ccdb5aaa2a.

Signed-off-by: Compute-Runtime-Validation <compute-runtime-validation@intel.com>
 2022-10-03 19:27:21 +02:00
Fabian Zwolinski
ccdb5aaa2a Include dynamic SLM in clGetKernelWorkGroupInfo 
Current implementation only takes static slmInlineSize into account.
With this change we also include dynamic SLM passed as a kernel arguments.

Related-To: NEO-5761
Signed-off-by: Fabian Zwolinski <fabian.zwolinski@intel.com>
 2022-09-29 17:38:44 +02:00
Igor Venevtsev
43676ed02a L0Debug Win: initialize device with empty submission 
In case of debuggable context device should be additionally
initialized by early empty submission issue.

Signed-off-by: Igor Venevtsev <igor.venevtsev@intel.com>
 2022-09-21 12:02:34 +02:00
Dunajski, Bartosz
1a28c2a154 Add threads count queries 
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2022-08-24 13:18:20 +02:00
Krystian Chmielewski
18adbed233 feat(zebin): add thread scheduling mode support 
Resolves: NEO-7197

Signed-off-by: Krystian Chmielewski <krystian.chmielewski@intel.com>
 2022-08-18 16:10:18 +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
649cd3441a Rename TestBodyImpl->testBodyImpl 
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2022-08-17 10:47:05 +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
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
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
Rafal Maziejuk
ed0c36117e Apply heuristics when setting TG dispatch size on XE_HPC_CORE 
The default TG dispatch size can be changed
to a better value based on number of threads in TG or
currently available amount of threads on GPU.
Decision on what TG dispatch size should be are based on
implemented heuristics.

Signed-off-by: Rafal Maziejuk <rafal.maziejuk@intel.com>
Related-To: NEO-6989
 2022-08-08 16:43:10 +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
Compute-Runtime-Validation
0eb2001d8f Revert "Check indirect access from igc" 
This reverts commit e5d63cd303.

Signed-off-by: Compute-Runtime-Validation <compute-runtime-validation@intel.com>
 2022-07-22 04:39:16 +02:00
Dominik Dabek
e5d63cd303 Check indirect access from igc 
Also add workaround for app passing svm pointers by value

Related-To: NEO-7182

Signed-off-by: Dominik Dabek <dominik.dabek@intel.com>
 2022-07-21 12:25:24 +02:00
Lukasz Jobczyk
4ac6e09117 Do not reuse mem obj's allocation 
Signed-off-by: Lukasz Jobczyk <lukasz.jobczyk@intel.com>
 2022-07-19 11:42:17 +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
Zbigniew Zdanowicz
e07f9f0698 Add kernel algorithm to check any argument is using system memory 
Related-To: NEO-6959

Signed-off-by: Zbigniew Zdanowicz <zbigniew.zdanowicz@intel.com>
 2022-07-12 13:08:49 +02:00
Katarzyna Cencelewska
25ce4d0c04 Clean unused code 
remove parts with device queue

Signed-off-by: Katarzyna Cencelewska <katarzyna.cencelewska@intel.com>
 2022-07-07 14:52:26 +02:00
Artur Harasimiuk
4bdd8860a1 test.h refactor 
Signed-off-by: Artur Harasimiuk <artur.harasimiuk@intel.com>
 2022-07-04 18:20:07 +02:00
Bartosz Dunajski
4fb4a1d77b Add LogicalStateHelper getter for CommandQueue. 
Refactor Kernel handling

Signed-off-by: Bartosz Dunajski <bartosz.dunajski@intel.com>
 2022-07-04 13:21:15 +02:00
Artur Harasimiuk
a8e2bd3f98 hw_cmds.h usage cleanup 
Signed-off-by: Artur Harasimiuk <artur.harasimiuk@intel.com>
 2022-06-29 11:15:45 +02:00
Artur Harasimiuk
2cc2d05c37 remove unused include 
Signed-off-by: Artur Harasimiuk <artur.harasimiuk@intel.com>
 2022-06-28 10:59:30 +02:00
Artur Harasimiuk
09d160910d remove unused includes 
Signed-off-by: Artur Harasimiuk <artur.harasimiuk@intel.com>
 2022-06-27 22:59:18 +02:00
Maciej Plewka
6ab6e1abff Fix mutex order for event task and move args to gpu 
This commit fixes problem with untransfered shared usm memory to gpu
when there is submit to gpu trigerred by user event. Also there is a fix
for dead lock problem caused by mixed orders of locking mutexes in csr
and in direct submission controller.

Related-To: NEO-6762

Signed-off-by: Maciej Plewka <maciej.plewka@intel.com>
 2022-06-21 11:28:25 +02:00
Krzysztof Gibala
c229ace4df Adjust GmmHelper to be HW aware 
Related-To: NEO-6523
Signed-off-by: Krzysztof Gibala <krzysztof.gibala@intel.com>
 2022-06-13 18:33:06 +02:00
Artur Harasimiuk
6d43e96dee style: configure readability-identifier-naming.ClassCase 
Signed-off-by: Artur Harasimiuk <artur.harasimiuk@intel.com>
 2022-06-13 18:02:39 +02:00
John Falkowski
620bb970f4 Resubmit fix for task count hang 
Signed-off-by: John Falkowski <john.falkowski@intel.com>
 2022-06-07 16:28:17 +02:00
Krzysztof Gibala
81899c4477 Add canonized gpuAddress to GraphicsAllocation constructor 
Related-To: NEO-6523
Signed-off-by: Krzysztof Gibala <krzysztof.gibala@intel.com>
 2022-06-06 18:17:36 +02:00
Krzysztof Gibala
e146a8e8ca Correct wrong constructor pattern in GraphicsAllocation 
Related-To: NEO-6523
Signed-off-by: Krzysztof Gibala <krzysztof.gibala@intel.com>
 2022-06-01 18:06:56 +02:00
Kacper Nowak
1b8ceb2bbc Enhance kernel arg info ULTs 
Manually set values expected by given kernel arg info query.
This prevents issues which incoming zebin switch.

Related-To: NEO-6646
Signed-off-by: Kacper Nowak <kacper.nowak@intel.com>
 2022-05-18 22:36:09 +02:00
Artur Harasimiuk
3f04769f07 style: configure readability-identifier-naming.FunctionCase 
Signed-off-by: Artur Harasimiuk <artur.harasimiuk@intel.com>
 2022-05-17 20:55:56 +02:00
Artur Harasimiuk
819e0f5515 style: configure readability-identifier-naming.LocalVariableCase 
Signed-off-by: Artur Harasimiuk <artur.harasimiuk@intel.com>
 2022-05-16 12:39:44 +02:00
Patryk Wrobel
9b2ad0c5df Detect GPU hangs in flushBcsTask() 
This change introduces detection of GPU hangs in flushBcsTask()
function. The new code has been covered with ULTs.

Related-To: NEO-6681
Signed-off-by: Patryk Wrobel <patryk.wrobel@intel.com>
 2022-05-12 16:17:16 +02:00
Artur Harasimiuk
e9be9b64c6 clang-tidy configuration cleanup 
Define single .clang-tidy configuration with all used checks and use
NOLINT to selectively silence tool. That way cleanup should be easier.
third_part/ has its own configuration that disables clang-tidy for this
folder.

Signed-off-by: Artur Harasimiuk <artur.harasimiuk@intel.com>
 2022-05-11 14:02:04 +02:00
Krzysztof Gibala
2fcda0a528 Refactor: Change decanonize method accessing point 
Accessing decanonize method as a member of GmmHelper class object

Signed-off-by: Krzysztof Gibala <krzysztof.gibala@intel.com>
 2022-05-11 12:57:02 +02:00
Filip Hazubski
1088bfd837 Move shared ULT helper files to shared directory 
Signed-off-by: Filip Hazubski <filip.hazubski@intel.com>
 2022-05-06 09:20:27 +02:00
Krzysztof Gibala
9b778863b4 Store GmmHelper in Gmm class 
Store GmmHelper in Gmm class instead of GmmClientContext

Related-To: NEO-6523
Signed-off-by: Krzysztof Gibala <krzysztof.gibala@intel.com>
 2022-04-27 15:45:49 +02:00
Compute-Runtime-Validation
903cf766b3 Revert "Move shared helper files to shared directory" 
This reverts commit 459524f129.

Signed-off-by: Compute-Runtime-Validation <compute-runtime-validation@intel.com>
 2022-04-27 13:12:16 +02:00
Filip Hazubski
459524f129 Move shared helper files to shared directory 
Signed-off-by: Filip Hazubski <filip.hazubski@intel.com>
 2022-04-27 10:34:42 +02:00
Zbigniew Zdanowicz
fd45ac133d Unify append calls 
Related-To: NEO-6242

Signed-off-by: Zbigniew Zdanowicz <zbigniew.zdanowicz@intel.com>
 2022-04-07 10:18:55 +02:00
Dominik Dabek
76289be8c1 Avoid unnecessary allocation in enqueueHandler 
Related-To: NEO-6837

kernelObjsForAuxTranslation will allocate only if needed

Signed-off-by: Dominik Dabek <dominik.dabek@intel.com>
 2022-04-06 13:03:41 +02:00
Zbigniew Zdanowicz
f2a18370e8 Split command queue hw tests 
Signed-off-by: Zbigniew Zdanowicz <zbigniew.zdanowicz@intel.com>
 2022-04-01 08:35:40 +02:00
Dominik Dabek
308f9ccfff Do not allocate dynamic state heap if not needed 
Dynamic state heap is only used for sampler data.

Related-To: NEO-6821

Signed-off-by: Dominik Dabek <dominik.dabek@intel.com>
 2022-03-31 12:13:13 +02:00
Konstanty Misiak
174c27eb31 Fix CFEFusedEUDispatch debug flag 
Signed-off-by: Konstanty Misiak <konstanty.misiak@intel.com>
 2022-03-28 12:32:05 +02:00