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

268 Commits

Author SHA1 Message Date
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
Artur Harasimiuk 412c88cf9b fix function argument name to comply with naming convention 
Change-Id: I126e0a8d86a888fa1bdf19fffd4c803bb6d6e9e5
Signed-off-by: Artur Harasimiuk <artur.harasimiuk@intel.com>
 2019-11-25 17:16:44 +01:00
Artur Harasimiuk cf8283cc9a clang-tidy improvements and code fixes 
Related-To: NEO-562
Change-Id: Iab9d1ed35e64c9fce849e1b0654ec65f731302e8
Signed-off-by: Artur Harasimiuk <artur.harasimiuk@intel.com>
 2019-11-25 16:06:34 +01:00
Filip Hazubski 026d1324a4 Move AllocationProperties::noDeviceSpecified to SubDevice 
Change-Id: Idfc1efa4e39168ca32b613201aac8ccd0aa3219a
Signed-off-by: Filip Hazubski <filip.hazubski@intel.com>
 2019-11-25 14:23:37 +01:00
Dunajski, Bartosz 684b3e1774 Improve aux translation restrictions check 
Change-Id: I6e5bd014fef60f89365f536c219ab7d399c51265
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2019-11-25 12:58:12 +01:00
Pawel Wilma 9b84d8f5ba Use RCS as default engine for TGL LP A0 
Related-To: NEO-3741

Change-Id: Iac79ff5e7142a3ee74990048fcc84565639a2da2
Signed-off-by: Pawel Wilma <pawel.wilma@intel.com>
 2019-11-25 12:24:20 +01:00
Maciej Plewka 49cde627c4 Adding Command container implementation 
Change-Id: Ic2c4b9128fa0275fd10db6e37b89a1f36aee60bc
Signed-off-by: Maciej Plewka <maciej.plewka@intel.com>
 2019-11-22 15:52:22 +01:00
Artur Harasimiuk caa16ea81b suppress clang-tidy warning 
there is check for null but not visible by clang-tidy (v8).

Change-Id: I9cf1403b5c9f8ecbeda0cd7a600f46aa2e41736e
Signed-off-by: Artur Harasimiuk <artur.harasimiuk@intel.com>
 2019-11-22 15:29:22 +01:00
Dunajski, Bartosz abdde5acb2 Improve aux translation mode helper 
Change-Id: Id9949fb3030386d7fe498a767c038a252cc28626
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2019-11-21 21:41:30 +01:00
Jobczyk, Lukasz 61e91a376b Add unified memory aub tests 
Related-To: NEO-2998

Change-Id: I1d047bc98de3cafe50ed7f54bfd3a6b695ec4dbd
Signed-off-by: Jobczyk, Lukasz <lukasz.jobczyk@intel.com>
 2019-11-21 10:14:04 +01:00
Gibala 9cebd45ccb Fix regression in TGLLP 
Remove conditions for UNCOVERABLE_IF

Related-To: NEO-3887
Change-Id: Ib6466956dd0669c6223cf5a4bbae163fb5c00862
Signed-off-by: Gibala <krzysztof.gibala@intel.com>
 2019-11-20 15:21:01 +01:00
Mateusz Jablonski bccfa1df38 Add cmake macro to append sources from properties 
Change-Id: I06771c56ebca2e7a0dc5b65d6ea53aca95a70797
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2019-11-20 11:58:10 +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
Pawel Wilma ae0cefc834 Add patchToken OffsetToSkipSetFFIDGP in device execution 
Change-Id: I0634836b787fa371f0b64779732941396a6ba804
Signed-off-by: Pawel Wilma <pawel.wilma@intel.com>
Related-To: NEO-3892
 2019-11-19 17:26:22 +01:00
Mateusz Jablonski 13921f698e Move files to core 
- OsLibrary class
- sku_info directory
- gmm_lib.h header

Change-Id: Ia86280e61cd2913c546afc40c3751b42e04ab137
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2019-11-19 16:19:52 +01:00
Mateusz Jablonski e7ee6daaa0 Remove runtime/gen_common from include paths 
Change-Id: I4d1f9e64e0f4099e7903234e62b070ad4235347a
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2019-11-19 13:37:34 +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
Filip Hazubski a070c08b2d Update alignUp and alignDown 
Do not return reference type in alignUp and alignDown

Change-Id: I819e434aadc3f2bf4647db87e7caaeda4c89ca25
Signed-off-by: Filip Hazubski <filip.hazubski@intel.com>
 2019-11-18 23:39:46 +01:00
Jablonski, Mateusz f5f1e64ea9 Remove not needed destructor 
Change-Id: I5cecf60eb55d69a185229f36a93cd22d6bf5ad46
Signed-off-by: Jablonski, Mateusz <mateusz.jablonski@intel.com>
 2019-11-18 22:59:15 +01:00
Dunajski, Bartosz 46b5513028 Initial Blit aux translation support 
Change-Id: I67fb71be57cff28a3736d5ffb9e1c39b2498feb8
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2019-11-16 11:42:10 +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
Dunajski, Bartosz 9ecd43fe88 Fix compilation warnings 
Change-Id: I2eda2617a60e54794490f932a80703e22e72a276
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2019-11-15 11:34:43 +01:00
Filip Hazubski 487c4c6e4b Add UNUSED_VARIABLE helper macro 
Change-Id: If293ad33899ee4feb79424c351b13ea85306c603
Signed-off-by: Filip Hazubski <filip.hazubski@intel.com>
 2019-11-14 17:42:56 +01:00
Dunajski, Bartosz d9bf9151cb Fix compilation warning 
Change-Id: Ibdebb496336d103e7cc78db2bf06134ef70cd002
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2019-11-13 19:10:32 +01:00
Filip Hazubski 4b2a8e99d8 Add clGetExecutionInfoIntel API 
This API allows querying for execution related information.
CL_EXECUTION_INFO_MAX_WORKGROUP_COUNT_INTEL parameter allows to query for
maximal work group count that is possible to run concurrently on the device.

Related-To: NEO-2712

Change-Id: I4e6b4c80aeb06ff966fb543c0a7f05ed54416dab
Signed-off-by: Filip Hazubski <filip.hazubski@intel.com>
 2019-11-13 12:09: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
Dunajski, Bartosz af8ce96ab4 Add move logic to TimestampPacketContainer 
Change-Id: Ib666fd57b4ca9123e324a82c3e648b0da49abffc
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2019-11-12 08:50:00 +01:00
Gibala Krzysztof b0e7994bb4 Fix regression in TGLLP RENDER_SURFACE_STATE command 
Resore previous version by changing
UNRECOVERABLE_IF to DEBUG_BREAK_IF

Change-Id: I02c743f8e13a759d82a03797c0d821b6879be7a0
Signed-off-by: Gibala Krzysztof <krzysztof.gibala@intel.com>
 2019-11-08 10:00:59 +01:00
Jaroslaw Chodor fa41f32b0b Disabling lint check for some cornercases 
Change-Id: I48dd87da1e12884ad2774319800a60303a932e1e
 2019-11-06 23:13:55 +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
Gibala Krzysztof 8631e93c69 Fix regression in TGLLP generated command 
Change-Id: Icc6dd0be105c4aa432328577532a5bedb20deb57
Signed-off-by: Gibala Krzysztof <krzysztof.gibala@intel.com>
 2019-11-05 09:52:13 +01:00
Zbigniew Zdanowicz aa7058a2a9 Enable thread-group preemption for GEN12LP 
Related-To: NEO-3880

Change-Id: Ia8ffc54f923578d3e7334d414e0087feff42eb7d
Signed-off-by: Zbigniew Zdanowicz <zbigniew.zdanowicz@intel.com>
 2019-11-04 18:30:58 +01:00
Artur Harasimiuk 52a0ddf0f4 adding .clang-tidy configuration for core/unit-tests 
Related-To: NEO-3676
Change-Id: Iebd1571011081796862fa64a75d0b176527ff8cc
Signed-off-by: Artur Harasimiuk <artur.harasimiuk@intel.com>
 2019-11-04 16:47:45 +01:00
Gibala Krzysztof ae5c75c807 Add shifts in RENDER_SURFACE_STATE command for TGLLP 
Related-To: NEO-3861
Change-Id: I2726807b5792e378071b6271dbb79a3d3f2a02ad
Signed-off-by: Gibala Krzysztof <krzysztof.gibala@intel.com>
 2019-11-04 14:24:24 +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
Gibala Krzysztof a6f8a19290 Update GEN12LP commands 7/n 
- RENDER_SURFACE_STATE

Related-To: NEO-3861
Change-Id: I758ad27906b77ad3167d59623bafc40e649d17b2
Signed-off-by: Gibala Krzysztof <krzysztof.gibala@intel.com>
 2019-10-31 14:22:48 +01:00
kamdiedrich 987dfdba07 Add additionalData member to GA 
Add core path to included files

Change-Id: I8c697dd00a1f37b9af469292367cd090d4fd4875
 2019-10-31 12:41:19 +01:00
Gibala Krzysztof 127654a340 Update GEN12LP commands 5/n 
- MEDIA_SURFACE_STATE
- PIPE_CONTROL
- MI_SEMAPHORE_WAIT
- MI_STORE_DATA_IMM

Related-To: NEO-3861
Change-Id: Ia8d6fe4364ea51d77a91776d055854eecbfc0939
Signed-off-by: Gibala Krzysztof <krzysztof.gibala@intel.com>
 2019-10-31 11:17:02 +01:00
Gibala Krzysztof 98305bd582 Remove not needed code, add missing files 
Change-Id: I0ffba91d5f2df1d6b6e362896de93928a6f54fb6
Signed-off-by: Gibala Krzysztof <krzysztof.gibala@intel.com>
 2019-10-31 08:09:41 +01:00
Gibala Krzysztof d48f1aaedc Update GEN12LP commands 6/n 
- STATE_SIP
- GPGPU_CSR_BASE_ADDRESS

Related-To: NEO-3861
Change-Id: If0e6cd2c78f9501c08cd4599fbf65c7b39e7eeb2
Signed-off-by: Gibala Krzysztof <krzysztof.gibala@intel.com>
 2019-10-30 15:44:18 +01:00
Gibala Krzysztof 0db28144ec Update GEN12LP commands 4/n 
- MI_NOOP
- MI_STORE_REGISTER_MEM
- PIPELINE_SELECT
- SAMPLER_STATE
- MI_REPORT_PERF_COUNT
- STATE_COMPUTE_MODE
- MI_USER_INTERRUPT
- XY_SRC_COPY_BLT
- MI_FLUSH_DW

Related-To: NEO-3861
Change-Id: Ie1cb736087e2e21ad8596b86775c213a8abec244
Signed-off-by: Gibala Krzysztof <krzysztof.gibala@intel.com>
 2019-10-29 23:50:40 +01:00
Dunajski, Bartosz 74a5e50339 Fix GENXTEST_P macro 
Change-Id: I60ce62ccaf1aa59293de5c4e4bd3f89ab891c0aa
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2019-10-29 08:36:10 +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
Maciej Plewka 51dcf2b6d2 add support for packed simd1 dispatch 
Change-Id: I3f2bf8e62e0a38d358fb87f02c88c387c874f6b3
Signed-off-by: Maciej Plewka <maciej.plewka@intel.com>
 2019-10-28 11:58:25 +01:00
Dunajski, Bartosz 542da0ecf7 Support Gmm::GetMipTailStartLodSurfaceState() 
Change-Id: I804061066c1a5c46bd3366ada525511885b2586f
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2019-10-28 08:56:48 +01:00
Gibala Krzysztof 440520ffdc Update GEN12LP commands 3/n 
- MI_LOAD_REGISTER_IMM
- MI_LOAD_REGISTER_MEM
- MI_LOAD_REGISTER_REG

Related-To: NEO-3861
Change-Id: Id2fc45f54b61205fb8454fdfc86e16112384843d
Signed-off-by: Gibala Krzysztof <krzysztof.gibala@intel.com>
 2019-10-25 14:26:51 +02:00
Gibala 7df55ba061 Update GEN12LP commands 2/n 
- MI_ARB_CHECK
- MI_ATOMIC
- MI_BATCH_BUFFER_END
- MI_BATCH_BUFFER_START

Related-To: NEO-3861
Change-Id: I6ce9788302f0c79bea3314703f33086c443757f7
Signed-off-by: Gibala Krzysztof <krzysztof.gibala@intel.com>
 2019-10-25 13:25:57 +02:00
Gibala 9fc82fdb08 Update GEN12LP commands 1/n 
- GPGPU_WALKER
- INTERFACE_DESCRIPTOR_DATA
- MEDIA_INTERFACE_DESCRIPTOR_LOAD
- MEDIA_STATE_FLUSH

Related-To: NEO-3861
Change-Id: I2efb0dfa9d941f674b7c27f1a79ac7b821942353
Signed-off-by: Gibala Krzysztof <krzysztof.gibala@intel.com>
 2019-10-24 12:04:51 +02:00
Jobczyk, Lukasz bfc9863179 [1/N] Make the execution environment adapter agnostic 
-Create a structure for adapter specific data
-Store an array of adapter data in the execution environment

Related-To: NEO-3857

Change-Id: Ia5b52a7bfa53198f0ca5124bcaa0669dd3601faf
Signed-off-by: Jobczyk, Lukasz <lukasz.jobczyk@intel.com>
 2019-10-23 15:51:35 +02:00
Gibala e22ce2f757 Prevent null allocation in createSharedUnifiedMemoryAllocation 
Related-To: NEO-3860
Change-Id: I3954279414b226ea332da4a3fd1580853e59bd54
Signed-off-by: Gibala <krzysztof.gibala@intel.com>
 2019-10-23 15:29:40 +02:00
Jaroslaw Chodor 28464ab2d4 [N/N] compiler interface refactor - move to core 
Change-Id: I029e3cd7a6adde9df97a0a7760ecbf5d25d8f501
 2019-10-22 19:14:09 +02:00
Gibala c6e13fdc67 Prevent null allocation in createUnifiedMemoryAllocation 
Related-To: NEO-3860
Change-Id: I4b11db679385393a9059af41d71a8ce9c3f9fdc7
Signed-off-by: Gibala <krzysztof.gibala@intel.com>
 2019-10-22 13:32:52 +02:00
Jaroslaw Chodor 3181939892 [3/N] compiler interface refactor - cache 
Change-Id: Iac1f36f7f505b100e65c2b44dff7f1689f99bfe5
 2019-10-21 23:29:49 +02:00
Daria Hinz 2196f7e216 Move ElfLib to core 
Change-Id: I57987e871aac9c72dc786661c1d24f5024dd367b
Signed-off-by: Daria Hinz <daria.hinz@intel.com>
 2019-10-18 08:31:12 +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
Artur Harasimiuk 7864c03b0a clang-tidy cleanup 
Related-To: NEO-3676
Change-Id: I538c4ee3a370a71a7e470a441cd101c9ed1b285d
Signed-off-by: Artur Harasimiuk <artur.harasimiuk@intel.com>
 2019-10-15 19:55:43 +02:00
Maciej Plewka a1c4283e0c Add method for checking if deferr deleter is enabled 
Change-Id: I5949a01ac312669824b8738f4bb7f8aedb2a056b
Signed-off-by: Maciej Plewka <maciej.plewka@intel.com>
 2019-10-15 13:28:14 +02:00
Barreyra, Bruno R d7c56eb7d6 Fix GPU debugging on gen11+ 
Format of debug mode register changed for gen11+ projects. Without this
change, the SIP is never invoked.

Change-Id: Ie8314acbee1ead527deeea45cb5689b4a39df24c
 2019-10-14 11:28:20 +02:00
Maciej Dziuban 100f888b85 Enable setting additional params for gen12lp image compression 
Signed-off-by: Maciej Dziuban <maciej.dziuban@intel.com>
Change-Id: I6228413938930f36c120523818649cde1a717cf2
Related-To: NEO-3564
 2019-10-11 07:25:38 +02:00
Mateusz Jablonski 2d5abc6702 Correct setBarrierEnable definition for gen8 
Change-Id: I3b61e0875f342fa63669a7860d94a8593a6351b7
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2019-10-10 17:00:05 +02:00
Jacek Danecki fab1601394 Fix compilation errors on clang 4 and 5 
Signed-off-by: Jacek Danecki <jacek.danecki@intel.com>

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

Change-Id: Id51310a4787b32e80de567d29960072d826b02df
 2019-10-10 16:07:45 +02:00
Koska fc067c823b Added test to read the debug int value 
Change-Id: I97e90320498b0abbdeeeb92c82e962bb411111c6
Signed-off-by: Koska <andrzej.koska@intel.com>
Related-To: NEO-3239
 2019-10-10 14:54:33 +02:00
Filip Hazubski 96031e7bba Update programming BarrierEnable 
Related-To: NEO-3211

Change-Id: I27d04d12414738c8e4a3eef1d29967e47a61c0fb
Signed-off-by: Filip Hazubski <filip.hazubski@intel.com>
 2019-10-10 13:07:23 +02:00
Koska b9e0411c18 Support for environment variables 
Change-Id: Ie52580703d3db36e3993d9e91cbbeb1fbb8cc1ae
Signed-off-by: Koska <andrzej.koska@intel.com>
Related-To: NEO-3239
Current order of reading debug variables:
- igdrcl.config file
- registry (under Windows)
- Environment variables
 2019-10-10 11:47:45 +02:00
Filip Hazubski 8ba7a0ea4e Move test.h to a separate directory 
Change-Id: Iceb14d701612d5b7814602ab0742ba1110b44a85
Signed-off-by: Filip Hazubski <filip.hazubski@intel.com>
 2019-10-10 10:58:23 +02:00
Daria Hinz 053896c525 Move Preamble tests to core 
Change-Id: I57a53ee68022e3f6d7558a56e0001c8126e135a9
Signed-off-by: Daria Hinz <daria.hinz@intel.com>
 2019-10-09 16:29:17 +02:00
Andrzej Koska 0ae977015d Adding a debug variable to select a test device 
Change-Id: Icf28d456590d532db44119d95be35ec6933a2647
Signed-off-by: Andrzej Koska <andrzej.koska@intel.com>
Related-To: NEO-3239
 2019-10-09 14:25:41 +02:00
Filip Hazubski 81cd28e0f4 Add Math::divideAndRoundUp helper function 
Add usage of the function where applicable

Change-Id: I9c41ad37009d1f088fa1917d30525194a10d3061
Signed-off-by: Filip Hazubski <filip.hazubski@intel.com>
 2019-10-09 13:25:39 +02:00
Jobczyk, Lukasz 419916f1b4 Add debug variable to measure processGenBinary execution time 
Related-To: NEO-3773

Change-Id: I79df8e6639ce775329307f4bfb25cbac5606e8c3
Signed-off-by: Jobczyk, Lukasz <lukasz.jobczyk@intel.com>
 2019-10-08 13:07:27 +02:00
Kamil Kopryk 50f40296c4 Add WaDisableFusedThreadScheduling 
Change-Id: I5ad09fc7d366b8062ff7b10f86718f3afe28ba0b
Signed-off-by: Kamil Kopryk <kamil.kopryk@intel.com>
 2019-10-08 12:11:16 +02:00
Daria Hinz 375681ae12 Move Preamble Helper to core 
Change-Id: I7d1bf567a67dc93c10d396aeb48ad1179b5b8ecb
Signed-off-by: Daria Hinz <daria.hinz@intel.com>
 2019-10-03 13:54:17 +02:00
Jobczyk, Lukasz 627c359798 Move Host Ptr Manager to the core dir 
Change-Id: I48c521acdcd4b3a78eb539026af5ffa840cf2181
Signed-off-by: Jobczyk, Lukasz <lukasz.jobczyk@intel.com>
 2019-09-30 19:07:09 +02:00
Jobczyk, Lukasz 62d5ed2c08 Store a unified memory flags 
Related-To: NEO-3610

Change-Id: Ie9f924f188d4024c7355b7655fea231229b4bf6a
Signed-off-by: Jobczyk, Lukasz <lukasz.jobczyk@intel.com>
 2019-09-30 16:06:39 +02:00
Jobczyk, Lukasz 3bd4baeba3 Move a unified memory manager to the core dir 
Related-To: NEO-3677

Change-Id: Ib60dea2bcaaf5feea97d61cb9f54baee4c6b4b64
Signed-off-by: Jobczyk, Lukasz <lukasz.jobczyk@intel.com>
 2019-09-27 10:46:35 +02:00
Dunajski, Bartosz d18d1b6ce4 Opensource TGLLP 
Change-Id: I1685057a641d938170b8c7ec860d2f53f45b1d6d
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2019-09-27 09:20:41 +02:00
Dunajski, Bartosz 235268aef5 Add missing pragma 
Change-Id: Id06ac0741d626cceaafa79f592f3ed9e69136464
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2019-09-23 10:47:06 +02:00
Andrew Friedley 67ba9d2b00 Fill in MMIO reg consts for ALU, PREDICATE_RESULT 
Change-Id: Iba1b88a6bd5fbbc900bed14cf90bed69557539a4
Signed-off-by: Andrew Friedley <andrew.friedley@intel.com>
 2019-09-19 08:59:50 +02:00
Kamil Diedrich 115070767c Move graphics_allocation to core folder 
Change-Id: I16b8dbb57c2a40126826a232332c18ba9f563220
 2019-09-18 05:26:55 +02:00
Daria Hinz 51e0c19f79 Suppressing Undesired Diagnostics 
Change-Id: Ifd0c096c0e2d62132b55b399ef90cc98fe3f8d03
Signed-off-by: Daria Hinz <daria.hinz@intel.com>
 2019-09-17 13:00:48 +02:00
Daria Hinz 6d21c2a422 Remove not used include 
Change-Id: I8aa14342cf78ef6b5df0ad5e3017a45f0f24cb2f
Signed-off-by: Daria Hinz <daria.hinz@intel.com>
 2019-09-17 06:16:05 +02:00
Venevtsev, Igor 3fab76d95e Add GfxPartition::initAdditionalRange() stub 
Related-To: NEO-2941

Change-Id: Iec74652a5ee2cc79af9093d520e892cb30045cdf
Signed-off-by: Venevtsev, Igor <igor.venevtsev@intel.com>
 2019-09-16 16:47:28 +02:00
Jobczyk, Lukasz cbc04629fd Move memory pool to the core dir 
Related-To: NEO-3677

Change-Id: I04fce78640cb0bfc26ad8950261324d997cd113a
Signed-off-by: Jobczyk, Lukasz <lukasz.jobczyk@intel.com>
 2019-09-13 09:56:21 +02:00
Daria Hinz ae4425351f Preamble Helper Refactor 
Change-Id: Iacd05dcb6d9047fc2814895fa87d1cd9be6df446
Signed-off-by: Daria Hinz <daria.hinz@intel.com>
 2019-09-13 08:29:03 +02:00
Jobczyk, Lukasz 2e8e6bdb18 Move majority of utilities to the core dir 
Related-To: NEO-3677

Change-Id: If2e876028b765ad3ecf5f75db8755623b82955b8
Signed-off-by: Jobczyk, Lukasz <lukasz.jobczyk@intel.com>
 2019-09-12 15:07:02 +02:00
Krzysztof Gibala 04e1d73fcc Remove duplicate enums in RENDER_SURFACE_STATE 
Remove:
- tagSHADER_CHANNEL_SELECT_ALPHA
- tagSHADER_CHANNEL_SELECT_BLUE
- tagSHADER_CHANNEL_SELECT_GREEN
- tagSHADER_CHANNEL_SELECT_RED
Replace:
- tagSHADER_CHANNEL_SELECT

Change-Id: Ia08ac5920107e0c2f4c3e3ef64622f1cd5254174
Signed-off-by: Krzysztof Gibala <krzysztof.gibala@intel.com>
 2019-09-11 16:58:12 +02:00
Andrew Friedley 21309f7cc1 Fill in missing ALU register constants 
Change-Id: I94a3c2bdfc90791b7f8eef7614967b19a964e9df
Signed-off-by: Andrew Friedley <andrew.friedley@intel.com>
 2019-09-11 10:51:23 +02:00
Jobczyk, Lukasz 3fe91e6d69 Move host_ptr_defines to the core dir 
Related-To: NEO-3677

Change-Id: Ic973fb65f584563cc3fbcfa20eb81fe687dc5435
Signed-off-by: Jobczyk, Lukasz <lukasz.jobczyk@intel.com>
 2019-09-11 09:35:55 +02:00
Jobczyk, Lukasz fa8fc3fc43 Move a LocalMemoryUsageBankSelector to the core dir 
Related-To: NEO-3677

Change-Id: Ie9fff1b353b8c2432305b44063861767e44add32
Signed-off-by: Jobczyk, Lukasz <lukasz.jobczyk@intel.com>
 2019-09-10 10:53:58 +02:00
Jobczyk, Lukasz fab659f4a9 Move residency to the core dir 
Related-To: NEO-3677

Change-Id: Ib4aaa7dcfc46d9bb515c4881ddb6adb974990ca9
Signed-off-by: Jobczyk, Lukasz <lukasz.jobczyk@intel.com>
 2019-09-10 10:50:20 +02:00
Jobczyk, Lukasz 4c1adc4d47 Move engine limits to the core dir 
Related-To: NEO-3677

Change-Id: Ib36d24e8e6f0605033cfbc79afea45e85a058aad
Signed-off-by: Jobczyk, Lukasz <lukasz.jobczyk@intel.com>
 2019-09-09 12:30:59 +02:00
Krzysztof Gibala c100db4333 Remove duplicate enums in SAMPLER_STATE command 
Remove:
- tagTCZ_ADDRESS_CONTROL_MODE
- tagTCY_ADDRESS_CONTROL_MODE
- tagTCX_ADDRESS_CONTROL_MODE
Replace:
- tagTEXTURE_COORDINATE_MODE

Change-Id: I26fb654628360f107378c7bdd531951f196c35cf
Signed-off-by: Krzysztof Gibala <krzysztof.gibala@intel.com>
 2019-09-09 09:15:53 +02:00
Jobczyk, Lukasz bdd81fcc85 Annotate MockPageFaultManager's destructor with override 
Change-Id: I7687fe56b4c4ea737fd5b77936f9e82e0f136b18
Signed-off-by: Jobczyk, Lukasz <lukasz.jobczyk@intel.com>
 2019-09-09 07:04:49 +02:00
Mrozek, Michal d4571d685a Improve Windows page fault handler. 
- Re-throw exception if not access violation exception.
- If pointer is not within known pointers also re-throw.

Change-Id: I01461f550994e32c9e8757b0344e70f2195612fb
Signed-off-by: Mrozek, Michal <michal.mrozek@intel.com>
 2019-09-06 13:19:24 +02:00
Jobczyk, Lukasz 882a216688 Move Debug helpers to the core dir 
Related-To: NEO-3677

Change-Id: I2c98595190fadfa8ffd9e378e774c0d4485cbf9e
Signed-off-by: Jobczyk, Lukasz <lukasz.jobczyk@intel.com>
 2019-09-05 16:00:35 +02:00
Jobczyk, Lukasz a79b682fc2 Move a GfxPartition to the core dir 
Related-To: NEO-3677

Change-Id: Ia89ba93eefbb2921ef7d64bde7ed4114a0c78e0d
Signed-off-by: Jobczyk, Lukasz <lukasz.jobczyk@intel.com>
 2019-09-04 15:42:25 +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
Jobczyk, Lukasz 86edfea3bf Fix OCL specific registry path in a core dir 
Change-Id: I5b7792582e6c77a29ffb42b8fe024bc826ae1867
Signed-off-by: Jobczyk, Lukasz <lukasz.jobczyk@intel.com>
 2019-09-02 17:33:50 +02:00
Maciej Plewka 7827501b91 Add returned status to MemoryOperationsHandler 
Change-Id: Ic8685e3711cec03d8f83d371fa7152ee095a47a0
Signed-off-by: Maciej Plewka <maciej.plewka@intel.com>
 2019-09-02 08:42:50 +02:00
Mrozek, Michal 33f6c7f0da Add new flag to disable L3 for stateful accesses. 
- With this flag resource will not be cached in L3 for stateful accesses.

Change-Id: Icf9a393ab92d55c2cdf30444420ea40da0d5630c
Signed-off-by: Mrozek, Michal <michal.mrozek@intel.com>
 2019-08-29 23:38:26 -07:00
Mrozek, Michal bb55023ba0 Do not set property under Unix flag. 
Change-Id: Ibd95ef445262e185efd6abcb43d3f18bc20ff897
Signed-off-by: Mrozek, Michal <michal.mrozek@intel.com>
 2019-08-29 16:28:34 +02:00
Jobczyk, Lukasz 10795c716f Move DebugSettingsReader to a core dir 
Related-To: NEO-3677

Change-Id: I3374abde6717be20c064ec6d65c0751a783f5138
Signed-off-by: Jobczyk, Lukasz <lukasz.jobczyk@intel.com>
 2019-08-29 13:49:40 +02:00
Krzysztof Gibala 84c801e28b Remove OCL object from MemoryProperties 8/n 
Refactor MemoryPropertiesFlags to bitfield

Related-To: NEO-3132
Change-Id: I7092b16d15cec962e94c992696bd9845ce86f642
Signed-off-by: Krzysztof Gibala <krzysztof.gibala@intel.com>
 2019-08-27 17:28:47 +02:00
Maciej Plewka 90266b4a37 Move autogenerated files to core directory 
Change-Id: Ie23411f9cfce068390f116c557000a665a62a337
Signed-off-by: Maciej Plewka <maciej.plewka@intel.com>
 2019-08-27 17:19:39 +02:00
Maciej Plewka 7a5bc461eb Add residency handler for TBX 
Change-Id: I6c01d065ff3372fe7583ed50ed51595ebeb53e54
Signed-off-by: Maciej Plewka <maciej.plewka@intel.com>
 2019-08-27 07:59:47 +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
Krzysztof Gibala f8818c5984 Remove OCL object from MemoryProperties 3/n 
Wire in MemoryPropertiesFlags support to:
-getGraphicsAllocationType
-isSuitableForRenderCompression
Add variable to MemoryPropertiesFlags:
-forceSharedPhysicalMemory

Related-To: NEO-3132
Change-Id: I41d91877877437993621577717c274ba3a77336e
Signed-off-by: Krzysztof Gibala <krzysztof.gibala@intel.com>
 2019-08-12 16:05:02 +02:00
Maciej Plewka 5ab8748fc5 Move registers offsets to seperate header 
Change-Id: I48487943c1cd0354fb38801a1504c503a5bc4d80
Signed-off-by: Maciej Plewka <maciej.plewka@intel.com>
 2019-08-09 14:48:32 +02:00