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
44fb2a1672
Infra update.
...
Change-Id: I287b9e05765fbdb424253061843a09b9db4faea4
Signed-off-by: Pawel Cieslak <pawel.cieslak@intel.com >
2020-01-27 15:13:57 +01:00
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
d6f4520599
ProgramInfo cleanup - explicitly delete copying
...
Change-Id: I2691d272b5248e62b2dd3eb1e5995f664e8a94a2
2020-01-27 11:15:52 +01:00
1606f2d267
Manifest update
...
Change-Id: Idbea4a5f162e4835e38027bf9562c89e7a925c16
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com >
2020-01-27 10:44:27 +01:00
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
5ddabac3c0
New command encoders
...
Change-Id: I39b0f8a0bff4fa4ff5072e6a6893fb8b41df1768
Signed-off-by: Mateusz Hoppe <mateusz.hoppe@intel.com >
2020-01-27 10:07:04 +01:00
2e64471f58
Fixing regression in arg_info tests
...
Resolves: NEO-4188
Change-Id: I375d0efc084b95d4a93a987b87d9e5635d7ec26b
2020-01-25 19:09:21 +01:00
b74d502052
Moving patchtokens decoder to core
...
Change-Id: I61d9f3ec7a1bca55df5b3b8c1884014acff1a4c0
2020-01-25 15:16:01 +01:00
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
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
570b09850d
removing clean_on_sync attribute
...
Change-Id: I7970b0587f04d71c0d741a6ad04c44e9eeb10e78
Signed-off-by: Artur Harasimiuk <artur.harasimiuk@intel.com >
2020-01-25 00:37:42 +01:00
39198dfda2
Add flag for forcing usage of hostPtrTracking
...
Change-Id: I1a7c27145fcb23a54d49edf24659225621dd4496
2020-01-24 15:54:31 +01:00
715e32b6a5
Change Memory Constants into constexpr
...
Change-Id: Ic3c675b6343d362879b71e9071d720c46efe8c43
Signed-off-by: Zbigniew Zdanowicz <zbigniew.zdanowicz@intel.com >
2020-01-24 15:10:52 +01:00
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
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
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
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
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
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
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
fba25e696c
ocloc adding '-ignore_isa_padding' flag
...
Change-Id: I5e77d1005cd5057cb796a945c18998e6ce91e4ed
2020-01-23 16:04:50 +01:00
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
a5f875e5d1
dependencies update
...
Change-Id: Ia19ed2c254aca9571e3313befba821412e94dcba
2020-01-23 15:43:21 +01:00
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
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
98006aa2bf
Add support for SVM pointer reuse to enqueueReadBuffer.
...
Change-Id: I7a6718b2ebe48912a19af3da5e233acd84bdd3ef
Signed-off-by: Michal Mrozek <michal.mrozek@intel.com >
20.04.15428
2020-01-23 11:09:13 +01:00
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
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
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
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
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
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
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
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
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
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
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
00f667723f
Create commandContainer encoders
...
Change-Id: I2f27c4de6af9ebbc0210bc5e08bbfa9cb6beec0e
Signed-off-by: Maciej Plewka <maciej.plewka@intel.com >
2020-01-21 16:07:42 +01:00
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
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
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
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
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
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
3c27e97c43
Extract gl mocks to windows directory
...
Change-Id: I963032bfad880e42100f6233b9570cefb607f26c
2020-01-21 12:07:13 +01:00
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
ca84ebfe4c
Add const suffix
...
Change-Id: I128a710a889aa6a7ead7867400a8b1ec6e781729
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com >
2020-01-21 10:15:32 +01:00
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
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