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,654 Commits 42 Branches 655 Tags
5b11a4a5faabd461beaf450b3aae7f7c212695bb
Commit Graph

205 Commits

Author SHA1 Message Date
Maciej Plewka
7f38c5e633 Revert "Return error code for unsuported image arg in gen12lp" 
This reverts commit bbc31e6aac


Signed-off-by: Maciej Plewka maciej.plewka@intel.com
 2022-11-02 12:57:16 +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
Dominik Dabek
526ba1bde5 Fix l0 kernel set arg buffer caching 
Fix for incorrect cache hit if alloc id was uninitialized
and allocations counter was the same.

Signed-off-by: Dominik Dabek <dominik.dabek@intel.com>
 2022-10-27 17:25:10 +02:00
Maciej Plewka
bbc31e6aac Return error code for unsuported image arg in gen12lp 
Signed-off-by: Maciej Plewka <maciej.plewka@intel.com>
 2022-10-24 16:54:10 +02:00
Jim Snow
f976c7a313 Revert "Allocate RTDispatchGlobals as unboxed array" 
This reverts commit eaa4965ae8.

Signed-off-by: Jim Snow <jim.m.snow@intel.com>
 2022-10-24 05:16:03 +02:00
Compute-Runtime-Validation
7c6783c4a1 Revert "Return error when image arg does not support media block commands" 
This reverts commit e56d18b69f.

Signed-off-by: Compute-Runtime-Validation <compute-runtime-validation@intel.com>
 2022-10-12 03:58:33 +02:00
Maciej Plewka
e56d18b69f Return error when image arg does not support media block commands 
Signed-off-by: Maciej Plewka <maciej.plewka@intel.com>
 2022-10-11 15:47:27 +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
Jim Snow
eaa4965ae8 Allocate RTDispatchGlobals as unboxed array 
Previously we used an array-of-pointers approach, but using an
array-of-structures is in some ways simpler.

We also split out the RTStack as a separate allocation.

Related-To: LOCI-2966

Signed-off-by: Jim Snow <jim.m.snow@intel.com>
 2022-09-28 03:42:14 +02:00
Dominik Dabek
52ae228535 Add missing unit test 
Missing ult for isDebuggerActive
Move inline function to .inl file

Related-To: NEO-7003

Signed-off-by: Dominik Dabek <dominik.dabek@intel.com>
 2022-09-16 15:55:03 +02:00
Dominik Dabek
8cc0177f1c Change DG2 l1 cache policy to WB 
With compiler LSC WAs this gives better performance.

If debugger is active, policy will not be changed ie.
will be WBP.

Related-To: NEO-7003

Signed-off-by: Dominik Dabek <dominik.dabek@intel.com>
 2022-08-31 14:31:23 +02:00
Compute-Runtime-Validation
2621460e80 Revert "Change DG2 l1 cache policy to WB" 
This reverts commit a820e73dd7.

Signed-off-by: Compute-Runtime-Validation <compute-runtime-validation@intel.com>
 2022-08-27 08:04:19 +02:00
Dominik Dabek
a820e73dd7 Change DG2 l1 cache policy to WB 
With compiler LSC WAs this gives better performance.

If debugger is active, policy will not be changed ie.
will be WBP.

Related-To: NEO-7003

Signed-off-by: Dominik Dabek <dominik.dabek@intel.com>
 2022-08-26 12:58:45 +02:00
Compute-Runtime-Validation
a5b4a13452 Revert "Return error when image arg does not support media block commands" 
This reverts commit 8388e6cf4a.

Signed-off-by: Compute-Runtime-Validation <compute-runtime-validation@intel.com>
 2022-08-24 06:23:22 +02:00
Maciej Plewka
8388e6cf4a Return error when image arg does not support media block commands 
Related-To: NEO-7168

Signed-off-by: Maciej Plewka <maciej.plewka@intel.com>
 2022-08-23 12:07:29 +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
Wrobel, Patryk
dda5b19859 Adjust the implementation of strncpy_s() for Linux 
This change:
- prevents writing memory out of the range of the destination buffer
- prevents calling strlen() with non-null terminated c-string
- corrects the logic, which validates passed range to proceed
when real length fits the destination buffer

Related-To: NEO-7264
Signed-off-by: Wrobel, Patryk <patryk.wrobel@intel.com>
 2022-08-17 18:37:46 +02:00
Neil R Spruit
0101e80b00 Verify L0 Image Format Support for SPIRv 
- Check that the Image Format is valid for the image
argument to a SPIRv module. If the Image is invalid
return ZE_RESULT_ERROR_UNSUPPORTED_IMAGE_FORMAT.

Signed-off-by: Neil R Spruit <neil.r.spruit@intel.com>
 2022-08-12 17:57:17 +02:00
Jim Snow
6b4375efcd Re-enable use case where application allocates own RTDispatchGlobals. 
Implementation was assuming that if HasRTCalls is true then the
RTDispatchGlobals patch token is also valid, but that isn't the case
when the application is using its own RTDispatchGlobals instead of the
one provided by the L0 UMD.

Related-To: LOCI-3323

Signed-off-by: Jim Snow <jim.m.snow@intel.com>
 2022-08-04 23:19:43 +02:00
Rafal Maziejuk
af91f94098 Improve calculateAvailableThreadCount implementation 
Signed-off-by: Rafal Maziejuk <rafal.maziejuk@intel.com>
 2022-07-28 11:43:14 +02:00
Kamil Kopryk
d4d54f5093 Cleanup includes 
Signed-off-by: Kamil Kopryk <kamil.kopryk@intel.com>
 2022-07-25 09:58:38 +02:00
Kamil Kopryk
d29abb7955 Fix typo 
Signed-off-by: Kamil Kopryk <kamil.kopryk@intel.com>
 2022-07-25 08:21:16 +02:00
Jim Snow
f4879f064f Allocate per-tile RTDispatchGlobals, handle ray tracing patch tokens. 
Related-to: NEO-6711

Signed-off-by: Raiyan Latif <raiyan.latif@intel.com>
 2022-07-22 06:29:29 +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
Compute-Runtime-Validation
f9888db0fb Revert "Check indirect access from igc" 
This reverts commit e14c91fa6c.

Signed-off-by: Compute-Runtime-Validation <compute-runtime-validation@intel.com>
 2022-07-16 07:36:49 +02:00
Dominik Dabek
e14c91fa6c Check indirect access from igc 
Related-To: NEO-7182

Signed-off-by: Dominik Dabek <dominik.dabek@intel.com>
 2022-07-15 15:01:48 +02:00
Tratnack, Geoffrey
16bd39650f Adding Implementation of zetKernelGetProfileInfo 
Signed-off-by: Tratnack, Geoffrey <geoffrey.tratnack@intel.com>
 2022-07-07 21:45:08 +02:00
Mateusz Hoppe
673bf3b553 Move DebuggerL0 to shared 
Related-To: NEO-7075

Signed-off-by: Mateusz Hoppe <mateusz.hoppe@intel.com>
 2022-06-23 10:05:45 +02:00
Compute-Runtime-Validation
c45ddab1c3 Revert "Move DebuggerL0 to shared" 
This reverts commit 7eba4db2e7.

Signed-off-by: Compute-Runtime-Validation <compute-runtime-validation@intel.com>
 2022-06-22 04:38:32 +02:00
Mateusz Hoppe
7eba4db2e7 Move DebuggerL0 to shared 
Related-To: NEO-7075

Signed-off-by: Mateusz Hoppe <mateusz.hoppe@intel.com>
 2022-06-21 17:10:46 +02:00
Jaime Arteaga
de4b42118d Fix kernelBaseAddress extension 
Signed-off-by: Jaime Arteaga <jaime.a.arteaga.molina@intel.com>
 2022-06-03 18:35:13 +02:00
Mateusz Jablonski
747c2d3d83 Cleanup includes in cmdlist, cmdqueue, context, device, driver and module 
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2022-06-03 02:54:41 +02:00
Mateusz Jablonski
2a4c68dc38 Remove not needed dependencies from device_imp.h 
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2022-06-02 18:35:34 +02:00
Filip Hazubski
35d1f2e341 Add debug flag to control programming of thread arbitration policy with SCM 
Related-To: NEO-6801

Signed-off-by: Filip Hazubski <filip.hazubski@intel.com>
 2022-05-27 11:35:41 +02:00
Katarzyna Cencelewska
96e1eb7467 Move variables baseDieRev and baseDieA0Masked from xe_hpc to pvc 
Pvc specific variables should be located in pvc struct

Related-To: NEO-6738
Signed-off-by: Katarzyna Cencelewska <katarzyna.cencelewska@intel.com>
 2022-05-17 12:19:16 +02:00
Krystian Chmielewski
a5d8a22bac Add option for extending kernel 
Signed-off-by: Krystian Chmielewski <krystian.chmielewski@intel.com>
 2022-05-16 12:08:41 +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
Dominik Dabek
d0a32b1437 Fix: svm pointer caching 
Given a following sequence of setting kernel arg svm pointers: A, nullptr, A
the kernel arg was not being set to A

Related-To: NEO-6895

Signed-off-by: Dominik Dabek <dominik.dabek@intel.com>
 2022-04-25 07:59:47 +02:00
Bartosz Dunajski
9959896957 Add RT calls support to Kernel descriptor 
Signed-off-by: Bartosz Dunajski <bartosz.dunajski@intel.com>
 2022-04-22 16:33:59 +02:00
Compute-Runtime-Validation
a5e0167c1e Revert "Report Unsupported Image Format for invalid types for L0" 
This reverts commit d6ac8cdd03.

Signed-off-by: Compute-Runtime-Validation <compute-runtime-validation@intel.com>
 2022-04-15 07:49:25 +02:00
Neil R Spruit
d6ac8cdd03 Report Unsupported Image Format for invalid types for L0 
- If channel type or channel order is invalid for the layout, type, or
swizzle passed by the the user, then return unsupported image format.

Signed-off-by: Neil R Spruit <neil.r.spruit@intel.com>
 2022-04-14 00:33:55 +02:00
Krystian Chmielewski
2c1bfbb5b2 Encode number barriers 
When programming number of barriers use BARRIER_SIZE enumeration.
Resolves: NEO-6785

Signed-off-by: Krystian Chmielewski <krystian.chmielewski@intel.com>
 2022-04-08 10:32:23 +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
Jaime Arteaga
e8a6842b7e Add method to read kernel base address 
Signed-off-by: Jaime Arteaga <jaime.a.arteaga.molina@intel.com>
 2022-03-25 21:49:22 +01:00
Dominik Dabek
b03119b964 Add setArgBuffer caching to l0 
When trying to set the same values we don't need to set it again.
The pointer and allocId need to be the same.

Related-To: NEO-6737

Signed-off-by: Dominik Dabek <dominik.dabek@intel.com>
 2022-03-17 10:39:45 +01:00
Compute-Runtime-Validation
cee7ded064 Revert "Add setArgBuffer caching to l0" 
This reverts commit e6460e5534.

Signed-off-by: Compute-Runtime-Validation <compute-runtime-validation@intel.com>
 2022-03-13 00:50:42 +01:00
Dominik Dabek
e6460e5534 Add setArgBuffer caching to l0 
When trying to set the same values we don't need to set it again.
The pointer and allocId need to be the same.

Related-To: NEO-6737

Signed-off-by: Dominik Dabek <dominik.dabek@intel.com>
 2022-03-11 14:20:15 +01:00