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

3604 Commits

Author SHA1 Message Date
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
ocldev cd198fac0a igc revision update 
Change-Id: I4bb4db57c1e2798f5b6c2492465f9b84de90cda3
 2019-12-06 11:27:08 +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
Pawel Wilma baeac08662 Remove unused method obtainGpuAddressIfNeeded() 
Change-Id: I0b0ff5c793d31c97f488339dcb75aba617871f88
Signed-off-by: Pawel Wilma <pawel.wilma@intel.com>
 2019-12-04 17:22:43 +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
Filip Hazubski 7be937c226 Update clCreateSubDevices implementation 
Make it possible to get SubDevices from given RootDevice.

Resolves: NEO-3977

Change-Id: I9cf06f17b45299009ab6953b9ad7d5cb0bbe848f
Signed-off-by: Filip Hazubski <filip.hazubski@intel.com>
 2019-12-04 16:38:07 +01:00
Mateusz Jablonski 73dad03c66 Fix clSVMAlloc function: use device from context 
Related-To: NEO-4000

Change-Id: Iefad9d7a8908a584b98801bdbe13aa1e0be2e47f
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2019-12-04 16:27:54 +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
Pawel Cieslak 2070bd8970 Fix build_spec.py script. 
Change-Id: I0485d6be5f68b3200621de9bcaeaf0289c970a92
Signed-off-by: Pawel Cieslak <pawel.cieslak@intel.com>
 2019-12-04 14:37:38 +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
ocldev 48f3f10396 dependencies update 
Change-Id: I33b431ba8f10029bb6756db550180fc028e9919d
 2019-12-04 12:59:07 +01:00
Dunajski, Bartosz c8a34e65f0 Revert "Dont make Surfaces resident on GPGPU CSR for blit enqueue" 
This reverts commit d74edb3d3f.

Change-Id: Idd4fb27afd0b8a30be1dba1630ecd81932963fae
 2019-12-04 12:18:26 +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
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
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
Michal Mrozek e234c89ee4 Change makeResident to be non virtual function. 
- remove wddm version, not a lot of value there as residency is logged
in processResidency anyway.

Change-Id: Icb2814cfce0e8f3cd75445f1fd2e2f8535d476cc
Signed-off-by: Michal Mrozek <michal.mrozek@intel.com>
 2019-12-04 07:29:00 +01:00
Kamil Kopryk ec63a03337 Added support for stateless enqeueueSVMMemcpy 
Change-Id: I1690735b7888b29572b75756d38698305805b7cb
Signed-off-by: Kamil Kopryk <kamil.kopryk@intel.com>
Related-To: NEO-3314
 2019-12-03 19:00:47 +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
Pawel Cieslak 1d4d806933 Refactor python scripts. 
Change-Id: I442f5bf081d89369f7c71b0de2c99fd39b3ff942
Signed-off-by: Pawel Cieslak <pawel.cieslak@intel.com>
 2019-12-03 14:20:53 +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
Dunajski, Bartosz b308906999 Return 1 as PreferredTagPoolSize for CSR with aub dump 
Change-Id: I33fbd8131bdd8579cf3e5bbfdc5ea6d66a5c74b6
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2019-12-03 13:42:36 +01:00
Filip Hazubski 2ead0e6910 Update Device::getDeviceBitfield() 
Related-To: NEO-2712

Change-Id: I609f55c9a0ee637dcef7cb176728f2ae65499a58
Signed-off-by: Filip Hazubski <filip.hazubski@intel.com>
 2019-12-03 12:45:23 +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
Mateusz Jablonski ee544e2515 Reorder members and methods in Device class 
Related-To: NEO-3938

Change-Id: I18e6ed4b301d5e221263ced5a3213b54dd21745a
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2019-12-03 10:22:31 +01:00
Dunajski, Bartosz 4bcbd476d9 Add missing override 
Change-Id: I8bddaf940b5f7f3920da350cbedb9af9a5cbbd97
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2019-12-03 06:48:50 +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
Artur Harasimiuk b49424772f infrastructure update 
Change-Id: I0aa5dc783bc5e1bdd690e5619fc0e6b665f8269f
Signed-off-by: Artur Harasimiuk <artur.harasimiuk@intel.com>
 2019-12-02 19:05:38 +01:00
Dunajski, Bartosz 821a83aa24 Use helper method to program DSH size 
Change-Id: I2c6502b58f83941f547b53bbd8fa44748cbd2746
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2019-12-02 16:57:09 +01:00
Dunajski, Bartosz 0527c9113c Disable TimestampPacket optimizations in Aub/Tbx mode 
Avoid removing semaphores and reusing returned tags

Change-Id: Ic26167953c5d5a9ccceaae49f4921af11a375fab
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2019-12-02 15:38:13 +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
Marcin Naczk c6354c8741 add output_file_list flag 
Change-Id: I8cec83eaf39db306622ac9d399399ef54397d613
 2019-12-02 13:57:16 +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 04b4198228 Use castToUint64 while casting form void* to uint64_t. 
- Otherwise the uint64_t GPU address may not be proper
- The sign bit is propagated while reinterpret_cast is happening
causing wrong address to be generated.

i.e. in 32 bit application:
void* address = 0xffff0000;
unit64_t gpuAddress = reinterpret_cast<uint64_t>(address);

gpuAddress is equal to 0xffffffffffff0000 instead of 0x00000000ffff0000.

Change-Id: I36665651d615c3ab612b2cea375fa539edc7d08d
 2019-12-02 12:50:33 +01:00
Filip Hazubski c1ba471053 Add minor improvements 
Change-Id: I39b9b91a73d5fc8a88cfbbe6ba0ceb65e13a2779
Signed-off-by: Filip Hazubski <filip.hazubski@intel.com>
 2019-12-02 09:22:55 +01:00
Adam Cetnerowski 8f46761262 ULT renaming: Flush tests 
Related-To: NEO-2236

Change-Id: I86fbac1205dba63d4b8918d4eeec215428bb5949
Signed-off-by: Adam Cetnerowski <adam.cetnerowski@intel.com>
 2019-12-02 09:08:33 +01:00
Gibala 43dd16e1b8 Add unit tests to check value shift 
Related-To: NEO-3962
Change-Id: Ia3ba560201dd495a22742ef9fef767d6aa4c35f9
Signed-off-by: Gibala <krzysztof.gibala@intel.com>
 2019-11-29 15:23:34 +01:00
Dunajski, Bartosz b1fbced81f Fix completion check for TimestampPacketStorage 
Change-Id: If15d2bbc49a1dc2dfb29e3b6cdc3ad1523997cd5
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2019-11-29 14:43:11 +01:00
Dunajski, Bartosz 8784491abe Manifest update 
Change-Id: I8d553ee900288290e3aa90512fc0e2128fc4bd86
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2019-11-29 13:21:32 +01:00
Mateusz Jablonski 244146c203 Move Device::getProductAbbrev method to MockDevice 
Change-Id: Ia146d0198039b526e563a44d76710ac175ea3b88
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2019-11-29 11:12:08 +01:00
ocldev 273a416f28 igc revision update 
Change-Id: If8bb6a41ebed2f7b6f00fc6f904bdd47918f7e20
 2019-11-29 04:21:13 +01:00
Filip Hazubski 4da2b1b3f5 Update internal 
Change-Id: I452d17321819acb9b83512316d6cdaac10e64b34
Signed-off-by: Filip Hazubski <filip.hazubski@intel.com>
 2019-11-28 19:07:12 +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
Jaroslaw Chodor 102bceb4c9 Adding bindless compilation toggles 
Change-Id: I35e37e9319a660fe0e4588f7abdc821557948b18
 2019-11-28 15:23:24 +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 5bed747e33 Update Program::extractInternalOptions 
Change-Id: Ie67a8ef7b6f010a44b252666e9d9ef48fdeac9e0
Signed-off-by: Filip Hazubski <filip.hazubski@intel.com>
 2019-11-28 15:04:28 +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