AI/rocm-systems
2
0
Fork 0
Code Issues Pull Requests Actions Packages Projects Releases Wiki Activity
5,651 Commits 3 Branches 0 Tags
9f81811fd2efc9ab731bf22f3cd660243fa2c310
Commit Graph

4937 Commits

Author SHA1 Message Date
foreman 0da954f20e P4 to Git Change 1778949 by michliao@hliao-dev-00-hip.rocm-workspace on 2019/05/06 16:36:53 
SWDEV-144570 - Fix build failure after switching to gcc-7

	- Hex representation of float needs gnu++11. We'd better not relying on
	  that. Change the float in hex format into alternative representation.

	RBT: http://ocltc.amd.com/reviews/r/17300/

Affected files ...

... //depot/stg/opencl/drivers/opencl/api/hip/hip_platform.cpp#29 edit
 2019-05-06 17:20:00 -04:00
Maneesh Gupta 2f43f110d9 Implement hipExtGetLinkTypeAndHopCount for ROCm devices 
Change-Id: Ie5bb4f640ac6d189c7fceeab22627a7494fd10bd
 2019-05-06 15:54:31 +05:30
Michael LIAO 32f69c8bc4 [test] Add device variant of std::declval. 
- Current clang disallows any invocation of wrong-side functions even
  under context with type-inspection only. Work around that by adding a
  variant of `std::decl` with `__device__` attribute.
 2019-05-03 15:58:31 -04:00
Michael LIAO a27877794f [test] Use explicit cast for address space cast. 2019-05-03 14:56:00 -04:00
Maneesh Gupta 2eafa5dcf9 Merge pull request #1062 from mhbliao/hliao/master/icmp 
[hip] Re-implement ballot using AMDGCN builtins
 2019-05-03 17:48:19 +05:30
Maneesh Gupta ad070d4da5 Merge pull request #1058 from mhbliao/hliao/master/devfunc 
[Device Function] Fix implementation
 2019-05-03 17:47:51 +05:30
Konstantin Pyzhov e04e408a37 hipMultiThreadDevice test: Reduced maximum number of created HIP streams on Windows. 2019-05-03 05:43:30 -04:00
Konstantin Pyzhov 29fd3812e5 Refined hipSetDevice test. 2019-05-03 05:39:45 -04:00
Michael LIAO aad19f6171 [test] Remove unused common routines. 
- Remove used common routines, which variadic functions, not supported
  feature, are used.
 2019-05-02 12:34:07 -04:00
Michael LIAO a9f90713f3 [devfunc] Add necessary __device__ and __host__ attributes. 
- Minor clean up to keep consistent function declaration.
 2019-05-01 22:26:35 -04:00
foreman b39d02b166 P4 to Git Change 1777225 by cpaquot@cpaquot-ocl-lc-lnx on 2019/05/01 18:47:25 
SWDEV-188233 - [HIP] Implemented hipGetChannelDesc.

Affected files ...

... //depot/stg/opencl/drivers/opencl/api/hip/hip_texture.cpp#11 edit
 2019-05-01 19:53:29 -04:00
foreman ef45e9ab42 P4 to Git Change 1777158 by cpaquot@cpaquot-ocl-lc-lnx on 2019/05/01 17:12:01 
SWDEV-188219 - [HIP] Add hipStreamCreateWithPriority. NOP right now.

Affected files ...

... //depot/stg/opencl/drivers/opencl/api/hip/hip_device_runtime.cpp#14 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_hcc.def.in#13 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_hcc.map.in#14 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_stream.cpp#17 edit
... //depot/stg/opencl/drivers/opencl/runtime/platform/commandqueue.hpp#21 edit
 2019-05-01 18:43:47 -04:00
emankov d5c3e5ea71 [HIPIFY][tests] Add cuSPARSE CSR-BCSR-SPMV-conversions example 2019-04-30 17:37:34 +03:00
Michael LIAO 2380eb8ecc [Device Function] Fix implementation of __bitinsert_u64 
- It's a common mistake by assuming 1 << shamt would be promoted to
  64-bit, if shamt is a 64-bit integer. That's not the case. Replace
  that left shift to a 64-bit one to ensure it won't fall into undefined
  behavior.
- Fix the host-side implementation as well for device function testing.
 2019-04-30 08:59:13 -04:00
Michael LIAO a7a4d80f54 [devfunc] Re-implement ballot using AMDGCN builtins 
- As the signature of `amdgcn.icmp` is changed for next-gen chip, using
  clang builtins is portable way to hide that details.
 2019-04-29 17:21:25 -04:00
Michael LIAO 92f90c3651 [hipcc] Repace --rpath with --rpath-link 
- With `--rpath`, app's RUNPATH is set to the temporary library path
  during build. Instead, `--rpath-link` should be used to leave RUNPATH
  untouched. User should set LD_LIBRARY_PATH or system ld.so.conf to
  proper setting.
 2019-04-29 16:01:16 -04:00
foreman 7101fd9ed2 P4 to Git Change 1775995 by gandryey@gera-w8 on 2019/04/29 13:46:53 
SWDEV-79445 - OCL generic changes and code clean-up
	- Enable P2P extension for PAL path, currently it's staging copy only
	- Fix P2P staging copy

Affected files ...

... //depot/stg/opencl/drivers/opencl/api/hip/hip_memory.cpp#55 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/device.cpp#243 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/device.hpp#336 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/paldevice.cpp#130 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palsettings.cpp#77 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palvirtual.cpp#131 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palvirtual.hpp#59 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocdevice.cpp#124 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocdevice.hpp#36 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocvirtual.cpp#74 edit
... //depot/stg/opencl/drivers/opencl/runtime/platform/command.cpp#92 edit
 2019-04-29 13:58:26 -04:00
Evgeny Mankov 116daa3a1f [HIPIFY][doc] Update Readme.md: latest cuDNN 7.5.1.10 is supported 
+ tested with CUDA 9.0, 9,2, 10.0 and 10.1
 2019-04-29 15:41:08 +03:00
Aaron Enye Shi 235c6877c8 Revert "Use COMgr to read Kernel Args Metadata (#1006)" 
This reverts commit 2c80975e9c.
 2019-04-26 16:04:56 -04:00
Aaron Enye Shi acfa46bbbc Revert "Add COMGR relative path for build machines" 
This reverts commit 6b3095f7cb.
 2019-04-26 16:04:56 -04:00
Aaron Enye Shi 2378c7a20b Revert "Add dependency on amd_comgr in hip-config-*.cmake.in" 
This reverts commit b8fe5ba572.
 2019-04-26 16:04:56 -04:00
foreman 33ebadc935 P4 to Git Change 1775366 by kjayapra@99_HIPWS_SLV_CHECKIN on 2019/04/26 14:48:23 
SWDEV-144570 - hipFuncGetAttributes() API changes.

Affected files ...

... //depot/stg/opencl/drivers/opencl/api/hip/hip_internal.hpp#29 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_module.cpp#23 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_platform.cpp#28 edit
 2019-04-26 15:15:48 -04:00
Maneesh Gupta b8fe5ba572 Add dependency on amd_comgr in hip-config-*.cmake.in 
Change-Id: Iac1d851a8cfb99224e9c5926780273d9b9b08426
 2019-04-25 15:26:33 -04:00
Sameer Sahasrabuddhe c74a97f756 minor cleanup: eliminate repetition 2019-04-25 20:41:16 +05:30
Evgeny Mankov f0c2fdc6d7 [HIPIFY][perl][fix][258] Memory fence device functions are supported now 2019-04-25 13:27:30 +03:00
Evgeny Mankov 72a809caf6 [HIPIFY][DNN] cudnnSetFilter4dDescriptor support 2019-04-25 12:18:51 +03:00
Evgeny Mankov df9418c3cd [HIPIFY][fix][#204] Suppress warning message: #pragma once in main file 2019-04-24 20:35:52 +03:00
Evgeny Mankov 1049031d98 [HIPIFY][doc] Update README.md 
+ A few words about clang patches to work with CUDA 9.2 - 10.0 on Windows;
+ Fix cuDNN versions with correct values.
 2019-04-24 17:40:35 +03:00
Maneesh Gupta 7f81c72f1c Merge pull request #1043 from mhbliao/hliao/master/fp16 
[hip] Fix including of hip_fp16.h
 2019-04-24 16:50:46 +05:30
Maneesh Gupta 63ab2ea945 Merge pull request #1042 from mhbliao/hliao/master/ldg 
[hip] Fix use of `__HIP_CLANG_ONLY__` in `hip_ldg.h`.
 2019-04-24 16:50:37 +05:30
Maneesh Gupta 54cdeabe6e Merge pull request #1040 from eshcherb/roctracer-hip-frontend-190422 
hip_prof_api.h include under __cplusplus
 2019-04-24 16:50:27 +05:30
Maneesh Gupta 7edb43bc83 Merge pull request #1039 from gargrahul/fix_ptrgetattr_nvcc 
Fix hipPointerGetAttributes for NVCC
 2019-04-24 16:50:18 +05:30
Rahul Garg 94769fc8dd Add hipMallocManaged default functional support (#1036) 
* Add hipMallocManaged default functional support

* Fix build error

* Add dtest
 2019-04-24 16:50:03 +05:30
Maneesh Gupta 61861faddc Merge pull request #1034 from kpyzhov/master 
Minor fixes for 64-bit device functions.
 2019-04-24 16:49:36 +05:30
Maneesh Gupta 3ac21336eb Merge pull request #1031 from yxsamliu/fix-init 
Fix missing arg in HIP_INIT_API
 2019-04-24 16:49:23 +05:30
Maneesh Gupta 3ba7afcfc1 Merge pull request #1028 from gargrahul/fix_d2d_async_test 
[dtest] Fix D2DAsync test
 2019-04-24 16:49:13 +05:30
Aaron Enye Shi 6b3095f7cb Add COMGR relative path for build machines 2019-04-23 17:16:26 -04:00
Evgeny Mankov 87fa81f7be [HIPIFY][doc] Provide patches for clang's bug 38811 
+ Update Readme.md accordingly
 2019-04-23 21:13:00 +03:00
Evgeny Mankov 65dd1d4c7d [HIPIFY][hipify-perl] Formatting 2019-04-23 17:55:47 +03:00
Michael LIAO d086dbd0e5 [hip] Fix including of hip_fp16.h 
- Separate the definition of `__HCC_OR_HIP_CLANG__`, `__HCC_ONLY__`, and
  `__HIP_CLANG_ONLY__` into hip_common.h so that it could be included in
  hip_fp16.h, which may be included separately in app.
 2019-04-23 09:16:00 -04:00
Michael LIAO ca6a5c07eb [hip] Fix use of __HIP_CLANG_ONLY__ in hip_ldg.h. 
- Check its value instead of whether it's defined or not.
 2019-04-22 23:22:32 -04:00
Evgeny 165c42483b hip_prof_api.h include under __cplusplus 2019-04-22 21:14:18 -05:00
Rahul Garg c0e0f0b7fd Fix hipPointerGetAttributes for NVCC 2019-04-23 03:22:25 +05:30
foreman b07f3f0de7 P4 to Git Change 1772785 by cpaquot@cpaquot-ocl-lc-lnx on 2019/04/22 14:31:18 
SWDEV-144570 - [HIP] Lazy build kernels to avoid overfilling dev memory.

Affected files ...

... //depot/stg/opencl/drivers/opencl/api/hip/hip_internal.hpp#28 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_platform.cpp#27 edit
 2019-04-22 15:19:24 -04:00
foreman 02b4ec115b P4 to Git Change 1772349 by mshivama@mshivama_tf on 2019/04/20 07:35:24 
SWDEV-187020 - Basic "Hello World" Tensorflow program fails to execute on HIP/VDI/PAL/LINUX

	Make sure that the size of `dest` is big enough to hoid `src` including trailing zero byte

Affected files ...

... //depot/stg/opencl/drivers/opencl/api/hip/hip_device.cpp#19 edit
 2019-04-21 21:50:04 -04:00
foreman 4538956a99 P4 to Git Change 1772193 by mshivama@mshivama_tf on 2019/04/19 09:39:39 
SWDEV-187020 -  Basic "Hello World" Tensorflow program fails to execute on HIP/VDI/PAL/LINUX

	the API hiDeviceGetName() should pass the length of device name as argument to strncpy() instead
	of total (dest) memory size which is being passed to it by its caller. Also, bit of a code clean-up.

Affected files ...

... //depot/stg/opencl/drivers/opencl/api/hip/hip_device.cpp#18 edit
 2019-04-19 09:49:37 -04:00
Konstantin Pyzhov f6fbf8751d Fix for __popcll() device function implementation. 2019-04-19 08:53:22 -04:00
Yaxun (Sam) Liu 710e633bdd Fix missing arg in HIP_INIT_API 2019-04-18 16:18:31 -04:00
Konstantin Pyzhov 5664ed3206 Fix for __ffsll() device functions. 2019-04-18 13:07:24 -04:00
foreman 8b60833e6e P4 to Git Change 1771752 by cpaquot@cpaquot-ocl-lc-lnx on 2019/04/18 11:54:18 
SWDEV-145570 - [HIP] Use isAsync flag for async cases.

Affected files ...

... //depot/stg/opencl/drivers/opencl/api/hip/hip_memory.cpp#54 edit
 2019-04-18 12:15:25 -04:00