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

2736 Commits

Author SHA1 Message Date
kamdiedrich c7274c60e7 Add USM support flags 
Change-Id: I36ef2eaf22ea75c28efd83a91ac3ef9e8961a824
 2020-01-31 14:42:14 +01:00
Jablonski, Mateusz 8bbb719a97 Stop using platformDevices to setup hw info on Linux 
Related-To: NEO-4207
Change-Id: I6ab136c8cddf9652ba05b3ef4e81fb6ad594831b
Signed-off-by: Jablonski, Mateusz <mateusz.jablonski@intel.com>
 2020-01-31 14:34:29 +01:00
Mateusz Jablonski 0e3ab96298 Move compiler extensions to cl device 
Related-To: NEO-4207
Change-Id: Ia220085260fbafb062e0e0aedca863eb64b079bd
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2020-01-31 14:11:05 +01:00
Mateusz Jablonski 0a0b1ce1d8 Pass platform to ClDevice 
Related-To: NEO-4207
Change-Id: I1c70d209df2b378573a41fa991ab594746691adb
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2020-01-31 14:10:29 +01:00
Mateusz Hoppe e0fe796115 Create core library 
- include only enabled gen files

Change-Id: Id3251b72253d25f92c83f6ca465903366d9e78e7
Signed-off-by: Mateusz Hoppe <mateusz.hoppe@intel.com>
 2020-01-31 13:05:43 +01:00
Dunajski, Bartosz 36f11d4d0e Enhance cmd parser for custom commands parsing 
Change-Id: I54bd48db5c99e0196d556fe14882a071c3f04b3b
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2020-01-31 12:35:33 +01:00
Artur Harasimiuk 8fd1e8c511 change config storage from string to uint 
Change-Id: If206fe823541fb2a64f0a555934788eef5a05da7
Signed-off-by: Artur Harasimiuk <artur.harasimiuk@intel.com>
 2020-01-31 11:14:05 +01:00
Igor Venevtsev a34268fc54 Split Standard 64KB heap for multiple root devices 
Resolves: NEO-4196

Change-Id: Ibd76eb2447791e34ba3e1c27bbc7f5cd09325e98
Signed-off-by: Igor Venevtsev <igor.venevtsev@intel.com>
 2020-01-31 08:29:06 +01:00
Adam Cetnerowski dbd12dbaff ULT renaming: context negative tests 
Related-To: NEO-2236

Change-Id: Ib4be5397f09924e0899397e2d4f3928714bf7e4f
Signed-off-by: Adam Cetnerowski <adam.cetnerowski@intel.com>
 2020-01-30 15:26:29 +01:00
Jobczyk, Lukasz 39cb48024a Initialize root command stream receiver 
Change-Id: I90c4ee9c0e24b1f9182f100213bf6a1ec70df3a8
Signed-off-by: Jobczyk, Lukasz <lukasz.jobczyk@intel.com>
 2020-01-30 15:01:11 +01:00
Filip Hazubski f80480de7f Move ClDevice to a separate file 
Related-To: NEO-3938

Change-Id: I275b9285b70dac2c9bc52878f6e517e4f3e083b3
Signed-off-by: Filip Hazubski <filip.hazubski@intel.com>
 2020-01-30 12:46:10 +01:00
Jablonski, Mateusz adc3a97503 Pass RootDeviceEnvironment to Drm 
Related-To: NEO-4207
Change-Id: Ic59abf9221702333efea69213391b9646ae0864e
Signed-off-by: Jablonski, Mateusz <mateusz.jablonski@intel.com>
 2020-01-30 10:57:03 +01:00
Adam Cetnerowski 918cae0188 Device ID cleanup 
Change-Id: I257c56bc4f4ac53759a4da0724eea33c66012aa5
Signed-off-by: Adam Cetnerowski <adam.cetnerowski@intel.com>
 2020-01-30 09:43:36 +01:00
Pawel Wilma 9cbafe8bdd Add per-DSS backed buffer programming to dispatch flags 
Related-To: NEO-3220

Change-Id: I16711af6d5b2ca51ab2c92b680d253124774534f
Signed-off-by: Pawel Wilma <pawel.wilma@intel.com>
 2020-01-30 08:40:59 +01:00
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