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
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
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
971cbd55f3
Add new SVM types
...
Related-To: NEO-2917
Change-Id: Ica127129799c1e617a326a110348c2f70160b15c
Signed-off-by: Zbigniew Zdanowicz <zbigniew.zdanowicz@intel.com>
2019-04-11 15:27:38 +02:00
Mrozek, Michal
a21f921dcf
Do not validate platform for add comment call.
...
Change-Id: I1f4c28541aea8e13ac1a63511acb5528b3047fe5
Signed-off-by: Mrozek, Michal <michal.mrozek@intel.com>
2019-04-11 10:25:18 +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
Jobczyk, Lukasz
d6367f02aa
Add INTEL suffix to the clEnqueueVerifyMemory
...
Related-To: NEO-3082
Change-Id: Ia15ab39545144198b2db745a0a61757b6b1caf47
Signed-off-by: Jobczyk, Lukasz <lukasz.jobczyk@intel.com>
2019-04-09 11:00:48 +02:00
Jobczyk, Lukasz
2393aceca6
Add dispatchable object to the clAddCommentINTEL
...
Related-To: NEO-3082
Change-Id: Iae0117b32a81c97a37fb30e79bd4b9547c50c95c
Signed-off-by: Jobczyk, Lukasz <lukasz.jobczyk@intel.com>
2019-04-08 16:05:29 +02:00
Maciej Plewka
4eb48e3d06
Add function to flush caches
...
Related-To: NEO-2536
Change-Id: Ifbf7e7a42514dd66eb0914f9d13407287481e123
Signed-off-by: Maciej Plewka <maciej.plewka@intel.com>
2019-04-05 09:48:50 +02:00
Jobczyk, Lukasz
e926a6d037
Adjust error handling in the clAddCommentINTEL
...
Related-To: NEO-3047
Change-Id: Ic9ecfff8358c43a37a1c4ea4ccf4aec8d09acde8
Signed-off-by: Jobczyk, Lukasz <lukasz.jobczyk@intel.com>
2019-04-04 18:58:39 +02:00
Jobczyk, Lukasz
c2e5831c1c
Add the clAddCommentINTEL function
...
Related-To: NEO-3047
Change-Id: I4def3e4866e0bf53c00f18d42b3c32c0d0c8a746
Signed-off-by: Jobczyk, Lukasz <lukasz.jobczyk@intel.com>
2019-04-04 11:05:10 +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
Filip Hazubski
9bbf1daa0e
Update CommandStreamReceiver::expectMemory()
...
Change-Id: I3362f8beee2430f2bf5ff797ec804448682e41ea
Signed-off-by: Filip Hazubski <filip.hazubski@intel.com>
2019-03-29 08:52:02 +01: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
Dunajski, Bartosz
a7d66b0365
Improve clGetDeviceIDs
...
Change-Id: If7df41e0c2bae5c615f6fea286baf5d7e740cfc7
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
2019-03-20 14:54:21 +01:00
Filip Hazubski
01ff1accfa
Refactor queue extra properties validation
...
Change-Id: If95190159b3885653507c0ffc243d8b45aaa6cc7
Signed-off-by: Filip Hazubski <filip.hazubski@intel.com>
2019-03-19 12:27:52 +01:00
Filip Hazubski
40541e4faa
Update Image compression
...
Change-Id: I3a15dba343a80716b57cdda6b74f2142814021f3
Signed-off-by: Filip Hazubski <filip.hazubski@intel.com>
2019-03-13 13:59:50 +01:00
Mateusz Hoppe
72a5c2c6c4
Fix compilation with OCL_RUNTIME_PROFILING
...
Change-Id: Ib07543fb5f6048e99cdd198111ba88309da2c3e8
Signed-off-by: Mateusz Hoppe <mateusz.hoppe@intel.com>
2019-03-04 10:55:38 +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
Filip Hazubski
ec03210687
Update clEnqueueVerifyMemory
...
- return success also for non aub CSRs
Change-Id: Iac7fdcd58e4b76a325ef67fd266f183d779ca956
Signed-off-by: Filip Hazubski <filip.hazubski@intel.com>
2019-01-14 14:37:09 +01:00
Kamil Diedrich
8feab5e570
Remove commandStreamReceiver lock in clSetUserEventStatus
...
Change-Id: I9a095e2b34aef33f8c8fb210445727dec3aefbfa
2019-01-09 12:46:45 +01:00
Filip Hazubski
7e3884e22d
Add clEnqueueVerifyMemory API
...
Change-Id: I15a514b14b9efdaeb182c7abd98b8e236932d50f
Signed-off-by: Filip Hazubski <filip.hazubski@intel.com>
2019-01-04 08:30:02 +01:00
Filip Hazubski
9d9b11734d
Enhance processing Queue properties
...
Change-Id: I53ab00bdbfb6b11a7d9fdcaec816eead625ae737
Signed-off-by: Filip Hazubski <filip.hazubski@intel.com>
2019-01-02 14:52:02 +01:00
Zdanowicz, Zbigniew
3dca095ccf
Add cache flush command after WALKER command
...
Change-Id: I3983dc6c0797047e17cc8189655a22a22e85892b
2018-12-19 13:15:33 +01:00
Dunajski, Bartosz
1f7448425d
Allow Device creating multiple CSRs [7/n]
...
Create and initialize all supported Engines
Change-Id: If0adf1a06b5005ef2698cebc6f1aaa6eacf562ec
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
2018-11-30 15:48:44 +01:00
Dunajski, Bartosz
3ad33bf1b8
Allow Device creating multiple CSRs [3/n]
...
Add CSR from Device to CommandQueue
Change-Id: Iaccf3c73d25e357242837677777d0513e81f520e
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
2018-11-23 10:51:34 +01:00
Mrozek, Michal
1c6fb9def4
Return pointer to clCreateBufferWithPropertiesINTEL.
...
Change-Id: I36c5e1e0ed9a9032e7f5d3653b413ad1911c37a5
2018-11-19 15:13:32 +01:00
Filip Hazubski
ea2e634f7e
Add clCreateBufferWithPropertiesIntel() API
...
Change-Id: Icfbbbc2479c1bc94008e0ccf90bcb25adddf0b61
Signed-off-by: Filip Hazubski <filip.hazubski@intel.com>
2018-11-06 11:03:04 +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
Adam Cetnerowski
7a476b7bc1
Correct HostPtr and flag usage in clCreateImage:
...
- Disallow HostPtr flags, when HostPtr is null
- Require HostPtr flag, when HostPtr is not null
Change-Id: I8f198b7c3d4052128032e1f0575b19e7af6ffac9
Signed-off-by: Adam Cetnerowski <adam.cetnerowski@intel.com>
2018-10-16 17:43:59 +02:00
Piotr Fusik
9e8af5e045
Validate the numKernels argument to clCreateKernelsInProgram.
...
Change-Id: I9b4ad4497c6cb090caa9b29fd7c92d0477e7f6c0
2018-10-10 21:14:13 +02:00
Mrozek, Michal
12b4d44375
Add new debug flag to limit the number of returned devices.
...
Change-Id: I01e1b6804291956fb62b84ff5df68c57b51bd17d
2018-10-09 00:35:51 +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
Artur Harasimiuk
8334d424ba
add script to set copyright header for source files
...
this works for:
- C/C++ files
- files where comment is #
Change include set of simple tests.
Change-Id: I1c08c6c359e2a48957d5d81397c439508ae06c42
Signed-off-by: Artur Harasimiuk <artur.harasimiuk@intel.com>
2018-09-18 19:12:13 +02:00
Hoppe, Mateusz
5f7b6db893
Validate buffer flags with helper
...
Change-Id: Iaaf04bbe6e5237da0183556fa1ee10817faaf5c0
2018-09-05 14:10:21 +02:00
Mateusz Jablonski
6096263d2a
Process extra tokens when create command queue with properties
...
Change-Id: I8f7d1aeaa7ed1a21e9c35794e5453ffa1ab67d5f
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
2018-08-30 15:20:49 +02:00
Maciej Dziuban
b91c14f70e
Delete Device::getBuiltIns()
...
Change-Id: I9d1968dfb2ba4a56020fd17152119add726106e1
Signed-off-by: Maciej Dziuban <maciej.dziuban@intel.com>
2018-08-22 16:54:53 +02:00
Maciej Dziuban
e0e48203d2
Move BuiltIns to ExecutionEnvironment
...
Change-Id: Ib2a1b82cc7858c898bb32820aad106a01d1325ad
Signed-off-by: Maciej Dziuban <maciej.dziuban@intel.com>
2018-08-21 23:15:47 +02:00
Maciej Dziuban
524737af39
Add executionEnvironment field to Program
...
Change-Id: Id624177aa3f0b5525bac86e2e0a935ebaf53480e
Signed-off-by: Maciej Dziuban <maciej.dziuban@intel.com>
2018-08-16 16:52:41 +02:00
Woloszyn, Wojciech
93c1a7b51b
Fix mipmaps return values
...
Change-Id: I6e7cdc69edc80010a0c6f5f337e6b530278a6606
2018-08-13 11:56:07 +02:00
Lukasz Towarek
23a7ec5ef9
Return CL_INVALID_PROGRAM_EXECUTABLE instead of CL_INVALID_KERNEL
...
- clCreateKernel can't return CL_INVALID_KERNEL according to OpenCL spec
Change-Id: I379218fe20bd13eef52e5a17b1fd3f91fdda06c0
2018-08-13 11:43:33 +02:00
Lukasz Towarek
20aa362a7d
Support CL_INVALID_PROGRAM_EXECUTABLE in clCreateKernel
...
Change-Id: I7ff5b988d0e6187931ea4ad35a7aaeb92e37907a
2018-08-10 09:58:33 +02:00
Lukasz Towarek
d9aad44434
Handle kernel name set to nullptr
...
Change-Id: Ifeb6923c8df948de94b0771de0f37e628013d8db
2018-08-09 16:05:03 +02:00
Katarzyna Cencelewska
32b25ff08b
Add missing API_ENTER and DBG_LOG_INPUTS logging in functions:
...
clEnqueueReadImage, clEnqueueFillImage,
clEnqueueWriteImage, clEnqueueCopyImage,
clEnqueueCopyImageToBuffer, clEnqueueMapImage,
clEnqueueUnmapMemObject, clEnqueueMigrateMemObjects,
clEnqueueNDRangeKernel, clEnqueueTask,
clEnqueueNativeKernel, clEnqueueMarker,
clEnqueueWaitForEvents, clEnqueueBarrier,
clEnqueueMarkerWithWaitList
Change-Id: Ifde3290f8dcd9758235018a97fc080798d3b9de0
2018-08-09 13:00:36 +02:00
Hoppe, Mateusz
69820ab51f
Log created image cl_mem objects in api calls
...
Change-Id: Ic304b5971ddb93057afa47a5205e11e0110b037e
2018-08-09 12:44:39 +02:00
Katarzyna Cencelewska
955aaccb74
Add missing API_ENTER and DBG_LOG_INPUTS logging in functions:
...
clEnqueueSVMMap, clEnqueueSVMUnmap,
clSetKernelArgSVMPointer, clSetKernelExecInfo,
clGetPipeInfo, clCreateCommandQueueWithProperties,
clCreateSamplerWithProperties, clGetKernelSubGroupInfoKHR,
clGetDeviceAndHostTimer, clGetHostTimer,
clGetKernelSubGroupInfo, clSetDefaultDeviceCommandQueue,
clEnqueueSVMMigrateMem, clCloneKernel
Change-Id: Ic5ef808b4fd331b32173c176f498974fc9506a5d
2018-08-09 11:41:11 +02:00
Katarzyna Cencelewska
4afa8fb6ca
Add missing API_ENTER and DBG_LOG_INPUTS logging in functions:
...
clCreatePerfCountersCommandQueueINTEL, clSetPerformanceConfigurationINTEL,
clCreateCommandQueueWithPropertiesKHR, clCreateAcceleratorINTEL,
clRetainAcceleratorINTEL, clGetAcceleratorInfoINTEL,
clReleaseAcceleratorINTEL, clCreateProgramWithILKHR,
clGetExtensionFunctionAddress, clGetExtensionFunctionAddressForPlatform,
clSVMAlloc, clSVMFree,
clEnqueueSVMFree, clEnqueueSVMFree,
clEnqueueSVMMemcpy, clEnqueueSVMMemFill
Change-Id: I40db218af43a9379af173d08cba78c051e169352
2018-08-09 09:50:21 +02:00
Mrozek, Michal
d80dbb1ae0
Do not take ownership on device.
...
- Command Stream Receiver should be used instead for locking.
- Remove not needed synchronization in clSetUserEventStatus
Change-Id: I17050dc70cb0be03b2003043a9666ba8df1a83c9
2018-08-07 09:29:50 +02:00