intel/compute-runtime
1
0
Fork 0
mirror of https://github.com/intel/compute-runtime.git synced 2026-01-13 10:14:36 +08:00
Code Issues Packages Projects Releases Wiki Activity
4,105 Commits 43 Branches 656 Tags
ea172d2f246bdfa5a19ea0ab4c507ffa316c3c4b
Commit Graph

254 Commits

Author SHA1 Message Date
Filip Hazubski
3e3d2d3b3a Update sub devices related device info 
Following parameter values are updated:
- CL_DEVICE_PARENT_DEVICE
- CL_DEVICE_PARTITION_AFFINITY_DOMAIN
- CL_DEVICE_PARTITION_MAX_SUB_DEVICES
- CL_DEVICE_PARTITION_PROPERTIES
- CL_DEVICE_PARTITION_TYPE

Change-Id: I6e2312f3a35aad038a0bebd430ca8f362f01f2a1
Signed-off-by: Filip Hazubski <filip.hazubski@intel.com>
 2020-02-18 20:17:29 +01:00
Jobczyk, Lukasz
70322b858f Make enableLocalMemory and enable64kbpages flags root device specific 
Change-Id: I2f0c601bae83a1c4b69fb2ee04255e1d73c1ab7f
Signed-off-by: Jobczyk, Lukasz <lukasz.jobczyk@intel.com>
 2020-02-18 11:22:21 +01:00
Katarzyna Cencelewska
ab5449acb4 Disable cl_khr_3d_image_writes when image are not supported 
Change-Id: I1a9fc02135dac60156de3d7cc2abe61d685149df
Signed-off-by: Katarzyna Cencelewska <katarzyna.cencelewska@intel.com>
 2020-02-18 10:58:18 +01:00
Katarzyna Cencelewska
541e161898 Change error code from CL_INVALID_VALUE to CL_SUCCESSS 
when image are not suppoorted

Change-Id: I8350558ada1ab048b02b68cb372a22fdadf8c2f5
Signed-off-by: Katarzyna Cencelewska <katarzyna.cencelewska@intel.com>
 2020-02-13 16:04:18 +01:00
Maciej Plewka
df59101dae Create base class for debugger in core 
Resolves: NEO-4176

Change-Id: Iba48676fe145538c8213d21d514be38c702525c9
Signed-off-by: Maciej Plewka <maciej.plewka@intel.com>
 2020-02-11 08:38:48 +01:00
kamdiedrich
f3fc466f5b Move memory_manager to core folder 
Change-Id: I8d84d6982fea3cd785f1e15af0ee7fa361258a23
 2020-02-08 15:24:13 +01:00
Filip Hazubski
d023d9ff02 Move core device objects to core 
Change-Id: Iab6f00ea5cf2595cebc34c18286a6900b90aef92
Signed-off-by: Filip Hazubski <filip.hazubski@intel.com>
 2020-02-07 14:35:14 +01:00
Milczarek, Slawomir
8560b2b262 Create dedicated allocation for global fence purposes 
Related-To: NEO-3216

Change-Id: I0483a99ea1095c7a10b1318f51569e479386cac4
Signed-off-by: Milczarek, Slawomir <slawomir.milczarek@intel.com>
 2020-02-07 10:50:47 +01:00
Maciej Plewka
52931156ed Move execution environment to Core 
Change-Id: I3f5a1f5ef97f058f91d0be7e3c33df7fff04062e
Signed-off-by: Maciej Plewka <maciej.plewka@intel.com>
 2020-02-06 15:00:37 +01:00
Jobczyk, Lukasz
d810067048 Create dedicated engine for internal usage 
Related-To: NEO-4149

Change-Id: I1641866429cfa87b457a808b22917d191c482a7e
Signed-off-by: Jobczyk, Lukasz <lukasz.jobczyk@intel.com>
 2020-02-05 13:48:04 +01:00
Mateusz Jablonski
c7ed76a169 Don't use global platform in cl device 
Related-To: NEO-4207
Change-Id: I5e478a9aa8e0acab925cd0159db1ec36a28dd729
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2020-02-05 11:54:59 +01:00
Mateusz Jablonski
66754c4849 Remove platformDevices from runtime 
Related-To: NEO-4207

Change-Id: I70781b44e7d14360a581808049baf8b61fd1b4e4
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2020-02-05 09:59:13 +01:00
Filip Hazubski
eb72ea8677 Rename DeviceHelper to ClDeviceHelper 
Related-To: NEO-3938

Change-Id: I6c518c25d9868d7a94a20d3a1fcaf9a3631ebc0b
Signed-off-by: Filip Hazubski <filip.hazubski@intel.com>
 2020-02-04 20:30:25 +01:00
Filip Hazubski
5495a4b458 Add specializedDevice pointer to Device 
Related-To: NEO-3938

Change-Id: Ic3386580a22c41f34c67949ccb7f7c6957c8f60d
Signed-off-by: Filip Hazubski <filip.hazubski@intel.com>
 2020-02-04 12:32:14 +01:00
Filip Hazubski
e5f3824740 Rename device_vector.h to cl_device_vector.h 
Related-To: NEO-3938

Change-Id: I06850fc5e03e86e8c1e0fa7348454fdcbe838ed7
Signed-off-by: Filip Hazubski <filip.hazubski@intel.com>
 2020-02-04 09:20:20 +01:00
kamdiedrich
0fff56b656 Move wddm files to core folder 
Change-Id: I28cb7ee6f63275e5b44697e22259023354b9311e
 2020-01-31 20:10:01 +01:00
Michal Mrozek
ca5baf6d89 Add flag to override max work group size. 
Change-Id: I525f9382bc7764f0611acaee202b40800a5836a1
Signed-off-by: Michal Mrozek <michal.mrozek@intel.com>
 2020-01-31 15:48:33 +01:00
Mateusz Jablonski
0e3ab96298 Move compiler extensions to cl device 
Related-To: NEO-4207
Change-Id: Ia220085260fbafb062e0e0aedca863eb64b079bd
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2020-01-31 14:11:05 +01:00
Mateusz Jablonski
0a0b1ce1d8 Pass platform to ClDevice 
Related-To: NEO-4207
Change-Id: I1c70d209df2b378573a41fa991ab594746691adb
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2020-01-31 14:10:29 +01:00
Jobczyk, Lukasz
39cb48024a Initialize root command stream receiver 
Change-Id: I90c4ee9c0e24b1f9182f100213bf6a1ec70df3a8
Signed-off-by: Jobczyk, Lukasz <lukasz.jobczyk@intel.com>
 2020-01-30 15:01:11 +01:00
Filip Hazubski
f80480de7f Move ClDevice to a separate file 
Related-To: NEO-3938

Change-Id: I275b9285b70dac2c9bc52878f6e517e4f3e083b3
Signed-off-by: Filip Hazubski <filip.hazubski@intel.com>
 2020-01-30 12:46:10 +01:00
Kamil Kopryk
bb8dd181a7 Disable sharing extensions on specific configs 
Change-Id: Ib2be6e797095bf771c618ba3515236e3f3eb16c6
Signed-off-by: Kamil Kopryk <kamil.kopryk@intel.com>
Resolves: NEO-4010
 2020-01-29 13:52:48 +01:00
Michal Mrozek
63bfd36232 Add function to query minimal SIMD size. 
Change-Id: I9b6815b3559f7cdd8eddd05ad78c721a360814ef
Signed-off-by: Michal Mrozek <michal.mrozek@intel.com>
 2020-01-27 18:13:43 +01:00
Konstanty Misiak
fc5b98970c Moved files from gmm_helper to core 
Related-To: NEO-4138

Change-Id: Ib7aecb1531cebbe34abb5c8e57067464726e9009
Signed-off-by: Konstanty Misiak <konstanty.misiak@intel.com>
 2020-01-25 11:49:17 +01:00
Mateusz Hoppe
3c89cfc753 Move os_interface files to core 
Change-Id: Ie708a944130884248499091854ebc483953fa828
Signed-off-by: Mateusz Hoppe <mateusz.hoppe@intel.com>
 2020-01-22 14:50:51 +01:00
Filip Hazubski
807a52f3cf Pass ClDevice in DeviceHelper::getExtraDeviceInfo 
Change-Id: I2e7395b86f6c281d976928d9afd2fedf1e1ef4c9
Signed-off-by: Filip Hazubski <filip.hazubski@intel.com>
 2020-01-21 16:26:09 +01:00
Michal Mrozek
686f885e13 Remove debug breaks. 
-They hit each time retain/release is called on root device, which is actually
not an error.

Change-Id: I374752f56ae6750c85ac4750eb997dc66a33d0af
Signed-off-by: Michal Mrozek <michal.mrozek@intel.com>
 2020-01-21 08:04:02 +01:00
Mateusz Hoppe
42858acb32 Move methods from DeviceHelper to HwHelper 
- getSubDevicesCount()
- getEnginesCount()

Change-Id: I59e2d5e8552db5d30767edf8382b846b5ca683d8
Signed-off-by: Mateusz Hoppe <mateusz.hoppe@intel.com>
 2020-01-21 07:20:55 +01:00
Katarzyna Cencelewska
6ffbf55e43 Add new function to set max threads for workgroup 
Resolves: NEO-4116

Change-Id: I8b9faf582c42edcb6f616a2f4662200d0d5b73d3
Signed-off-by: Katarzyna Cencelewska <katarzyna.cencelewska@intel.com>
 2020-01-20 17:05:14 +01:00
Filip Hazubski
17aee4da95 Remove constexpr from ClDevice::getDevice 
Change-Id: Iba4bd324a36c368b2711f5e1ec478acd210dbc14
Signed-off-by: Filip Hazubski <filip.hazubski@intel.com>
 2020-01-20 15:40:20 +01:00
Filip Hazubski
8fcff2241f Add ClDevice 
Decouple cl_device_id from Device class.

Related-To: NEO-3938

Change-Id: I68543a753aea562f3b47ba0d23a059ff3cffa906
Signed-off-by: Filip Hazubski <filip.hazubski@intel.com>
 2020-01-17 12:43:11 +01:00
Katarzyna Cencelewska
1b072cf170 Add error code for get device info relative to images 
if image are not supported

Related-To: NEO-3931
Change-Id: I527da2dc857cd15dae6535dd389378511eb71b6d
Signed-off-by: Katarzyna Cencelewska <katarzyna.cencelewska@intel.com>
 2020-01-16 16:30:13 +01:00
Jobczyk, Lukasz
172e75147e Make OsInterface root device specific 
Related-To: NEO-3857

Change-Id: Ibcd80c731b5d3755b62e0e03d0ffeedb08b52ca0
Signed-off-by: Jobczyk, Lukasz <lukasz.jobczyk@intel.com>
 2020-01-15 11:07:25 +01:00
Katarzyna Cencelewska
c436e8ab77 Add cl_intel_spirv_media_block_io to device extensions 
Resolved: NEO-4140
Change-Id: I6784a3a32ef5a3ba70e4b927e9c99dc3e5a5aa3d
Signed-off-by: Katarzyna Cencelewska <katarzyna.cencelewska@intel.com>
 2020-01-14 13:52:29 +01:00
Katarzyna Cencelewska
0f6248d7ac Modify restrictions to support some extensions 
Change-Id: I7d94249654b5e6aedcf48a4626f59b780dfebf53
Signed-off-by: Katarzyna Cencelewska <katarzyna.cencelewska@intel.com>
 2020-01-13 19:29:59 +01:00
Mateusz Hoppe
01d8532f52 Move files to core 
- wddm_allocation.h/.cpp
- os_context.h
- residency_container.h

Change-Id: I9f933a09d1142f86550c0d67626f0719b6450303
Signed-off-by: Mateusz Hoppe <mateusz.hoppe@intel.com>
 2020-01-13 18:25:00 +01:00
Mateusz Hoppe
51f7ca1601 Move files to core 
- runtime/gmm_helper files
- engine_control.h
- allocation_properties.h

Change-Id: I108888d639c8fdb298eda00fb1e7961b2ccb26cd
Signed-off-by: Mateusz Hoppe <mateusz.hoppe@intel.com>
 2020-01-02 15:57:05 +01:00
Mateusz Jablonski
14c013f53b Dont create multiple page table managers within single root device 
Resolves: NEO-4090
Change-Id: I148b9a5a2755edbcd15ead5f4a0d5d799ee815e1
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2019-12-27 04:36:51 -08: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
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