intel/compute-runtime
1
0
Fork 0
mirror of https://github.com/intel/compute-runtime.git synced 2025-12-30 09:58:55 +08:00
Code Issues Packages Projects Releases Wiki Activity
11,937 Commits 42 Branches 655 Tags
1fa5710dffcac4d22b23c74982b586ec4792c81b
Commit Graph

216 Commits

Author SHA1 Message Date
Kamil Kopryk
91d39ad5bf Rename ClHwHelper -> ClGfxCoreHelper 
Related-To: NEO-6853
Signed-off-by: Kamil Kopryk <kamil.kopryk@intel.com>
 2022-12-05 11:26:20 +01:00
Dunajski, Bartosz
85da0ee184 Enable flushTask path for BCS 
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2022-12-01 20:10:21 +01:00
Zbigniew Zdanowicz
c0c9ce548a Validate level zero events in TBX mode 
Related-To: NEO-7545

Signed-off-by: Zbigniew Zdanowicz <zbigniew.zdanowicz@intel.com>
 2022-11-28 16:45:02 +01:00
Maciej Plewka
4b42b066f8 Use dedicated using type for TaskCount 
Related-To: NEO-7155

Signed-off-by: Maciej Plewka <maciej.plewka@intel.com>
 2022-11-28 16:44:44 +01:00
Andrzej Koska
90034d4173 Added scratch size check 
Related-To: NEO-7508
Signed-off-by: Andrzej Koska <andrzej.koska@intel.com>
 2022-11-22 14:14:33 +01:00
Fabian Zwolinski
f6eb2e753a Error check total SLM size not only inline 
Related-To: NEO-7280
Signed-off-by: Fabian Zwolinski <fabian.zwolinski@intel.com>
 2022-11-21 15:30:25 +01:00
Kamil Kopryk
0e47bcde1d Move ClCoreHelper ownership to RootDeviceEnvironment 4/n 
Related-To: NEO-6853
Signed-off-by: Kamil Kopryk <kamil.kopryk@intel.com>

Use RootDeviceEnvironment getHelper<ClCoreHelper> for
- isSupportedKernelThreadArbitrationPolicy
- getSupportedThreadArbitrationPolicies
 2022-11-15 17:24:11 +01:00
Kamil Kopryk
1d4240a0c8 Move ClCoreHelper ownership to RootDeviceEnvironment 1/n 
Related-To: NEO-6853
Signed-off-by: Kamil Kopryk <kamil.kopryk@intel.com>

Use RootDeviceEnvironment getHelper<ClCoreHelper> for
- requiresNonAuxMode
- requiresAuxResolves
 2022-11-15 10:35:22 +01:00
Mateusz Jablonski
dffe5fd604 Propagate flush error to initializeDeviceWithFirstSubmission method 
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2022-11-10 19:33:38 +01:00
Kamil Kopryk
002a90c717 Move hwHelper ownership to RootDeviceEnvironment 2/n 
Related-To: NEO-6853
Signed-off-by: Kamil Kopryk <kamil.kopryk@intel.com>

UseRootDeviceEnvironment getHelper<CoreHelper> for:
- getMaxBarrierRegisterPerSlice
- getPaddingForISAAllocation
 2022-11-10 16:39:39 +01:00
Mateusz Jablonski
57cea7365e Return submission status from flushTagUpdate method 
Related-To: NEO-7412
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2022-11-09 14:04:16 +01:00
Mateusz Jablonski
1c3d5c3892 Prepare mechanism for returning GPU execution error on OCL API 
translate task count value to OCL error

Related-To: NEO-7412
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2022-11-04 15:54:19 +01:00
Maciej Plewka
ff01b9361e Return error code when there is no space for scratch/private 
Signed-off-by: Maciej Plewka <maciej.plewka@intel.com>
 2022-11-02 11:55:18 +01:00
Compute-Runtime-Validation
052164c559 Revert "Use total SLM instead of inline in error checking" 
This reverts commit e1c49d0f23.

Signed-off-by: Compute-Runtime-Validation <compute-runtime-validation@intel.com>
 2022-10-22 09:41:36 +02:00
Fabian Zwolinski
e1c49d0f23 Use total SLM instead of inline in error checking 
Related-To: NEO-7280
Signed-off-by: Fabian Zwolinski <fabian.zwolinski@intel.com>
 2022-10-21 12:39:48 +02:00
Compute-Runtime-Validation
c2ce19ff36 Revert "Include dynamic SLM in clGetKernelWorkGroupInfo" 
This reverts commit 320b020dd6.

Signed-off-by: Compute-Runtime-Validation <compute-runtime-validation@intel.com>
 2022-10-12 22:58:58 +02:00
Fabian Zwolinski
320b020dd6 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-10-11 09:59:05 +02:00
Fabian Zwolinski
35b3a6ae1e Fix uncaptured debug output 
This commit fixes bug in which we print debug message to stderr stream. We
don't want any test to print any message out. Every output should be
captured.

Signed-off-by: Fabian Zwolinski <fabian.zwolinski@intel.com>
 2022-10-10 16:44:20 +02:00
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
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
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
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
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
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
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
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
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
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
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
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
Lukasz Jobczyk
a230f267e1 Poll task count indefinitely on high throttle command queue 
Resolves: NEO-6781

Signed-off-by: Lukasz Jobczyk <lukasz.jobczyk@intel.com>
 2022-03-25 10:06:16 +01:00
Fabian Zwolinski
3d8effcd69 Clean-Up unused code related to GMock 
This commit:
- Removes usings e.g. ::testing::Return
- Removes unnecessary gmock inclues
- Replaces Gmock macros (e.g. EXPECT_THAT) with our custom implementations

Related-To: NEO-4941
Signed-off-by: Fabian Zwolinski <fabian.zwolinski@intel.com>
 2022-03-22 16:16:34 +01:00
Konstanty Misiak
cf1bc3a2ba Disable EU fusion based on kernel properties from compiler 
Related-To: NEO-6633

Signed-off-by: Konstanty Misiak <konstanty.misiak@intel.com>
 2022-02-28 18:50:38 +01:00