Media
/
compute-runtime
mirror of https://github.com/intel/compute-runtime.git
1
0
Fork 0
Code Issues Packages Projects Releases Wiki Activity
11,745 Commits 36 Branches 610 Tags 175 MiB
Commit Graph

324 Commits

Author SHA1 Message Date
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
Kacper Nowak a12251d464 feat(zebin): code improvements 
- Set initial value for ArgIndexT index in
KernelArgMiscInfoT struct
- Add check for arg index in extended metadata in order to avoid OOB
accesses
- Fix missing: populating ArgTypeTraits + refactor ULTs in order to
check it
- Add missing ULTs for Program::callPopulateZebinExtendedArgsMetadataOnce

Signed-off-by: Kacper Nowak <kacper.nowak@intel.com>
 2022-11-08 14:10:55 +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
Krystian Chmielewski 78d75dee0f Use mock in KernelArgInfoTest 
Signed-off-by: Krystian Chmielewski <krystian.chmielewski@intel.com>
 2022-11-04 14:09:47 +01:00
Kacper Nowak 709e322a4a feat(zebin): get extended args metadata on clGetKernelArgInfo API call 
This commit adds support for retrieving extended args metadata passed in
.kernel_misc_info zeInfo's section on clGetKernelArgInfo call.

Related-To: NEO-7372
Signed-off-by: Kacper Nowak <kacper.nowak@intel.com>
 2022-11-03 13:15:09 +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
Kacper Nowak f06df021b5 feat(zebin): Add support for indirect stateless count 
Add support for newly added indirect statelss count check;
populate related field in kernelInfo.
- Move hasIndirectStatelessAccess check from KernelInfo to
KernelDescriptor.

Related-To: NEO-7428
Signed-off-by: Kacper Nowak <kacper.nowak@intel.com>
 2022-10-19 07:58:02 +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 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