Media/compute-runtime
1
0
Fork 0
mirror of https://github.com/intel/compute-runtime.git synced 2025-09-15 13:01:45 +08:00
Code Issues Packages Projects Releases Wiki Activity
3,060 Commits 39 Branches 642 Tags
f4008336f8dea2fb840080beb3ced4e173c6a979
Commit Graph

62 Commits

Author SHA1 Message Date
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
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
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
Filip Hazubski
552a1268eb Refactor blit buffer call 
Resolves: NEO-3241

Change-Id: I726135ae55d1e0fcbacd80620e827ee5c7c0c8dc
Signed-off-by: Filip Hazubski <filip.hazubski@intel.com>
 2019-08-09 16:43:40 +02:00
Jim Snow
4360aff03c Move runtime/helpers/aligned_memory.h to core/helpers 
Signed-off-by: Jim Snow <jim.m.snow@intel.com>
Change-Id: I15de094c51d4eb18bfff4d17fd34e817b5525fda
 2019-08-06 23:56:24 +02:00
Piotr Fusik
a141911e19 Correct misspelled identifiers. 
Change-Id: Ifa629c0d6bb1b04b5cfde908f2672ef1843043f0
Signed-off-by: Piotr Fusik <piotr.fusik@intel.com>
 2019-07-17 17:45:52 +02:00
Mrozek, Michal
fe26b0b406 Move debug_manager_state_restore.h to core. 
Change-Id: I3ef4a1aec40efa4bbc8346a5b517336c42c06519
Signed-off-by: Mrozek, Michal <michal.mrozek@intel.com>
 2019-07-15 17:21:38 +02:00
Mrozek, Michal
9d723a10aa Move enumerateLeak to core. 
- remove not used parameter.
- remove the usage of default parameters.
- move some constants to memory management as well.

Change-Id: Iedf374568fa3594ffad6b53534e4483485863324
Signed-off-by: Mrozek, Michal <michal.mrozek@intel.com>
 2019-07-15 13:53:03 +02:00
Mrozek, Michal
0440b86d05 Rename SVM Memory Manager to Unified Memory Manager. 
Change-Id: I1d7637a5aaca3ef5190c4f6303c81060f95744a9
 2019-07-12 11:22:09 +02:00
Andrzej Swierczynski
2e2d5d53b4 Provide compression performance hints during resource allocation 
Change-Id: I1f8076b9c7cc51e16c25a554673a19c4a0c87d63
Resolves: NEO-3243
Signed-off-by: Andrzej Swierczynski <andrzej.swierczynski@intel.com>
 2019-07-11 16:52:07 +02:00
Jobczyk, Lukasz
329d940285 Add multiStorageResource flag to AllocationProperties 
Related-To: NEO-3242

Change-Id: If31adaead389acd3bef6af1931b91396c43b305e
Signed-off-by: Jobczyk, Lukasz <lukasz.jobczyk@intel.com>
 2019-06-14 06:59:28 +02:00
Dunajski, Bartosz
f6bf2c5d0b Simplify read/write enqueue operations on CPU 
Change-Id: I7f59b04d484be2699e325d10e16298016231faf2
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2019-06-03 09:56:26 +02:00
Hoppe, Mateusz
d15174d7c5 Block SVMAllocsManager creation in Context when SVM is not supported 
- skip SVM tests when SVM is not supported

Related-To: NEO-3157

Change-Id: Ie5d5ef4778749f60537084fc7f388714954a4873
Signed-off-by: Hoppe, Mateusz <mateusz.hoppe@intel.com>
 2019-05-17 08:59:00 +02:00
Zdunowski, Piotr
bfea41c85b Revert change to image alignment performance hint. 
This reverts commit 1262b67e17.

Change-Id: I0935c43e065e4543ad70a6178ceb3773d6c8a65b
Related-To: NEO-2366
Signed-off-by: Zdunowski, Piotr <piotr.zdunowski@intel.com>
 2019-05-15 14:58:17 +02:00
Zdunowski, Piotr
1262b67e17 Image alignment performance hint should report the same values it checks. 
Related-To: NEO-2366

Change-Id: I0bbbd4bbe2940ef89fdc9cadcf1d3894ca4fb5ad
Signed-off-by: Zdunowski, Piotr <piotr.zdunowski@intel.com>
 2019-05-14 16:29:24 +02:00
Dunajski, Bartosz
0f87e9aa1a Rename HardwareInfo members 
Change-Id: I85f56b677bafdd75dd958b488522393fc18b68af
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2019-05-09 09:13:55 +02:00
Dunajski, Bartosz
bb80d327c7 Move HardwareInfo ownership to ExecutionEnvironment [1/n] 
Change-Id: I5e5b4cc45947a8841282c7d431fb69d9c397a2d4
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2019-05-08 16:11:01 +02:00
Jobczyk, Lukasz
27c52714bb Add performance hints when kernel's argument requires aux translation 
Resolves: NEO-2931

Change-Id: I3756265d0d8a774805b0b35088b7477b09b5a7bf
Signed-off-by: Jobczyk, Lukasz <lukasz.jobczyk@intel.com>
 2019-04-29 15:55:42 +02:00
Filip Hazubski
fae1d882f8 Add SvmAllocationProperties 
Change-Id: Ie96aeab5597a1b3f2db8611a8a04597516730ce8
Related-To: NEO-2535
Signed-off-by: Filip Hazubski <filip.hazubski@intel.com>
 2019-04-23 10:30:04 +02:00
Zbigniew Zdanowicz
0c6823afd6 Add map allocation for images 
Related-To: NEO-3097

Change-Id: I5bfd89fd597a8d55597ff7a2aa05b2abd278d5bd
Signed-off-by: Zbigniew Zdanowicz <zbigniew.zdanowicz@intel.com>
 2019-04-18 14:46:06 +02:00
Zbigniew Zdanowicz
e201725dd5 Add dedicated map allocation 
Related-To: NEO-2917

Change-Id: Ieeca40f5faf29433a5c464d2c3ca3b8910695a9b
Signed-off-by: Zbigniew Zdanowicz <zbigniew.zdanowicz@intel.com>
 2019-04-09 16:16:31 +02:00
Filip Hazubski
b2e16b7897 Update allocationForCacheFlush method 
Related-To: NEO-2535

Change-Id: Ia24556814188263e2ebb54b6419feddd5d8ed707
Signed-off-by: Filip Hazubski <filip.hazubski@intel.com>
 2019-04-03 18:07:13 +02:00
Maciej Plewka
9e52684f5b Change namespace from OCLRT to NEO 
Change-Id: If965c79d70392db26597aea4c2f3b7ae2820fe96
Signed-off-by: Maciej Plewka <maciej.plewka@intel.com>
 2019-03-26 15:48:19 +01:00
Filip Hazubski
8b57d28116 clang-format: enable sorting includes 
Include files are now grouped and sorted in following order:
1. Header file of the class the current file implements
2. Project files
3. Third party files
4. Standard library

Change-Id: If31af05652184169f7fee1d7ad08f1b2ed602cf0
Signed-off-by: Filip Hazubski <filip.hazubski@intel.com>
 2019-02-27 11:50:07 +01:00
Chodor, Jaroslaw
43856e88b5 Refactor around cache flush and command queue 
Change-Id: I277e27cbc60fbbb015c0024f171697408879ec0b
 2019-02-10 17:59:33 +01:00
Mrozek, Michal
acc5e87b40 Change CL_MEM_USE_HOST_PTR buffer allocation scheme. 
- Choose BUFFER type if local memory is present.
- add CL_MEM_FORCE_SHARED_PHYSICAL_MEMORY_INTEL for allocations that
require host pointer storage.

Change-Id: Ifd3c74800cd53a2a9bb2171212a47ef5bcffe2a1
 2019-01-08 16:24:10 +01:00
Zdanowicz, Zbigniew
3dca095ccf Add cache flush command after WALKER command 
Change-Id: I3983dc6c0797047e17cc8189655a22a22e85892b
 2018-12-19 13:15:33 +01:00
Mrozek, Michal
5336e87590 Remove limit to 256 work items for local workgroup size. 
Change-Id: I30accf0dbf8086a10fb96d29924a7a2c4ef15eb0
 2018-11-05 17:17:59 +01:00
Mateusz Jablonski
ead2e2ea6d Move createAllocationForHostPtr method to command stream receiver 
Remove not needed includes from command_queue.h

Change-Id: I45963bf005471bd7716d55471474299a15e27b62
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2018-10-30 17:49:08 +01:00
Mrozek, Michal
41e77d2fdf Add context types. 
Change-Id: Ie8f76de97ce2a41c55e78b715b0ab7db039f5b3b
 2018-10-24 16:54:56 +02:00
Mateusz Jablonski
4f028d13a1 Command stream receiver: use memory manager from execution environment 
Change-Id: I236218a73bd7dac6e5744e3596f146b77b5ca1c8
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2018-10-16 12:14:55 +02:00
Maciej Godek
2ad5108380 Clarified dependencies in Context::getSupportedImageFormats 
Change-Id: Iaa09a2b572b3ae6d0533378f0ecf227bd90b1a10
 2018-09-27 18:41:18 +02:00
Artur Harasimiuk
40146291ad Update copyright headers 
Updating files modified in 2018 only. Older files remain with old style
copyright header

Change-Id: Ic99f2e190ad74b4b7f2bd79dd7b9fa5fbe36ec92
Signed-off-by: Artur Harasimiuk <artur.harasimiuk@intel.com>
 2018-09-20 18:02:35 +02:00
Katarzyna Cencelewska
962b6ce883 Add support for cl-gl sharing 
Change-Id: I08d7608722746baa3be61846e05eecb5419cc136
 2018-09-18 11:18:46 +02:00
Kamil Diedrich
d3d8b6f905 change ARRAY_COUNT macro to constexpr 
Change-Id: I027c4e70e3b901f3ffb3c0971935ae67e971db07
 2018-08-14 10:04:58 +02:00
Mateusz Jablonski
98061903aa Remove device helper 
Change-Id: Ie66c029359a62b81c8658d804dcf8565647100f1
 2018-07-26 14:10:05 +02:00
Dunajski, Bartosz
eead3ec683 Abort execution when registering invalid sharing object 
Change-Id: Ie6091eb659c423ffe5deb4a3ffe55ae0ef66797d
 2018-07-05 08:35:49 +02:00
Mrozek, Michal
887df5a90d Add reference on device while creating a context 
- Context uses device, it needs to make sure it exists.

Change-Id: I1aeaabc53b6198965dc8f4e6fa37585490774a3f
 2018-06-28 08:53:23 +02:00
Mrozek, Michal
686209874a Remove not used parameters in PlatformFixture SetUp function 
Change-Id: Ib58c97e377218350cea19373dd1f193c4cc32a45
 2018-06-26 15:00:27 +02:00
Artur Harasimiuk
75ab0c6fe1 Switch clang-format to 6.0 
Change-Id: Id96d1f47fb3d479d10d1022f1259dc030a148192
Signed-off-by: Artur Harasimiuk <artur.harasimiuk@intel.com>
 2018-06-14 09:45:00 +02:00
Mateusz Jablonski
180de340d8 Define variable with binary name suffix 
use this variable in tests as it is set once in main.cpp
create function to get binary kernel filename

Change-Id: Ibf7b4c2d390caefda4a5d7fc4667006e7f2edde8
 2018-04-25 15:34:34 +02:00
Mrozek, Michal
ce8c44cae3 Add check for local work group size in clEnqueueNDRangeKernel call. 
- Incoming local work group size cannot exceed device capabilities.

Change-Id: I89a7503155c71443e3ebc630debb5d5b466c6cb5
 2018-04-20 08:16:16 +02:00
Artur Harasimiuk
b42e19110b more ULTs cleanup 
- removing not used BuiltInsFixture

Change-Id: Iba35db629d155522070a143da26ee2ac44fc9568
Signed-off-by: Artur Harasimiuk <artur.harasimiuk@intel.com>
 2018-04-17 10:25:12 +02:00
Jacek Danecki
e43c345e07 sharing: add context tests 
Change-Id: I1dc504f6931ab0ae5645e9460ae0c0284704404c
 2018-04-12 11:26:58 +02:00
Zdanowicz, Zbigniew
b6b92ae808 Create GpgpuWalkerHelper class 
Change-Id: Ia9aa7b816356aff57234b46ea3509b6bd9b7f14b
 2018-04-04 16:42:16 +02:00
Jacek Danecki
d8199a4ebe refactor context creation 
- createContextOsProperties is not needed anymore
- replace invalid context property value
  0x200D as invalid context property value should not be used,
  as it can be use in future as valid property

Change-Id: I569433b0f37bbce083f0d64ecf1dc80ff83bfb46
 2018-04-04 08:07:28 +02:00
Artur Harasimiuk
bdcaf332ce ULTs: more MemoryManagementFixture cleanup 
Change-Id: Iaeb60c9c9e22baf63ff01419a5a6dde1e1652a47
 2018-03-30 10:52:50 +02:00
Mateusz Jablonski
0afd7a9ec1 Cmake refactor part 8 
igdrcl_tests: define sources in subdirectories A-C

Change-Id: Iad8e4e866c4b0b8ccf679313e46ef6f0e5deac50
 2018-03-06 20:53:43 +01:00
Mrozek, Michal
bee295415f Add debug flag to print driver diagnostics to cout. 
- New registry flags can be used for applications that wants to dump driver
diagnostics without using any additional tools
- When flag is on , context is being created with driver diagnostics and
hint level is being set to debug variable
- If application is already using driver diagnostics the hint level is
overwritten

Change-Id: I9912c0a7e8f23adb8372997144e5b75f9cc05b1d
 2018-03-05 09:18:10 +01:00
mplewka
e738e6aa48 Hint for map/unmap when queue is blocked 
Change-Id: I8b2c79fac77325e26e2ead663177cef09b17e00b
 2018-02-16 15:57:44 +01:00