intel/compute-runtime
1
0
Fork 0
mirror of https://github.com/intel/compute-runtime.git synced 2026-01-05 18:00:01 +08:00
Code Issues Packages Projects Releases Wiki Activity
1,034 Commits 43 Branches 655 Tags
e102f6c36b55b1836434a087ec5671291cd81b22
Commit Graph

1034 Commits

This Branch
This Branch
All Branches
Author SHA1 Message Date
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
Maciej Dziuban
3edb738051 Decrease number of classes deriving from Program 2/n 
Change-Id: I67a6e26f62c4bfdcdcea591ca4af3d4ce4f9980e
Signed-off-by: Maciej Dziuban <maciej.dziuban@intel.com>
 2018-08-08 13:01:45 +02:00
Dunajski, Bartosz
f80b020401 Add existing files to cmake 
Change-Id: I23f6b976326464489b1f41136088027e8b207952
 2018-08-08 09:29:17 +02:00
Dunajski, Bartosz
b4f53fdfa7 Pick applicable buffers for aux translation 
Change-Id: I60a28cd9e0dec61120b1ae5c42dfe0cb852eb387
 2018-08-08 09:23:51 +02:00
Chodor, Jaroslaw
428fdb4ed4 Fix for clang compilation error 
Adding missing braces for array initialization

Change-Id: Ic816237af68e0189718f07a617371f131da67c44
 2018-08-08 07:20:03 +02:00
Mrozek, Michal
79708fdbd3 Update internal. 
Change-Id: Ibfba6e854040cf0005f5eb18079f883ee371f5b7
 2018-08-07 18:07:31 +02:00
Kamil Diedrich
8226269bbe Reimplementation of Elf Writer 
- remove is_initialize pattern
- add RAII
- replace dynamic arrays with std::vector<char>
- use fixed width integer types
- remove c-style casting
- reducing the number of code checks
- add camelCase style

Change-Id: If24a595f03865c59c86fed29db280de0084b5663
 2018-08-07 17:35:39 +02:00
Plewka, Maciej
392277ff00 Enable 'Pass info between GT-Pin and IGC', after being reverted 
This reverts commit ea92874a66.

Change-Id: I4994b30f059012a5e89d899665af5c24b8ac8b18
 2018-08-07 17:28:54 +02:00
Mrozek, Michal
d17879d412 Pass ExecutionEnvironment to get devices. 
- this would allow for further re-use of objects allocated here.

Change-Id: I73b62ae3991ebd786dea3c085e1391194b8de6ba
 2018-08-07 15:17:06 +02:00
Mrozek, Michal
4eb2e64231 Remove OsInterface creation from getDevices on Windows. 
Change-Id: I33a141803c336eeaaa6b2702b92515420de97cc1
 2018-08-07 14:41:31 +02:00
Chodor, Jaroslaw
02216e198d Adding spirv to cloc 
cloc will now accept spirv as input
when spirv_input command line argument
is present

Change-Id: Iaca88e1bd11ec2e4b2bfbac3e372ba97fa7efc8e
 2018-08-07 14:08:34 +02:00
Chodor, Jaroslaw
c10d0d79f5 Workgroup walk order 
Change-Id: Id02db6a383e21dc17be64655e7f51a84103b2e0b
 2018-08-07 13:54:10 +02:00
Mrozek, Michal
dfd331c568 Add logic to detect if kernel is using only images as arguments. 
Change-Id: Ia897a1838761c452c36c3f7821149b5867c3cd70
 2018-08-07 13:39:41 +02:00
Hoppe, Mateusz
8123c8b08f Log and print computed SchedulerKernel GWS 
Change-Id: I5781ffc0dcc8cd762d433384f250173b6aee42a4
 2018-08-07 13:32:31 +02:00
Stefanowski, Adam
4df9cf638f Remove device use by memory manager 
Change-Id: Ia9dffb322d7b9f96e5698eb85fcff22a60051f74
 2018-08-07 10:58:15 +02:00
Mrozek, Michal
dd407a3bf1 Move header setting to Wddm csr creation. 
- This is constant setting and will not change in device lifetime.
- This is a part of device removal from memory manager.

Change-Id: Ib80559bac67d65c1bcc488fb033be7343839a108
 2018-08-07 10:35:40 +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
Dunajski, Bartosz
ec6f0f9f86 Aux translation [1/n] 
- Mark Kernel for aux translation
- Initial implementation of dispatchAuxTranslation for future use

Change-Id: Ifca1c9a893876eecc5678cdc4f564b2bfcae959a
 2018-08-07 09:07:25 +02:00
Maciej Dziuban
72740fc048 Cleanup program_tests.cpp 
Reduce number of local classes deriving from Program

Change-Id: I713790c6ea0e034971fa90c6cb8f9c0a6bd6b6cd
 2018-08-06 16:05:25 +02:00
Mrozek, Michal
2711e19986 Do not seek extension presensce in sharing builder. 
- Do it in sharing functions instead
- remove incorrect interface

Change-Id: I6319a341e311217d41e151c332808442db561587
 2018-08-06 10:57:18 +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
Jacek Danecki
de5c3a4ad6 ci: split Ubuntu 18.04 builds with gcc 7 
- use separate builds for each gen to limit builds times

Signed-off-by: Jacek Danecki <jacek.danecki@intel.com>

https://github.com/intel/compute-runtime/pull/73

Change-Id: Icb3d8539011d1919c48f263e1caf45cccee516ea
 2018-08-04 14:12:01 +02:00