intel/compute-runtime
1
0
Fork 0
mirror of https://github.com/intel/compute-runtime.git synced 2026-01-03 23:03:02 +08:00
Code Issues Packages Projects Releases Wiki Activity
3,976 Commits 43 Branches 655 Tags
8a6cb1e5ca428a97ee8b62c38dfea665d646db32
Commit Graph

278 Commits

Author SHA1 Message Date
Jobczyk, Lukasz
bfa1164675 Make unified memory allocations multistorage resources 
Related-To: NEO-2998

Change-Id: I61e831568a6bbf6e751d7a2ef9c7171c633a128a
Signed-off-by: Jobczyk, Lukasz <lukasz.jobczyk@intel.com>
 2019-12-19 11:06:17 +01:00
Mateusz Hoppe
ff30a66624 Use correct macros for enabling tests 
Change-Id: I51f51464918a487001200337b97a542ab4e65f1a
Signed-off-by: Mateusz Hoppe <mateusz.hoppe@intel.com>
 2019-12-18 15:38:51 +01:00
Mateusz Jablonski
3aa454a771 Move SysCalls to core 
Related-To: NEO-3982
Change-Id: Ie4797e0c83891d689dd8903716bce9292702938d
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2019-12-18 10:02:53 +01:00
Dunajski, Bartosz
7b18a919e7 Refactor heaps 
- Remove GENERAL_STATE
- Change allocation types
- IOH can be utilized as 4GB heap

Change-Id: I1c2a7bc284217a26d740b504bf92834d39f3ace2
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2019-12-18 09:50:22 +01:00
Maciej Plewka
8803b4cd4e Move grf size to HwInfo 
Change-Id: I65ee879644573586d63092b487f8b5ea0cedf1e3
Signed-off-by: Maciej Plewka <maciej.plewka@intel.com>
 2019-12-17 17:27:21 +01:00
Dunajski, Bartosz
73697b7ab4 Add debug flag to override gpu address space 
Change-Id: Ifce09cf2b0f1935ce15f1a718cff36b0c44848ca
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2019-12-17 15:01:35 +01:00
Mateusz Hoppe
f0a6f6b057 Move DebugSettingsManager to core 
- pass registry path in constructor

Change-Id: I2a121da2c9483a0df088989feea490a638c63016
Signed-off-by: Mateusz Hoppe <mateusz.hoppe@intel.com>
 2019-12-17 10:39:53 +01:00
Pawel Wilma
0643a89ff9 Move TGLLP specific workarounds to HwInfo 
Related-To: NEO-3914

Change-Id: I115b28ea6e796dcc69b32105e39a68da0e5af7df
Signed-off-by: Pawel Wilma <pawel.wilma@intel.com>
 2019-12-16 16:25:18 +01:00
Krzysztof Gibala
03252ee9fe Add support for write combined in unified memory 
Related-To: NEO-3374
Change-Id: I610ad2d71b056f2bc5b8f4bda72e7f08a45cf59d
Signed-off-by: Krzysztof Gibala <krzysztof.gibala@intel.com>
 2019-12-16 08:59:40 +01:00
Artur Harasimiuk
b78c9ecb39 moving auto-generated files to dedicated folders 
Related-To: NEO-126
Change-Id: I18e3ebac769fb5a8866392eb627625cace6597dd
Signed-off-by: Artur Harasimiuk <artur.harasimiuk@intel.com>
 2019-12-13 21:44:20 +01:00
Mateusz Hoppe
5685b285f3 Extract logging logic from DebugSettingsManager 
Change-Id: I0ccc68216c1c3bb23d0389bec17124e09e4f98e1
Signed-off-by: Mateusz Hoppe <mateusz.hoppe@intel.com>
 2019-12-13 15:34:45 +01:00
Krzysztof Gibala
dded0aa3bc Remove unnecessary program of default value for allocation flags 
According to regression, remove setting value
for CL_MEM_ALLOC_DEFAULT_INTEL in MemoryPropertiesFlags

Related-To: NEO-4053
Change-Id: I1761bbf2ed8b977b7e96cebd38040c3977998b63
Signed-off-by: Krzysztof Gibala <krzysztof.gibala@intel.com>
 2019-12-13 14:33:32 +01:00
kamdiedrich
b737ed5219 Fix for heapHelper 
-add mockable_virtual for memoryManager class

Change-Id: Ie3ff592c7d61759efa7c2955de6b4e8d1731a2c4
 2019-12-13 12:01:02 +01:00
Mateusz Jablonski
9f5152e823 Move linux files to core 
memory_info
engine_info
os_inc

Related-To: NEO-3982
Change-Id: I52ef357f790497fc6efcd590db277ce96ec1e579
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2019-12-13 09:23:33 +01:00
Jacek Danecki
fb8df1a328 fix compilation with clang 9 
ci: add build with clang on Arch

Signed-off-by: Jacek Danecki <jacek.danecki@intel.com>

https://github.com/intel/compute-runtime/pull/241

Change-Id: I1a8620c9f8146e7108098d18e9db75b9ff178f44
 2019-12-12 11:45:08 +01:00
Mateusz Jablonski
c7755c2c48 Move files to core 
engine_node_helper
kmdaf_listener
wddm_engine_mapper
windows_defs

Related-To: NEO-3982
Change-Id: Ia39342059bdeafa97d17f286c167138e5c40553c
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2019-12-11 17:39:14 +01:00
Mateusz Jablonski
ab2134ae8f Change subDeviceIndex to subDevicesBitfield in allocation properties 
Related-To: NEO-3691
Change-Id: I11d235107bf9b4cee75b910c114795b5df76d9c7
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2019-12-11 15:15:04 +01:00
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
Dunajski, Bartosz
c6a202ab87 Refactor programBindingTableBaseAddress 
Change-Id: I5a1d29ef3551717c7d28617c8af4d5f3bfbe3dbd
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2019-12-10 10:50:32 +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
Dunajski, Bartosz
3014b304ca Refactor STATE_BASE_ADDRESS programming 
Change-Id: I977867678ea980f17cbe6ceef51c4f05096c809f
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2019-12-07 19:00:45 +01:00
Jaroslaw Chodor
72a1542140 [2/N] Program refactor - gather compiler options 
Change-Id: I0a614be73fbd87184be2dfea407582a58c27b0bc
 2019-12-06 22:17:19 +01:00
Dunajski, Bartosz
232dc59cde Make specific SBA heaps programming optional 
Change-Id: I852a9e1d9bcc5d6227b1e8a81ab81ad896d6586f
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2019-12-06 12:52:21 +01:00
Pawel Wilma
632134db30 Disable host ptr tracking for GEN12LP 
Related-To: NEO-3661

Change-Id: I1774aad8ef32f294192a9b679cb9f66e4091198c
Signed-off-by: Pawel Wilma <pawel.wilma@intel.com>
 2019-12-06 11:57:32 +01:00
Dunajski, Bartosz
566b845bbc Move state_base_address to core 
Change-Id: I2b64fff4eed31054ae29b7b14ecb9f147914049a
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2019-12-06 09:01:24 +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
c0cafccacb Fix command container tests cmake generation 
Change-Id: Ie7dcad6aefc375aa0c344764f10683d4b22ace8c
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2019-12-04 15:22:01 +01:00
Mateusz Hoppe
dfce56d634 Cleanup headers in print_formatter and move to core 
Change-Id: I2ef5498927b02e0371dc4e484f94b00b4f86721c
Signed-off-by: Mateusz Hoppe <mateusz.hoppe@intel.com>
 2019-12-04 13:37:11 +01:00
Mateusz Hoppe
96cc1081c0 Moving print.h/.cpp files to core 
Change-Id: I4972f87a007c7183acdaf79f48ece4ff0a6cf087
Signed-off-by: Mateusz Hoppe <mateusz.hoppe@intel.com>
 2019-12-04 11:05:44 +01:00
Michal Mrozek
6847893e02 Add support for querying device from usm allocations. 
Change-Id: I8aad69622e3af1ebec74ee9d325340b02ca9a6b2
Signed-off-by: Michal Mrozek <michal.mrozek@intel.com>
 2019-12-04 09:28:06 +01:00
Jaime Arteaga
98884d99af Move USM allocationWithDeviceStorage methods to public 
Change-Id: I98ec3cf133e716fe325e51f2664a057f25b30976
Signed-off-by: Jaime Arteaga <jaime.a.arteaga.molina@intel.com>
 2019-12-04 08:36:59 +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
Michal Mrozek
6cc84c7bc4 Unify 2 functions. 
Change-Id: I9c179e8a458474ded0bc48b18f57987d3f407dba
Signed-off-by: Michal Mrozek <michal.mrozek@intel.com>
 2019-12-03 14:03:41 +01:00
Maciej Plewka
620c2ade18 Add wrapper for hwMapper 
Change-Id: I11382de91758617cfd16cd457954fc51f65e4932
Signed-off-by: Maciej Plewka <maciej.plewka@intel.com>
 2019-12-03 12:18:27 +01:00
Michal Mrozek
83c0f80431 Avoid casting void* to uint64_t. 
- Add new wrapper that accepts const void *.

Change-Id: I1cea088b563cf704b6673844b533ce44f388e5fc
Signed-off-by: Michal Mrozek <michal.mrozek@intel.com>
 2019-12-03 11:55:26 +01:00
Dunajski, Bartosz
9522734801 Improve dirtyHeaps check in CommandContainer 
Change-Id: I798c916ff267671650a30d06d67aa1c1162c567f
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2019-12-02 20:59:04 +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
Filip Hazubski
0270ad8015 Add pointer checks 
Change-Id: I37a6898670a4d9e66f0eff404b5282714f293956
Signed-off-by: Filip Hazubski <filip.hazubski@intel.com>
 2019-12-02 12:57:02 +01:00
Michal Mrozek
b937b54064 Remove 32 bit code. 
- Enable local memory in 32 bit scenarios.

Change-Id: I091570a3d0aa6043febf2721480196425e058978
Signed-off-by: Michal Mrozek <michal.mrozek@intel.com>
 2019-11-28 17:50:42 +01:00
Dunajski, Bartosz
6dddcbd812 Simplify block copy command interface 
Change-Id: I9c89fdb05bc7734e29678fd396bb6f5bc58e919a
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2019-11-28 15:06:35 +01:00
Filip Hazubski
0193b3ea69 Change maxNBitValue to a constexpr function 
Now maxNBitValue can be used with run time variables.

Change-Id: I323071400305e05e6303a33e24e90c521246d73f
Signed-off-by: Filip Hazubski <filip.hazubski@intel.com>
 2019-11-28 14:40:16 +01:00
Zbigniew Zdanowicz
7781650586 Simplify Preemption interface and get device preemption once 
Change-Id: Iaab9b9b60a71651125df27dece1a68e9c9435143
Signed-off-by: Zbigniew Zdanowicz <zbigniew.zdanowicz@intel.com>
 2019-11-27 16:28:45 +01:00
Jaroslaw Chodor
fd0d69e144 Fixing race condition in compiler interface 
Change-Id: Iba3e4c3213cff7750260539849c630b3c66d98ca
 2019-11-27 13:29:34 +01:00
Jobczyk, Lukasz
00243a455d Fix page fault handling on linux 
Change-Id: Ic7c2697d9e143c9e4d668974fce0ade3fe060a46
Signed-off-by: Jobczyk, Lukasz <lukasz.jobczyk@intel.com>
 2019-11-27 10:24:56 +01:00
Zbigniew Zdanowicz
9727de58b0 Aggregate preemption flags into single structure 
Change-Id: Ia087931a7a9eb2850644e00ffaa302dae54c95f1
Signed-off-by: Zbigniew Zdanowicz <zbigniew.zdanowicz@intel.com>
 2019-11-26 14:44:47 +01:00
Maciej Plewka
f262900bbd Create allocations for cmdContainer with device root index 0 
Change-Id: Icb0034e87bc27f9c0435f066eebe6a9af3ed9f66
Signed-off-by: Maciej Plewka <maciej.plewka@intel.com>
 2019-11-26 12:03:06 +01:00
Jaroslaw Chodor
c2bc814ac9 Adding support for new relocation types 
Change-Id: I52e20542b8d7a6ca46e6d8b8ce715cc5b5ace428
 2019-11-25 23:39:59 +01:00
Jaroslaw Chodor
355e8d3e5a [1/N] Program refactor - decouple from patchokens 
Change-Id: I63bbf6c31a5db9e788124f22b6105e65c16c86d4
 2019-11-25 19:46:21 +01:00