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

5367 Commits

This Branch
This Branch
All Branches
Author SHA1 Message Date
Aryan Salmanpour 75572a4175 code clean up 2020-01-31 13:08:25 -05:00
Laurent Morichetti 2f1305b9a4 Merge branch 'origin/pghafari/hip-vdi' into lmoriche/amd-master-next 
Change-Id: I22c145d39f430ca571a981687bcb034ea6e3b8a2
 2020-01-31 07:33:12 -08:00
jujiang-del cb632005bc [dtest] Avoid resViewDesc for non-array resource in texture creation (#1823) 2020-01-30 14:04:41 -08:00
Aryan Salmanpour 6db9b782be [HIP][HIPIFY] Add some missing flags for cooperative launch and occupancy APIs 2020-01-30 15:05:53 -05:00
Evgeny Mankov f1c70ea6ba Merge pull request #1700 from scchan/object_load_error_check 
add error checking for code object loading
 2020-01-30 21:31:03 +03:00
Laurent Morichetti 6f3e18a764 Merge HIP/VDI branch 'amd-staging' into lmoriche/amd-master-next 
Change-Id: Iabaab4e72815ba483a1330ec6a1130f2b86676f0
 2020-01-29 15:02:13 -08:00
satyanveshd 262ad13dd5 Match Occupancy APIs syntax with CUDA (#1625) 
* Match Occupancy APIs syntax with CUDA and fix tests using these APIs
 2020-01-29 13:05:53 -08:00
vsytch 6da0c82b78 Add missing texturePitchAlignment member to the hipDeviceProp_t struct. (#1802) 
* Add missing texturePitchAlignment member to the hipDeviceProp_t struct.

* Add missing hipDeviceAttributeTexturePitchAlignment enumerator to the hipDeviceAttribute_t enum.

* Initialize texturePitchAlignment to 256. This works for gfx9+, but is technically overaligned in most cases for pre-gfx9.

* Add the texturePitchAlignment property to the NVCC path.
 2020-01-27 16:37:00 -08:00
Evgeny Mankov e419d738e7 Merge pull request #1820 from emankov/HIP 
[HIPIFY] Update Readme.md
 2020-01-27 17:23:06 +03:00
Evgeny Mankov 5a788eb048 [HIPIFY] Update Readme.md 
Restructure contents in order to have separated same-level information about hipify-clang and hipify-perl.
 2020-01-27 17:21:32 +03:00
Evgeny Mankov 37da8171bc Merge pull request #1813 from emankov/HIP 
[HIP][HIPIFY] Readmes actualization
 2020-01-27 12:50:48 +03:00
Evgeny Mankov 5fae88f84b [HIPIFY][#1819] Fix for not found clang's system header files 
Use absolute paths instead of relative ones.
 2020-01-27 12:37:26 +03:00
Evgeny Mankov e57c2b3147 Merge branch 'master' of https://github.com/ROCm-Developer-Tools/HIP into HIP 2020-01-27 12:08:22 +03:00
vsytch e419a1609f Update the HIP_TRSF_* flags to match their Cuda equivalents. (#1801) 2020-01-24 11:41:15 -08:00
Evgeny Mankov 2b77ca7d2e Merge branch 'master' of https://github.com/ROCm-Developer-Tools/HIP into HIP 2020-01-24 16:14:16 +03:00
aakanksha555 ef3dbc1f91 Fix for a syntax error in deb packages (#1814) 2020-01-24 16:23:47 +05:30
mshivama 0605426049 SWDEV-220503: this_grid().thread_rank() gives incorrect result (#1808) 
* fix a minor bug while computing this.grid()::thread_rank()
 2020-01-24 16:23:28 +05:30
paulfreddy 5cd5c62f29 Fix install script syntax error (#1805) 
Fix hip-nvcc install warning on postinstall and prerm script
 2020-01-24 16:22:57 +05:30
Siu Chi Chan 8fc7cad90f Fix associate code object symbols with host allocation bug (#1799) 
The current implementation skips this procedure for a given device
object when a global symbol is found in the cache.  This is incorrect:

 - There could be other undefined globals that have not been previously
encountered further down the list
 - If a symbol is found in the cache, it doesn't need to be pinned again
but it still need to be defined for the current executable

Added special case for the printf buffer symbol (already pinned by HCC)

The bug was exposed by running printf on different GPUs.
 2020-01-24 16:22:49 +05:30
Alexey Chernov 9f5a4148ce Clear HIP_PATH before version detection (#1786) 
Don't allow `HIP_PATH` to be propagated to `hipconfig`,
when run by CMake to detect the package version, as it
leads to the wrong version is detected: when there's
already HIP of some different version installed in the
system and `HIP_PATH` points to its location, `hipconfig`
tends to return the version of the installed HIP, rather
than the value defined for the distribution. The compiled
results report wrong version and spoils the rest of the
stack in this case.
 2020-01-24 16:21:49 +05:30
foreman 1fe8cc8a7e P4 to Git Change 2062258 by cpaquot@cpaquot-ocl-lc-lnx on 2020/01/23 16:04:59 
SWDEV-145570 - [hip] hipMallocManaged
	Basic implementation of hipMallocManaged behaving like hipHostMalloc for hipMemAttachGlobal.
	Return hipErrorInvalidValue for the hipMemAttachHost for now.

Affected files ...

... //depot/stg/opencl/drivers/opencl/api/hip/hip_hcc.def.in#39 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_hcc.map.in#37 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_memory.cpp#97 edit
 2020-01-23 16:13:57 -05:00
Evgeny Mankov 0a380694c5 [HIP][HIPIFY] Readmes actualization 2020-01-23 20:55:10 +03:00
Evgeny Mankov 9f40056297 Merge pull request #1812 from emankov/HIP 
[HIPIFY][doc] Readme - update versions
 2020-01-23 18:04:39 +03:00
Evgeny Mankov 85b76bac70 [HIPIFY][doc] Readme - update versions 2020-01-23 18:01:48 +03:00
Evgeny Mankov ea9307b60b Merge pull request #1811 from emankov/HIP 
[HIPIFY][cmake] Formatting
 2020-01-23 17:48:52 +03:00
Evgeny Mankov 584ce03173 [HIPIFY][cmake] Formatting 2020-01-23 17:47:11 +03:00
Evgeny Mankov e563b67207 Merge pull request #1810 from emankov/HIP 
[HIPIFY][cmake] Send error on CUDA 10.2 and higher as yet unsupported
 2020-01-23 17:29:38 +03:00
Evgeny Mankov 9b739bfa15 [HIPIFY][cmake] Send error on CUDA 10.2 and higher as yet unsupported 2020-01-23 16:37:25 +03:00
Rahul Garg 8b8e4a66b4 Simplify hipDispatchLatency sample (#1793) 
* Use hipExtLaunchKernelGGL in dispatchlatency sample

* Let it run on NVCC path too

* Refactoring

* Add test_kernel source

* Remove ResultDB

* Remove error checks
 2020-01-22 14:37:47 -08:00
Jenkins c00154541a Merge 'master' into 'amd-master' 
Change-Id: I747654bdd481c906a88bd6bb65f6ba1a5f38142e
 2020-01-22 10:25:03 +00:00
foreman 0096cc552b P4 to Git Change 2061101 by skudchad@skudchad_test2_win_opencl on 2020/01/21 16:47:25 
SWDEV-219917 - [VDI Cleanup] Remove some direct OpenCL references, introduce a common functionality.

	ReviewBoardURL = http://ocltc.amd.com/reviews/r/18488/diff/

Affected files ...

... //depot/stg/opencl/drivers/opencl/api/hip/build/Makefile.hip#30 edit
... //depot/stg/opencl/drivers/opencl/api/hip/fixme.cpp#3 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_internal.hpp#51 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hiprtc_internal.hpp#3 edit
... //depot/stg/opencl/drivers/opencl/api/opencl/amdocl/build/Makefile.api#190 edit
... //depot/stg/opencl/drivers/opencl/api/opencl/amdocl/cl_common.hpp#25 edit
... //depot/stg/opencl/drivers/opencl/api/opencl/amdocl/cl_context.cpp#61 edit
... //depot/stg/opencl/drivers/opencl/api/opencl/amdocl/cl_device.cpp#75 edit
... //depot/stg/opencl/drivers/opencl/api/opencl/amdocl/cl_execute.cpp#31 edit
... //depot/stg/opencl/drivers/opencl/api/opencl/amdocl/cl_icd.cpp#36 edit
... //depot/stg/opencl/drivers/opencl/api/opencl/amdocl/cl_platform_amd.cpp#3 edit
... //depot/stg/opencl/drivers/opencl/api/opencl/amdocl/cl_program.cpp#54 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/gpu/gpudevice.cpp#610 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/paldevice.cpp#180 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocdevice.cpp#150 edit
... //depot/stg/opencl/drivers/opencl/runtime/include/vdi_agent_amd.h#1 add
... //depot/stg/opencl/drivers/opencl/runtime/include/vdi_common.hpp#1 add
... //depot/stg/opencl/drivers/opencl/runtime/os/os.hpp#32 edit
... //depot/stg/opencl/drivers/opencl/runtime/os/os_posix.cpp#49 edit
... //depot/stg/opencl/drivers/opencl/runtime/os/os_win32.cpp#50 edit
... //depot/stg/opencl/drivers/opencl/runtime/platform/agent.cpp#9 edit
... //depot/stg/opencl/drivers/opencl/runtime/platform/agent.hpp#7 edit
... //depot/stg/opencl/drivers/opencl/runtime/platform/context.cpp#54 edit
... //depot/stg/opencl/drivers/opencl/runtime/runtimedefs#54 edit
 2020-01-21 16:52:40 -05:00
paulfreddy c5ed5c71a3 Changes for multiple ROCm installation (#1771) 
* FBA-29, FBA-69, multiple rocm support, shared library conflicts
Changes to resolve:
1) Multiple rocm release installation support
2) Multiple rocm shared lib conflicts
3) Add the so versioning also
 2020-01-21 14:17:35 +05:30
foreman 37bb58b556 P4 to Git Change 2060446 by vsytchen@vsytchen-ocl-win10-2 on 2020/01/20 18:58:37 
SWDEV-215533 - [HIP][Windows]Output mismatch with tex3D()

	When calculating the pitch for hipMallocPitch() align it to the device's image pitch alignment. If we don't, PAL backend will overalign the pitch when creating an image buffer.

	ReviewBoardURL = http://ocltc.amd.com/reviews/r/18496/diff/

Affected files ...

... //depot/stg/opencl/drivers/opencl/api/hip/hip_memory.cpp#96 edit
 2020-01-20 19:05:16 -05:00
Evgeny Mankov 30baf8fdf4 Merge pull request #1795 from aakanksha555/master 
[HIPIFY][cmake] Packaging for hipify-clang
 2020-01-20 19:10:20 +03:00
Jenkins 5d0b11543b Merge 'master' into 'amd-master' 
Change-Id: I35af993320b9694efb88ba6a8567c58b62213fb9
 2020-01-19 05:27:18 -05:00
ansurya 688b6e6af0 Fix texture tests, always pass row pitch to HSA API for linear layout images (#1785) 
=> New ROCr calculates pitch as per HSA specification and addrlib is used to check whether HW can support that configuration. Hence few texture tests are failing with HSA_EXT_STATUS_ERROR_IMAGE_PITCH_UNSUPPORTED.

=> Determine pitch for linear images and always pass rowpitch to HSA API's.
 2020-01-16 08:54:30 +05:30
kpyzhov 1d6a2fb064 Don't use accelerated vector element access for hip-clang. (#1796) 2020-01-15 18:17:08 -08:00
foreman 37c900f2a1 P4 to Git Change 2057410 by skudchad@skudchad_rocm on 2020/01/15 18:24:33 
SWDEV-219341 - Free memory correctly. hiprtcProgram is a pointer by itself. So release *prog

Affected files ...

... //depot/stg/opencl/drivers/opencl/api/hip/hip_rtc.cpp#10 edit
 2020-01-15 18:32:44 -05:00
Aakanksha Patil 545ad0dad3 [HIPIFY][cmake] Packaging for hipify-clang 2020-01-15 11:39:02 -05:00
kpyzhov 0918614615 Add missing constructors for Scalar_accessor class. (#1792) 2020-01-14 11:30:21 -08:00
Evgeny Mankov 84ee66314e Merge pull request #1788 from emankov/HIP 
[HIPIFY][fix] Add "--" separator in-place if needed
 2020-01-13 18:53:02 +03:00
Evgeny Mankov df563c966c [HIPIFY][fix] Add "--" separator in-place if needed 2020-01-13 18:49:28 +03:00
Evgeny Mankov 083bfaeb6b Merge pull request #1787 from emankov/HIP 
[HIPIFY] Sync with hipSPARSE
 2020-01-13 18:40:10 +03:00
Evgeny Mankov 41beed4839 [HIPIFY] Sync with hipSPARSE 
+ Update hipify-perl and doc accordingly
 2020-01-13 18:34:10 +03:00
foreman ec3fbfd60c P4 to Git Change 2055228 by jujiang@JJ-HIP on 2020/01/10 16:36:01 
SWDEV-205925 - Update HIP texture APIs for issue in hipTexRefSetAddress in HIP/PAL on Windows
	-Update HIP texture function parameter to use hipChannelFormatDesc& desc

	http://ocltc.amd.com/reviews/r/18456/

Affected files ...

... //depot/stg/opencl/drivers/opencl/api/hip/hip_texture.cpp#33 edit
 2020-01-10 16:43:46 -05:00
Jenkins e7aaac2ccd Merge 'master' into 'amd-master' 
Change-Id: I59a0793711937b997b97735d6ab10dee889cc1f9
 2020-01-10 17:19:54 +00:00
Jatin Chaudhary 0b211478dd Remove filesystem dependency in hipRTC (#1749) 
Removing dependency on filesystem, so libstdc++fs is no longer required to link
 2020-01-10 13:47:54 +05:30
Evgeny Mankov 9c2fcff9ce [HIP] Unify hipError_t (Step 3): Sync nvcc path (#1778) 
* [HIP] Unify hipError_t (Step 3): Sync nvcc path

* [HIP][fix] Add CUDA 10.x support to nvcc path
 2020-01-10 13:47:18 +05:30
Yaxun (Sam) Liu 55525fa466 Fix test hip_bitextract.cpp (#1784) 
The randomly generated offset+width may exceeds 32, which causes
a left shift operation with 32-offset-width. As an unsigned number
that is greater than 32 and causes undefined behavior. When the
test is compiled without -mavx it is still OK. However when
the test is compiled with -mavx, the undefined behavior causes
wrong results and test failure.

This patch adjusts width so that offset+width<=32 always.
 2020-01-10 13:46:57 +05:30
Jenkins e27b0c8129 Merge 'master' into 'amd-master' 
Change-Id: I09eb56a50f07d30b6bd0e03e5ee72e92d373c904
 2020-01-09 06:06:58 -05:00