intel/compute-runtime
1
0
Fork 0
mirror of https://github.com/intel/compute-runtime.git synced 2026-01-03 06:49:52 +08:00
Code Issues Packages Projects Releases Wiki Activity
3,918 Commits 43 Branches 655 Tags
15930487359f7f9250095af1617934b5625e15fa
Commit Graph

2722 Commits

Author SHA1 Message Date
Jaroslaw Chodor
33ac782f03 Allow empty kernel arg info 
Change-Id: I0e45e342148dfb4dceca1e7fdba885280e4ab597
 2020-01-29 17:58:22 +01:00
Dunajski, Bartosz
483cd71a20 Remove not used helper method 
Change-Id: I32e7d9c23ecd21e7ef45092ef8abd6571049f93d
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2020-01-29 15:23:11 +01:00
Mateusz Jablonski
b2c8574e28 Allow to create context with nondefault platform 
Related-To: NEO-3007
Change-Id: Iceeee6458431e77fe54724369144e7b4025aab2d
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2020-01-29 15:00:49 +01:00
Kamil Kopryk
bb8dd181a7 Disable sharing extensions on specific configs 
Change-Id: Ib2be6e797095bf771c618ba3515236e3f3eb16c6
Signed-off-by: Kamil Kopryk <kamil.kopryk@intel.com>
Resolves: NEO-4010
 2020-01-29 13:52:48 +01:00
Mateusz Hoppe
522dedfbd2 Move files to core 
Change-Id: I78bf6a82df3399a2b79143333989bac81e7a392a
Signed-off-by: Mateusz Hoppe <mateusz.hoppe@intel.com>
 2020-01-29 12:21:40 +01:00
Jobczyk, Lukasz
395444c5cc Do not override a CsrDispatchMode debug flag 
Change-Id: Ib483c1f60ce76228baf562be8ad0f4f454ac92d3
Signed-off-by: Jobczyk, Lukasz <lukasz.jobczyk@intel.com>
 2020-01-29 11:13:36 +01:00
Milczarek, Slawomir
7fe6a2fbed Add oclock option to force stateless to stateful optimization 
Related-To: NEO-2993

Change-Id: I9668053aa749534d09501bfccb1a9b93e69f0e4e
Signed-off-by: Milczarek, Slawomir <slawomir.milczarek@intel.com>
 2020-01-29 10:23:47 +01:00
Michal Mrozek
7af5aa274f Adjust tests. 
- do not use hard coded value, rely on HwHelper.

Change-Id: Icc269b46d44880453b2092b323de93c673c0658b
Signed-off-by: Michal Mrozek <michal.mrozek@intel.com>
 2020-01-28 14:52:20 +01:00
Mateusz Hoppe
a2b123a058 Pass CsrDependencies from events to BlitProperties 
- move files to core
- extract struct and enums to headers

Change-Id: Id5509f284dfa9ffc5e5d9173124af8a860f5a6f4
Signed-off-by: Mateusz Hoppe <mateusz.hoppe@intel.com>
 2020-01-28 12:31:59 +01:00
Michal Mrozek
63bfd36232 Add function to query minimal SIMD size. 
Change-Id: I9b6815b3559f7cdd8eddd05ad78c721a360814ef
Signed-off-by: Michal Mrozek <michal.mrozek@intel.com>
 2020-01-27 18:13:43 +01:00
Adam Cetnerowski
c9b845e72f ULT renaming: Context Multi Device tests 
Related-To: NEO-2236

Change-Id: I40b7b0462e8b78dbb44399f97f6aa1f8b89e57a6
Signed-off-by: Adam Cetnerowski <adam.cetnerowski@intel.com>
 2020-01-27 17:57:09 +01:00
Mateusz Hoppe
60c7587c2b Simplify HardwareCommandsHelper 
Related-To: NEO-4175

Change-Id: I39b08353514ea0bf384b6b592f24952d0ed631e6
Signed-off-by: Mateusz Hoppe <mateusz.hoppe@intel.com>
 2020-01-27 17:10:33 +01:00
Dunajski, Bartosz
fd8c5ba67f Fix unit test configurations 
Change-Id: Ia2a2ac7d67b5836ad2da8db747f06c71d7a71636
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2020-01-27 16:37:13 +01:00
Filip Hazubski
07c4682668 Respect KernelExecutionType in enqueue kernel calls 
Change-Id: I9de07f9e3b77c4a44f6a0127e0ae3bd7e1ab97f8
Signed-off-by: Filip Hazubski <filip.hazubski@intel.com>
 2020-01-27 13:51:49 +01:00
Mateusz Jablonski
f030f6c67a Dont access global platform in GmmMemory 
Related-To: NEO-3007
Change-Id: I5c8ed5cd9a3f78b3b67a63e9281f6cc6af4ffd1b
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2020-01-27 10:21:51 +01:00
Jaroslaw Chodor
2e64471f58 Fixing regression in arg_info tests 
Resolves: NEO-4188

Change-Id: I375d0efc084b95d4a93a987b87d9e5635d7ec26b
 2020-01-25 19:09:21 +01:00
Jaroslaw Chodor
b74d502052 Moving patchtokens decoder to core 
Change-Id: I61d9f3ec7a1bca55df5b3b8c1884014acff1a4c0
 2020-01-25 15:16:01 +01:00
Konstanty Misiak
fc5b98970c Moved files from gmm_helper to core 
Related-To: NEO-4138

Change-Id: Ib7aecb1531cebbe34abb5c8e57067464726e9009
Signed-off-by: Konstanty Misiak <konstanty.misiak@intel.com>
 2020-01-25 11:49:17 +01:00
Jaroslaw Chodor
f057712fa7 Program refactor 
* decouple program_info
* move global allocations relocation to linker
* remove obsolete tests
* initial cleanup to kernel_info kernelInfo
* unified patchtoken validation

Change-Id: I0567cd6d607b4f3cf44e6caf33681f6210760f76
 2020-01-25 10:56:30 +01:00
kamdiedrich
39198dfda2 Add flag for forcing usage of hostPtrTracking 
Change-Id: I1a7c27145fcb23a54d49edf24659225621dd4496
 2020-01-24 15:54:31 +01:00
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
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
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
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
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
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
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
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
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