AI/rocm-systems
2
0
Fork 0
Code Issues Pull Requests Actions Packages Projects Releases Wiki Activity
2,533 Commits 3 Branches 0 Tags
2caff650a91222cc09fc3c89c00aada3d65a86e3
Commit Graph

1128 Commits

Author SHA1 Message Date
foreman 2caff650a9 P4 to Git Change 1577357 by gandryey@gera-w8 on 2018/07/06 17:44:59 
SWDEV-158017 - CL_DEVICE_GLOBAL_FREE_MEMORY_AMD doesn't work correctly on PAL backend
	- Adjust system memory calculation for APU systems

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/gpu/gpudevice.cpp#594 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/gpu/gpuresource.hpp#89 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/paldevice.cpp#95 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palresource.hpp#26 edit
 2018-07-06 17:53:44 -04:00
foreman e2b18eda3e P4 to Git Change 1576542 by jatang@jatang-opencl-hsa-stg5 on 2018/07/05 09:29:34 
SWDEV-126897 - Remove un-necessary synchronize() for Device Enqueue in LC/ROCm path.

	We don't need it since we have a hsa_signal_wait_acquire() to wait for the scheduler to finish. Moreover, synchronize() sends a barrier packet that could get stuck for some reason.

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocblit.cpp#25 edit
 2018-07-05 09:39:08 -04:00
foreman 7e185b873e P4 to Git Change 1576247 by gandryey@gera-w8 on 2018/07/04 16:55:54 
SWDEV-158017 - CL_DEVICE_GLOBAL_FREE_MEMORY_AMD doesn't work correctly on PAL backend
	- Change the free memory detection to account possible memory allocation with oversubscription.
	- Make sure resource cache isn't counted as allocated memory

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/gpu/gpudevice.cpp#593 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/gpu/gpuresource.cpp#244 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/gpu/gpuresource.hpp#88 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/paldevice.cpp#94 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/paldevice.hpp#31 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palresource.cpp#68 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palresource.hpp#25 edit
 2018-07-04 17:04:53 -04:00
foreman 6e589b7de6 P4 to Git Change 1576209 by vsytchen@vsytchen-win10 on 2018/07/04 15:37:58 
SWDEV-79445 - OCL generic changes and code clean-up

	1. Purge redundant AllocMapTarget function

	ReviewBoardURL = http://ocltc.amd.com/reviews/r/15346/diff/

Affected files ...

... //depot/stg/opencl/drivers/opencl/api/opencl/amdocl/cl_memobj.cpp#84 edit
... //depot/stg/opencl/drivers/opencl/api/opencl/amdocl/cl_svm.cpp#28 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/device.cpp#223 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/device.hpp#309 edit
 2018-07-04 15:50:23 -04:00
foreman 0bc34b7062 P4 to Git Change 1576208 by vsytchen@vsytchen-win10 on 2018/07/04 15:36:47 
SWDEV-154903 - [Vega10][PAL] clSVMAlloc is failing to create allocations greater than 2GB

	1. Uncommit coarse grain SVM from system memory when calling clEnqueueSVMUnmap

	ReviewBoardURL = http://ocltc.amd.com/reviews/r/15336/diff/

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/gpu/gpumemory.cpp#133 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palmemory.cpp#22 edit
... //depot/stg/opencl/drivers/opencl/runtime/platform/memory.cpp#133 edit
... //depot/stg/opencl/drivers/opencl/runtime/platform/memory.hpp#106 edit
 2018-07-04 15:45:29 -04:00
foreman 1c17b90822 P4 to Git Change 1575517 by gandryey@gera-w8 on 2018/07/03 11:55:33 
SWDEV-133815 - PAL support for Linux Pro w/OpenCL 2.0 support
	- Reenable OCL2.0 support on Linux.

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palsettings.cpp#53 edit
 2018-07-03 12:03:24 -04:00
foreman a5bf56e9bc P4 to Git Change 1573627 by skudchad@skudchad_test2_win_opencl on 2018/06/27 18:26:38 
SWDEV-145570 - [HIP] Report 64KB LDS for Linux

	ReviewBoardURL = http://ocltc.amd.com/reviews/r/15296/diff/

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palsettings.cpp#52 edit
 2018-06-27 18:36:59 -04:00
foreman 7bb3d41155 P4 to Git Change 1573623 by gandryey@gera-w8 on 2018/06/27 18:23:10 
SWDEV-155433 - Add OpenCL API type for RGP files generated from OpenCL
	- Add API type events to the SQTT

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/pal/paldevice.cpp#93 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/paldevice.hpp#30 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palgpuopen.cpp#3 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palgpuopen.hpp#3 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palvirtual.cpp#112 edit
 2018-06-27 18:32:23 -04:00
foreman 717c0e3e6c P4 to Git Change 1572945 by jatang@jatang-opencl-hsa-stg5 on 2018/06/26 16:09:41 
SWDEV-155654 - TDR\BSOD observed while running Nuke Performance Benchmark test on Hawaii Asics.

	Need to support the new power-related appprofile parameters for gfx8 ASICs.

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/gpu/gpuappprofile.cpp#14 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/gpu/gpuappprofile.hpp#8 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/gpu/gpudevice.cpp#592 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/gpu/gslbe/src/rt/GSLDevice.cpp#183 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/gpu/gslbe/src/rt/GSLDevice.h#64 edit
 2018-06-26 16:18:18 -04:00
foreman c7bbeca0d5 P4 to Git Change 1572344 by jatang@jatang-opencl-hsa-stg5 on 2018/06/25 13:05:15 
SWDEV-126897 - Enable 'OPENCL_VERSION=210' in LC/ROCm path.

	For testing purpose.

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocdevice.cpp#91 edit
... //depot/stg/opencl/drivers/opencl/tests/conformance/devel/2.0/test_conformance/device_execution/main.c#10 edit
 2018-06-25 13:16:30 -04:00
foreman 75b68a5dac P4 to Git Change 1571962 by skeely@skeely_HSA_linux on 2018/06/22 17:51:21 
SWDEV-157321 - Mesa interop interface update.

	Interop in/out structs and header updated to match version at git://anongit.freedesktop.org/mesa/mesa
	Mostly minor changes, cleans up include structure avoiding GLX on Windows.

	Larger change is version tracking (now by numbers rather than struct size),
	added a field to mesa_glinterop_export_out giving the size of data written to out_driver_data,
	and corrected spelling of mesa_glinterop_export_out::internal_format.

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/mesa_glinterop.h#5 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocdevice.cpp#90 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocglinterop.cpp#6 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocglinterop.hpp#6 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocmemory.cpp#36 edit
 2018-06-22 18:00:13 -04:00
foreman 64fd3e50a0 P4 to Git Change 1570202 by gandryey@gera-w8 on 2018/06/19 13:58:38 
SWDEV-155436 - Write dispatch dimensions to COMPUTE registers for OpenCL support for RGP
	- Add the dispatch dimensions to the RGP trace

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palgpuopen.cpp#2 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palgpuopen.hpp#2 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palvirtual.cpp#111 edit
... //depot/stg/opencl/drivers/opencl/runtime/utils/flags.hpp#290 edit
 2018-06-19 14:06:00 -04:00
foreman 8d82c5e97b P4 to Git Change 1570053 by jatang@jatang-opencl-hsa-stg5 on 2018/06/19 09:47:32 
SWDEV-155306 - Restore ClockMode when the last queue is destroyed.

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palvirtual.cpp#110 edit
 2018-06-19 09:53:09 -04:00
foreman 1e1aa59aed P4 to Git Change 1569647 by gandryey@gera-lnx-rcf-lc on 2018/06/18 14:04:00 
SWDEV-79445 - OCL generic changes and code clean-up
	 -Following CL#1568521. Correct LDS size look-up.

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocvirtual.cpp#57 edit
 2018-06-18 14:15:59 -04:00
foreman f6d8feabeb P4 to Git Change 1568521 by gandryey@gera-w8 on 2018/06/14 17:43:52 
SWDEV-79445 - OCL generic changes and code clean-up
	- Change LDS setup to account the size, since LC forces 4 bytes for LDS offsets always

	http://ocltc.amd.com/reviews/r/15197/

Affected files ...

... //depot/stg/opencl/drivers/opencl/api/opencl/amdocl/cl_execute.cpp#28 edit
... //depot/stg/opencl/drivers/opencl/api/opencl/amdocl/cl_program.cpp#49 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/gpu/gpublit.cpp#130 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/gpu/gpukernel.cpp#327 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palblit.cpp#25 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palkernel.cpp#56 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palvirtual.cpp#109 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocblit.hpp#11 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rockernel.cpp#38 edit
... //depot/stg/opencl/drivers/opencl/runtime/platform/command.cpp#88 edit
... //depot/stg/opencl/drivers/opencl/runtime/platform/kernel.cpp#34 edit
... //depot/stg/opencl/drivers/opencl/runtime/platform/kernel.hpp#25 edit
 2018-06-14 17:51:35 -04:00
foreman c149902a4d P4 to Git Change 1568474 by asalmanp@asalmanp-ocl-stg on 2018/06/14 16:29:06 
SWDEV-132899 - [OCL][GFX10] OCLGLDepthTex[0] and OCLGLDepthTex[4] subtests of OCLTST/OCLGL are failing on gfx10 Emulator
	extending the Depth24_Stencil8 workaround for gfx10 based on gfx10 Image SRDs

	ReviewBoardURL = http://ocltc.amd.com/reviews/r/15194/

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palresource.cpp#67 edit
 2018-06-14 16:39:10 -04:00
foreman b7b121fa27 P4 to Git Change 1567935 by gandryey@gera-w8 on 2018/06/13 16:49:10 
SWDEV-79445 - OCL generic changes and code clean-up
	- Remove array of hidden parameters. Hidden parameters will be placed together with OCL kernel arguments.

	http://ocltc.amd.com/reviews/r/15178/

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/device.cpp#222 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/device.hpp#308 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/gpu/gpukernel.cpp#326 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palkernel.cpp#55 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rockernel.cpp#37 edit
... //depot/stg/opencl/drivers/opencl/runtime/platform/kernel.cpp#33 edit
 2018-06-13 17:09:22 -04:00
foreman 1eb9ba3640 P4 to Git Change 1567812 by jatang@jatang-opencl-hsa-stg4 on 2018/06/13 12:23:13 
SWDEV-126897 - Change OCL version in ROCm/LC path back to 1.2.

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocdevice.cpp#89 edit
 2018-06-13 12:38:01 -04:00
foreman ec029f4a40 P4 to Git Change 1567789 by gandryey@gera-w8 on 2018/06/13 11:45:56 
SWDEV-79445 - OCL generic changes and code clean-up
	Following CL#1567428. Fix "pass by reference" logic:
	- Make sure we add the offset to the struct location
	- Adjust assert condition

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palkernel.cpp#54 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palvirtual.cpp#108 edit
... //depot/stg/opencl/drivers/opencl/runtime/platform/kernel.cpp#31 edit
 2018-06-13 12:01:00 -04:00
foreman 1f1b062117 P4 to Git Change 1567767 by jatang@jatang_rocm_lc2 on 2018/06/13 11:06:09 
SWDEV-126897 - Support OpenCL Device Enqueue on ROCm.

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocblit.cpp#24 edit
 2018-06-13 11:41:03 -04:00
foreman 1be400ff01 P4 to Git Change 1567428 by gandryey@gera-w8 on 2018/06/12 18:39:23 
SWDEV-79445 - OCL generic changes and code clean-up
	- Optimize setup of kernel arguments. Stage 2.
	- Add HW ABI support in the abstraction layer
	- Remove arguments parsing loop from the kernel launch. Memory processing will be responsible for dependency tracking and  patching of arguments.

	http://ocltc.amd.com/reviews/r/15122/

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/device.cpp#221 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/device.hpp#307 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/gpu/gpukernel.cpp#325 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palblit.cpp#24 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palkernel.cpp#53 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palkernel.hpp#17 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palmemory.hpp#9 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palvirtual.cpp#107 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palvirtual.hpp#53 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rockernel.cpp#36 edit
... //depot/stg/opencl/drivers/opencl/runtime/platform/kernel.cpp#30 edit
... //depot/stg/opencl/drivers/opencl/runtime/platform/kernel.hpp#23 edit
... //depot/stg/opencl/drivers/opencl/runtime/platform/program.cpp#95 edit
 2018-06-12 18:57:20 -04:00
foreman 6321912698 P4 to Git Change 1567349 by jatang@jatang_rocm_lc2 on 2018/06/12 16:09:03 
SWDEV-126897 - Support OpenCL Device Enqueue on ROCm.

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocblit.cpp#23 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocblit.hpp#10 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocdefs.hpp#17 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocdevice.cpp#88 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rockernel.cpp#35 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rockernel.hpp#22 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocprogram.hpp#32 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocsched.hpp#1 add
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocschedcl.cpp#1 add
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocsettings.cpp#33 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocsettings.hpp#13 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocvirtual.cpp#56 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocvirtual.hpp#16 edit
 2018-06-12 16:17:29 -04:00
foreman aa7316a8eb P4 to Git Change 1564341 by gandryey@gera-w8 on 2018/06/05 16:37:09 
SWDEV-79445 - OCL generic changes and code clean-up
	- Follwoing CL#1564298. Delete the old array

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/gpu/gpuvirtual.cpp#421 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palvirtual.cpp#106 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocvirtual.cpp#55 edit
 2018-06-05 16:44:03 -04:00
foreman 1130565901 P4 to Git Change 1564298 by gandryey@gera-w8 on 2018/06/05 15:43:17 
SWDEV-79445 - OCL generic changes and code clean-up
	- Add reallocation logic for memory dependency. SVM path can send the amount of SVM ptrs over the max size of arguments

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/gpu/gpuvirtual.cpp#420 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palvirtual.cpp#105 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocvirtual.cpp#54 edit
 2018-06-05 15:48:18 -04:00
foreman 4214c42b59 P4 to Git Change 1562960 by skudchad@skudchad_test2_win_opencl on 2018/06/01 14:46:26 
SWDEV-145570 - [HIP] - Rename SVManager to be more genric. The same functionality can be used for HIP without needing additonal map

	ReviewBoardURL = http://ocltc.amd.com/reviews/r/15054/diff/

Affected files ...

... //depot/stg/opencl/drivers/opencl/api/opencl/amdocl/cl_memobj.cpp#83 edit
... //depot/stg/opencl/drivers/opencl/api/opencl/amdocl/cl_svm.cpp#27 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/device.cpp#220 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/device.hpp#306 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/gpu/gpudevice.cpp#591 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/gpu/gpuvirtual.cpp#419 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/paldevice.cpp#92 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palvirtual.cpp#104 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocdevice.cpp#87 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocvirtual.cpp#53 edit
... //depot/stg/opencl/drivers/opencl/runtime/platform/kernel.cpp#29 edit
 2018-06-01 14:57:43 -04:00
foreman 97223251ca P4 to Git Change 1562330 by gandryey@gera-w8 on 2018/05/31 14:48:10 
SWDEV-79445 - OCL generic changes and code clean-up
	- Restore reatain/release methods in the device object, removed in CL#1398097. There is a crash in the old SHOC11_DeviceMemory test on TC.

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/device.hpp#305 edit
 2018-05-31 14:55:04 -04:00
foreman d703ef373a P4 to Git Change 1561847 by gandryey@gera-w8 on 2018/05/30 17:34:28 
SWDEV-79445 - OCL generic changes and code clean-up
	- Replace resize(0) with clear() for std::vector. Clear() should preserve the original memory for data.

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palvirtual.cpp#103 edit
 2018-05-30 18:48:09 -04:00
foreman b8a9cdb20e P4 to Git Change 1561794 by gandryey@gera-w8 on 2018/05/30 16:14:30 
SWDEV-79445 - OCL generic changes and code clean-up
	- Move memory sync logic to processMemObjectsHSA() to simplify the arguments setup

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palkernel.cpp#52 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palvirtual.cpp#102 edit
 2018-05-30 16:22:34 -04:00
foreman 818a6d46d2 P4 to Git Change 1561359 by todli@todli-win-opencl-kv1 on 2018/05/30 01:19:53 
SWDEV-152361 - add memory reference to MainEngine queue before initializing BusAddressable memory

	http://ocltc.amd.com/reviews/r/14978/

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palvirtual.cpp#101 edit
 2018-05-30 01:27:28 -04:00
foreman 12315470b7 P4 to Git Change 1561216 by gandryey@gera-w8 on 2018/05/29 18:05:31 
SWDEV-79445 - OCL generic changes and code clean-up
	- Remove parent_ field from the device object, since it was used for subdevices only.

Affected files ...

... //depot/stg/opencl/drivers/opencl/api/opencl/amdocl/cl_device.cpp#72 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/device.cpp#219 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/device.hpp#304 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/gpu/gpudevice.cpp#590 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/paldevice.cpp#91 edit
... //depot/stg/opencl/drivers/opencl/runtime/platform/context.cpp#52 edit
... //depot/stg/opencl/drivers/opencl/runtime/platform/program.cpp#94 edit
... //depot/stg/opencl/drivers/opencl/runtime/platform/program.hpp#45 edit
 2018-05-29 18:13:40 -04:00
foreman a36ef232f2 P4 to Git Change 1561039 by gandryey@gera-w8 on 2018/05/29 13:29:24 
SWDEV-79445 - OCL generic changes and code clean-up
	- Move modified_ fleld initialization to fix g++ compilation

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/pal/paldefs.hpp#36 edit
 2018-05-29 13:50:48 -04:00
foreman 51a4d1865c P4 to Git Change 1561015 by gandryey@gera-w8 on 2018/05/29 13:10:06 
SWDEV-79445 - OCL generic changes and code clean-up
	Optimize memory dependency tracking logic:
	1. Add modified_ filed to the event object to track memory writes into device memory.
	2. Check memory dependency only if a write operation is currently requested or previously performed.

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/pal/paldefs.hpp#35 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palresource.cpp#66 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palresource.hpp#24 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palvirtual.cpp#100 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palvirtual.hpp#52 edit
 2018-05-29 13:18:29 -04:00
foreman 4e1c25c90d P4 to Git Change 1559770 by gandryey@gera-w8 on 2018/05/25 12:44:43 
SWDEV-79445 - OCL generic changes and code clean-up
	- Switch to USWC memory for command buffers

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palvirtual.cpp#99 edit
 2018-05-25 12:49:57 -04:00
foreman be77b7fac1 P4 to Git Change 1559383 by gandryey@gera-w8 on 2018/05/24 18:38:36 
SWDEV-79445 - OCL generic changes and code clean-up
	- Remove memory reallocation interfaces. It was used for AMDIL path with HW constant buffers support. It seems AMDIL with SI+ doesn't enable HW const buffers.

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/device.hpp#303 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/gpu/gpudevice.cpp#589 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/gpu/gpudevice.hpp#166 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/gpu/gpukernel.cpp#324 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/gpu/gpukernel.hpp#129 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/gpu/gpumemory.cpp#132 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/gpu/gpumemory.hpp#52 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/paldevice.cpp#90 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/paldevice.hpp#29 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palkernel.cpp#51 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palkernel.hpp#16 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palmemory.cpp#21 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palmemory.hpp#8 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocdevice.hpp#29 edit
... //depot/stg/opencl/drivers/opencl/runtime/platform/memory.hpp#105 edit
 2018-05-24 18:49:01 -04:00
foreman f095889106 P4 to Git Change 1559253 by gandryey@gera-w8 on 2018/05/24 15:44:23 
SWDEV-79445 - OCL generic changes and code clean-up
	- Following CL#1558704. Fix a regression with AMDIL path. Allocate default device sampler

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/gpu/gpudevice.cpp#588 edit
 2018-05-24 15:56:10 -04:00
foreman bcea58f07f P4 to Git Change 1559096 by gandryey@gera-w8 on 2018/05/24 10:34:47 
SWDEV-79445 - OCL generic changes and code clean-up
	- Remove obsolete logic for aliased kernels, since it was a pre-SI optimization

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/gpu/gpuvirtual.cpp#418 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palvirtual.cpp#98 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocvirtual.cpp#52 edit
... //depot/stg/opencl/drivers/opencl/runtime/platform/kernel.cpp#27 edit
... //depot/stg/opencl/drivers/opencl/runtime/platform/kernel.hpp#21 edit
... //depot/stg/opencl/drivers/opencl/runtime/platform/program.cpp#93 edit
... //depot/stg/opencl/drivers/opencl/runtime/platform/program.hpp#44 edit
 2018-05-24 10:45:00 -04:00
foreman 2176dc3b19 P4 to Git Change 1558704 by gandryey@gera-w8 on 2018/05/23 17:20:01 
SWDEV-79445 - OCL generic changes and code clean-up
	- ABI clean-up. Stage 1: Separate kernel arguments and OCL objects. OCL objects will be passed in the new arrays of mem objects, samplers and device queue objects. The kernel arguments will contain GPU virtual addresses.

	http://ocltc.amd.com/reviews/r/14881/

Affected files ...

... //depot/stg/opencl/drivers/opencl/api/opencl/amdocl/cl_program.cpp#48 edit
... //depot/stg/opencl/drivers/opencl/api/opencl/amdocl/cl_svm.cpp#25 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/device.hpp#302 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/gpu/gpublit.cpp#129 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/gpu/gpukernel.cpp#323 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/gpu/gpukernel.hpp#128 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/gpu/gpumemory.hpp#51 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/gpu/gpuvirtual.cpp#417 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palblit.cpp#23 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palkernel.cpp#50 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palmemory.hpp#7 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palvirtual.cpp#97 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocblit.cpp#22 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocblit.hpp#9 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocdevice.hpp#28 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocmemory.hpp#12 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocvirtual.cpp#51 edit
... //depot/stg/opencl/drivers/opencl/runtime/platform/command.cpp#86 edit
... //depot/stg/opencl/drivers/opencl/runtime/platform/kernel.cpp#26 edit
... //depot/stg/opencl/drivers/opencl/runtime/platform/kernel.hpp#20 edit
 2018-05-23 17:24:32 -04:00
foreman 05fc09fe2c P4 to Git Change 1558617 by vsytchen@vsytchen-win10 on 2018/05/23 15:39:19 
SWDEV-153682 - Report cl_amd_planar_yuv extension in OpenCL

	1. Enable cl_amd_planar_yuv extension for mainline.

	ReviewBoardURL = http://ocltc.amd.com/reviews/r/14948/diff/

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/device.hpp#301 edit
 2018-05-23 15:50:44 -04:00
foreman 4bff7e6b91 P4 to Git Change 1558428 by vsytchen@vsytchen-win10 on 2018/05/23 10:55:37 
SWDEV-153051 - Maya 2018 unable to load OpenCL device on Vega 10 Lnx-Pro

	1. Enable SVM on Lnx-Pro

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/pal/paldevice.cpp#89 edit
 2018-05-23 12:19:25 -04:00
foreman f17ee3da60 P4 to Git Change 1557880 by vsytchen@vsytchen-win10 on 2018/05/22 14:37:35 
SWDEV-153682 - Report cl_amd_planar_yuv extension in OpenCL

	ReviewBoardURL = http://ocltc.amd.com/reviews/r/14917/diff/

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/device.hpp#300 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/gpu/gpusettings.cpp#360 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palsettings.cpp#51 edit
... //depot/stg/opencl/drivers/opencl/tests/ocltst/module/dx/OCLDX11Common.cpp#4 edit
... //depot/stg/opencl/drivers/opencl/tests/ocltst/module/dx/OCLDX11Common.h#2 edit
... //depot/stg/opencl/drivers/opencl/tests/ocltst/module/dx/OCLDX11NV12.cpp#4 delete
... //depot/stg/opencl/drivers/opencl/tests/ocltst/module/dx/OCLDX11NV12.h#2 delete
... //depot/stg/opencl/drivers/opencl/tests/ocltst/module/dx/OCLDX11YUY2.cpp#1 add
... //depot/stg/opencl/drivers/opencl/tests/ocltst/module/dx/OCLDX11YUY2.h#1 add
... //depot/stg/opencl/drivers/opencl/tests/ocltst/module/dx/TestList.cpp#2 edit
... //depot/stg/opencl/drivers/opencl/tests/ocltst/module/dx/build/Makefile.dx#2 edit
 2018-05-22 14:44:23 -04:00
foreman 80fc091f0d P4 to Git Change 1556517 by gandryey@gera-w8 on 2018/05/17 18:37:46 
SWDEV-153682 - Report cl_amd_planar_yuv extension in OpenCL
	- Correct bytePitch for P010 format

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/gpu/gpuresource.cpp#243 edit
 2018-05-17 18:42:59 -04:00
foreman 1b7d26cd88 P4 to Git Change 1555866 by cpaquot@cpaquot-ocl-lc-lnx on 2018/05/16 16:27:00 
SWDEV-145570 - [HIP] Store HIP mem flags inside amd::Buffer's flags
	Use the 16 upper bits of amd::Buffer's flags field instead of adding a new field.

Affected files ...

... //depot/stg/opencl/drivers/opencl/api/hip/hip_memory.cpp#26 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocdevice.cpp#86 edit
 2018-05-16 16:35:53 -04:00
foreman e56e3ce677 P4 to Git Change 1553193 by gandryey@gera-lnx-rcf-lc on 2018/05/10 13:55:21 
SWDEV-79445 - OCL generic changes and code clean-up
	- Following CL#1552596. Add a flag to skip memory allocation. ROCr backend requires access to the parent object in the blit manager, but it's not fully initialized and a view creation is required. However a view creation with not fully initialized object can cause a dead lock if device memory is allocated during the object create.

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocmemory.cpp#35 edit
... //depot/stg/opencl/drivers/opencl/runtime/platform/memory.cpp#132 edit
... //depot/stg/opencl/drivers/opencl/runtime/platform/memory.hpp#104 edit
 2018-05-10 14:03:44 -04:00
foreman 522de89190 P4 to Git Change 1553162 by asalmanp@asalmanp-ocl-stg on 2018/05/10 12:34:13 
SWDEV-132899 - [OCL][GFX10] Adding perfcounter support

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palcounters.cpp#16 edit
 2018-05-10 12:42:46 -04:00
foreman c11b2d52b7 P4 to Git Change 1552704 by gandryey@gera-w8 on 2018/05/09 15:11:23 
SWDEV-79445 - OCL generic changes and code clean-up
	- Following CL#1552596. Make sure virtual GPU is set for the internal allocations before the create() call, since the deferred alloc is disabled.

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/gpu/gpublit.cpp#128 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/gpu/gpuvirtual.cpp#416 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/gpu/gpuvirtual.hpp#144 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palblit.cpp#22 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palvirtual.cpp#96 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palvirtual.hpp#51 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocblit.cpp#21 edit
 2018-05-09 15:16:40 -04:00
foreman 862d478fc6 P4 to Git Change 1551931 by gandryey@gera-w8 on 2018/05/08 12:56:00 
SWDEV-151981 - Removal of CPU support on Windows
	- Remove missed prototype

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocdevice.hpp#27 edit
 2018-05-08 13:05:02 -04:00
foreman ac50335c91 P4 to Git Change 1551928 by gandryey@gera-w8 on 2018/05/08 12:42:43 
SWDEV-151981 - Removal of CPU support on Windows
	- Part 3. Remove device fission extension

Affected files ...

... //depot/stg/opencl/drivers/opencl/api/opencl/amdocl/cl_common.hpp#20 edit
... //depot/stg/opencl/drivers/opencl/api/opencl/amdocl/cl_context.cpp#59 edit
... //depot/stg/opencl/drivers/opencl/api/opencl/amdocl/cl_device.cpp#71 edit
... //depot/stg/opencl/drivers/opencl/api/opencl/amdocl/cl_icd.cpp#32 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/device.cpp#218 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/device.hpp#299 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/gpu/gpudevice.hpp#165 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/paldevice.hpp#28 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocdevice.hpp#26 edit
 2018-05-08 12:50:31 -04:00
foreman 20257bd78b P4 to Git Change 1551379 by skeely@skeely_HSA_linux on 2018/05/07 19:08:50 
SWDEV-147388 - Ignore metadata for TEXTURE_BUFFER objects.

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocmemory.cpp#34 edit
 2018-05-07 19:19:26 -04:00
foreman 4c3d52ab29 P4 to Git Change 1549971 by skudchad@skudchad_rocm on 2018/05/03 18:39:37 
SWDEV-145570 - [HIP] -  Fix build

Affected files ...

... //depot/stg/opencl/drivers/opencl/api/hip/hip_memory.cpp#21 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rockernel.hpp#21 edit
 2018-05-03 18:56:01 -04:00
foreman 8495a06967 P4 to Git Change 1549969 by skudchad@skudchad_rocm on 2018/05/03 18:37:35 
SWDEV-145570 - [HIP] -  Fix build

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rockernel.hpp#20 edit
 2018-05-03 18:49:22 -04:00