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,141 Commits 39 Branches 642 Tags
578a03e417c516b422177f2a2fa762f058431dc5
Commit Graph

129 Commits

Author SHA1 Message Date
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
Woloszyn, Wojciech
44fbbaee24 Implement clEnqueueWaitForEvents 
Change-Id: I54a1f75ed2935d75fa3d6e07d52ea0831b355dd7
 2018-08-07 09:14:46 +02:00
Katarzyna Cencelewska
831532bf14 Add missing API_ENTER logging in functions: 
clCreateImage2D, clCreateImage3D,
clGetSupportedImageFormats, clGetMemObjectInfo,
clGetImageInfo, clGetImageParamsINTEL,
clSetMemObjectDestructorCallback, clCreateSampler,
clRetainSampler, clReleaseSampler,
clGetSamplerInfo, clCreateProgramWithSource,
clCreateProgramWithBinary

Change-Id: I37214fe5f815c0cc39ec29082ed1f4efb52af4c7
 2018-08-04 14:18:24 +02:00
Katarzyna Cencelewska
a2a2eaf5dd Add missing API_ENTER logging in functions: 
clGetEventInfo, clCreateUserEvent,
clRetainEvent, clReleaseEvent,
clSetUserEventStatus, clSetEventCallback,
clGetEventProfilingInfo, clEnqueueReadBufferRect,
clEnqueueWriteBufferRect, clEnqueueFillBuffer

Change-Id: Ie1fd337d926fa28474157f97390b9c3aece0a782
 2018-08-02 13:18:50 +02:00
Katarzyna Cencelewska
8f18841f38 Add missing API_ENTER logging in function: 
clRetainContext, clReleaseContext,
clGetContextInfo, clCreateCommandQueue,
clRetainCommandQueue, clReleaseCommandQueue,
clGetCommandQueueInfo, clSetCommandQueueProperty,
clCreateBuffer, clCreateSubBuffer

Change-Id: I70c0b57d6f5ff335145593f1a81bc5055b1d0c0c
 2018-08-02 13:10:53 +02:00
Katarzyna Cencelewska
ccbbebdf75 Add missing API_ENTER logging in functions: 
clCreateProgramWithIL, clCreateProgramWithBuiltInKernels,
clRetainProgram, clReleaseProgram,
clLinkProgram, clGetProgramInfo,
clGetProgramBuildInfo, clCreateKernelsInProgram,
clCreateKernelsInProgram, clRetainKernel,
clReleaseKernel, clSetKernelArg,
clGetKernelInfo, clGetKernelArgInfo,
clGetKernelWorkGroupInfo

Change-Id: I4cbe68dd8593e6d42b6e1e4c25a7155a477aa7d0
 2018-08-01 17:13:19 +02:00
Katarzyna Cencelewska
00a62f204a Add missing API_ENTER logging in functions: 
clGetPlatformIDs, clIcdGetPlatformIDsKHR,
 clGetPlatformInfo, clGetDeviceIDs,
 clCreateSubDevices, clRetainDevice,
 clCreateContextFromType

Change-Id: I571b036cc6b64a66d768d7f3f8eb55e7d69b9aa7
 2018-08-01 14:29:10 +02:00
Mrozek, Michal
121376b248 Remove redundant cast. 
Change-Id: I72734ba38d7dd9a5d0055340e6de5709d2de635c
 2018-07-17 19:13:45 +02:00
Mrozek, Michal
513d23ca1d Return error if invalid context is passed. 
Change-Id: Icff0b6658badb08183340375abd1e68fc582c25d
 2018-07-17 18:51:45 +02:00
Mrozek, Michal
d69f23dc10 Enhance validation of properties when command queue is created. 
Change-Id: I1735ef8d9fbc17a09b9711f8f881c27c5de6b82c
 2018-07-10 14:44:15 +02:00
Mrozek, Michal
a21c0a0074 Add control on platform life cycle. 
Change-Id: I5c24b41747d822b71dd57e9a949cf25fcc78a453
 2018-06-27 10:09:26 +02:00
Mrozek, Michal
5c0a562a6b Simplify platform initialize. 
- Remove not required parameters
- move the logic to ult directories

Change-Id: I913f1048489137a61220d96fa9f2798572cd4f56
 2018-06-21 12:46:35 +02:00
Zdunowski, Piotr
157ffbceb5 Revert "Builtins increase context refcount." 
This reverts commit 39d55e5257.

Change-Id: Ib5b38e5a508c5e56e61c7f0ac0b5b8a965d6170d
 2018-05-28 16:35:45 +02:00
Zdunowski, Piotr
39d55e5257 Builtins increase context refcount. 
Change-Id: I146852092e1cb374b816875ae9a90ac03a8f205e
 2018-05-23 17:56:20 +02:00