AI/rocm-systems
2
0
Garpu 0
Kode Masalah Tarik Permintaan Actions Packages Projects Rilis Wiki Kegiatan
4.111 Melakukan 3 Cabang 0 Tag
5c8a7521f41ab650e36ebd25e0ea5449e83d0e1e
Grafik Komit

4111 Melakukan

This Branch
This Branch
All Branches
Penulis SHA1 Pesan Tanggal
Michael LIAO 5c8a7521f4 [HIP] Correct headers and add missing function templates for hip-clang. 
- Fix 2 runtime API prototypes
  `hipOccupancyMaxActiveBlocksPerMultiprocessor` and
  `hipOccupancyMaxActiveBlocksPerMultiprocessorWithFlags`
- Add missing function templates of them in hip-clang.
 2019-10-29 22:00:11 -04:00
Rahul Garg 4d04baf0cd Merge pull request #1602 from ROCm-Developer-Tools/revert-1560-satyanveshd/hipoccupy 
Revert "Cooperative groups match with cuda SWDEV-205006"
 2019-10-29 16:54:36 -07:00
Evgeny Mankov 7d0a10cf00 Merge pull request #1604 from emankov/hipify 
[HIPIFY][#1603] Fix
 2019-10-29 22:12:39 +03:00
Evgeny Mankov 389b5ec957 [HIPIFY][#1603] Fix 2019-10-29 22:10:36 +03:00
Rahul Garg e4a1e44162 Revert "Fix occupany APIs (#1560)" 
This reverts commit af351d7e1b.
 2019-10-29 11:41:08 -07:00
Evgeny Mankov 265d34e160 Merge pull request #1601 from emankov/hipify 
[HIPIFY][Linux] Rollback --cuda-compile-host-device on Linux
 2019-10-29 20:55:29 +03:00
Evgeny Mankov 85087644da [HIPIFY][Linux] Rollback --cuda-compile-host-device on Linux 
[Reason] It doesn't work with LLVM 9 and higher; Windows is fine
 2019-10-29 20:53:54 +03:00
Evgeny Mankov 764a1f0023 Merge pull request #1600 from emankov/hipify 
[HIPIFY] Introduce --cuda-compile-host-device for LLVM >= 9
 2019-10-29 19:47:15 +03:00
Evgeny Mankov 3f2eefa82a [HIPIFY] Introduce --cuda-compile-host-device for LLVM >= 9 
* LLVM < 9 continues using --cuda-host-only
 2019-10-29 19:42:53 +03:00
Evgeny Mankov bce616e037 Merge pull request #1599 from emankov/hipify 
[HIPIFY] cudaMemcpy2DFromArray(Async) support
 2019-10-29 19:14:00 +03:00
Evgeny Mankov 315a10a59d [HIPIFY] cudaMemcpy2DFromArray(Async) support 2019-10-29 19:12:42 +03:00
Evgeny Mankov 542fa41a9a Merge pull request #1594 from emankov/HIP 
[HIP][doc] Fix typo: AMD-clang -> HIP-clang
 2019-10-28 23:22:57 +03:00
Evgeny Mankov 3a4165779a [HIP][doc] NVIDIA-nvcc -> HIP-nvcc 2019-10-28 22:46:33 +03:00
Evgeny Mankov 46b164c17a [HIP][doc] AMD-hcc -> HIP-hcc 2019-10-28 21:41:12 +03:00
Evgeny Mankov 06d9e426e0 [HIP][doc] Fix typo: AMD-clang -> HIP-clang 
HIP-clang is already used below instead of AMD-clang
 2019-10-28 21:19:21 +03:00
Evgeny Mankov 954d1847b2 Merge pull request #1590 from emankov/doc 
[HIPIFY][tests] Fix ambiguous call to cusparseGetErrorString declared in cusparse.h
 2019-10-25 16:08:22 +03:00
Evgeny Mankov 70c5072302 [HIPIFY][tests] Rename the ambiguous call as well 2019-10-25 16:07:31 +03:00
Evgeny Mankov 0410d5dcd2 [HIPIFY][tests] Fix ambiguous call to cusparseGetErrorString declared in cusparse.h 2019-10-25 16:04:20 +03:00
Alex Voicu dabd939048 Add missing operators, fix GCC compilation. (#1589) 2019-10-25 15:44:24 +05:30
Alex Voicu a855a13c22 Fix deadlock, remove old __sync_* use. (#1584) 
This fixes a deadlock introduced by the switch to TTAS loops, and is therefore mildly urgent (to prevent the CI from hoovering in the broken code).
 2019-10-25 15:44:17 +05:30
Rahul Garg 12e1a86ec1 [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.
 2019-10-25 15:44:05 +05:30
Rahul Garg 356765a223 Add hipMemcpy2DfromArray (#1510) 
Adds hipMemcpy2DFromArray and hipMemcpy2DFromArrayAsync equivalent to cudaMemcpy2DFromArray and cudaMemcpy2DFromArrayAsync.
 2019-10-25 15:43:33 +05:30
Rahul Garg 70f2cd1317 Update profiling doc (#1576) 2019-10-24 17:51:55 +05:30
Jatin Chaudhary 770d3412f8 Adding New Analyze Target Merging with cppcheck (#1583) 2019-10-24 17:46:06 +05:30
Rahul Garg 04e10814d8 Add HIP checks in texture driver sample (#1581) 2019-10-24 17:45:51 +05:30
gandryey 81952ce5a7 Hip vdi profiling header (#1577) 
Add HIP-VDI profiling interface for GPU timing collection.
 2019-10-24 17:45:42 +05:30
Alex Voicu 9ba25b42c8 Make CAS loops use the TTAS idiom. (#1573) 
* Make CAS loops use the TTAS idiom.

* More efficient re-formulation of TTAS.

* Fix typo.

* The typo was not quite a typo
 2019-10-24 17:45:20 +05:30
satyanveshd af351d7e1b Fix occupany APIs (#1560) 
Addresses SWDEV-205006
 2019-10-24 17:44:47 +05:30
searlmc1 c4a51f3679 Improve performance of v2 arg handling (#1539) 
* Improve performance of v2 arg handling

* Missing change to `std::string`
 2019-10-24 17:44:05 +05:30
Alex Voicu 4a635add45 Improve scalar access into vector types. (#1531) 
The improvement is based on the ideas here: https://t0rakka.silvrback.com/simd-scalar-accessor. It yields significantly better ISA when the base's .xyzw members are used.
 2019-10-24 17:43:49 +05:30
Aryan Salmanpour 359dc79101 [hip] add support for implicit kernel argument for multi-grid sync (#1456) 
* [hip] add support for implicit kernel argument for multi-grid sync

* modified code for calculating the prev_sum

* change the impCoopArg type to size_t

* add memory clean up

* launch init_gws and main kernels into two separate loops
 2019-10-24 17:43:30 +05:30
Rahul Garg fe5f7d4245 Merge pull request #1559 from vsytch/win10_aligned_alloc 
Fixes for hipMemcpy_simple on Windows
 2019-10-23 13:10:59 -07:00
Evgeny Mankov 29e04f99b5 Merge pull request #1578 from emankov/doc 
[HIPIFY][cmake][#1571] Take into account building hipify-clang as a part of building HIP while installing
 2019-10-23 21:23:05 +03:00
Evgeny Mankov 75d70a6714 [HIPIFY][cmake][#1571] Take into account building hipify-clang as a part of building HIP while installing 
[Algorithm]
  [Release]
    If CMAKE_INSTALL_PREFIX is set by the user:
       If BIN_INSTALL_DIR is set by HIP, use it as CMAKE_INSTALL_PREFIX, otherwise CMAKE_INSTALL_PREFIX is used unchanged.
    If the user does not set CMAKE_INSTALL_PREFIX (CMAKE_INSTALL_PREFIX_INITIALIZED_TO_DEFAULT):
       If BIN_INSTALL_DIR is set by HIP, use it as CMAKE_INSTALL_PREFIX, otherwise use PROJECT_BINARY_DIR/bin for installation.
  [Debug]
    If CMAKE_INSTALL_PREFIX is set by the user:
       CMAKE_INSTALL_PREFIX is used unchanged.
    If the user does not set CMAKE_INSTALL_PREFIX (CMAKE_INSTALL_PREFIX_INITIALIZED_TO_DEFAULT):
       use CMAKE_CURRENT_SOURCE_DIR/bin for installation.

Standalone build left unchanged: CMAKE_INSTALL_PREFIX is used if set.
 2019-10-23 18:54:45 +03:00
Evgeny Mankov cc9efa707c Merge pull request #1574 from emankov/hipify-clang 
[HIPIFY] Disable delayed template parsing
 2019-10-22 19:09:13 +03:00
Evgeny Mankov b6e6f12b54 [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.
 2019-10-22 19:07:37 +03:00
Evgeny Mankov 76c8406449 Merge pull request #1570 from emankov/doc 
[HIPIFY][#1569] Fix
 2019-10-22 11:13:47 +03:00
Evgeny Mankov 6f88c81a78 [HIPIFY][#1569] Fix 2019-10-22 11:08:37 +03:00
Evgeny Mankov 239fb0a098 Merge pull request #1568 from emankov/hipify-clang 
[HIPIFY][tests] Set max clang's CudaArch for corresponding CUDA major…
 2019-10-21 17:52:02 +03:00
Evgeny Mankov 39e7d213cf [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.
 2019-10-21 17:50:00 +03:00
Evgeny Mankov 2ddde17039 Merge pull request #1567 from emankov/hipify-clang 
[HIPIFY][perl] Support of 'using namespace cub'
 2019-10-21 17:16:32 +03:00
Evgeny Mankov b08f29a6fa [HIPIFY][perl] Support of 'using namespace cub' 2019-10-21 17:15:05 +03:00
Evgeny Mankov 1caeb5613d Merge pull request #1566 from emankov/hipify-clang 
[HIPIFY][tests] Set max clang's CudaArch for corresponding CUDA version
 2019-10-21 15:54:34 +03:00
Evgeny Mankov 14b4df126c [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)
 2019-10-21 15:51:25 +03:00
Evgeny Mankov abb34bab8e Merge pull request #1565 from emankov/hipify-clang 
[HIPIFY][tests] Set -I for CUDA path instead of --cuda-path for LLVM < 4
 2019-10-20 20:10:25 +03:00
Evgeny Mankov 6cfea9b600 [HIPIFY][tests] Set -I for CUDA path instead of --cuda-path for LLVM < 4 2019-10-20 20:08:56 +03:00
Evgeny Mankov 7fb633bcc7 Merge pull request #1564 from emankov/hipify-clang 
[HIPIFY][tests] Exclude all CUB tests if CUDA_CUB_ROOT_DIR is not set
 2019-10-20 20:04:18 +03:00
Evgeny Mankov ccb075b1db [HIPIFY][tests] Exclude all CUB tests if CUDA_CUB_ROOT_DIR is not set 2019-10-20 20:03:18 +03:00
Vladislav Sytchenko 664b115c44 Remove extra #endif. 2019-10-18 16:40:29 -04:00
Evgeny Mankov 3baf7f8d93 Merge pull request #1562 from emankov/doc 
[HIPIFY][CUB][#1460] Add "using namespace cub" translation support
 2019-10-18 18:56:34 +03:00