intel/compute-runtime
1
0
Fork 0
mirror of https://github.com/intel/compute-runtime.git synced 2025-12-30 01:34:43 +08:00
Code Issues Packages Projects Releases Wiki Activity
3,880 Commits 42 Branches 655 Tags
d5cedc4fd5edc31999727870fa1c98daefc4789f
Commit Graph

2461 Commits

Author SHA1 Message Date
Mateusz Jablonski
d5cedc4fd5 Fail castToObject when icdDispatch is invalid 
Change-Id: Ieacf183c2c57d321f4399b7bc92020002b32bb8f
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2020-01-24 12:51:17 +01:00
Pawel Wilma
315df91d9d Builtin kernels refactoring 
Related-To: NEO-3220
Change-Id: Ib85a1f4fd69b47bc8e819a29cc4adec73bda72e0
Signed-off-by: Pawel Wilma <pawel.wilma@intel.com>
 2020-01-24 11:56:02 +01:00
Filip Hazubski
9c16c1a425 Add clGetKernelMaxConcurrentWorkGroupCountINTEL 
clGetKernelMaxConcurrentWorkGroupCountINTEL replaces clGetExecutionInfoINTEL
function.

Change-Id: I7e3461695de7ee4c0e43c3e9770724b025c0e2be
Signed-off-by: Filip Hazubski <filip.hazubski@intel.com>
 2020-01-24 11:55:28 +01:00
Mateusz Jablonski
2c568542f1 Pass GmmClientContext to page table manager 
Change-Id: If326696eef7fc6ef81a13afc9dcebb3cd8bcba9d
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2020-01-24 08:20:23 +01:00
Mateusz Hoppe
b6825933f8 Replace Event::eventNotReady with CompletionStamp::levelNotReady 
- move some files to core
- remove unnecessary includes

Related-To: NEO-4175

Change-Id: Ib33dff644452c7cfd6fda7e9bb4b68cd6eb3a61c
Signed-off-by: Mateusz Hoppe <mateusz.hoppe@intel.com>
 2020-01-23 16:16:23 +01:00
Filip Hazubski
a60aa092f8 Rename clEnqueueNDRangeKernelINTEL to clEnqueueNDCountKernelINTEL 
Change-Id: Ibe46bd94a93290b0b6cef0c10aa98e024fc17324
Signed-off-by: Filip Hazubski <filip.hazubski@intel.com>
 2020-01-23 15:46:13 +01:00
Zbigniew Zdanowicz
5727b8081f Add parameters to disable programming general and instruction base adresses 
Change-Id: If4380a0d3b281dbd2c5e3f2275e8f7960ce1acc7
Signed-off-by: Zbigniew Zdanowicz <zbigniew.zdanowicz@intel.com>
 2020-01-23 14:49:59 +01:00
Filip Hazubski
8d34f40aad Add clGetKernelSuggestedLocalWorkSizeINTEL 
This function can be used to query local work size that would be used in
case of querying ND range kernel with local_work_size set to NULL.

Change-Id: I86ac7c97cffb6c3e11b673a28285739edfabb4a6
Signed-off-by: Filip Hazubski <filip.hazubski@intel.com>
 2020-01-23 13:50:37 +01:00
Michal Mrozek
98006aa2bf Add support for SVM pointer reuse to enqueueReadBuffer. 
Change-Id: I7a6718b2ebe48912a19af3da5e233acd84bdd3ef
Signed-off-by: Michal Mrozek <michal.mrozek@intel.com>
 2020-01-23 11:09:13 +01:00
Maciej Dziuban
c50d8e3eb9 Add 'windows' suffix to windows specific files 
Related-To: NEO-3599
Change-Id: I42535735142a240844c87a7b8170328a32f359b5
Signed-off-by: Maciej Dziuban <maciej.dziuban@intel.com>
 2020-01-23 10:07:02 +01:00
Michal Mrozek
ac4041d906 Add more robust validation of inputs. 
- prevent USM device pointers on transfer calls
- prevent pointers that do not hold enough storage to service transfer.

Change-Id: I678808c034f708e9d0ae477d632788aae7f70452
Signed-off-by: Michal Mrozek <michal.mrozek@intel.com>
 2020-01-23 10:00:00 +01:00
Mateusz Hoppe
915a6fa14f Refactor CsrDependencies 
Related-To: NEO-4175

Change-Id: If7e02235c1545e3e8ddf254c31523dd57286088d
Signed-off-by: Mateusz Hoppe <mateusz.hoppe@intel.com>
 2020-01-23 08:38:13 +01:00
Michal Mrozek
35b59b7cbe Reuse SVM storage on writeBuffer call. 
- Instead of creating new allocation, look if it already exists if so
re-use it.

Change-Id: I23bc4ac8b8e59e96fce7d48546b76289bedc157f
Signed-off-by: Michal Mrozek <michal.mrozek@intel.com>
 2020-01-22 15:31:48 +01:00
Mateusz Hoppe
3c89cfc753 Move os_interface files to core 
Change-Id: Ie708a944130884248499091854ebc483953fa828
Signed-off-by: Mateusz Hoppe <mateusz.hoppe@intel.com>
 2020-01-22 14:50:51 +01:00
Filip Hazubski
0b141ed4ea Add KernelExecutionType 
Add possibility to set Kernel execution type via clSetKernelExecInfo.

Change-Id: I2de0bf4e067921440e34e14c6975f640d3f47162
Signed-off-by: Filip Hazubski <filip.hazubski@intel.com>
 2020-01-22 14:40:36 +01:00
Mateusz Jablonski
257275fa26 Add missing gen specific headers to solution 
Change-Id: I2d733db057e265efa4493597927d7f9baeb94e2b
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2020-01-22 11:45:24 +01:00
Filip Hazubski
807a52f3cf Pass ClDevice in DeviceHelper::getExtraDeviceInfo 
Change-Id: I2e7395b86f6c281d976928d9afd2fedf1e1ef4c9
Signed-off-by: Filip Hazubski <filip.hazubski@intel.com>
 2020-01-21 16:26:09 +01:00
Maciej Plewka
00f667723f Create commandContainer encoders 
Change-Id: I2f27c4de6af9ebbc0210bc5e08bbfa9cb6beec0e
Signed-off-by: Maciej Plewka <maciej.plewka@intel.com>
 2020-01-21 16:07:42 +01:00
Daria Hinz
278efbdfe6 Split structures into core and OCL-specific ones 
Change-Id: I349ed52bcc7ed26eb0ff892acadc456ae285b92e
Signed-off-by: Daria Hinz <daria.hinz@intel.com>
 2020-01-21 15:36:11 +01:00
Mateusz Hoppe
b5e2f322f6 Move files from runtime/memory_manager to core 
- remove TbxMemoryManager

Change-Id: I554feff51f08e108b2e9ee22ecaa2cb75a1eead7
Signed-off-by: Mateusz Hoppe <mateusz.hoppe@intel.com>
 2020-01-21 15:28:47 +01:00
Maciej Dziuban
4d3dfa9514 Add helper for casting to osHandle 
Change-Id: I61d397d68a7be304f314b272905323339318856b
Signed-off-by: Maciej Dziuban <maciej.dziuban@intel.com>
 2020-01-21 14:27:52 +01:00
Zbigniew Zdanowicz
7b4b4eaeb1 Add static getter to retrieve platform level SIP kernel allocation 
Change-Id: I2220c3b027ccb6ab52169077ef522c29476b3e68
Signed-off-by: Zbigniew Zdanowicz <zbigniew.zdanowicz@intel.com>
 2020-01-21 13:53:06 +01:00
Dunajski, Bartosz
054f2b503a Remove not used method 
Change-Id: I6109d4f1521de157f449cad92ecfbab3d133f815
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2020-01-21 11:14:45 +01:00
Dunajski, Bartosz
ca84ebfe4c Add const suffix 
Change-Id: I128a710a889aa6a7ead7867400a8b1ec6e781729
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2020-01-21 10:15:32 +01:00
Michal Mrozek
686f885e13 Remove debug breaks. 
-They hit each time retain/release is called on root device, which is actually
not an error.

Change-Id: I374752f56ae6750c85ac4750eb997dc66a33d0af
Signed-off-by: Michal Mrozek <michal.mrozek@intel.com>
 2020-01-21 08:04:02 +01:00
Mateusz Hoppe
42858acb32 Move methods from DeviceHelper to HwHelper 
- getSubDevicesCount()
- getEnginesCount()

Change-Id: I59e2d5e8552db5d30767edf8382b846b5ca683d8
Signed-off-by: Mateusz Hoppe <mateusz.hoppe@intel.com>
 2020-01-21 07:20:55 +01:00
Maciej Dziuban
142a38ea9d Move ClGl api to windows directory 
Functions will be gradually moved to cross-platform directory as linux
functionality gets implemented.

Change-Id: I566c6aca063f1fa4bdb0dbc0655d4de69b7f1f42
Signed-off-by: Maciej Dziuban <maciej.dziuban@intel.com>
 2020-01-21 07:02:52 +01:00
Katarzyna Cencelewska
6ffbf55e43 Add new function to set max threads for workgroup 
Resolves: NEO-4116

Change-Id: I8b9faf582c42edcb6f616a2f4662200d0d5b73d3
Signed-off-by: Katarzyna Cencelewska <katarzyna.cencelewska@intel.com>
 2020-01-20 17:05:14 +01:00
Filip Hazubski
17aee4da95 Remove constexpr from ClDevice::getDevice 
Change-Id: Iba4bd324a36c368b2711f5e1ec478acd210dbc14
Signed-off-by: Filip Hazubski <filip.hazubski@intel.com>
 2020-01-20 15:40:20 +01:00
Misiak
b498fea989 Removed unused atomic latestTaskCountWaited 
Related-To: NEO-3869

Change-Id: If7e9db2645c9c9c38d65a0b200960e387441c9ca
Signed-off-by: Konstanty Misiak <konstanty.misiak@intel.com>
 2020-01-20 11:43:56 +01:00
Maciej Dziuban
bd9cd46ab9 Unified memory sharing 10/n 
Enable creating allocations from non-NT handles

Change-Id: Ifd8c67dfd5624182aed76457b1d80bcc2659dd45
Signed-off-by: Maciej Dziuban <maciej.dziuban@intel.com>
Related-To: NEO-3771
 2020-01-20 11:27:33 +01:00
Mateusz Jablonski
9562daa2d0 Create wrapper for Gmm exported functions 
Related-To: NEO-2551

Change-Id: I6d2912b2cb020e9544e52af7c46f54d5174a1a52
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2020-01-20 11:15:24 +01:00
Jobczyk, Lukasz
cccb95bc4e Do not pass device ordinal in drm creation 
Change-Id: I8376a8eace1109772c516d7a3daadfa709495171
Signed-off-by: Jobczyk, Lukasz <lukasz.jobczyk@intel.com>
 2020-01-20 11:01:27 +01:00
Filip Hazubski
a7dba34814 Update api.cpp 
Use UNRECOVERABLE_IF when checking for nullptr.
Remove redundant object checks.

Change-Id: I004663bcab9e682927206242fdd567a05c30992d
Signed-off-by: Filip Hazubski <filip.hazubski@intel.com>
 2020-01-20 10:26:36 +01:00
Filip Hazubski
94a8345d3b Update GTPin functions 
Do not use Platform to acquire Devices.

Change-Id: I00d7c6f9903e0daefff98ec6292dc682444de45f
Signed-off-by: Filip Hazubski <filip.hazubski@intel.com>
 2020-01-20 10:11:35 +01:00
Maciej Dziuban
9865003cc2 Move GL sharing to windows directory 
Change-Id: I9aeb60d31d5c49c0464b2cd8296dc5d79ec41d63
Signed-off-by: Maciej Dziuban <maciej.dziuban@intel.com>
 2020-01-20 09:34:08 +01:00
Mateusz Hoppe
2e95ef42ae Move thread_arbitration_policy.h to core 
- extract QueueThrottle to core

Change-Id: I954732a44ae4fdd5f227ec6be4e27b879ca6eece
Signed-off-by: Mateusz Hoppe <mateusz.hoppe@intel.com>
 2020-01-17 18:09:00 +01:00
Filip Hazubski
8fcff2241f Add ClDevice 
Decouple cl_device_id from Device class.

Related-To: NEO-3938

Change-Id: I68543a753aea562f3b47ba0d23a059ff3cffa906
Signed-off-by: Filip Hazubski <filip.hazubski@intel.com>
 2020-01-17 12:43:11 +01:00
Dunajski, Bartosz
b982fb058c Obtain BCS engine type through helper method 
Change-Id: I8a8bf99f3a73a4293013ab3bc73911e25a12b57e
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2020-01-17 08:22:58 +01:00
Katarzyna Cencelewska
1b072cf170 Add error code for get device info relative to images 
if image are not supported

Related-To: NEO-3931
Change-Id: I527da2dc857cd15dae6535dd389378511eb71b6d
Signed-off-by: Katarzyna Cencelewska <katarzyna.cencelewska@intel.com>
 2020-01-16 16:30:13 +01:00
Dunajski, Bartosz
318d9620ae Improve debug logs 
Change-Id: I17f68beedd3e4fcf8e6e546fa507188d8ba99e0e
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2020-01-16 15:40:18 +01:00
Wesierski, Lukasz
5a1d78b3ce Correction in fill_buffer_stateless.igdrcl_built_in 
Corrected kernel FillBufferLeftLeftover argument type.

Change-Id: Iba17d5430aaa57c6871e6a09eaa66d56b2b5fe8b
 2020-01-16 05:02:52 -08:00
Andrzej Koska
8502df41aa Add JSL device IDs 
Change-Id: I69f31d26dfcf0d5d7b9e72969ed720775b702e8f
Signed-off-by: Andrzej Koska <andrzej.koska@intel.com>
Related-To: NEO-3770
 2020-01-15 21:27:02 +01:00
Krzysztof Gibala
e2d7634dd5 Remove limitation for write combined flag 
Allow usage of WC in clHostMemAllocINTEL & clSharedMemAllocINTEL

Related-To: NEO-3374
Change-Id: I82f0be3f67b26bd19195d374b40f73e8f8a50b01
Signed-off-by: Krzysztof Gibala <krzysztof.gibala@intel.com>
 2020-01-15 17:42:53 +01:00
kamdiedrich
05cf673279 Move files to core and cleanup headers 
gmm_callbacks
cleanup headers in wddm

Change-Id: Idc64ed7a6df1afd46aea08493c33cca12b62b861
 2020-01-15 15:07:10 +01:00
Zbigniew Zdanowicz
84d6a25b7f Replace instrisic pause call with NEO and ULT function 
Change-Id: I40707ecc77ea59d5bb3ae6f7f505ef8168847f1a
Signed-off-by: Zbigniew Zdanowicz <zbigniew.zdanowicz@intel.com>
 2020-01-15 14:55:11 +01:00
Mateusz Jablonski
28511bbc50 Remove not needed dependencies on gmm library target 
target_link_libraries applies the dependency implicitly

Change-Id: Ie989e8edbcfeecfb15b3512dac6026ea5e9eb3eb
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2020-01-15 12:18:02 +01:00
Jobczyk, Lukasz
172e75147e Make OsInterface root device specific 
Related-To: NEO-3857

Change-Id: Ibcd80c731b5d3755b62e0e03d0ffeedb08b52ca0
Signed-off-by: Jobczyk, Lukasz <lukasz.jobczyk@intel.com>
 2020-01-15 11:07:25 +01:00
Mateusz Jablonski
d24735b38f Rename cmake variables 
IGDRCL__* to NEO__*
UMKM_SHAREDDATA_INCLUDE_PATHS to NEO__GMM_INCLUDE_DIR

Change-Id: I565eedfbf572badd6bdbfaf9e09e62dbb2efb017
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2020-01-15 08:46:10 +01:00
Mateusz Jablonski
78187655eb Windows: load gmm lib via LoadLibrary 
Resolves: NEO-4144

Change-Id: Iae9d170a43872a93d36e84e93709a23951b4ac35
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2020-01-14 22:23:01 +01:00