intel/compute-runtime
1
0
Fork 0
mirror of https://github.com/intel/compute-runtime.git synced 2025-12-30 01:35:20 +08:00
Code Issues Packages Projects Releases Wiki Activity
3,711 Commits 42 Branches 655 Tags
07cacd4e70b894264a55d770ff4881b46a03037c
Commit Graph

216 Commits

Author SHA1 Message Date
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
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
Andrzej Koska
d135944ae0 Improving reporting VME extensions 
Change-Id: Ia7ed2d1587603d8cfed391d8d5f7c1cd1faa1c21
Signed-off-by: Andrzej Koska <andrzej.koska@intel.com>
Related-To: NEO-4047
 2019-12-13 15:34:13 +01:00
Mateusz Hoppe
195f610fa3 Return CL_DEVICE_HOST_UNIFIED_MEMORY cap based on local memory 
Change-Id: Ic896d9aca60a36618b30745db5bd38f98a0bd2e9
Signed-off-by: Mateusz Hoppe <mateusz.hoppe@intel.com>
 2019-12-10 17:43:17 +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
Mateusz Jablonski
e27c5a9475 Change signature of clAddCommentINTEL function: pass device instead of platform 
Resolves: NEO-3939
Change-Id: I394ef7c2370771569a0ec50ac4644782ce8a384f
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2019-12-09 17:20:04 +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
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
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
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
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
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
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
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
Mateusz Jablonski
d617219665 Add getter for sub device index 
Related-To: NEO-3691

Change-Id: I1375b3b422997d280e2006b00af8f6fab2314f8b
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2019-11-05 13:17:05 +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
Mateusz Jablonski
472b1627a2 Rename DeviceHelper's method getDevicesCount- > getSubDevicesCount 
Related-To: NEO-3691

Change-Id: Ifc7956aa284f88647fab1423f9d5ebc4f5183d07
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2019-10-23 15:21:28 +02:00
Mateusz Jablonski
b93817fe7c Use DeviceHelper to calculate number of sub devices 
Related-To: NEO-3691

Change-Id: I390b7919fe8960b74cf290923f5daf128d824674
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2019-10-21 15:40:18 +02:00
Jobczyk, Lukasz
77d7d9f740 Add a getRootDeviceIndex method 
Change-Id: I7f46a42b5ce25a53365b9faaeba62f2c3232f104
Signed-off-by: Jobczyk, Lukasz <lukasz.jobczyk@intel.com>
 2019-10-21 15:35:26 +02:00
Cetnerowski, Adam
dbad1d7081 Revert "Disable cl_khr_subgroups extension" 
This reverts commit 332e02ef27.

Change-Id: I913d0a00286f46b9c08913d925e1be08b31c367f
 2019-10-16 13:11:04 +02:00
Jobczyk, Lukasz
332e02ef27 Disable cl_khr_subgroups extension 
Related-To: NEO-3807

Change-Id: I03d6a72f897b883c10cff4f31c152d7c9f100b43
Signed-off-by: Jobczyk, Lukasz <lukasz.jobczyk@intel.com>
 2019-10-15 17:26:41 +02:00
Mateusz Jablonski
c86fa7763a Add method to get device from device 
Related-To: NEO-3691

Change-Id: I710d740d82803e2a844b30a5cd3e4b017192f6f1
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2019-10-11 12:50:22 +02:00
Mateusz Jablonski
ea64a3fbc3 Add method for getting number of available devices 
Related-To: NEO-3691

Change-Id: Ida2454adbfc9b177acbbb320f3f9577849a6fd74
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2019-09-24 06:29:25 +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
Mateusz Jablonski
af80a61db3 Add debug flag to create multiple sub devices 
Related-To: NEO-3691

Change-Id: Ia3554424221e102094c40cdd5941680c6a253b18
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2019-09-11 10:25:21 +02:00
Koska, Andrzej
ccea3f497c Enhance VME registry support 
Related-To: NEO-3583
Change-Id: I4ddad40348d276cb4f52ceedadf77ab615c85db9
Signed-off-by: Andrzej Koska <andrzej.koska@intel.com>
 2019-09-10 14:40:03 +02:00
Mateusz Jablonski
9c200530c8 Remove not needed inclusions of device.h 
Change-Id: Idfd8122592f58539a569143146443c08a18dace9
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2019-09-09 15:05:29 +02:00
Mrozek, Michal
29613a2b1a Allow to set shared system memory pointers in constant buffers. 
Change-Id: Ie2a811c0f50abf667df82517abf2291e00a18460
Signed-off-by: Mrozek, Michal <michal.mrozek@intel.com>
 2019-09-05 07:36:02 +02:00
Mrozek, Michal
bf3210c1cd Add debug flag to override shared system memory capabilities. 
Change-Id: I241221757aaab8780c1f2542ed835a03e710adb6
Signed-off-by: Mrozek, Michal <michal.mrozek@intel.com>
 2019-09-04 17:24:38 +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
db8cd0e575 Report 64 bit integer atomic extension basing on caps. 
Change-Id: Ib4241c082eb03edcb43bb79d2eef3af8b5bbe00d
Signed-off-by: Mrozek, Michal <michal.mrozek@intel.com>
 2019-09-02 17:58:05 +02:00
Mateusz Jablonski
18982bd016 Move memory for slm window to memory manager 
remove redundant methods from MockDevice

Related-To: NEO-3007

Change-Id: I9cc819b9c9118dbb667f5bf87d1bf15787f9b67f
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2019-08-28 12:09:17 +02:00
Mateusz Jablonski
c7c6068d1f Add classes for sub devices concept 
Related-To: NEO-3007

Change-Id: I27dd4b91e286ba1b75f4b50bec96d98df37983e1
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2019-08-27 15:38:10 +02:00
Mateusz Jablonski
7749f28f70 Remove not needed methods from Device. 
Change-Id: I179089a4b248ba1ebd6502e001fda18238c4767b
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2019-08-27 09:07:10 +02:00
Mrozek, Michal
3528179434 Add preview to Unified Shared Memory extension name. 
Change-Id: I1fba3b275a280823abc9f57ed76c130bfa5f44a9
Signed-off-by: Mrozek, Michal <michal.mrozek@intel.com>
 2019-08-23 08:37:00 +02:00
Krzysztof Gibala
026f06cc50 Add function getPitchAlignmentForImage 
Related-To: NEO-3207
Change-Id: I39ef8624ad7172a3e2acf9072e1e3d5d1b6fcc34
Signed-off-by: Krzysztof Gibala <krzysztof.gibala@intel.com>
 2019-08-23 00:59:13 +02:00
Mrozek, Michal
68134974c5 Expose unified shared memory extension. 
-Available only when device already supports OpenCL 2.0

Related-To: NEO-3148
Change-Id: Ie2bce908c5e49666d5a18c4b0eb21ff39a3e5a68
Signed-off-by: Mrozek, Michal <michal.mrozek@intel.com>
 2019-08-19 13:49:02 +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
Milczarek, Slawomir
4198e8f24f Add interface to get local memory size 
Related-To: NEO-2687

Change-Id: I8d9913e925f88de34d71da9371d25ec04d2e02d5
Signed-off-by: Milczarek, Slawomir <slawomir.milczarek@intel.com>
 2019-07-29 14:40:56 +02:00
Filip Hazubski
4410ebe74d Remove unused function 
Related-To: NEO-3503

Change-Id: I787907e73f1237295594d3a2620f8459f8698eee
Signed-off-by: Filip Hazubski <filip.hazubski@intel.com>
 2019-07-25 01:31:14 +02:00
Koska, Andrzej
1bff5a7bcb Dynamically expose VME extensions 
Change-Id: Ia562361aeea70020cd99f813ea325fa88ca37006
Signed-off-by: Koska, Andrzej <andrzej.koska@intel.com>
Related-To: NEO-3416
 2019-07-24 16:07:13 +02:00
Zdunowski, Piotr
1460713d69 Fail build program if local mem size is higher then device capabilities. 
Resolves: NEO-3411

Change-Id: I04e0b97bfeb9e66e4ea730a15e0c6bfd764cab62
Signed-off-by: Zdunowski, Piotr <piotr.zdunowski@intel.com>
 2019-07-22 17:48:23 +02:00
Mateusz Jablonski
1114361994 Add API for querying number of slices 
Related-To: NEO-3426

Change-Id: I2893be858de9f0f6516ca6ded61123c2c15f1494
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2019-07-17 14:07:30 +02:00
Dunajski, Bartosz
23e9e9e02e Register Blit CSR to CommandQueue 
Change-Id: Ib22ef934492b702990ca549bab576993b0684e98
Related-To: NEO-3020
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2019-07-17 08:04:03 +02:00
Cencelewska
e4e5b5ccdf Add check for vme support 
Change-Id: Ic51e87e1e049bce4ce8ce111e35b94d3806db21b
Signed-off-by: Cencelewska <katarzyna.cencelewska@intel.com>
 2019-07-16 14:35:32 +02:00
Mrozek, Michal
5dc20f50d1 Change max mem alloc size deduction. 
- make it half of global mem
- change buffer input validation, look for hw limitations instead of
computed value of max mem alloc size.

Change-Id: Ibbe7eb16d01299b02cef3b1e7234efefbced2197
Signed-off-by: Mrozek, Michal <michal.mrozek@intel.com>
 2019-07-16 13:47:21 +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
Mrozek, Michal
6abb6523c2 Make max mem alloc size equal to global mem size. 
Change-Id: Ia2b2ec9d66e0b9d7ee33d8e194a42c71fc01fc97
Signed-off-by: Mrozek, Michal <michal.mrozek@intel.com>
 2019-07-11 16:10:53 +02:00
Venevtsev, Igor
4403796f58 Use GfxPartition for GPU address range allocations 
[4/n] - Remove allocator32Bit

Related-To: NEO-2877

Change-Id: I0772a7fe1fda19daa12699c546587bd3cdd84f2c
Signed-off-by: Venevtsev, Igor <igor.venevtsev@intel.com>
 2019-07-08 12:09:07 +02:00