AI/rocm-systems
2
0 Fork 0
Code Issues Pull Requests Actions Packages Projects Releases Wiki Activity
2,678 Commits 3 Branches 0 Tags
c4c871ba6ce92893e60dbdd059a9c71e2ad63fbb
Commit Graph
1205 Commits
Author SHA1 Message Date
foreman c4c871ba6c P4 to Git Change 1611614 by wchau@wchau_OCL_boltzmann on 2018/09/27 12:54:16 
SWDEV-164014 - OCLPerfCounters results in "LLVM ERROR: out of memory"
	- use generic hsa_ven_amd_aqlprofile_pfn_t to point to extension function table

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/roccounters.hpp#3 edit


[ROCm/clr commit: 5616270bbd]
 2018-09-27 13:15:51 -04:00
foreman ef66c429a4 P4 to Git Change 1611613 by gandryey@gera-w8 on 2018/09/27 12:54:08 
SWDEV-79445 - OCL generic changes and code clean-up
	Program compilation clean-up. Step#5:
	- Move the first linkImpl() method to the abstraciton layer. Utilize the new method in GPU/PAL/ROCr backends

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/devprogram.cpp#7 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/devprogram.hpp#5 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/gpu/gpuprogram.cpp#244 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/gpu/gpuprogram.hpp#77 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palprogram.cpp#78 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palprogram.hpp#34 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocprogram.cpp#90 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocprogram.hpp#39 edit


[ROCm/clr commit: e428107060]
 2018-09-27 13:10:59 -04:00
foreman 7edb3642a2 P4 to Git Change 1611191 by wchau@wchau_OCL_boltzmann on 2018/09/26 17:00:31 
SWDEV-164014 - OCLPerfCounters results in "LLVM ERROR: out of memory"
	- replace deprecated  'hsa_system_get_extension_table()' call with 'hsa_system_get_major_extension_table() with table size of “hsa_ven_amd_aqlprofile_1_00_pfn_t”

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/roccounters.hpp#2 edit


[ROCm/clr commit: b1eed992e1]
 2018-09-26 17:14:11 -04:00
foreman dfe67fa6da P4 to Git Change 1611180 by gandryey@gera-ocl-lc on 2018/09/26 16:54:02 
SWDEV-79445 - OCL generic changes and code clean-up
	- Fix Ellesmere compilation with LC path. Switch to multiple device info fields to support LC and HSAIL at the same time

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/pal/paldefs.hpp#40 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/paldevice.cpp#110 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palprogram.cpp#77 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palprogram.hpp#33 edit


[ROCm/clr commit: 42e7f37f69]
 2018-09-26 17:10:57 -04:00
foreman e2a6a8e8ba P4 to Git Change 1610640 by gandryey@gera-w8 on 2018/09/25 17:34:09 
SWDEV-79445 - OCL generic changes and code clean-up
	Program compilation clean-up. Step#4:
	- Add common method FindGlobalVarSize() and metadata setup to the abstraction layer

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/devprogram.cpp#6 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/devprogram.hpp#4 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palprogram.cpp#76 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palprogram.hpp#32 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocprogram.cpp#89 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocprogram.hpp#38 edit


[ROCm/clr commit: 40bfc4cf20]
 2018-09-25 17:47:26 -04:00
foreman 17234d5abb P4 to Git Change 1610625 by gandryey@gera-w8 on 2018/09/25 17:00:40 
SWDEV-79445 - OCL generic changes and code clean-up
	- Fix RGP capture. Add the engine mask.

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palgpuopen.cpp#7 edit


[ROCm/clr commit: f24fdb6d53]
 2018-09-25 17:14:51 -04:00
foreman addd208e25 P4 to Git Change 1610376 by gandryey@gera-w8 on 2018/09/25 11:50:37 
SWDEV-79445 - OCL generic changes and code clean-up
	- Fix HIP failures

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/devprogram.cpp#5 edit


[ROCm/clr commit: 90339a205f]
 2018-09-25 12:03:21 -04:00
foreman 7cf7b1d6eb P4 to Git Change 1610362 by gandryey@gera-w8 on 2018/09/25 11:39:08 
SWDEV-79445 - OCL generic changes and code clean-up
	- Attempt to fix HIP failures with VDI/ROCm

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/devprogram.cpp#4 edit


[ROCm/clr commit: dfe166ffc1]
 2018-09-25 11:48:56 -04:00
foreman 0821f2167f P4 to Git Change 1610043 by gandryey@gera-w8 on 2018/09/24 18:08:36 
SWDEV-79445 - OCL generic changes and code clean-up
	Program compilation clean-up. Step#3:
	- Move getCompilationStagesFromBinary and getNextCompilationStageFromBinary to the abstraction layer.
	- Share the same functionality across GSL, PAL and ROCr backends

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/devprogram.cpp#3 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/devprogram.hpp#3 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/gpu/gpuprogram.cpp#243 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/gpu/gpuprogram.hpp#76 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/paldefs.hpp#39 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palprogram.cpp#75 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palprogram.hpp#31 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocprogram.cpp#88 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocprogram.hpp#37 edit


[ROCm/clr commit: dee2f4bd71]
 2018-09-24 18:21:56 -04:00
foreman c5b9715a6b P4 to Git Change 1608975 by gandryey@gera-w8 on 2018/09/20 18:14:01 
SWDEV-79445 - OCL generic changes and code clean-up
	Program compilation clean-up. Follwoing CL#1608319:
	- Switch HSAIL GSL path to the common compilation method

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/gpu/gpucompiler.cpp#160 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/gpu/gpudevice.hpp#168 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/gpu/gpukernel.cpp#332 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/gpu/gpuprogram.cpp#242 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/gpu/gpuprogram.hpp#75 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palprogram.cpp#74 edit


[ROCm/clr commit: dbe7f3201d]
 2018-09-20 18:26:16 -04:00
foreman 1238139fab P4 to Git Change 1608319 by gandryey@gera-lnx-rcf-lc on 2018/09/19 16:55:11 
SWDEV-79445 - OCL generic changes and code clean-up
	Program compilation clean-up. Step#2:
	- Combine PAL and ROCr implementations of compilation under common methods in device::Program for HSAIL and LC.

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/device.hpp#319 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/devprogram.cpp#2 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/devprogram.hpp#2 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/gpu/gpuprogram.hpp#74 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palcompiler.cpp#26 delete
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/paldevice.hpp#34 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palprogram.cpp#73 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palprogram.hpp#30 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/roccompiler.cpp#46 delete
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocdevice.hpp#31 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocprogram.cpp#87 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocprogram.hpp#36 edit


[ROCm/clr commit: e132af9cad]
 2018-09-19 17:06:20 -04:00
foreman bc0ac6bd43 P4 to Git Change 1607675 by gandryey@gera-w8 on 2018/09/18 18:42:34 
SWDEV-79445 - OCL generic changes and code clean-up
	Program compilation clean-up. Step#1:
	- Move device::Program implementation into a separate file
	- Combine the common fields accros all 3 layers into the abstract device::Program

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/device.cpp#230 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/device.hpp#318 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/devprogram.cpp#1 add
... //depot/stg/opencl/drivers/opencl/runtime/device/devprogram.hpp#1 add
... //depot/stg/opencl/drivers/opencl/runtime/device/gpu/gpucompiler.cpp#159 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/gpu/gpuprogram.cpp#241 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/gpu/gpuprogram.hpp#73 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palprogram.cpp#72 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palprogram.hpp#29 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palvirtual.cpp#125 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocprogram.cpp#86 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocprogram.hpp#35 edit


[ROCm/clr commit: 0253c1afb3]
 2018-09-18 18:53:08 -04:00
foreman c1913716c2 P4 to Git Change 1607596 by jatang@jatang_win_pal_lc on 2018/09/18 16:37:51 
SWDEV-126897 - Remove calling setDynamicParallelFlag() from submitKernelInternal() in LC/ROCm path.

	For LC, setDynamicParallelFlag() is now called at Kernel::InitParameters().

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocvirtual.cpp#69 edit


[ROCm/clr commit: f8e1706822]
 2018-09-18 16:47:41 -04:00
foreman ebe30e5da9 P4 to Git Change 1607329 by jatang@jatang_win_pal_lc on 2018/09/18 10:34:41 
SWDEV-148809 - Device Enqueue on LC/PAL.

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/devkernel.cpp#7 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/paldevice.cpp#109 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palkernel.cpp#66 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palprogram.cpp#71 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palprogram.hpp#28 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palvirtual.cpp#124 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palvirtual.hpp#55 edit


[ROCm/clr commit: 41facdb089]
 2018-09-18 10:42:05 -04:00
foreman 62f0035220 P4 to Git Change 1605680 by gandryey@gera-ocl-lc on 2018/09/13 19:07:27 
SWDEV-79445 - OCL generic changes and code clean-up
	- Fix test_basic progvar_prog_scope_uninit with LC. Detect global variables usage in the program and add the code object allocation to the memory dependency tracking

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palprogram.cpp#70 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palprogram.hpp#27 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palvirtual.cpp#123 edit


[ROCm/clr commit: 45fb4ac8f6]
 2018-09-13 19:25:30 -04:00
foreman 320bfd429b P4 to Git Change 1605385 by gandryey@gera-w8 on 2018/09/13 11:53:28 
SWDEV-79445 - OCL generic changes and code clean-up
	- Don't call backing store destruction if segment wasn't created at all. It could occur during library link.

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palprogram.hpp#26 edit


[ROCm/clr commit: 55cf1727b2]
 2018-09-13 12:03:30 -04:00
foreman 9cd6136461 P4 to Git Change 1605085 by skudchad@skudchad_test2_win_opencl on 2018/09/12 17:44:09 
SWDEV-145570 - [HIP] - Enable largest possible allocation on HIP

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

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palsettings.cpp#56 edit


[ROCm/clr commit: c35c82f394]
 2018-09-12 17:55:29 -04:00
foreman a2af1d68ae P4 to Git Change 1604422 by gandryey@gera-ocl-lc on 2018/09/11 16:51:04 
SWDEV-79445 - OCL generic changes and code clean-up
	- Don't call backing store destruction for Null programs

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palprogram.hpp#25 edit


[ROCm/clr commit: 9bb9312630]
 2018-09-11 17:08:39 -04:00
foreman b7ec7ccfb7 P4 to Git Change 1604296 by jatang@jatang-opencl-hsa-stg5 on 2018/09/11 14:13:12 
SWDEV-126897 - Fix a regression of Device Enqueue in LC path.

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/devkernel.cpp#6 edit


[ROCm/clr commit: e615155636]
 2018-09-11 14:37:55 -04:00
foreman 3f05dba83f P4 to Git Change 1603998 by eboumaou@eboumaou_ugl_stg on 2018/09/11 03:45:45 
SWDEV-164509 - [Dassault][Catia] Adding 8-bits internal format support for sL8 format in OpenGL

	For glTextureView support, GL_LUMINANCE8 internal format needs to return 8_BITS view compatibility class.

	Add 3 new surface formats, CM_SURF_FMT_L8_SRGB, CM_SURF_FMT_R8_SRGB and CM_SURF_FMT_RG8_SRGB. For the moment, only L8_SRGB is supported by GLL.
	Keep L8_X24_SRGB format because of side effects, especially outside the GL driver (CAL)

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

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/gpu/gslbe/src/rt/GSLDeviceGL.cpp#32 edit


[ROCm/clr commit: 8914124cc8]
 2018-09-11 03:58:48 -04:00
foreman 9e9f191c98 P4 to Git Change 1603686 by lmoriche@lmoriche_opencl_dev2 on 2018/09/10 14:36:15 
SWDEV-1 - Cleanups required to build with gcc-5.4
	- Fix the Windows build

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palprintf.cpp#12 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palprintf.hpp#5 edit


[ROCm/clr commit: bda4d20a58]
 2018-09-10 15:02:41 -04:00
foreman 73b444c681 P4 to Git Change 1603633 by lmoriche@lmoriche_opencl_dev2 on 2018/09/10 13:24:30 
SWDEV-1 - Cleanups required to build with gcc-5.4

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palprintf.cpp#11 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/roccompiler.cpp#45 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocdevice.cpp#100 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocprogram.cpp#85 edit
... //depot/stg/opencl/drivers/opencl/support/libcxx/build/Makefile.libcxx#7 edit


[ROCm/clr commit: fea536eea4]
 2018-09-10 13:33:24 -04:00
foreman 08dd8e0f64 P4 to Git Change 1603601 by jatang@jatang-opencl-hsa-stg5 on 2018/09/10 11:55:05 
SWDEV-126897 - Fix segfault in HSAIL/ROCm path.

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocvirtual.cpp#68 edit


[ROCm/clr commit: 03e6266c64]
 2018-09-10 12:09:51 -04:00
foreman bae6f34b08 P4 to Git Change 1603595 by gandryey@gera-ocl-lc on 2018/09/10 11:45:44 
SWDEV-79445 - OCL generic changes and code clean-up
	- Make a fallback to system memory without device access if USWC allocation failed
	- Destroy the backing store after the load of all kernels

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palkernel.cpp#65 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palkernel.hpp#24 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palprogram.cpp#69 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palprogram.hpp#24 edit


[ROCm/clr commit: 8e02d82368]
 2018-09-10 11:57:07 -04:00
foreman 787fdc49a3 P4 to Git Change 1602604 by gandryey@gera-ocl-lc on 2018/09/06 15:25:43 
SWDEV-79445 - OCL generic changes and code clean-up
	- Combine opencl compiler options under a single function.

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/device.cpp#229 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/device.hpp#317 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/gpu/gpusettings.hpp#102 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palcompiler.cpp#25 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palprogram.cpp#68 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palprogram.hpp#23 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palsettings.cpp#55 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palsettings.hpp#19 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/roccompiler.cpp#44 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocprogram.cpp#84 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocprogram.hpp#34 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocsettings.hpp#17 edit


[ROCm/clr commit: 1d5f2b6dac]
 2018-09-06 15:37:37 -04:00
foreman c1e0ad299d P4 to Git Change 1602019 by marsenau@marsenau-fiji on 2018/09/05 14:33:40 
SWDEV-79445 - Remove use of irif.
	     This is now directly linked in the library build and will be
	  removed as a standalone library.

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palprogram.cpp#67 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocprogram.cpp#83 edit


[ROCm/clr commit: 1380df62d9]
 2018-09-05 14:45:11 -04:00
foreman 4208e8e04b P4 to Git Change 1601829 by marsenau@marsenau-fiji on 2018/09/05 09:00:19 
SWDEV-79445 - Stop using -opencl component of triple. This
	  hasn't been needed in a while.

	  Also stop redundantly defining extension macros.

Affected files ...

... //depot/stg/opencl/drivers/opencl/opencldefs#231 edit
... //depot/stg/opencl/drivers/opencl/runtime/CMakeLists.txt#10 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palcompiler.cpp#24 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/CMakeLists.txt#12 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/roccompiler.cpp#43 edit


[ROCm/clr commit: b0396b47e1]
 2018-09-05 09:11:51 -04:00
foreman 29c39ade39 P4 to Git Change 1601516 by asalmanp@asalmanp-ocl-stg on 2018/09/04 16:37:05 
SWDEV-132899 - [OCL][GFX10.1] Adding gfx1010 support and use  Pal::GfxIpLevel::GfxIp10_1/Pal::AsicRevision::Navi10 for gfx1010 and Pal::GfxIpLevel::GfxIp10/Pal::AsicRevision::Navi10Lite for Ariel (gfx1000)

	ReviewRequestURL = http://ocltc.amd.com/reviews/r/15740/

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/gpu/gpudefs.hpp#152 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/gpu/gpuprogram.cpp#240 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palcounters.cpp#17 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/paldefs.hpp#38 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/paldevice.cpp#108 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palsettings.cpp#54 edit


[ROCm/clr commit: 42f5788b2e]
 2018-09-04 16:57:45 -04:00
foreman dd5aa956a1 P4 to Git Change 1601331 by jatang@jatang_rocm_lc2 on 2018/09/04 11:32:49 
SWDEV-126897 - Use the new __amd_scheduler_rocm.

	It's only a name change.

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocschedcl.cpp#2 edit


[ROCm/clr commit: 6ffc12c7c8]
 2018-09-04 11:42:41 -04:00
foreman d5f3e9341f P4 to Git Change 1600140 by gandryey@gera-w8 on 2018/08/30 15:10:58 
SWDEV-79445 - OCL generic changes and code clean-up
	- It's not necessary to have backend specific  binary objects in HSAIL or LC paths.

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/device.cpp#228 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/device.hpp#316 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/gpu/gpubinary.hpp#28 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/gpu/gpuprogram.cpp#239 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/gpu/gpuprogram.hpp#72 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palbinary.cpp#3 delete
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palbinary.hpp#4 delete
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palprogram.cpp#66 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palprogram.hpp#22 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocbinary.hpp#7 delete
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocprogram.cpp#82 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocprogram.hpp#33 edit


[ROCm/clr commit: 5c4478fa22]
 2018-08-30 15:31:56 -04:00
foreman 5467692316 P4 to Git Change 1600013 by gandryey@gera-w8 on 2018/08/30 11:12:14 
SWDEV-79445 - OCL generic changes and code clean-up
	- Fix a typo from CL#1599699

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/devkernel.cpp#5 edit


[ROCm/clr commit: 03a81d46b7]
 2018-08-30 11:27:16 -04:00
foreman ad1839e9ee P4 to Git Change 1599701 by gandryey@gera-w8 on 2018/08/29 18:48:36 
SWDEV-79445 - OCL generic changes and code clean-up
	- Use SDMA staging transfers for data upload if pinning fails. Fixes HIP failure in a test that uses the code segment data for uppload.

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palblit.cpp#26 edit


[ROCm/clr commit: 45d50bb738]
 2018-08-29 18:57:40 -04:00
foreman 0a5f1257f5 P4 to Git Change 1599699 by gandryey@gera-w8 on 2018/08/29 18:43:02 
SWDEV-79445 - OCL generic changes and code clean-up
	- Move WaveLimiter logic to the abstract layer. PAL version was taken as the base, thus performance of GSL path can be affected by this change

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/device.hpp#315 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/devkernel.cpp#4 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/devkernel.hpp#4 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/devwavelimiter.cpp#1 move/add
... //depot/stg/opencl/drivers/opencl/runtime/device/devwavelimiter.hpp#1 move/add
... //depot/stg/opencl/drivers/opencl/runtime/device/gpu/gpudevice.cpp#598 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/gpu/gpukernel.cpp#331 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/gpu/gpukernel.hpp#133 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/gpu/gpuwavelimiter.cpp#15 delete
... //depot/stg/opencl/drivers/opencl/runtime/device/gpu/gpuwavelimiter.hpp#11 delete
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/paldevice.cpp#107 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palkernel.cpp#64 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palkernel.hpp#23 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palwavelimiter.cpp#8 move/delete
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palwavelimiter.hpp#8 move/delete


[ROCm/clr commit: 6cc75de90f]
 2018-08-29 18:54:19 -04:00
foreman 5f5ea9af64 P4 to Git Change 1599472 by gandryey@gera-w8 on 2018/08/29 12:25:34 
SWDEV-79445 - OCL generic changes and code clean-up
	- Move FindLocalWorkSize() logic to the abstraction layer
	- Replace the ROCr path with the common FindLocalWorkSize() functionality

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/device.cpp#227 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/device.hpp#314 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/devkernel.cpp#3 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/devkernel.hpp#3 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/gpu/gpukernel.cpp#330 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/gpu/gpukernel.hpp#132 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palkernel.cpp#63 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palkernel.hpp#22 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rockernel.cpp#42 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocsettings.cpp#36 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocsettings.hpp#16 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocvirtual.cpp#67 edit


[ROCm/clr commit: 5ee211e801]
 2018-08-29 12:35:08 -04:00
foreman 6d60a084ba P4 to Git Change 1599194 by gandryey@gera-w8 on 2018/08/28 18:38:33 
SWDEV-79445 - OCL generic changes and code clean-up
	- Move printf setup in the kernels to the abstraction layer

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/devkernel.cpp#2 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/devkernel.hpp#2 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/gpu/gpukernel.cpp#329 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/gpu/gpukernel.hpp#131 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/gpu/gpuprintf.cpp#47 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/gpu/gpuprintf.hpp#16 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/gpu/gpuprogram.cpp#238 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/gpu/gpuprogram.hpp#71 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palkernel.cpp#62 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palkernel.hpp#21 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palprintf.cpp#10 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palprintf.hpp#4 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rockernel.cpp#41 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rockernel.hpp#25 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocprintf.cpp#11 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocprintf.hpp#6 edit


[ROCm/clr commit: ef83d84899]
 2018-08-28 18:48:05 -04:00
foreman 0eb2d36332 P4 to Git Change 1599157 by gandryey@gera-ocl-lc on 2018/08/28 17:11:04 
SWDEV-79445 - OCL generic changes and code clean-up
	- Add devkerenle.cpp/hpp files for device::Kernel object
	- Move generic code for the arguments setup from the device layer to the abstraction layer
	- Update ROCr and PAL paths to utilize the generic logic for the arguments setup

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/device.cpp#226 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/device.hpp#313 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/devkernel.cpp#1 add
... //depot/stg/opencl/drivers/opencl/runtime/device/devkernel.hpp#1 add
... //depot/stg/opencl/drivers/opencl/runtime/device/gpu/gpukernel.cpp#328 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/gpu/gpukernel.hpp#130 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palkernel.cpp#61 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palkernel.hpp#20 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rockernel.cpp#40 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rockernel.hpp#24 edit
... //depot/stg/opencl/drivers/opencl/runtime/runtimedefs#51 edit


[ROCm/clr commit: 5cfeb120ed]
 2018-08-28 17:30:29 -04:00
foreman 323a56ec40 P4 to Git Change 1598525 by gandryey@gera-ocl-lc on 2018/08/27 14:28:05 
SWDEV-79445 - OCL generic changes and code clean-up
	- Setup KernelParameterDescriptor directly from the binary's metadata without any intermediate arguments presentation.

Affected files ...

... //depot/stg/opencl/drivers/opencl/api/opencl/amdocl/cl_program.cpp#50 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/device.hpp#312 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palkernel.cpp#60 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palkernel.hpp#19 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palvirtual.cpp#122 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocvirtual.cpp#66 edit


[ROCm/clr commit: 4d46463948]
 2018-08-27 14:44:08 -04:00
foreman 1388921e3e P4 to Git Change 1598045 by skudchad@skudchad_test2_win_opencl on 2018/08/24 14:07:44 
SWDEV-145570 - [HIP] Output threadID along with kernel info with LOG_LEVEL=3

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

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palvirtual.cpp#121 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocvirtual.cpp#65 edit


[ROCm/clr commit: cf0504da19]
 2018-08-24 14:21:35 -04:00
foreman a658f61cb1 P4 to Git Change 1597965 by wchau@wchau_OCL_boltzmann on 2018/08/24 11:07:49 
SWDEV-160377 - [OCL][ROCM] Add OpenCL Runtime Support for GFX10 in ROCm - disable XNACK for Navi10 and Ariel

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocdefs.hpp#19 edit


[ROCm/clr commit: 7384db1dd2]
 2018-08-24 11:23:24 -04:00
foreman 81122a4a9d P4 to Git Change 1597023 by vsytchen@vsytchen-win10 on 2018/08/22 15:12:23 
SWDEV-159881 - [OCL][ROCm] Add SVM coarse-grain buffer support with device memory

	1. Use the system memory pool for coarse grain allocations on APUs

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

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocmemory.cpp#39 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocvirtual.cpp#64 edit


[ROCm/clr commit: 1bf70582f0]
 2018-08-22 15:25:01 -04:00
foreman f160b50dc6 P4 to Git Change 1596631 by skudchad@skudchad-lnx on 2018/08/21 18:05:06 
SWDEV-145570 - [HIP] Fixes incorrect condition. Its not needed

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/pal/paldevice.cpp#106 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocdevice.cpp#99 edit


[ROCm/clr commit: 96acb578ad]
 2018-08-21 18:24:17 -04:00
foreman 509e1424a8 P4 to Git Change 1596548 by axie@axie_win_opencl_laptop on 2018/08/21 15:55:23 
SWDEV-161959 - [ROCm QA][RAVEN] QCDGPU-S test is having ERROR -61: (clCreateKernel failed) on RAVEN
	SWDEV-161983 - [ROCm QA][RAVEN] Cachebench test is failing with CL_INVALID_BUFFER_SIZE issue
	SWDEV-161978 - [ROCm QA][RAVEN] PCIeBW is failing on -with error : 61, OpenCL error creating buffer !
	SWDEV-161962 - [ROCm QA][RAVEN] rodinia->nw test has ERROR: clCreateBuffer input_item_set (size:67125249) => -61

	- We make the global memory size at least 1G byte. This is to avoid issue/regression if sysconf API misbehaves.

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

	Tests:
	1. ocltst -m oclruntime.so -A oclruntime.exclude - PASS except SVM test (non regression)
	2. TeamCity presubmission test (OpenCL) - PASS
	3. Run test qcdgpu-s.sh : PASS
	4. Run test cachebench-ocl : PASS
	5. Run test PCIeBandwidth -c 0 -g 0 :  PASS
	6. Run test Rodinia/opencl/nw/run : PASS

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocdevice.cpp#98 edit


[ROCm/clr commit: d886bbdb2c]
 2018-08-21 16:16:14 -04:00
foreman a99daf43d0 P4 to Git Change 1596446 by axie@axie_win_opencl_laptop on 2018/08/21 13:40:43 
SWDEV-161959 - [ROCm QA][RAVEN] QCDGPU-S test is having ERROR -61: (clCreateKernel failed) on RAVEN
	SWDEV-161983 - [ROCm QA][RAVEN] Cachebench test is failing with CL_INVALID_BUFFER_SIZE issue
	SWDEV-161978 - [ROCm QA][RAVEN] PCIeBW is failing on -with error : 61, OpenCL error creating buffer !
	SWDEV-161962 - [ROCm QA][RAVEN] rodinia->nw test has ERROR: clCreateBuffer input_item_set (size:67125249) => -61

	- Adjust Global memory size as half of the system physical memory size in APU for Rocm
	- Similar to current DGPU calculation, environment GPU_SINGLE_ALLOC_PERCENT can be used to adjust max memory allocation size.

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

	Tests:
	1. ocltst -m oclruntime.so -A oclruntime.exclude - PASS except SVM test (non regression)
	2. TeamCity presubmission test (OpenCL) - PASS
	    http://ocltc.amd.com:8111/viewModification.html?modId=106628&personal=true&init=1&tab=vcsModificationBuilds
	3. Run test qcdgpu-s.sh : PASS
	4. Run test cachebench-ocl : PASS
	5. Run test PCIeBandwidth -c 0 -g 0 :  PASS
	6. Run test Rodinia/opencl/nw/run : PASS

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocdevice.cpp#97 edit


[ROCm/clr commit: f84d1d2d03]
 2018-08-21 13:52:31 -04:00
foreman 5fc5595516 P4 to Git Change 1596023 by skudchad@skudchad_test2_win_opencl on 2018/08/20 18:40:38 
SWDEV-145570 - [HIP] Fixes to HIP env var logic

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

Affected files ...

... //depot/stg/opencl/drivers/opencl/api/hip/hip_device.cpp#16 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_internal.hpp#15 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_platform.cpp#18 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/device.cpp#225 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/device.hpp#311 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/paldevice.cpp#105 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocdevice.cpp#96 edit


[ROCm/clr commit: 26954707a4]
 2018-08-20 18:48:00 -04:00
foreman 57d3807f93 P4 to Git Change 1595251 by chui@chui-cnchuiw8-ocl-hsa-stg on 2018/08/17 17:06:54 
SWDEV-160930 - Back out CL1594730 as it is failing OCL/LC and HIP tests

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palkernel.cpp#59 edit


[ROCm/clr commit: c6280baa3c]
 2018-08-17 17:52:29 -04:00
foreman 3285fb68a5 P4 to Git Change 1595124 by skudchad@skudchad_test2_win_opencl on 2018/08/17 14:05:25 
SWDEV-145570 - [HIP] Implement environment variables and subsequent changes for HIP. This gets hipEnvVar passing

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

Affected files ...

... //depot/stg/opencl/drivers/opencl/api/hip/hip_device.cpp#15 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/device.cpp#224 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/device.hpp#310 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/paldevice.cpp#104 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocdevice.cpp#95 edit
... //depot/stg/opencl/drivers/opencl/runtime/utils/flags.hpp#297 edit


[ROCm/clr commit: 812ec48f9e]
 2018-08-17 14:28:54 -04:00
foreman fed5b102b1 P4 to Git Change 1594730 by asalmanp@asalmanp-ocl-stg on 2018/08/16 17:32:14 
SWDEV-160930 - SPECworkstation 3 benchmark GPU Compute tests fail
	Root cause: Caffe compute benchmark fails within SPECWorkstation app because one of the Caffe's OCL kernel tries to launch a kernel with the local_work_size of 1024 causing the clEnqueueNDRangeKernel API to return CL_INVALID_WORK_GROUP_SIZE (i.e., the maximum allowable number is 256)
	Proposed workaround: In order to run a kernel with a local_work_size of 1024, we check the number of used VGPRs in the Kernel and if the Kernel is not using all the available VGPRs we let the Kernel to use 1024 as the local_work_size.

	ReviewURLBoard = http://ocltc.amd.com/reviews/r/15638/

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palkernel.cpp#58 edit


[ROCm/clr commit: 1dcac07a7e]
 2018-08-16 17:49:03 -04:00
foreman 9c2c23a3a3 P4 to Git Change 1594574 by vsytchen@vsytchen-win10 on 2018/08/16 13:43:33 
SWDEV-159881 - [OCL][ROCm] Add SVM coarse-grain buffer support with device memory (Part 2)

	1. Implement clEnqueueSvmMap/Unmap using a staging buffer
	2. Enable device memory coarse grain SVM for OCL only with single device contexts.

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

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocdevice.cpp#94 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocdevice.hpp#30 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocmemory.cpp#38 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocvirtual.cpp#63 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocvirtual.hpp#19 edit
... //depot/stg/opencl/drivers/opencl/runtime/utils/flags.hpp#296 edit


[ROCm/clr commit: 8dcc948d37]
 2018-08-16 13:59:59 -04:00
foreman 834d54fac8 P4 to Git Change 1593708 by vsytchen@vsytchen-win10 on 2018/08/14 18:51:20 
SWDEV-145570 - [HIP] use IS_HIP variable to determine SVM size

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

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/pal/paldevice.cpp#103 edit
... //depot/stg/opencl/drivers/opencl/runtime/utils/flags.hpp#295 edit


[ROCm/clr commit: 3981cc165c]
 2018-08-14 19:06:08 -04:00
foreman 8ffad2579c P4 to Git Change 1593119 by skudchad@skudchad_test2_win_opencl on 2018/08/13 16:53:08 
SWDEV-145570 - [HIP] Output Kernel name and mem arguments passed with LOG_LEVEL=3 for PAL and ROCm backends

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

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palvirtual.cpp#120 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocvirtual.cpp#62 edit


[ROCm/clr commit: bc3e3217b6]
 2018-08-13 17:07:02 -04:00