intel/compute-runtime
1
0
Fork 0
mirror of https://github.com/intel/compute-runtime.git synced 2025-12-24 21:11:16 +08:00
Code Issues Packages Projects Releases Wiki Activity
1,056 Commits 42 Branches 655 Tags
815bd9e0277a460e64ea74df89577cb75f9f140c
Commit Graph

1056 Commits

This Branch
This Branch
All Branches
Author SHA1 Message Date
Mateusz Jablonski
815bd9e027 Cmake: Remove Windows requirement when copying gmm dynamic lib 
Change-Id: Ieba2f37fbb5aeca855a5ca3790efdaafe544b982
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2018-08-14 12:51:07 +02:00
Mateusz Jablonski
47f3dad619 Apply (2/4)x4x1 layout when generating local ids for kernel with images only 
- For SIMD8 apply 2x4x1 layout
- For SIMD16/SIMD32 apply 4x4x1 layout

Change-Id: I31bceb49387011c66da5f96ad2a71125b96d4cda
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
 2018-08-14 12:22:20 +02:00
Dunajski, Bartosz
cf971158c6 Improve compilation time: split api_tests_wrapper into 3 files 
Change-Id: I5ae90154fb9baa5fb60adceef1995097b4125b81
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2018-08-14 11:52:40 +02:00
Mrozek, Michal
6c5875f805 [2/n] Initialize Wddm interface in Wddm init. 
Change-Id: If7184e64df54b4e6840970fec67cb5bc11909b7c
 2018-08-14 11:02:27 +02:00
Dunajski, Bartosz
a5950500a3 Aux translation [4/n]: Lock BuiltIn Kernel + refactor BuiltIns locking 
Change-Id: Ic7dc9b86a4aa5f93f1c4bcdf80b9598ecdff9713
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2018-08-14 10:56:16 +02:00
Kamil Diedrich
d3d8b6f905 change ARRAY_COUNT macro to constexpr 
Change-Id: I027c4e70e3b901f3ffb3c0971935ae67e971db07
 2018-08-14 10:04:58 +02:00
Mrozek, Michal
d51c7ccdd4 [1/n] Move different wddm functions to dedicated helper. 
- This is first phase of moving wddm specific internals to Wddm
Interface helper
- Instead of having 2 different wddm classes driver will route interface
specific functions to dedicated helper
- Helper will be initialized when interface version will be known,
therefore we would not need to initialize wddm multiple times

Change-Id: Ic71788ccb2f8a71bf2f3f3c2a04117f16417d85e
 2018-08-14 09:08:25 +02:00
Lukasz Towarek
95e28faca0 Fix division by zero in enqueueKernel 
Change-Id: I8e7d3db39805133a5af545e65a94fb19433a2a41
 2018-08-14 09:02:17 +02:00
Mrozek, Michal
99829a3319 Prefetch binding table entries. 
- Significant performance boost for kernels utilizing surface states

Change-Id: I0cec91cb61bd19999847090b945810f798ed80d6
 2018-08-13 17:21:04 +02:00
Stefanowski, Adam
8598168355 Remove programCount from device 
Change-Id: I4edfabadd73166a27db73a120fc1380de52a33a5
 2018-08-13 13:45:55 +02:00
Lukasz Towarek
78f505f4f4 Return CL_INVALID_ARG_SIZE instead of CL_INVALID_ARG_VALUE 
Change-Id: Ia8792035e19a450f1399f8be3287ef46d0d6609d
 2018-08-13 13:31:55 +02:00
Chodor, Jaroslaw
29794db9d9 Refactor cloc UTLS - use inititializer list 
Using initializer list instead of C array

Change-Id: I0520fc8f782347b884b6134208e6b6edaea532dd
 2018-08-13 13:10:46 +02:00
Dunajski, Bartosz
6ca84c278a Aux translation [3/n]: Dispatch AuxTranslation builtin when required 
Change-Id: I9bd0294de7980ac01ebb3c2d696eba6fd6a456ec
 2018-08-13 12:15:30 +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
Chodor, Jaroslaw
59365ab854 Fix for cloc binary input 
Cloc was truncating binary input
at first 0.

Change-Id: I10e3c9dbbfb56fedfa768e19fdf4e7c71bc47dd1
 2018-08-13 11:05:18 +02:00
Woloszyn, Wojciech
53d99ead24 Fix sampler lifecycle 
- Add refcount to sampler to avoid use after free

Change-Id: I0f03d8ed29b5b9dc5bee355ed266ac7437e92509
 2018-08-13 10:13:08 +02:00
Dunajski, Bartosz
1a85f83235 Use std::make_unique for BuiltinDispatchInfoBuilder creation 
Change-Id: I6c28627201c22900502f8f0d481a606f887069bf
 2018-08-13 08:09:54 +02:00
Dunajski, Bartosz
117a7d15ad Aux translation [2/n]: Add new builtins 
Each Kernel arg for aux translation needs to have own builtin kernel.
This is required to build MultiDispatchInfo before copying into SSH

Change-Id: I4b2f42518cf06bb31c31fd5f83f7da927bde99c3
 2018-08-10 18:24:21 +02:00
Mrozek, Michal
9632d18071 Use make unique to construct an object. 
Change-Id: I4fd944869238c0a4c38676160cb752d523dc07a1
 2018-08-10 18:06:49 +02:00
Mrozek, Michal
1f3274e3dc Refactor some tests to not create csr twice. 
- There is no need to create command stream receiver twice.

Change-Id: Ic47e7460e608625c31ab0652ad269c08f45c2250
 2018-08-10 16:34:27 +02:00
Maciej Dziuban
b7bcd2dbac Move createFromGenBinary out from header 
Change-Id: I444c057d76308fcaf08c8f2e6af1590f4cced0b3
Signed-off-by: Maciej Dziuban <maciej.dziuban@intel.com>
 2018-08-10 15:59:26 +02:00
Woloszyn, Wojciech
e102f6c36b Add missing getMaxLod() gmm call 
Change-Id: I14e672b17ddfc9a7045ee66a694642f224a0f4e7
 2018-08-10 15:49:24 +02:00
ocldev
d9d90b3cbf igc revision update 
Change-Id: I1bbc7ceee0c87f3f6fea6fd709c01c43c42290d9
 2018-08-10 14:39:26 +02:00
Mrozek, Michal
ae9134233d OsInterface cleanup. 
- OsInterface is now a part of execution environment
- it is created when getDevice is being called
- move ownership of wddm from Wddm Memory manager to OSInterface
- reuse osInterface on Linux in Command Stream Receiver
- currently OsInterface is not reused upon command stream receiver creation
on Windows this will change in further commits.
- make enumAdapters non static function

Change-Id: I10f36c01e6729f48653e3b5c11cbc32e811ce754
 2018-08-10 14:25:53 +02:00
Dunajski, Bartosz
2845e34c12 Split api_test_wrapper into smaller files to avoid bigobj compile flag 
Change-Id: Idf1ef0816c537a8540ed26c689c2606f25480ce9
 2018-08-10 13:15:10 +02:00
Dunajski, Bartosz
70383c770c Change SourceLevelDebugger gmock object to NiceMock type 
Change-Id: I5f1257d09dec65bd9e0c4ecad94d04a31b0ad5ca
 2018-08-10 12:23:34 +02:00
Kowalczuk, Jakub
571babf1d5 Add new macro _RELEASE_BUILD_WITH_REGKEYS 
Change-Id: I679a17e99d7928b3caf10f80a581fb386aaf7751
 2018-08-10 11:17:22 +02:00
Maciej Dziuban
6f26ced3b5 Don't store MockProgram as member of fixture 
This is to prepare for adding argument to MockProgram constructor. It'll have
to be constructed after ExecutionEnvironment creation, for example after
DeviceFixture::SetUp.

Change-Id: I37b08f814679271820a07fb29cf1fb6b517c8376
Signed-off-by: Maciej Dziuban <maciej.dziuban@intel.com>
 2018-08-10 10:13:33 +02:00
Lukasz Towarek
20aa362a7d Support CL_INVALID_PROGRAM_EXECUTABLE in clCreateKernel 
Change-Id: I7ff5b988d0e6187931ea4ad35a7aaeb92e37907a
 2018-08-10 09:58:33 +02:00
Dunajski, Bartosz
8d80a84ac0 Rename api/api_tests.cpp 
Change-Id: Ieb4df016c8563bd6bc304b3e841cbeac52205094
 2018-08-10 08:17:03 +02:00
Artur Harasimiuk
c149144c97 Infrastructure update 
Change-Id: I4c3ed8f965c0fae1c4820f769d878b0613f68d1d
Signed-off-by: Artur Harasimiuk <artur.harasimiuk@intel.com>
 2018-08-09 17:24:10 +02:00
Mrozek, Michal
9776868aff Remove not used debug variable. 
Change-Id: I6e3a7d1340096383101b84148d772afd2d4f304e
 2018-08-09 16:12:44 +02:00
Lukasz Towarek
d9aad44434 Handle kernel name set to nullptr 
Change-Id: Ifeb6923c8df948de94b0771de0f37e628013d8db
 2018-08-09 16:05:03 +02:00
Slawomir Milczarek
55475c2848 Clang tidy: Call to virtual function during destruction 
Fix for clang tidy warning: Call to virtual function
during destruction will not dispatch to derived class

Change-Id: I000dacdbdfb486d2e35795d18ea9f5e4a00b7d6a
 2018-08-09 15:20:58 +02:00
ocldev
989044818c dependencies update 
Change-Id: Ib49a5cef5f3707fdd0aef0543df29566505970d0
 2018-08-09 14:49:53 +02:00
Dunajski, Bartosz
83dc651d3c Move api tests to single cpp 
Change-Id: Ie591e4680cfdeb68f47c7d16b5977bd03202c997
 2018-08-09 14:35:02 +02:00
Mrozek, Michal
8c0aa92048 Do not use device fixture in work group size tests. 
Change-Id: Id8aea4603c5228de1d8a7943c8a050e898f4ea42
 2018-08-09 14:27:17 +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
18.32.11249 		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
Maciej Dziuban
b9310afe76 Decrease number of classes deriving from Program 4/n 
Change-Id: I73a8616162b72e2dd29e4fa7facbd9bbe1932303
Signed-off-by: Maciej Dziuban <maciej.dziuban@intel.com>
 2018-08-09 12:19:46 +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
Artur Harasimiuk
d5b9cf5570 Infrastructure update 
Change-Id: If2a618da0ebbe2f9a9e20adb13b198d31bb61da0
Signed-off-by: Artur Harasimiuk <artur.harasimiuk@intel.com>
 2018-08-09 10:45:02 +02:00
Slawomir Milczarek
285af96dc2 getCpuGpuTime to return false when unavailable 
This commit addresses crash issue in AUB standalone mode
when queue profiling is enabled on Linux platform.

Change-Id: Ie2d02093d3628efac3a8925890f22afd6a49469d
 2018-08-09 10:10:47 +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
Katarzyna Cencelewska
e4f986a283 Add missing API_ENTER and DBG_LOG_INPUTS logging functions in api_win.cpp 
Change-Id: I7d604e2b6fbb9480a6f8949b64b7eba1fe34fe8b
 2018-08-09 09:34:36 +02:00
Mrozek, Michal
1599ea800e Pass execution environment to command stream receiver. 
Change-Id: I598f67f8b005b5ce8249b638e080657eb6dc3547
 2018-08-08 17:10:39 +02:00
Cetnerowski, Adam
287d33d87e Documentation: Fix broken link after build instructions refactoring 
Change-Id: I2a4b1af6f48fa7ce22a7d4772732cf82692b9665
Signed-off-by: Cetnerowski, Adam <adam.cetnerowski@intel.com>
 2018-08-08 17:04:02 +02:00
Maciej Dziuban
acc0ec539f Decrease number of classes deriving from Program 3/n 
Change-Id: Id5211d4acb46d770dd57b91896af81427d370e0c
Signed-off-by: Maciej Dziuban <maciej.dziuban@intel.com>
 2018-08-08 16:20:35 +02:00
Dunajski, Bartosz
f0e53d5cf1 Add UNRECOVERABLE_IF for unexpected builtIn setArgBuffer scenario 
Change-Id: I87a5c373eae9c833239e0eb4dca6f1660c763a86
 2018-08-08 13:18:34 +02:00