Commit Graph

2891 Commits

Author SHA1 Message Date
Yaxun Sam Liu 0471ce2da6 Fix hipLaunchKernelGGL for hip-clang
Do not decay function pointer type of the kernel argument passed to hipLaunchKernelGGL
and hipLaunchKernel, otherwise some type information is lost which may cause
type inference failure for the template.

This issue caused compilation error of FeatureLPPooling in Caffe2/PyTorch and this patch
fixes that.
2018-09-17 11:20:41 -04:00
Maneesh Gupta a5aa5cbcfa Merge pull request #606 from ROCm-Developer-Tools/add-test-global-var
Add HIP directed test hipTestGlobalVariable.cpp
2018-09-17 11:11:51 +05:30
Maneesh Gupta c47e2bc7ba Merge pull request #598 from ROCm-Developer-Tools/support-malloc
Support device-side malloc/free for hip-clang
2018-09-17 11:11:36 +05:30
Maneesh Gupta b23609ad42 Merge branch 'master' into support-malloc 2018-09-17 10:17:25 +05:30
Maneesh Gupta 4d0d1fb3f4 Merge pull request #639 from ROCm-Developer-Tools/skudchad-hip
Check for hipEnvVar at the same level if directed_tests location fails
2018-09-16 18:31:37 +05:30
Maneesh Gupta f9167cd2da Revert changes to runtime/stream/hipStreamSync2 2018-09-15 13:23:38 +05:30
Maneesh Gupta 9f553c0b40 Merge pull request #650 from ROCm-Developer-Tools/hip-clang-new
Support placement new in hip-clang
2018-09-15 11:21:01 +05:30
Maneesh Gupta a190b1ba01 Merge pull request #636 from ROCm-Developer-Tools/db-fatbin
Add HIP_DB=fatbin for debugging fat binary issues
2018-09-14 13:21:58 +05:30
Maneesh Gupta c6d0de2c21 Merge pull request #637 from ROCm-Developer-Tools/add-pthread
Let hipcc link -lpthread -lm by default
2018-09-14 13:21:47 +05:30
Maneesh Gupta 17d12bbfef Merge pull request #665 from aaronenyeshi/fix-min-funcs
Use templates for min to prevent ambiguity
2018-09-14 13:21:38 +05:30
Maneesh Gupta ac7f16613d Merge pull request #642 from ROCm-Developer-Tools/handle-obj
Let hipcc handle obj files in linker response file for hip-clang
2018-09-14 08:59:53 +05:30
Maneesh Gupta 2f794fd99f Merge pull request #658 from phani544/hipClangFrndClass
[HIP-Clang]Add friend class/function test
2018-09-14 08:59:40 +05:30
Aaron Enye Shi 6fa3ba3e12 Fix Tensorflow ambiguous min issue 2018-09-13 23:16:20 +00:00
Maneesh Gupta cb8a0e3a43 Merge pull request #633 from aaronenyeshi/hip-clang-remove-am
Remove few hcc specific cmake for hip-clang
2018-09-13 10:20:12 +05:30
Maneesh Gupta d7a832bce1 Merge pull request #669 from ROCm-Developer-Tools/feature_automatic_cast
Remove potential for mismatch between runtime passed actuals and defined formals
2018-09-13 07:54:22 +05:30
Maneesh Gupta 90833360d1 Merge pull request #670 from gargrahul/remove_adipose_launchkernelhcc
Remove adipose extn from launchKernelHcc sample
2018-09-13 07:54:11 +05:30
Maneesh Gupta 2081cc9bd4 Merge pull request #661 from yxsamliu/add-empty-printf
Add empty printf for hip-clang
2018-09-13 07:54:03 +05:30
Maneesh Gupta 09da85729b Merge pull request #648 from ROCm-Developer-Tools/yxsamliu-patch-2
Document kernel launching for hip-clang
2018-09-13 07:53:50 +05:30
Aaron Enye Shi ebf565819e Avoid AMP-retrict call to CPU-restrict 2018-09-12 14:54:31 +00:00
Rahul Garg 632b6f6b39 Remove adipose extn from launchKernelHcc sample 2018-09-12 16:41:24 +05:30
Alex Voicu 5a8eb9eba5 Remove potential for mismatch between runtime passed actuals and defined formals. 2018-09-12 10:30:48 +01:00
Maneesh Gupta 22cfe54e31 Merge pull request #664 from lcskrishna/master
added __host__ to float2half and half2float functions.
2018-09-12 14:50:01 +05:30
Maneesh Gupta ad5bc7f015 Merge pull request #663 from yxsamliu/fix-launch
Use template for hipLaunchKernelGGL for hip-clang
2018-09-12 14:49:38 +05:30
Maneesh Gupta 2eadadff94 Merge pull request #667 from carlushuang/longlong_as_double_fix
fix __longlong_as_double() problem, return the double value
2018-09-12 12:53:57 +05:30
Maneesh Gupta 74a13473f3 Merge pull request #666 from ROCm-Developer-Tools/mangupta-patch-2
[ci] Disable hipVectorTypes* tests in CI
2018-09-12 12:52:15 +05:30
carlushuang 15281b7b84 fix __longlong_as_double() problem, return the double value
previous version return a long long valus *as* double, hence we may get the wrong result.
this also affect atomicAdd(double * ...), which use long long pointer to mimic double pointer.

Signed-off-by: carlushuang <carlus.huang@amd.com>
2018-09-12 13:25:00 +08:00
Maneesh Gupta d45cf59fc4 [ci] Disable hipVectorTypes* tests in CI
Disable directed_tests/deviceLib/hipVectorTypes.tst & directed_tests/deviceLib/hipVectorTypesDevice.tst in CI due to HCC regressions. Once HCC fixes are in, the tests can be re-enabled in CI.
2018-09-12 10:32:15 +05:30
Aaron Enye Shi 7aa282897f Avoid host min func conflict with gcc min 2018-09-11 18:48:31 +00:00
Aaron Enye Shi 5f0838300e Use templates for min to prevent ambiguity 2018-09-11 18:21:54 +00:00
Yaxun Sam Liu 6f2201475d Use template for hipLaunchKernelGGL for hip-clang 2018-09-07 16:20:00 -04:00
Yaxun Sam Liu be4a8f6859 Add empty printf for hip-clang 2018-09-07 16:15:08 -04:00
lcskrishna fc2c8de816 added host for float2half and hlaf2float 2018-09-06 15:02:52 -07:00
fpadmin 9ca3401f8b [HIP-Clang]Add friend class/function test 2018-09-05 11:48:49 +05:30
Yaxun Sam Liu 7d1492ab61 Let hipcc link -lpthread -lm by default 2018-09-04 17:11:47 -04:00
Yaxun Sam Liu 627c179612 Let hipcc handle obj files in linker response file for hip-clang
If obj files in linker response file contains device code, pass them to hip-clang, otherwise keep them in the linker
response file.
2018-09-04 16:57:55 -04:00
Yaxun (Sam) Liu 139d76a4db Document kernel launching for hip-clang 2018-09-04 16:56:53 -04:00
Yaxun (Sam) Liu cc0fbc0e2e Support placement new in hip-clang 2018-09-04 16:53:46 -04:00
Maneesh Gupta 0a02ae19dc Merge pull request #654 from ROCm-Developer-Tools/fix-force-inline
__forceinline__ needs inline and always_inline
2018-09-03 16:35:34 +05:30
Maneesh Gupta 6dfb6fac8b Merge pull request #657 from yxsamliu/fix-clz
Fix ambiguity of __clz and __clzll
2018-09-03 16:34:42 +05:30
Maneesh Gupta 0957130a52 Merge pull request #656 from searlmc1/msearles-fixes
Add keyword 'explicit' to avoid ambiguity
2018-09-03 16:33:41 +05:30
Maneesh Gupta d515998ac4 Merge pull request #651 from yxsamliu/hip-clang-clock
Add clock() and clock64()
2018-09-03 16:32:30 +05:30
Maneesh Gupta 75a010fa3c Merge pull request #649 from ROCm-Developer-Tools/yxsamliu-patch-3
Documents hip-clang predefined macros
2018-09-03 16:32:12 +05:30
Maneesh Gupta 11d1b8d310 Merge pull request #640 from aaronenyeshi/hip-clang-add-bit-funcs
Add bitextract and bitinsert functions
2018-09-03 16:31:42 +05:30
Yaxun Sam Liu 701519d27d Fix ambiguity of __clz and __clzll 2018-08-31 18:07:57 -04:00
Saleel Kudchadker 3684975b91 Fix record_event and hipStreamSync2 tests. The test should expect null stream to complete if synchrionize is called as per the spec 2018-08-31 12:54:23 -07:00
Mark Searles 992c90079b Add keyword 'explicit' to avoid ambiguity
Older gcc, e.g., 5.x, see an ambiguity in some calls. Example error
output as seen with gcc 5.5:

In file included from benchmark_wino.cpp:1:
In file included from ./miopen.hpp:13:
In file included from /usr/lib/gcc/x86_64-linux-gnu/5.5.0/../../../../include/c++/5.5.0/regex:38:
In file included from /usr/lib/gcc/x86_64-linux-gnu/5.5.0/../../../../include/c++/5.5.0/algorithm:62:
In file included from /usr/lib/gcc/x86_64-linux-gnu/5.5.0/../../../../include/c++/5.5.0/bits/stl_algo.h:66:
In file included from /usr/lib/gcc/x86_64-linux-gnu/5.5.0/../../../../include/c++/5.5.0/random:51:
/usr/lib/gcc/x86_64-linux-gnu/5.5.0/../../../../include/c++/5.5.0/bits/random.tcc:1324:27: error: call to 'abs' is ambiguous
                    const double __y = -std::abs(__n) * __param._M_sm - 1;
                                        ^~~~~~~~
/opt/rocm/hip/include/hip/hcc_detail/hip_complex.h:345:31: note: candidate function
__DEFINE_HIP_COMPLEX_REAL_FUN(abs, hipCabs)
2018-08-31 11:10:58 -07:00
Saleel Kudchadker b76c94afb9 Merge branch 'master' of https://github.com/ROCm-Developer-Tools/HIP into skudchad-hip 2018-08-31 10:38:41 -07:00
Mark Searles 37cc117bd5 Add keyword 'explicit' to avoid ambiguity
Older gcc, e.g., 5.x, see an ambiguity in some calls. Example error
output as seen with gcc 5.5:

In file included from benchmark_wino.cpp:1:
In file included from ./miopen.hpp:13:
In file included from /usr/lib/gcc/x86_64-linux-gnu/5.5.0/../../../../include/c++/5.5.0/regex:38:
In file included from /usr/lib/gcc/x86_64-linux-gnu/5.5.0/../../../../include/c++/5.5.0/algorithm:62:
In file included from /usr/lib/gcc/x86_64-linux-gnu/5.5.0/../../../../include/c++/5.5.0/bits/stl_algo.h:66:
In file included from /usr/lib/gcc/x86_64-linux-gnu/5.5.0/../../../../include/c++/5.5.0/random:51:
/usr/lib/gcc/x86_64-linux-gnu/5.5.0/../../../../include/c++/5.5.0/bits/random.tcc:1324:27: error: call to 'abs' is ambiguous
                    const double __y = -std::abs(__n) * __param._M_sm - 1;
                                        ^~~~~~~~
/opt/rocm/hip/include/hip/hcc_detail/hip_complex.h:345:31: note: candidate function
__DEFINE_HIP_COMPLEX_REAL_FUN(abs, hipCabs)
2018-08-31 10:36:05 -07:00
Maneesh Gupta 0b8e209532 Merge pull request #564 from phani544/hipClangClass8B
Adding class size>8bytes tests
2018-08-30 10:33:47 +05:30
Maneesh Gupta 9060955c89 Merge pull request #647 from tdd11235813/fix-cmake-build-name
Fixes build-name bug due to reversed string() arguments in cmake.
2018-08-30 10:32:39 +05:30