cf1e71c5f6
Merge "Update copyright info for VDI files" into amd-master-next
...
[ROCm/hip commit: b57d64c22e
2020-02-04 17:19:31 -05:00
ed5081c945
Update copyright info for VDI files
...
Change-Id: Ib160fbf89ec89a5895321f73402a33b4d344a68f
[ROCm/hip commit: 2764aee583
2020-02-04 08:47:10 -08:00
db9a20e401
removing hip-vdi versioning dependency till we update the packaging
...
Change-Id: I8d97bf443f548c3a570a0ef5a068ad04c8d91021
[ROCm/hip commit: 322436574f
2020-02-04 00:36:06 -05:00
bc78a8529d
Merge branch 'origin/pghafari/hip-vdi' into lmoriche/amd-master-next
...
Change-Id: I22c145d39f430ca571a981687bcb034ea6e3b8a2
[ROCm/hip commit: a8b81e96b4
2020-01-31 07:33:12 -08:00
cbd1b27c5e
Merge HIP/VDI branch 'amd-staging' into lmoriche/amd-master-next
...
Change-Id: Iabaab4e72815ba483a1330ec6a1130f2b86676f0
[ROCm/hip commit: e604beeef4
2020-01-29 15:02:13 -08:00
0ef73d15c4
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
[ROCm/hip commit: 2fb1d6a604
2020-01-23 16:13:57 -05:00
402dbba182
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
[ROCm/hip commit: ca165f2fbb
2020-01-21 16:52:40 -05:00
e47b0a4152
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
[ROCm/hip commit: 3bc69394d0
2020-01-21 14:17:35 +05:30
8a5f3ecb50
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
[ROCm/hip commit: d18baabc70
2020-01-20 19:05:16 -05:00
7fdfabf210
Merge pull request #1795 from aakanksha555/master
...
[HIPIFY][cmake] Packaging for hipify-clang
[ROCm/hip commit: 955b88ef5a
2020-01-20 19:10:20 +03:00
ac41b1d0e0
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.
[ROCm/hip commit: df20c17f12
2020-01-16 08:54:30 +05:30
dabbde21c6
Don't use accelerated vector element access for hip-clang. ( #1796 )
...
[ROCm/hip commit: 566adc4594
2020-01-15 18:17:08 -08:00
8938270136
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
[ROCm/hip commit: 97a6164702
2020-01-15 18:32:44 -05:00
04b0bf0a1d
[HIPIFY][cmake] Packaging for hipify-clang
...
[ROCm/hip commit: 7f78630124
2020-01-15 11:39:02 -05:00
4c457c2bb5
Add missing constructors for Scalar_accessor class. ( #1792 )
...
[ROCm/hip commit: fae85cf6d2
2020-01-14 11:30:21 -08:00
7d42bb6fff
[HIPIFY][fix] Add "--" separator in-place if needed
...
[ROCm/hip commit: f0db2c761b
2020-01-13 18:49:28 +03:00
c688151a89
[HIPIFY] Sync with hipSPARSE
...
+ Update hipify-perl and doc accordingly
[ROCm/hip commit: d7f8654487
2020-01-13 18:34:10 +03:00
b4796d13fc
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
[ROCm/hip commit: d8c1215113
2020-01-10 16:43:46 -05:00
de58e1b43e
Remove filesystem dependency in hipRTC ( #1749 )
...
Removing dependency on filesystem, so libstdc++fs is no longer required to link
[ROCm/hip commit: aadb62f2c9
2020-01-10 13:47:54 +05:30
3d22f829f5
[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
[ROCm/hip commit: a005a8550d
2020-01-10 13:47:18 +05:30
5d17d5b029
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.
[ROCm/hip commit: 02848e0b80
2020-01-10 13:46:57 +05:30
6ebf5ca991
Revert PRs that break ROCm builds ( #1781 )
...
Fixes SWDEV-218626 and SWDEV-218629
Changes:
- Revert "`static inline` in a header, just like excess sugar in a diet, causes bloat (#1692 )"
This reverts commit b7803eb0c6#1777 )"
This reverts commit 9c8c3df29400bd5d1cec
2020-01-08 15:11:58 +05:30
e4e9475327
P4 to Git Change 2053320 by vsytchen@vsytchen-hip-win10 on 2020/01/07 15:54:34
...
SWDEV-215533 - [HIP][Windows]Output mismatch with tex3D()
1. Implement hipMemcpy3DAsync().
2. Add logic in hipMemcpy3D() to determine based on src/dst parameters if the user intended on calling cudaMemcpy3D() or cuMemcpy3D().
ReviewBoardURL = http://ocltc.amd.com/reviews/r/18444/diff/
Affected files ...
... //depot/stg/opencl/drivers/opencl/api/hip/hip_hcc.def.in#38 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_hcc.map.in#36 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_memory.cpp#95 edit
[ROCm/hip commit: 3cbd083c8d
2020-01-07 15:59:02 -05:00
fcf07e0b04
Detect when an explicit printf buffer flush is required ( #1766 )
...
* Detect when an explicit printf buffer flush is required
in a device/stream synchronization function.
* hip_module.cpp: add missing hc_am.hpp header
[ROCm/hip commit: f4555c835a
2020-01-07 09:06:38 -08:00
ebef1ff3c6
[HIPIFY] main source file refactoring
...
[ROCm/hip commit: e9de81fea7
2020-01-07 16:25:18 +03:00
9c8c3df294
Fix rocFFT build failure ( #1777 )
...
Fixes SWDEV-217761
[ROCm/hip commit: 753277422a
2020-01-07 08:12:37 +05:30
33b5e15e9a
hipMemcpy[To/From]Symbol(Async) fixes ( #1774 )
...
[ROCm/hip commit: 6b5ea15dfe
2020-01-07 08:11:53 +05:30
98a6bb683a
Fix minor explainations in the kernel guide ( #1775 )
...
[ROCm/hip commit: 7d27247814
2020-01-06 12:34:21 +05:30
327a45b18b
Add hipBindTexture2D on NVCC path ( #1773 )
...
[ROCm/hip commit: a5d7e7d8d3
2020-01-06 12:33:50 +05:30
b6a3c3a95e
Fix nested designator warnings ( #1768 )
...
[ROCm/hip commit: 785a4440c8
2020-01-06 12:33:34 +05:30
86dbb13897
Fix hipcc warning related to hipVersion ( #1767 )
...
* Fix hipcc warning related to hipVersion
* Rename hipVersion.h to hip_version.h
* Remove HIP_VERSION splitting
* Update .gitignore
- Ignore generated include/hip/hip_version.h
- Removed some stale entries
- Added executables from samples/1_Utils/*/ for consistency with bin/ entries.
[ROCm/hip commit: f3cafd5855
2020-01-06 12:33:23 +05:30
3dae7945ff
Update HIP-Clang build instruction ( #1764 )
...
[ROCm/hip commit: af697eaefe
2020-01-06 12:32:47 +05:30
2a70e452a5
Document FMA settings ( #1717 )
...
[ROCm/hip commit: 47525e72db
2020-01-06 12:32:38 +05:30
31e4b7e893
P4 to Git Change 2052191 by skudchad@skudchad_test2_win_opencl on 2020/01/03 15:54:23
...
SWDEV-213000 - Backout change to notifyCmdQueue as the real issue has been identified
Affected files ...
... //depot/stg/opencl/drivers/opencl/api/hip/hip_module.cpp#53 edit
[ROCm/hip commit: a42f6272f5
2020-01-03 16:02:59 -05:00
73263137b4
P4 to Git Change 2051060 by michliao@hliao-dev-00-hip.rocm-workspace on 2019/12/30 16:42:07
...
SWDEV-145570 - Clean up after `hipError_t` unification.
- Replace deprecated `hipError_t` enums.
Affected files ...
... //depot/stg/opencl/drivers/opencl/api/hip/hip_device_runtime.cpp#24 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_error.cpp#4 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_event.cpp#19 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_memory.cpp#94 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_module.cpp#52 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_stream.cpp#27 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_texture.cpp#32 edit
... //depot/stg/opencl/drivers/opencl/api/hip/trace_helper.h#5 edit
[ROCm/hip commit: 9386736b41
2019-12-30 16:46:39 -05:00
6ac4d18753
Merge pull request #1759 from emankov/master
...
[HIP] Unify hipError_t (Step 2)
[ROCm/hip commit: 0dadb23327
2019-12-30 19:21:09 +03:00
6d2ec032fe
Change to generate hipVersion.h ( #1726 )
...
HIP_VERSION_MAJOR, HIP_VERSION_MINOR, HIP_VERSION_PATCH and HIP_VERSION pre-processor macros are now defined in hipVersion.h instead of being set by hipcc.
[ROCm/hip commit: aa4aea0754
2019-12-30 12:44:24 +05:30
ffea90f865
[hip] refactoring cooperative kernel launch APIs ( #1737 )
...
This PR is a follow-up on PR# #1698 and it makes two more APIs (hipLaunchCooperativeKernel/hipLaunchCooperativeKernelMultiDevice) inline so that they can work correctly with lazy binding.
[ROCm/hip commit: 6968aeb841
2019-12-30 12:42:17 +05:30
8f0daf4019
Fix texture 3D & 2D layered with N components ( #1746 )
...
SWDEV-151670: Issue with 3D texture with 4 components
SWDEV-151671: Issue with 2D layered texture with 4 components
Fixed memcpy when memory is allocated with driver API's.
Github issues: #1755
Fixed 3D default case when array type is not set during memory allocation.
[ROCm/hip commit: 391e99cd12
2019-12-30 12:41:42 +05:30
3966a475bd
P4 to Git Change 2049729 by skudchad@skudchad_test2_win_opencl on 2019/12/23 12:36:57
...
SWDEV-203814 - Change the return type of the hiprtcGetTypeName to have compatibility across ABIs
ReviewBoardURL = http://ocltc.amd.com/reviews/r/18392/diff/
Affected files ...
... //depot/stg/opencl/drivers/opencl/api/hip/hip_rtc.cpp#9 edit
[ROCm/hip commit: 2989140f78
2019-12-23 12:42:24 -05:00
6ebd0592da
[HIPIFY][doc] LLVM 9.0.1 is the latest stable release now
...
+ Tested on Windows and Linux: no changes are needed
[ROCm/hip commit: 3254c3e2c1
2019-12-23 20:00:33 +03:00
abef353b5b
[HIP] Clean-up deprecated HIP error codes
...
hipErrorMemoryAllocation -> hipErrorOutOfMemory
hipErrorInitializationError -> hipErrorNotInitialized
hipErrorMapBufferObjectFailed -> hipErrorMapFailed
hipErrorInvalidResourceHandle -> hipErrorInvalidHandle
[ROCm/hip commit: 4921678b6c
2019-12-23 17:01:35 +03:00
d10837db9d
Add macro __HIP_ENABLE_CUDA_WRAPPER_FOR_OPENMP__ ( #1761 )
...
This is to allow force enable cuda wrapper for OpenMP for flexibility
[ROCm/hip commit: 3c90d57072
2019-12-23 19:24:54 +05:30
bb7fa73dcc
Fix the return type of demangle function so that its compatible across ABIs ( #1744 )
...
[ROCm/hip commit: 080b0b9a68
2019-12-23 19:11:40 +05:30
1f5ecc0f6a
Fix late-coming issues. ( #1724 )
...
Implementation for hipMemcpyWithStream.
[ROCm/hip commit: 75a11330aa
2019-12-23 19:11:24 +05:30
91f82210fb
replace array designator C99 ( #1694 )
...
* replace array designator C99
* Update texture_functions.h
Highlight valid and invalid values in texFormatToSize
Co-authored-by: Maneesh Gupta <maneesh.gupta@amd.com >
[ROCm/hip commit: 7d6634ce9d
2019-12-23 19:10:24 +05:30
b7803eb0c6
static inline in a header, just like excess sugar in a diet, causes bloat (#1692 )
...
[ROCm/hip commit: be70b9f7e7
2019-12-23 19:09:38 +05:30
97535f3e97
[HIP] Fix typo
...
[ROCm/hip commit: 9544682e2c
2019-12-23 12:06:44 +03:00
30ae3942dc
[HIP] Unify hipError_t (Step 2)
...
Step 2. Make a few hipError codes deprecated
Update hipify-clang, hipify-perl, docs and samples accordingly
[ROCm/hip commit: dbad4d9b7f
2019-12-22 02:05:31 +03:00
bf2f77846e
Merge pull request #1734 from vsytch/win10-hipMemcpy-fixes
...
Fix OOM issues with hipMemcpy test on Windows
[ROCm/hip commit: 9c91632194
2019-12-21 22:02:34 +03:00
Laurent Morichetti
Payam
foreman
paulfreddy
Evgeny Mankov
ansurya
kpyzhov
Aakanksha Patil
Jatin Chaudhary
Yaxun (Sam) Liu
Maneesh Gupta
Siu Chi Chan
satyanveshd
Rick Ho
Rahul Garg
Sarbojit2019
Aryan Salmanpour
saleelk
Alex Voicu