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

895 Commits

Author SHA1 Message Date
Rahul Garg cf648f7dbe Rename hip/hip_hcc.h to hip/hip_ext.h (#1341) 
* Rename hip/hip_hcc.h to hip/hip_ext.h

* Deprecate hip_hcc.h


[ROCm/clr commit: dfee3ae279]
 2019-11-07 13:17:10 +05:30
Evgeny Mankov ecad81b794 Merge pull request #1624 from emankov/hipify 
[HIPIFY][#1409] Fix for kernel launch macro expansion

[ROCm/clr commit: cf5d1caab3]
 2019-11-05 14:04:51 +03:00
Evgeny Mankov 3889be3031 [HIPIFY][#1409] Fix for kernel launch macro expansion 
+ Add a corresponding test kernel_launch_01.cu
+ Add isBefore() check to avoid crash on Replacement with negative length

TODO:
+ Compatibility with former LLVM versions
+ More complicated kernel launch tests


[ROCm/clr commit: a1c380f38d]
 2019-11-05 14:00:13 +03:00
Aryan Salmanpour 92a06b531d [hip][tests] Add two more workgroup sizes for testing hipLaunchCooperativeKernel (#1613) 
[ROCm/clr commit: 7a3d592ed0]
 2019-11-05 12:32:46 +05:30
Rahul Garg 2cf205bc7b Merge pull request #1582 from amd-lthakur/hipExtMLK 
Adding a directed test case for hipExtModuleLaunchKernel() api.

[ROCm/clr commit: 1bec1445bb]
 2019-10-31 17:13:26 -07:00
Rahul Garg 31fc374120 Formatting changes 
[ROCm/clr commit: 07f4431de8]
 2019-10-30 18:12:51 -07:00
Rahul Garg 5bcc1f66c5 Formatting changes ,variable name and check update 
[ROCm/clr commit: cd1435cbc7]
 2019-10-30 18:09:21 -07:00
Rahul Garg 04785f2d54 Merge pull request #1515 from ansurya/tex_unbind_issue_fix 
Fix undefined ref to hipUnbindTexture for texture types

[ROCm/clr commit: aeb7cebbad]
 2019-10-30 17:54:15 -07:00
Rahul Garg 72c686ed67 Revert "Fix occupany APIs (#1560)" 
This reverts commit ad1e409a24.


[ROCm/clr commit: 27221bc823]
 2019-10-29 11:41:08 -07:00
Evgeny Mankov bcc9d88b20 [HIPIFY][tests] Rename the ambiguous call as well 
[ROCm/clr commit: f68bee02f5]
 2019-10-25 16:07:31 +03:00
Evgeny Mankov 91732f98c0 [HIPIFY][tests] Fix ambiguous call to cusparseGetErrorString declared in cusparse.h 
[ROCm/clr commit: 9529e1d91d]
 2019-10-25 16:04:20 +03:00
Anusha Godavarthy Surya dfa019bdf6 Merge branch 'master' into tex_unbind_issue_fix 
[ROCm/clr commit: 9332a39838]
 2019-10-25 15:54:25 +05:30
amd-lthakur 6bb2cba965 Excluded the test case for nvcc platform 
[ROCm/clr commit: 626cd5d07a]
 2019-10-25 15:52:11 +05:30
Anusha Godavarthy Surya 0140ea8e1a merge from master 
[ROCm/clr commit: ae838f8cee]
 2019-10-25 15:52:09 +05:30
Rahul Garg 9c599a3581 [dtest] Fix hipMemset2D test (#1579) 
Reverts changes made in #1399. This is a RT api test. For testing hipMemAllocPitch , a new test should be written and that should use correct memset API.

[ROCm/clr commit: 66a3c874c8]
 2019-10-25 15:44:05 +05:30
Anusha Godavarthy Surya 2d538b702d Merge branch 'master' into tex_unbind_issue_fix 
[ROCm/clr commit: c0fc5e718c]
 2019-10-25 15:36:55 +05:30
amd-lthakur 796566f156 Refactored the file as suggested 
[ROCm/clr commit: b2238bacd4]
 2019-10-25 10:44:38 +05:30
amd-lthakur 40c7970293 Update matmul.cpp 
[ROCm/clr commit: 84fb936dfe]
 2019-10-25 09:22:07 +05:30
amd-lthakur 42fe3f5247 Update hipExtModuleLaunchKernel.cpp 
[ROCm/clr commit: 9a860e6766]
 2019-10-25 09:19:49 +05:30
satyanveshd ad1e409a24 Fix occupany APIs (#1560) 
Addresses SWDEV-205006 

[ROCm/clr commit: 6c5fbf9b4a]
 2019-10-24 17:44:47 +05:30
amd-lthakur 5189d287eb Adding a directed test case for hipExtModuleLaunchKernel() api. 
[ROCm/clr commit: 0adcc890b0]
 2019-10-24 15:06:28 +05:30
Rahul Garg 764135d242 Merge pull request #1559 from vsytch/win10_aligned_alloc 
Fixes for hipMemcpy_simple on Windows

[ROCm/clr commit: 465581612e]
 2019-10-23 13:10:59 -07:00
Evgeny Mankov 0896e41987 [HIPIFY] Disable delayed template parsing 
By implicit unconditional passing -fno-delayed-template-parsing option (which appeared in LLVM 3.8.0, thus doesn't need compatibility wrapping) to hipify-clang.

[Reason] To parse uncalled template functions otherwise they are not parsed without calling, thus not hipified.

Affects cub_03.cu test, which has uncalled global template function.


[ROCm/clr commit: 7ab06b3892]
 2019-10-22 19:07:37 +03:00
Evgeny Mankov 82222bf945 [HIPIFY][#1569] Fix 
[ROCm/clr commit: e2191e23e6]
 2019-10-22 11:08:37 +03:00
Evgeny Mankov e3cf10192c [HIPIFY][tests] Set max clang's CudaArch for corresponding CUDA major.minor version 
[Reason] To support maximum CUDA features in offline tests

+ Add defined(__CUDA_ARCH__) && __CUDA_ARCH__ >= 600 restriction for atomicAdd on doubles in atomics.cu.
  So if LLVM < 7 and --cuda-gpu-arch doesn't work, __CUDA_ARCH__ is unset too (350 by default in clang);
  if LLVM >= 7 --cuda-gpu-arch is used and __CUDA_ARCH__ is set based on it.


[ROCm/clr commit: 3233a845f6]
 2019-10-21 17:50:00 +03:00
Evgeny Mankov 665a200247 [HIPIFY][tests] Set max clang's CudaArch for corresponding CUDA version 
[Reason] To support maximum CUDA features in offline tests

+ Add CUDA_VERSION >= 800 restriction for atomics.cu

[TODO] Find a way to use or exclude atomicAdd for doubles if LLVM < 7, because
LLVM 6.0.1 and older do not use --cuda-gpu-arch in clang's Driver code at all (option is only declared)


[ROCm/clr commit: 9fc7afa738]
 2019-10-21 15:51:25 +03:00
Evgeny Mankov 3a45daed0a [HIPIFY][tests] Set -I for CUDA path instead of --cuda-path for LLVM < 4 
[ROCm/clr commit: ff6057d1ff]
 2019-10-20 20:08:56 +03:00
Evgeny Mankov e07be75489 [HIPIFY][tests] Exclude all CUB tests if CUDA_CUB_ROOT_DIR is not set 
[ROCm/clr commit: 5bf1ff19ff]
 2019-10-20 20:03:18 +03:00
Vladislav Sytchenko 33acfa17c1 Remove extra #endif. 
[ROCm/clr commit: 432380aa5d]
 2019-10-18 16:40:29 -04:00
Evgeny Mankov bb20336fa6 [HIPIFY][tests] Test clean-up 
[ROCm/clr commit: 44a897a146]
 2019-10-18 18:55:52 +03:00
Evgeny Mankov 85281b1d86 [HIPIFY][CUB][#1460] Add "using namespace cub" translation support 
+ Add cub_03.cu


[ROCm/clr commit: 86f6756b02]
 2019-10-18 18:51:40 +03:00
Vladislav Sytchenko 54eddfc8f0 _aligned_malloc() on Windows first takes size, then alignment, which is the opposite of how the similar function behaves on Linux. Memory allocated by it also has to be freed using _aligned_free(), unlike Linux where we can use regular free(). 
Edit aligned_alloc() macro and add a aligned_free() one to align with the above behaviour.


[ROCm/clr commit: f4440817cb]
 2019-10-17 18:58:32 -04:00
Rahul Garg 685a4cd182 Merge pull request #1544 from vsytch/master 
QoL changes to the hipMemset family

[ROCm/clr commit: a21fe1443b]
 2019-10-16 18:54:20 -07:00
Evgeny Mankov b357301610 [HIPIFY][CUB][#1460] Add cub:: namespace support in TemplateInstantiation of cudaLaunchKernel 
+ Update cub_02.cu test accordingly


[ROCm/clr commit: e557563947]
 2019-10-16 19:02:13 +03:00
Vladislav Sytchenko 577bac5de8 hipMemset2D and hipMemset3D tests should be passing by default. 
[ROCm/clr commit: 86d0c5fa5a]
 2019-10-16 11:02:38 -04:00
Evgeny Mankov 643a8bcf5b [HIPIFY][CUB][#1460] Implement cubFunctionTemplateDecl matcher 
+ Add cub_02.cu test
+ Partial fixes #1460


[ROCm/clr commit: 5555d46e66]
 2019-10-16 13:08:11 +03:00
vsytch 4b8d8034cf Update hipMathFunctions, hipTestHalf and hipTestNativeHalf tests to support Navi10 and Navi14. (#1545) 
[ROCm/clr commit: c2aadd4d12]
 2019-10-16 10:51:48 +05:30
Vladislav Sytchenko 2bc49fb55c In the hipMemset2D and hipMemset3D tests synchronize with the default stream after performing an async memset. 
[ROCm/clr commit: cc5abec092]
 2019-10-15 17:15:49 -04:00
Vladislav Sytchenko 91ceb7dd2b Update indentation in the hipMemset3D test. Replace all tabs with four spaces. 
[ROCm/clr commit: f402b6d01a]
 2019-10-15 15:29:14 -04:00
Vladislav Sytchenko d20c5251b1 Add async subtest to hipMemSet3D 
[ROCm/clr commit: c83b6adb33]
 2019-10-15 14:24:04 -04:00
Vladislav Sytchenko e6f426dee3 hipMemset2D test should pass only if both async and sync subtests pass. 
[ROCm/clr commit: 39e42d4056]
 2019-10-15 14:20:14 -04:00
Evgeny Mankov 4b0e9e9f05 [HIPIFY][tests] Exclude tests for the libs, which are not defined in cmake command line 
+ affects cuDNN and CUB tests, paths to libraries of which are defined by CUDA_DNN_ROOT_DIR and CUDA_CUB_ROOT_DIR
+ Warn about excluding and why, for instance:
  "WARN: cuDNN tests are excluded due to unset CUDA_DNN_ROOT_DIR"


[ROCm/clr commit: c0f7d02ced]
 2019-10-15 14:20:23 +03:00
Anusha Godavarthy Surya 712b6ccdc2 Added unbind texture to samples and tests 
[ROCm/clr commit: 20cfe17805]
 2019-10-15 11:34:15 +05:30
Evgeny Mankov cb245f763e [HIPIFY][CUB] Add missing unit test 
[ROCm/clr commit: 0dfe8423e7]
 2019-10-14 12:03:20 +03:00
Evgeny Mankov e066bba058 [HIPIFY][CUB] Initial support (hipify-clang only) 
+ Add one matcher (will be more)
+ Update Maps and Statistics
+ Add cub_01.cu unit test
+ Update lit harness to support standalone CUB
+ Update README.md
+ Update hipify-perl (only CUB header is supported for now)

[IMPORTANT]
clang (and hipify-clang) works correctly only with official NVLabs version on GitHub.
Compilation of CUB from official CUDA release has conflicts with THRUST.
Thus, to compile CUB sources, option "-I" should be specified to the cloned CUB from NVLAB on GitHub.


[ROCm/clr commit: 97df38903a]
 2019-10-14 11:55:55 +03:00
Jatin Chaudhary 90caf746e5 Re enable test RTC (#1516) 
Adding target resolution in hiprtc tests and reenable them.

[ROCm/clr commit: 444177ffac]
 2019-10-10 19:59:55 +05:30
ansurya 0abb25a2fe Fix for directed tests failure (#1511) 
directed_tests/runtimeApi/module/hipLaunchCooperativeKernel.tst - Disabling test temporarily until driver support is available.
directed_tests/runtimeApi/memory/hipArray.tst - Disabling test temporarily to reimplement it correctly.

[ROCm/clr commit: 9bb22c4e0f]
 2019-10-10 19:58:41 +05:30
Evgeny Mankov 0219b7c05d [HIPIFY][test] Update allocators.cu test 
[ROCm/clr commit: e3319acbf8]
 2019-10-10 17:20:41 +03:00
Anusha Godavarthy Surya c5fc879606 Fix undefine ref to hipUbindTexture for texture types 
[ROCm/clr commit: a5d9f56bef]
 2019-10-09 16:26:06 +05:30
Evgeny Mankov 808f59cd1c [HIPIFY][#1487][fix] Translate correctly kernel names prefixed with namespace 
+ Modify CUDA2HIP_perl for the fix
+ Add ns_kernel_launch.cu test
+ Update hipify-perl by hipify-clang -perl


[ROCm/clr commit: 4a2d87b70c]
 2019-10-08 15:58:48 +03:00