intel/compute-runtime
1
0
Fork 0
mirror of https://github.com/intel/compute-runtime.git synced 2026-01-12 17:33:00 +08:00
Code Issues Packages Projects Releases Wiki Activity
3,626 Commits 43 Branches 656 Tags
5fa53f4516973607c060f4ccc15caff8f8f37ded
Commit Graph

172 Commits

Author SHA1 Message Date
Mateusz Jablonski
5fa53f4516 Move headers to core 
- address_patch.h
- options.h
- registered_method_dispatcher.h
- grf_config.h

Rename OCL_RUNTIME_PROFILING -> KMD_PROFILING

Related-To: NEO-3982

Change-Id: I06cf72729e9d7d7d2ff0bd169fcbada00c4b509a
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2019-12-10 12:19:29 +01:00
Mateusz Jablonski
16c6d7eb9b Refactor ApiFixture 
- setup number of root devices
- define tested root device

Related-To: NEO-4000

Change-Id: I785d07a7f54932f66fe57637c8d10775743a871c
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2019-12-09 16:32:44 +01:00
Gibala
5ac1d1258c Connect UnifiedMemoryProperties with MemoryPropertiesFlags 
-Add support to SvmAllocationData
-Refactor parseMemoryProperties
-Add allocation flags

Related-To: NEO-4011
Change-Id: I3728d2319aeef983dbcc3f8702da9a303a4e2b9c
Signed-off-by: Gibala <krzysztof.gibala@intel.com>
 2019-12-09 14:23:46 +01:00
Jaroslaw Chodor
72a1542140 [2/N] Program refactor - gather compiler options 
Change-Id: I0a614be73fbd87184be2dfea407582a58c27b0bc
 2019-12-06 22:17:19 +01:00
Filip Hazubski
82bc594af0 Add clEnqueueNDRangeKernelINTEL API 
Related-To: NEO-2712

Change-Id: If1d16d9d626871a9dc4b19282f9edc5786ffa398
Signed-off-by: Filip Hazubski <filip.hazubski@intel.com>
 2019-12-04 17:11:28 +01:00
Dunajski, Bartosz
dfc50f3a75 Move gmm_helper to core 
Change-Id: I31ca317d10697ab884e04f443c8ccfdd6ca9d2ae
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2019-12-04 15:25:32 +01:00
Dunajski, Bartosz
ec21f06427 Move GMM-OCL types conversions to new helper + includes cleanup 
Change-Id: I13e5917a32a5cd894ee42a848407fe20bf1daa06
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2019-12-04 10:42:49 +01:00
Dunajski, Bartosz
1ecad5faed Move IndirectHeap to core and improve unit tests 
Change-Id: If7e329fc12fe934eb0f6b1762d3b0d86aab287e6
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2019-12-03 15:06:27 +01:00
Dunajski, Bartosz
614156dd8b Move cache_policy to core 
Change-Id: I16be70d15f329117539fe6dfcc07c6dc10d54977
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2019-12-03 14:53:49 +01:00
Mateusz Jablonski
54f65c0243 Move headers to core 
- hw_info
- hw_cmds
- kmd_notify_properties
- completion_stamp
- bxml_generator_glue

Related-To: NEO-3982
Change-Id: I3ed3ef81f42596f381e60c19250f6eb1296d47a4
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2019-12-02 14:20:45 +01:00
Jaroslaw Chodor
355e8d3e5a [1/N] Program refactor - decouple from patchokens 
Change-Id: I63bbf6c31a5db9e788124f22b6105e65c16c86d4
 2019-11-25 19:46:21 +01:00
Zbigniew Zdanowicz
8d7c965dd5 Move Preemption tests to core 
Change-Id: I717f2e485cac962373474c30e7ed7c52eab58e7f
Signed-off-by: Zbigniew Zdanowicz <zbigniew.zdanowicz@intel.com>
 2019-11-19 17:47:38 +01:00
Mateusz Jablonski
3e1b15c31d Move initialization of AubCenter to RootDeviceEnvironment 
make RootDeviceEnvironments vector of unique_ptr

Related-To: NEO-3857

Change-Id: I23998502198307c8535cdd5c9c4af5223a5d69a5
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2019-11-19 11:30:16 +01:00
Zbigniew Zdanowicz
b31e25dbb6 Move PreemptionHelper class to core 
Change-Id: I172c4beb8ea2576505d6192585d45cfa3d00da34
Signed-off-by: Zbigniew Zdanowicz <zbigniew.zdanowicz@intel.com>
 2019-11-18 23:59:28 +01:00
Igor Venevtsev
63fd26f6d6 Always specify rootDeviceIndex for graphics memory allocations 
Related-To: NEO-2941

Change-Id: Ia2362fd6b4e72ede02919152475f40b3edbc3658
Signed-off-by: Igor Venevtsev <igor.venevtsev@intel.com>
 2019-11-15 15:14:41 +01:00
Filip Hazubski
5f021afd6d Move HwHelper to core directory 
Change-Id: I2c78a8b737ee8e61b917b4918da37e77bbd9fe34
Signed-off-by: Filip Hazubski <filip.hazubski@intel.com>
 2019-11-15 14:06:40 +01:00
Mateusz Jablonski
5a8f455a84 Remove csrsContainer from root device environment 
improve mocking:
- add method to create RootDevice in Platform
- add method to create SubDevice in RootDevice
- add method to create CommandStreamReceiver in Device

Related-To: NEO-3691

Change-Id: Ie9fe3de260492604333c8ca93796bfbffae518c4
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2019-11-13 10:05:09 +01:00
Jobczyk, Lukasz
7b7ac67e47 Extend an allocation properties constructor 
Related-To: NEO-2998

Signed-off-by Jobczyk, Lukasz <lukasz.jobczyk@intel.com>

Change-Id: Ia2a99ff3bae574cc0cc40a973a30bdca126fe12d
Signed-off-by: Jobczyk, Lukasz <lukasz.jobczyk@intel.com>
 2019-11-12 16:21:54 +01:00
Igor Venevtsev
684d58d2aa Make GraphicsAllocation constructors unambiguous 
Related-To: NEO-2941

Change-Id: Iedd16d0dcb4158b5e7832043289e2e6aba1549d5
Signed-off-by: Igor Venevtsev <igor.venevtsev@intel.com>
 2019-11-06 10:12:26 +01:00
Jaroslaw Chodor
cab8968e1a Fixing regression in rebuildFromIr 
Change-Id: If1604861180d935575cd06fb2978df114453a070
 2019-11-02 21:52:16 +01:00
Igor Venevtsev
fed673861f Add multiple root devices support to memory manager 
Related-To: NEO-2941

Change-Id: If4977c19dbd083f2d1559a40f9b4e911eab4859c
Signed-off-by: Igor Venevtsev <igor.venevtsev@intel.com>
 2019-10-31 14:30:19 +01:00
Jobczyk, Lukasz
e784ba39fb [2/N] Make the execution environment adapter agnostic 
-add rootDeviceId to the command stream receiver

Related-To: NEO-3857

Change-Id: I6c7f334ebe3d19cf0c58a4db65d013b7a8b7f982
Signed-off-by: Jobczyk, Lukasz <lukasz.jobczyk@intel.com>
 2019-10-29 17:15:01 +01:00
Mateusz Jablonski
d408b82a19 Move aub center and command stream receivers to root device environment 
resize root device environments to 1 by default

Related-To: NEO-3691, NEO-3857

Change-Id: Idf3d61e84f8265f30381c18216632d0ffb2a16de
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2019-10-28 14:40:43 +01:00
Gibala
a32f537601 Remove OCL object from MemoryProperties 13/n 
Refactor parseMemoryProperties and createMemoryPropertiesFlags functions

Related-To: NEO-3132
Change-Id: I61aaae69b84d8b0f77c08a59010879cc3a93e6cf
Signed-off-by: Gibala <krzysztof.gibala@intel.com>
 2019-10-24 14:07:42 +02:00
Mateusz Jablonski
c8664b50a4 MemoryManager: don't access command stream receivers from execution environment 
Related-To: NEO-3691, NEO-3857

Change-Id: I8d83456f4164d2b25d78bffa368cffe988c498b0
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2019-10-22 17:38:24 +02:00
Gibala
5f02a0730b Remove OCL object from MemoryProperties 12/n 
Remove MemoryProperties from Buffer and Image classes and replaced it with
MemoryPropertiesFlags

Related-To: NEO-3132
Change-Id: Ib582cddf759bf501fa7dbbea3257640eb9f431e9
Signed-off-by: Gibala <krzysztof.gibala@intel.com>
 2019-10-22 14:26:21 +02:00
Jaroslaw Chodor
90e5cf164c Moving hash and file_io to core 
Change-Id: I1e6eece53fadf62a8919aa41e04deee3dac2ce60
 2019-10-17 13:16:20 +02:00
Chodor, Jaroslaw
856e5c6aaf [1/N] compiler interface refactor 
Decouple compiler interface from Program object

Change-Id: Ibd63c6eee01d85527318ccad52e52f5487d3402e
 2019-10-16 16:17:13 +02:00
Mateusz Jablonski
dccce00711 Remove redundant getters/setters from MockContext class 
Change-Id: I4283c1b5805141bf573fd433190e08d853ec7275
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2019-10-16 12:29:34 +02:00
Cencelewska
81d587e1f9 Change arguments in creation of DispatchFlags 
Change-Id: I150e0da2bc76a665e82c308ee2094742c13c2aa3
Signed-off-by: Cencelewska <katarzyna.cencelewska@intel.com>
 2019-09-30 13:53:58 +02:00
Cencelewska
03f910466e Remove default constructor of DispatchFlags 
Resolves: NEO-3394

Change-Id: I6d5d8e389e0680e698423e4e36b4f0d20d173522
Signed-off-by: Cencelewska <katarzyna.cencelewska@intel.com>
 2019-09-24 13:46:34 +02:00
Kamil Kopryk
b71e3a8bee Add aub test with stateless path 
Change-Id: I189deba70dbd9c7dfb33994b3a7876b3b889a47e
Signed-off-by: Kamil Kopryk <kamil.kopryk@intel.com>
Related-To: NEO-3627
 2019-09-20 12:13:40 +02:00
Kamil Diedrich
115070767c Move graphics_allocation to core folder 
Change-Id: I16b8dbb57c2a40126826a232332c18ba9f563220
 2019-09-18 05:26:55 +02:00
Mateusz Jablonski
dc949f6d18 Setup sub device's os context based on sub device id 
Move types defined by using to separated header file

Related-To: NEO-3691

Change-Id: I71dfca0644b7022c4a381fbe396d0e32ca7d1ce5
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2019-09-17 14:04:26 +02:00
Jobczyk, Lukasz
76fe09c2a9 Handle page faults while accessing unified memory 
Related-To: NEO-3330

Change-Id: I7e21f894e9d1c82598954c49342d1f65af07498f
Signed-off-by: Jobczyk, Lukasz <lukasz.jobczyk@intel.com>
 2019-09-04 13:28:53 +02:00
Dunajski, Bartosz
cf979c3bc0 Remove getWaTable() method 
Change-Id: I508103a0d46ae94b55891c8a7ef104fb47b0b3e0
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2019-09-04 11:32:55 +02:00
Mrozek, Michal
c1f0949a67 Return error on device queue creation attempts if not supported. 
Change-Id: I571433ec3f02ac7570c85949b636c86efc133abe
Signed-off-by: Mrozek, Michal <michal.mrozek@intel.com>
 2019-09-03 14:59:02 +02:00
Dunajski, Bartosz
386fa40241 Rename HWTEST_F_T to HWTEST_TEMPLATED_F 
Change-Id: I2db1eca61f180a3986e58a36fde7d8a523109303
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2019-08-29 08:32:51 +02:00
Dunajski, Bartosz
40d4314670 Templated SetUp and TearDown in fixtures 
Change-Id: I86b0e88db1ed52966ed5f0a6474deda09a415768
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2019-08-28 10:43:42 +02:00
Daria Hinz
6566eb3193 Move Linear Stream to core folder 
Change-Id: I962ebd6e9075fcab9d7b6211524093109e62d382
Signed-off-by: Daria Hinz <daria.hinz@intel.com>
 2019-08-26 17:00:53 +02:00
Mrozek, Michal
e851359e32 Start using real mocs index to call state base address programming. 
- After this change we start using real MOCS index as an argument to sba
programming
- We also start tracking real MOCS index in Command Stream Receiver.

Change-Id: Id34cffd7e58cb7363df02ac76f82bf377f4bbd77
Signed-off-by: Mrozek, Michal <michal.mrozek@intel.com>
 2019-08-26 16:14:36 +02:00
Piotr Maciejewski
9bb625185f Enable Linux performance counters. 
Change-Id: I688d3669d1791081074626ef474ab1edbc018034
 2019-08-13 10:52:32 +02:00
Jim Snow
4360aff03c Move runtime/helpers/aligned_memory.h to core/helpers 
Signed-off-by: Jim Snow <jim.m.snow@intel.com>
Change-Id: I15de094c51d4eb18bfff4d17fd34e817b5525fda
 2019-08-06 23:56:24 +02:00
Dunajski, Bartosz
51888bec7e Whitelisted registers cleanup 
Change-Id: Ifa704f4bd7c4f0bab3fc8565103af6da07a42ba7
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2019-08-05 10:31:16 +02:00
Andrzej Koska
dd777559ba Limiting VME tests to supporting platforms 
Change-Id: I06aac13fc69d74fc4db26dfdd3b2035e53405d08
Signed-off-by: Koska, Andrzej <andrzej.koska@intel.com>
Related-To: NEO-3416
 2019-07-30 12:06:02 +02:00
Piotr Fusik
2548bea71d Minor clean-up. 
Change-Id: Id1523930fc8aedf85506e254c67f6b1ca8dd020d
Signed-off-by: Piotr Fusik <piotr.fusik@intel.com>
 2019-07-30 11:53:20 +02:00
Dunajski, Bartosz
95c2dcd8b0 Improve obtaining LinearStream during enqueue call 
- Move logic to enqueueHandler to cover all scenarios
- Create BlockedCommandsData not only for Kernel enqueue
- KernelOperation cleanup

Change-Id: Ie4a673cbbc986c685996a38ab296444d38e7bbd5
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2019-07-22 18:52:14 +02:00
Raiyan Latif
ca74489172 Move string.h to core helpers 
Change-Id: Ibaaab077ef2867b5e0db3bd215c261de9294063f
Signed-off-by: Raiyan Latif <raiyan.latif@intel.com>
 2019-07-19 07:21:00 +02:00
Maciej Dziuban
00cb778553 Change ImageClearColorFixture 
Change-Id: I621056204879057d346b82e5bc264d3c8d151fa5
Signed-off-by: Maciej Dziuban <maciej.dziuban@intel.com>
Related-To: NEO-2942
 2019-07-17 15:00:41 +02:00
Kamil Kopryk
27b3c1fe7b clGetDeviceInfo support unified shared memory 2/n. 
Change-Id: I4f01ceb8d833393a9436ecd23f085f3dced91f27
Related-To: NEO-3344
Signed-off-by: Kamil Kopryk <kamil.kopryk@intel.com>
 2019-07-15 18:24:46 +02:00