58a18eaf0c
This corrects some interesting choices that were present in the HIP
...
unit tests such as e.g. de-allocating memory allocated with new[] using
free. All of these were identified via cppcheck.
2017-11-01 22:51:22 +00:00
b8a81d2b75
This corrects some interesting choices that were present in the HIP
...
unit tests such as e.g. de-allocating memory allocated with new[] using
free. All of these were identified via cppcheck.
[ROCm/hip commit: a619ac6f92
2017-11-01 22:51:22 +00:00
a619ac6f92
This corrects some interesting choices that were present in the HIP
...
unit tests such as e.g. de-allocating memory allocated with new[] using
free. All of these were identified via cppcheck.
2017-11-01 22:51:22 +00:00
840895525a
Correctly deal with functions from shared objects, wherein the program visible VA == so_base_va + st_value(function_symbol). Remove quaint usage of pfe for hipMemset (which is actually fill_n).
...
[ROCm/clr commit: 4693c5e56c
2017-11-01 22:33:13 +00:00
4693c5e56c
Correctly deal with functions from shared objects, wherein the program visible VA == so_base_va + st_value(function_symbol). Remove quaint usage of pfe for hipMemset (which is actually fill_n).
2017-11-01 22:33:13 +00:00
dab971370e
Correctly deal with functions from shared objects, wherein the program visible VA == so_base_va + st_value(function_symbol). Remove quaint usage of pfe for hipMemset (which is actually fill_n).
...
[ROCm/hip commit: 2cacda91bb
2017-11-01 22:33:13 +00:00
2cacda91bb
Correctly deal with functions from shared objects, wherein the program visible VA == so_base_va + st_value(function_symbol). Remove quaint usage of pfe for hipMemset (which is actually fill_n).
2017-11-01 22:33:13 +00:00
80e0bed02b
P4 to Git Change 1477581 by wchau@wchau_WIN_OCL_HSA on 2017/11/01 16:33:34
...
SWDEV-136305 - [OCL 2.1 Plat] API calls for all drivers
Affected files ...
... //depot/stg/opencl/drivers/opencl/api/opencl/amdocl/cl_command.cpp#15 edit
... //depot/stg/opencl/drivers/opencl/api/opencl/amdocl/cl_svm.cpp#22 edit
... //depot/stg/opencl/drivers/opencl/runtime/platform/command.hpp#87 edit
... //depot/stg/opencl/drivers/opencl/runtime/platform/context.hpp#27 edit
[ROCm/clr commit: ab934181fa
2017-11-01 16:53:27 -04:00
ab934181fa
P4 to Git Change 1477581 by wchau@wchau_WIN_OCL_HSA on 2017/11/01 16:33:34
...
SWDEV-136305 - [OCL 2.1 Plat] API calls for all drivers
Affected files ...
... //depot/stg/opencl/drivers/opencl/api/opencl/amdocl/cl_command.cpp#15 edit
... //depot/stg/opencl/drivers/opencl/api/opencl/amdocl/cl_svm.cpp#22 edit
... //depot/stg/opencl/drivers/opencl/runtime/platform/command.hpp#87 edit
... //depot/stg/opencl/drivers/opencl/runtime/platform/context.hpp#27 edit
2017-11-01 16:53:27 -04:00
d1584c846c
P4 to Git Change 1477581 by wchau@wchau_WIN_OCL_HSA on 2017/11/01 16:33:34
...
SWDEV-136305 - [OCL 2.1 Plat] API calls for all drivers
Affected files ...
... //depot/stg/opencl/drivers/opencl/api/opencl/amdocl/cl_command.cpp#15 edit
... //depot/stg/opencl/drivers/opencl/api/opencl/amdocl/cl_svm.cpp#22 edit
... //depot/stg/opencl/drivers/opencl/runtime/platform/command.hpp#87 edit
... //depot/stg/opencl/drivers/opencl/runtime/platform/context.hpp#27 edit
[ROCm/clr commit: bafc102e17
2017-11-01 16:53:27 -04:00
bafc102e17
P4 to Git Change 1477581 by wchau@wchau_WIN_OCL_HSA on 2017/11/01 16:33:34
...
SWDEV-136305 - [OCL 2.1 Plat] API calls for all drivers
Affected files ...
... //depot/stg/opencl/drivers/opencl/api/opencl/amdocl/cl_command.cpp#15 edit
... //depot/stg/opencl/drivers/opencl/api/opencl/amdocl/cl_svm.cpp#22 edit
... //depot/stg/opencl/drivers/opencl/runtime/platform/command.hpp#87 edit
... //depot/stg/opencl/drivers/opencl/runtime/platform/context.hpp#27 edit
2017-11-01 16:53:27 -04:00
725f46aa94
Merge pull request #237 from bensander/use_ctxptr_for_p2p
...
Use ctxptr for p2p
[ROCm/clr commit: fe32685fbc
2017-11-01 18:55:25 +01:00
fe32685fbc
Merge pull request #237 from bensander/use_ctxptr_for_p2p
...
Use ctxptr for p2p
2017-11-01 18:55:25 +01:00
2979a99888
Merge pull request #237 from bensander/use_ctxptr_for_p2p
...
Use ctxptr for p2p
[ROCm/hip commit: 09d866a639
2017-11-01 18:55:25 +01:00
09d866a639
Merge pull request #237 from bensander/use_ctxptr_for_p2p
...
Use ctxptr for p2p
2017-11-01 18:55:25 +01:00
6e82cc25df
Add HIP_DB=warn + message if sync on dangerous event.
...
[ROCm/clr commit: 172b9f96e6
2017-11-01 10:44:34 -07:00
172b9f96e6
Add HIP_DB=warn + message if sync on dangerous event.
2017-11-01 10:44:34 -07:00
6c60773e82
Add HIP_DB=warn + message if sync on dangerous event.
...
[ROCm/hip commit: 70c25bdf8e
2017-11-01 10:44:34 -07:00
70c25bdf8e
Add HIP_DB=warn + message if sync on dangerous event.
2017-11-01 10:44:34 -07:00
19935275ea
Merge pull request #245 from scchan/centos_fixes
...
various fixes for centos/rhel
[ROCm/clr commit: 5a80c4108e
2017-11-01 18:10:29 +01:00
5a80c4108e
Merge pull request #245 from scchan/centos_fixes
...
various fixes for centos/rhel
2017-11-01 18:10:29 +01:00
6f3b28d27c
Merge pull request #245 from scchan/centos_fixes
...
various fixes for centos/rhel
[ROCm/hip commit: 86f62accfd
2017-11-01 18:10:29 +01:00
86f62accfd
Merge pull request #245 from scchan/centos_fixes
...
various fixes for centos/rhel
2017-11-01 18:10:29 +01:00
7fa1b2c5b1
P4 to Git Change 1477431 by kzhuravl@kzhuravl-fiji-ocllc on 2017/11/01 12:56:46
...
SWDEV-102733 - Update cmake for CL 1455364
Testing: open source build, also here http://git.amd.com:8080/#/c/113674/
Affected files ...
... //depot/stg/opencl/drivers/opencl/CMakeLists.txt#18 edit
... //depot/stg/opencl/drivers/opencl/api/opencl/amdocl/CMakeLists.txt#12 edit
... //depot/stg/opencl/drivers/opencl/runtime/CMakeLists.txt#7 edit
[ROCm/clr commit: 6293fd1825
2017-11-01 13:01:29 -04:00
6293fd1825
P4 to Git Change 1477431 by kzhuravl@kzhuravl-fiji-ocllc on 2017/11/01 12:56:46
...
SWDEV-102733 - Update cmake for CL 1455364
Testing: open source build, also here http://git.amd.com:8080/#/c/113674/
Affected files ...
... //depot/stg/opencl/drivers/opencl/CMakeLists.txt#18 edit
... //depot/stg/opencl/drivers/opencl/api/opencl/amdocl/CMakeLists.txt#12 edit
... //depot/stg/opencl/drivers/opencl/runtime/CMakeLists.txt#7 edit
2017-11-01 13:01:29 -04:00
fa72a9a820
P4 to Git Change 1477431 by kzhuravl@kzhuravl-fiji-ocllc on 2017/11/01 12:56:46
...
SWDEV-102733 - Update cmake for CL 1455364
Testing: open source build, also here http://git.amd.com:8080/#/c/113674/
Affected files ...
... //depot/stg/opencl/drivers/opencl/CMakeLists.txt#18 edit
... //depot/stg/opencl/drivers/opencl/api/opencl/amdocl/CMakeLists.txt#12 edit
... //depot/stg/opencl/drivers/opencl/runtime/CMakeLists.txt#7 edit
[ROCm/clr commit: 6afeb11d56
2017-11-01 13:01:29 -04:00
6afeb11d56
P4 to Git Change 1477431 by kzhuravl@kzhuravl-fiji-ocllc on 2017/11/01 12:56:46
...
SWDEV-102733 - Update cmake for CL 1455364
Testing: open source build, also here http://git.amd.com:8080/#/c/113674/
Affected files ...
... //depot/stg/opencl/drivers/opencl/CMakeLists.txt#18 edit
... //depot/stg/opencl/drivers/opencl/api/opencl/amdocl/CMakeLists.txt#12 edit
... //depot/stg/opencl/drivers/opencl/runtime/CMakeLists.txt#7 edit
2017-11-01 13:01:29 -04:00
b738633bcb
This switches HIP from its currently convoluted macro + pfe based dispatch mechanism to a more natural one partially based on the existing module API. The basic idea is that HCC will always correctly emit __global__ functions: as empty-bodied stubs, on host, and as kernels, on device. It then becomes trivial to obtain the mangled name on host, at dispatch, from the function's address, and then to use the mangled name to retrieve the kernel. This should address all problems stemming from serialisation, dubious mismatches due to the manufactured functor, macro-isms et al. It also immediately enables support for generalised globals as a consequence of that being available in the module API. Finally, it will make debug much easier, since the actual names of the __global__ functions will automatically be used in traces etc. One detail is that due to how dispatch works now (hipLaunchKernel and hipLaunchKernelGGL are themselves variadic function templates which deduce the function type of the callee), in certain cases it may be necesssary to insert explicit casts to ensure that the variadic argument list selects a viable overload - this can be observed in some unit tests. Eventually we may be able to remove this limitation, but for now it does not appear terribly onerous. The code is not extremely HIPpie, nor is it fully optimised, but rather is intended as a starting point for the HIP team to make its own.
...
[ROCm/clr commit: 28f87f7d2e
2017-11-01 15:09:59 +00:00
28f87f7d2e
This switches HIP from its currently convoluted macro + pfe based dispatch mechanism to a more natural one partially based on the existing module API. The basic idea is that HCC will always correctly emit __global__ functions: as empty-bodied stubs, on host, and as kernels, on device. It then becomes trivial to obtain the mangled name on host, at dispatch, from the function's address, and then to use the mangled name to retrieve the kernel. This should address all problems stemming from serialisation, dubious mismatches due to the manufactured functor, macro-isms et al. It also immediately enables support for generalised globals as a consequence of that being available in the module API. Finally, it will make debug much easier, since the actual names of the __global__ functions will automatically be used in traces etc. One detail is that due to how dispatch works now (hipLaunchKernel and hipLaunchKernelGGL are themselves variadic function templates which deduce the function type of the callee), in certain cases it may be necesssary to insert explicit casts to ensure that the variadic argument list selects a viable overload - this can be observed in some unit tests. Eventually we may be able to remove this limitation, but for now it does not appear terribly onerous. The code is not extremely HIPpie, nor is it fully optimised, but rather is intended as a starting point for the HIP team to make its own.
2017-11-01 15:09:59 +00:00
70a41e7dac
This switches HIP from its currently convoluted macro + pfe based dispatch mechanism to a more natural one partially based on the existing module API. The basic idea is that HCC will always correctly emit __global__ functions: as empty-bodied stubs, on host, and as kernels, on device. It then becomes trivial to obtain the mangled name on host, at dispatch, from the function's address, and then to use the mangled name to retrieve the kernel. This should address all problems stemming from serialisation, dubious mismatches due to the manufactured functor, macro-isms et al. It also immediately enables support for generalised globals as a consequence of that being available in the module API. Finally, it will make debug much easier, since the actual names of the __global__ functions will automatically be used in traces etc. One detail is that due to how dispatch works now (hipLaunchKernel and hipLaunchKernelGGL are themselves variadic function templates which deduce the function type of the callee), in certain cases it may be necesssary to insert explicit casts to ensure that the variadic argument list selects a viable overload - this can be observed in some unit tests. Eventually we may be able to remove this limitation, but for now it does not appear terribly onerous. The code is not extremely HIPpie, nor is it fully optimised, but rather is intended as a starting point for the HIP team to make its own.
...
[ROCm/hip commit: c2482d1255
2017-11-01 15:09:59 +00:00
c2482d1255
This switches HIP from its currently convoluted macro + pfe based dispatch mechanism to a more natural one partially based on the existing module API. The basic idea is that HCC will always correctly emit __global__ functions: as empty-bodied stubs, on host, and as kernels, on device. It then becomes trivial to obtain the mangled name on host, at dispatch, from the function's address, and then to use the mangled name to retrieve the kernel. This should address all problems stemming from serialisation, dubious mismatches due to the manufactured functor, macro-isms et al. It also immediately enables support for generalised globals as a consequence of that being available in the module API. Finally, it will make debug much easier, since the actual names of the __global__ functions will automatically be used in traces etc. One detail is that due to how dispatch works now (hipLaunchKernel and hipLaunchKernelGGL are themselves variadic function templates which deduce the function type of the callee), in certain cases it may be necesssary to insert explicit casts to ensure that the variadic argument list selects a viable overload - this can be observed in some unit tests. Eventually we may be able to remove this limitation, but for now it does not appear terribly onerous. The code is not extremely HIPpie, nor is it fully optimised, but rather is intended as a starting point for the HIP team to make its own.
2017-11-01 15:09:59 +00:00
6f25720c66
Merge 'master' into 'amd-master'
...
Change-Id: Ic61bd45a4904ddb1645e90b9e8fb42ffeab4825a
[ROCm/clr commit: 4401c8c390
2017-11-01 04:42:40 -05:00
4401c8c390
Merge 'master' into 'amd-master'
...
Change-Id: Ic61bd45a4904ddb1645e90b9e8fb42ffeab4825a
2017-11-01 04:42:40 -05:00
267f2040f4
Merge 'master' into 'amd-master'
...
Change-Id: Ic61bd45a4904ddb1645e90b9e8fb42ffeab4825a
[ROCm/hip commit: 7d55fc385b
2017-11-01 04:42:40 -05:00
7d55fc385b
Merge 'master' into 'amd-master'
...
Change-Id: Ic61bd45a4904ddb1645e90b9e8fb42ffeab4825a
2017-11-01 04:42:40 -05:00
f1764ece0c
P4 to Git Change 1477155 by johtaylo@johtaylo-jtincrementor2-increment on 2017/11/01 03:00:04
...
SWDEV-2 - Change OpenCL version number from 2531 to 2532.
Affected files ...
... //depot/stg/opencl/drivers/opencl/runtime/utils/versions.hpp#2279 edit
[ROCm/clr commit: b3181d4b6c
2017-11-01 03:05:32 -04:00
b3181d4b6c
P4 to Git Change 1477155 by johtaylo@johtaylo-jtincrementor2-increment on 2017/11/01 03:00:04
...
SWDEV-2 - Change OpenCL version number from 2531 to 2532.
Affected files ...
... //depot/stg/opencl/drivers/opencl/runtime/utils/versions.hpp#2279 edit
2017-11-01 03:05:32 -04:00
f7ea0599f8
P4 to Git Change 1476932 by kzhuravl@kzhuravl-fiji-ocllc on 2017/10/31 16:10:43
...
SWDEV-102733 - Bring CMakeLists.txt in sync with open source
- Remove extra empty lines
- Add new lines at the end of files
Affected files ...
... //depot/stg/opencl/drivers/opencl/CMakeLists.txt#17 edit
... //depot/stg/opencl/drivers/opencl/tools/clinfo/CMakeLists.txt#4 edit
[ROCm/clr commit: 5c24331d20
2017-10-31 16:19:51 -04:00
5c24331d20
P4 to Git Change 1476932 by kzhuravl@kzhuravl-fiji-ocllc on 2017/10/31 16:10:43
...
SWDEV-102733 - Bring CMakeLists.txt in sync with open source
- Remove extra empty lines
- Add new lines at the end of files
Affected files ...
... //depot/stg/opencl/drivers/opencl/CMakeLists.txt#17 edit
... //depot/stg/opencl/drivers/opencl/tools/clinfo/CMakeLists.txt#4 edit
2017-10-31 16:19:51 -04:00
3698a97a23
P4 to Git Change 1476932 by kzhuravl@kzhuravl-fiji-ocllc on 2017/10/31 16:10:43
...
SWDEV-102733 - Bring CMakeLists.txt in sync with open source
- Remove extra empty lines
- Add new lines at the end of files
Affected files ...
... //depot/stg/opencl/drivers/opencl/CMakeLists.txt#17 edit
... //depot/stg/opencl/drivers/opencl/tools/clinfo/CMakeLists.txt#4 edit
[ROCm/clr commit: d52e0bf530
2017-10-31 16:19:51 -04:00
d52e0bf530
P4 to Git Change 1476932 by kzhuravl@kzhuravl-fiji-ocllc on 2017/10/31 16:10:43
...
SWDEV-102733 - Bring CMakeLists.txt in sync with open source
- Remove extra empty lines
- Add new lines at the end of files
Affected files ...
... //depot/stg/opencl/drivers/opencl/CMakeLists.txt#17 edit
... //depot/stg/opencl/drivers/opencl/tools/clinfo/CMakeLists.txt#4 edit
2017-10-31 16:19:51 -04:00
55fc06dac3
Add asic id for gfx906 on emulator
...
On thunk level, gfx906 works same as gfx900 chip
Change-Id: I727bd904284616f3b1b9b911e41ad0f19318b3ee
Signed-off-by: Shaoyun Liu <Shaoyun.Liu@amd.com >
2017-10-31 14:58:09 -04:00
a068301408
Add asic id for gfx906 on emulator
...
On thunk level, gfx906 works same as gfx900 chip
Change-Id: I727bd904284616f3b1b9b911e41ad0f19318b3ee
Signed-off-by: Shaoyun Liu <Shaoyun.Liu@amd.com >
[ROCm/ROCR-Runtime commit: 55fc06dac3
2017-10-31 14:58:09 -04:00
2094b92a3e
Centos/RHEL - remove usage of constexpr since libc++ doesn't enable ctor for constexpr pair in C++11
...
[ROCm/clr commit: c1a4ff7b20
2017-10-31 18:16:12 +00:00
c1a4ff7b20
Centos/RHEL - remove usage of constexpr since libc++ doesn't enable ctor for constexpr pair in C++11
2017-10-31 18:16:12 +00:00
d938703f9b
Centos/RHEL - remove usage of constexpr since libc++ doesn't enable ctor for constexpr pair in C++11
...
[ROCm/hip commit: 99d32a195f
2017-10-31 18:16:12 +00:00
99d32a195f
Centos/RHEL - remove usage of constexpr since libc++ doesn't enable ctor for constexpr pair in C++11
2017-10-31 18:16:12 +00:00
b04f17be8f
use libc++ on centos 7 and rhel 7.4
...
[ROCm/clr commit: cb454d5366
2017-10-31 18:14:07 +00:00
cb454d5366
use libc++ on centos 7 and rhel 7.4
2017-10-31 18:14:07 +00:00
b6265074fa
use libc++ on centos 7 and rhel 7.4
...
[ROCm/hip commit: cd6996614f
2017-10-31 18:14:07 +00:00
Alex Voicu
foreman
Ben Sander
Jenkins
Shaoyun Liu
Siu Chi Chan