intel/compute-runtime
1
0
Fork 0
mirror of https://github.com/intel/compute-runtime.git synced 2025-12-22 01:48:50 +08:00
Code Issues Packages Projects Releases Wiki Activity
2,268 Commits 42 Branches 655 Tags
91a64c85189a3f4fc1de0fca0d8ac22de4e4bb33
Commit Graph

77 Commits

Author SHA1 Message Date
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
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