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]
SWDEV-2 - Change OpenCL version number from 2729 to 2730.
Affected files ...
... //depot/stg/opencl/drivers/opencl/runtime/utils/versions.hpp#2477 edit
[ROCm/clr commit: 3150738ad2]
SWDEV-2 - Change OpenCL version number from 2728 to 2729.
Affected files ...
... //depot/stg/opencl/drivers/opencl/runtime/utils/versions.hpp#2476 edit
[ROCm/clr commit: 8404016f00]
SWDEV-143465 - HSAIL - Compiler Lib - Stop supporting SPIR binary on CI+ as well
This change plugs a hole when compiling from SPIR precompiled binary is possible on CI+ devices without option "-x spir" specified.
SPIR text has been already deprecated.
[Reviewers] Brian Sumner, Stanislav Mekhanoshin
[Testing] http://ocltc.amd.com:8111/viewModification.html?modId=107222&personal=true&tab=vcsModificationBuilds
Affected files ...
... //depot/stg/opencl/drivers/opencl/compiler/lib/backends/common/v0_8/if_acl.cpp#101 edit
[ROCm/clr commit: da2aa0859e]
SWDEV-2 - Change OpenCL version number from 2727 to 2728.
Affected files ...
... //depot/stg/opencl/drivers/opencl/runtime/utils/versions.hpp#2475 edit
[ROCm/clr commit: ce5e68844d]
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]
SWDEV-2 - Change OpenCL version number from 2726 to 2727.
Affected files ...
... //depot/stg/opencl/drivers/opencl/runtime/utils/versions.hpp#2474 edit
[ROCm/clr commit: 3f02c35aea]
SWDEV-2 - Change OpenCL version number from 2725 to 2726.
Affected files ...
... //depot/stg/opencl/drivers/opencl/runtime/utils/versions.hpp#2473 edit
[ROCm/clr commit: 0c5f415b5f]
SWDEV-2 - Change OpenCL version number from 2724 to 2725.
Affected files ...
... //depot/stg/opencl/drivers/opencl/runtime/utils/versions.hpp#2472 edit
[ROCm/clr commit: e2bbfbe758]
SWDEV-2 - Change OpenCL version number from 2723 to 2724.
Affected files ...
... //depot/stg/opencl/drivers/opencl/runtime/utils/versions.hpp#2471 edit
[ROCm/clr commit: 25a050c22b]
SWDEV-2 - Change OpenCL version number from 2722 to 2723.
Affected files ...
... //depot/stg/opencl/drivers/opencl/runtime/utils/versions.hpp#2470 edit
[ROCm/clr commit: 0fb56dbba0]
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]
SWDEV-2 - Change OpenCL version number from 2721 to 2722.
Affected files ...
... //depot/stg/opencl/drivers/opencl/runtime/utils/versions.hpp#2469 edit
[ROCm/clr commit: bd9a437016]
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]
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]
SWDEV-2 - Change OpenCL version number from 2720 to 2721.
Affected files ...
... //depot/stg/opencl/drivers/opencl/runtime/utils/versions.hpp#2468 edit
[ROCm/clr commit: ebd334d5bf]
SWDEV-2 - Change OpenCL version number from 2719 to 2720.
Affected files ...
... //depot/stg/opencl/drivers/opencl/runtime/utils/versions.hpp#2467 edit
[ROCm/clr commit: 52bbcd1d7b]
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]
SWDEV-2 - Change OpenCL version number from 2718 to 2719.
Affected files ...
... //depot/stg/opencl/drivers/opencl/runtime/utils/versions.hpp#2466 edit
[ROCm/clr commit: f9f39df8e3]
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]
SWDEV-2 - Change OpenCL version number from 2717 to 2718.
Affected files ...
... //depot/stg/opencl/drivers/opencl/runtime/utils/versions.hpp#2465 edit
[ROCm/clr commit: 481b6c2246]
SWDEV-2 - Change OpenCL version number from 2716 to 2717.
Affected files ...
... //depot/stg/opencl/drivers/opencl/runtime/utils/versions.hpp#2464 edit
[ROCm/clr commit: fe71f88909]
SWDEV-2 - Change OpenCL version number from 2715 to 2716.
Affected files ...
... //depot/stg/opencl/drivers/opencl/runtime/utils/versions.hpp#2463 edit
[ROCm/clr commit: 5f7432d495]
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]
SWDEV-2 - Change OpenCL version number from 2714 to 2715.
Affected files ...
... //depot/stg/opencl/drivers/opencl/runtime/utils/versions.hpp#2462 edit
[ROCm/clr commit: 8c7521debc]
SWDEV-2 - Change OpenCL version number from 2713 to 2714.
Affected files ...
... //depot/stg/opencl/drivers/opencl/runtime/utils/versions.hpp#2461 edit
[ROCm/clr commit: bf34297c34]
SWDEV-2 - Change OpenCL version number from 2712 to 2713.
Affected files ...
... //depot/stg/opencl/drivers/opencl/runtime/utils/versions.hpp#2460 edit
[ROCm/clr commit: 53e1b3b74f]
SWDEV-2 - Change OpenCL version number from 2711 to 2712.
Affected files ...
... //depot/stg/opencl/drivers/opencl/runtime/utils/versions.hpp#2459 edit
[ROCm/clr commit: 1575bb0507]
SWDEV-160552 - [CQE OCL][DTB][BD][Perf][QR][G] Soft hang is observed with ProRender after few subtests due to base driver.
- Reset the pointer to nullptr if PAL platform was destroyed
Affected files ...
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/paldevice.cpp#102 edit
[ROCm/clr commit: 1a61f6b9e5]
SWDEV-160552 - [CQE OCL][DTB][BD][Perf][QR][G] Soft hang is observed with ProRender after few subtests due to base driver.
- Delete PAL platform object if runtime didn't find any supported device.
Affected files ...
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/paldevice.cpp#101 edit
[ROCm/clr commit: 769cc7cddb]
SWDEV-159036 - HBCC is off by default in OCL on WX9100
- Disable HBCC, since it causes ocltst failures on TC
Affected files ...
... //depot/stg/opencl/drivers/opencl/runtime/utils/flags.hpp#293 edit
[ROCm/clr commit: 99cb78b186]
SWDEV-159036 - HBCC is off by default in OCL on WX9100
- Add HBCC size to the global memory. It seems KMD fixed all regressions.
Affected files ...
... //depot/stg/opencl/drivers/opencl/runtime/utils/flags.hpp#292 edit
[ROCm/clr commit: abefff3eb2]
foreman