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

4081 Commits

Author SHA1 Message Date
Michal Mrozek 94ebf4ac23 Allow device allocations for transfer calls. 
- make sure that transfer is not handled via cpu.

Change-Id: Ieffb1d8920b72d44cbe108410c00f76f4b110d83
Signed-off-by: Michal Mrozek <michal.mrozek@intel.com>
 2020-01-24 14:24:14 +01:00
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
Jaime Arteaga 0abd52fe9b Remove GraphicsAllocation::additionalData 
Change-Id: If128761a29e487edab4eed4f0e3de79563a482b0
Signed-off-by: Jaime Arteaga <jaime.a.arteaga.molina@intel.com>
 2020-01-24 12:09:44 +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
chmielew fba25e696c ocloc adding '-ignore_isa_padding' flag 
Change-Id: I5e77d1005cd5057cb796a945c18998e6ce91e4ed
 2020-01-23 16:04:50 +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
ocldev a5f875e5d1 dependencies update 
Change-Id: Ia19ed2c254aca9571e3313befba821412e94dcba
 2020-01-23 15:43:21 +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
Adam Cetnerowski 98ac4ca5fd ULT renaming: Get info tests 
Related-To: NEO-2236

Change-Id: Ia8396e55b89c62b7d9e5b932d1cc6267f1f47b46
Signed-off-by: Adam Cetnerowski <adam.cetnerowski@intel.com>
 2020-01-22 17:20:35 +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
Igor Venevtsev 0d7cc3a8c0 Infra update 
Related-To: NEO-2941

Change-Id: I40c6116730fe10b58b413c2ff317bfc8941cc8ac
Signed-off-by: Igor Venevtsev <igor.venevtsev@intel.com>
 2020-01-22 15:06:12 +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
Maciej Dziuban 6464fda1b2 Extract tests to windows directory 
Related-To: NEO-3599
Change-Id: Ibb5be80ae0e1096e21de2e08d900e0e7f15666bc
Signed-off-by: Maciej Dziuban <maciej.dziuban@intel.com>
 2020-01-22 11:30:28 +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
Mateusz Jablonski 877b82a8e7 Add tests for AdapterBDF/FileDescriptor passed to gmm 
Related-To: NEO-4168
Change-Id: Ic68ac8a6d8eb0c33cb51fc7ff10e85510d470241
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2020-01-21 12:32:16 +01:00
Adam Cetnerowski e50039b9f0 ULT renaming: Compiler Interface Cached tests 
Related-To: NEO-2236

Change-Id: I1003a6122420bb9e3d6cf56df838418f672484f5
Signed-off-by: Adam Cetnerowski <adam.cetnerowski@intel.com>
 2020-01-21 12:22:12 +01:00
Maciej Dziuban 3c27e97c43 Extract gl mocks to windows directory 
Change-Id: I963032bfad880e42100f6233b9570cefb607f26c
 2020-01-21 12:07:13 +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
Dunajski, Bartosz 4b2b1acbfd Move TGLLP tests to dedicated directory 
Change-Id: I62e0da2c984ae60a41e33cd061ec756fbd5704de
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2020-01-20 16:22:04 +01:00
ocldev 115c166d89 dependencies update 
Change-Id: I06b24891c8040ff95b489f3f4d5cba49d5510d2e
 2020-01-20 15:52:15 +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
Mateusz Jablonski 91c62dcc3a Initialize args for gmm library 
Related-To: NEO-4168

Change-Id: I62d9676887ac775c53863eb132de0d891da0314c
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2020-01-20 14:22:01 +01:00
Adam Cetnerowski b6a96323b3 ULT renaming: CSR tests 
Related-To: NEO-2236

Change-Id: I532c096b530d3da0ad11c58809ae9fdb8d82719b
Signed-off-by: Adam Cetnerowski <adam.cetnerowski@intel.com>
 2020-01-20 12:57:24 +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
Jaime Arteaga 48a87cb675 Enable shareable buffer support (2/N) 
Add shareable flag to UnifiedMemoryProperties.

Change-Id: Ia2767eaec183ad2b0f3fb6b64da4ba343f581fda
Signed-off-by: Jaime Arteaga <jaime.a.arteaga.molina@intel.com>
 2020-01-20 10:50:33 +01:00
Adam Cetnerowski 3180171208 ULT renaming: Aggregator tests 
Related-To: NEO-2236

Change-Id: Ie8522f42238cad03b7ba9a5e18404e8f6a96bd39
Signed-off-by: Adam Cetnerowski <adam.cetnerowski@intel.com>
 2020-01-20 10:35:56 +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