AI/rocm-systems
2
0
Fork 0
Code Issues Pull Requests Actions Packages Projects Releases Wiki Activity
6,995 Commits 3 Branches 0 Tags
77ed884c6f3cc87ea9ffda8fc232dede9ef996ca
Commit Graph

6995 Commits

This Branch
This Branch
All Branches
Author SHA1 Message Date
foreman e7931a8649 P4 to Git Change 2031768 by cpaquot@cpaquot-ocl-lc-lnx on 2019/11/16 17:21:58 
SWDEV-212440 - [HIP] Memory access fault observed on Pytorch while running performance tests with Microbenchmarking script
	We need to loop through all the default stream to sync them in case
	the app call hipFree on a different current stream and another current stream
	is using the memory.

Affected files ...

... //depot/stg/opencl/drivers/opencl/api/hip/hip_memory.cpp#85 edit


[ROCm/hip commit: 9529795fab]
 2019-11-16 17:25:59 -05:00
Maneesh Gupta 5536940e12 [ci] Fix failures on nvcc path (#1654) 
Change-Id: I97f6b51314e14965618ab510bf57a2b034183e78

[ROCm/hip commit: f9fec8fdca]
 2019-11-15 07:58:40 +05:30
Maneesh Gupta 8016fa32df [packaging] Conform to debian package naming rules (#1647) 
* [packaging] Conform to debian package naming rules

* Add hip_hcc metapackage for backward compatibility


[ROCm/hip commit: 2ca1a82036]
 2019-11-14 11:40:34 +05:30
foreman 4bfac94e66 P4 to Git Change 2029899 by kjayapra@0_HIPWS_LNX1_ROCM on 2019/11/13 12:29:19 
SWDEV-144570 - Implementing ihipUnbindTextureImpl API.

Affected files ...

... //depot/stg/opencl/drivers/opencl/api/hip/hip_hcc.def.in#35 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_hcc.map.in#33 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_texture.cpp#27 edit


[ROCm/hip commit: c4e4e370a9]
 2019-11-13 12:34:13 -05:00
Jenkins 61e9f00fe3 Merge 'master' into 'amd-master' 
Change-Id: I263f0f3c3e288df178a5313d2c142574a098dfa2


[ROCm/hip commit: 428083a5e4]
 2019-11-13 05:10:40 -05:00
foreman 4f54bb2285 P4 to Git Change 2029039 by kjayapra@0_HIPWS_LNX1_ROCM on 2019/11/12 12:52:46 
SWDEV-210844 - Implementing hipExtGetLinkTypeAndHopCount

Affected files ...

... //depot/stg/opencl/drivers/opencl/api/hip/hip_device_runtime.cpp#22 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/device.hpp#344 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/paldevice.hpp#47 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocdevice.cpp#141 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocdevice.hpp#44 edit


[ROCm/hip commit: ceebda15ef]
 2019-11-12 12:55:17 -05:00
Evgeny Mankov 8d9b8dc8c3 Merge pull request #1651 from emankov/hipify 
[HIPIFY][doc] A few words about LLVM's FileCheck in README.md

[ROCm/hip commit: 0a74d771b4]
 2019-11-12 16:06:25 +03:00
Evgeny Mankov 541e2a4935 [HIPIFY][doc] A few words about LLVM's FileCheck in README.md 
[ROCm/hip commit: 16c8ad0f99]
 2019-11-12 16:04:28 +03:00
Jenkins 41768352c2 Merge 'master' into 'amd-master' 
Change-Id: I3e1ce565f4faaeb5b53d6f8c7a4023c498fbf621


[ROCm/hip commit: fb312c701d]
 2019-11-11 05:10:19 -05:00
Maneesh Gupta 8723218421 Bump version to 3.0 (#1648) 
Change-Id: Id1e6eb222080a339af938212e74a52c39c305eab

[ROCm/hip commit: dae8630592]
 2019-11-10 20:23:58 -08:00
Rahul Garg 04cd46fed4 Merge pull request #1643 from mhbliao/hliao/master/remove.redundant.decl 
Remove redundant declarations.

[ROCm/hip commit: d80917d147]
 2019-11-07 11:16:40 -08:00
Michael LIAO 6318875ebc Remove redundant declarations. 
- The revised `hip/hip_ext.h` have that declarations.


[ROCm/hip commit: d6ff22510e]
 2019-11-07 10:11:22 -05:00
Jenkins 62a0771088 Merge 'master' into 'amd-master' 
Change-Id: Ia44cb648c8ae16ff424bcf64fb9a9338c7678c0c


[ROCm/hip commit: 425254aa13]
 2019-11-07 05:22:21 -05:00
Evgeny Mankov 4c66b0a5a9 Merge pull request #1642 from emankov/hipify 
[HIPIFY] Clang style formatting

[ROCm/hip commit: 3be0865cad]
 2019-11-07 12:49:52 +03:00
Evgeny Mankov 9e34880005 [HIPIFY] Clang style formatting 
[ROCm/hip commit: 93bc9c9195]
 2019-11-07 12:48:05 +03:00
Evgeny Mankov 615281a81a Merge pull request #1641 from emankov/hipify 
[HIPIFY][fix] Abandon canCompileHostAndDeviceInOneJob check for --cuda-compile-host-device option

[ROCm/hip commit: 67f787e74a]
 2019-11-07 11:35:15 +03:00
Evgeny Mankov 0ae791586b [HIPIFY][fix] Delete canCompileHostAndDeviceInOneJob declaration as well 
[ROCm/hip commit: 0c07b6b421]
 2019-11-07 11:32:53 +03:00
Evgeny Mankov 860e89df5e [HIPIFY][fix] Abandon canCompileHostAndDeviceInOneJob check for --cuda-compile-host-device option 
[Reason] It turned out that it is not so: 2 jobs are always


[ROCm/hip commit: c2c144ac04]
 2019-11-07 11:30:40 +03:00
Evgeny Mankov e6214fd60b Merge pull request #1640 from emankov/hipify 
[HIPIFY] Reorder options propagation to clang

[ROCm/hip commit: 8f33397d61]
 2019-11-07 11:23:38 +03:00
Evgeny Mankov 58fc750bf0 [HIPIFY] Reorder options propagation to clang 
[Reason] Leave overriding opportunity for -D, -std=c++XX, etc.


[ROCm/hip commit: 16a27213e4]
 2019-11-07 11:21:06 +03:00
Jeff Daily d4fe8ff822 General hipMemset improvements (#1495) 
* hipMemset et al can use HSA API directly for synchronous cases

* lock and flush stream in hipMemset, hold lock until complete

* move hipMemset async check to front of conditional

* use hsa_amd_memory_fill for additional sync memset cases

code cleanup/review for all memset calls

* Fix inversion of execution mutating value.

* ihipMemsetSync fall back to kernel if HSA memset fails

* Never fallback, never surrender.

* Allow NULL stream.

* Optimise memset kernel. Remove deadwood.

* Update hip_memory.cpp

* Clean up stream logic in sync memset

* Revert "Clean up stream logic in sync memset"

This reverts commit 6117dedf673367f44cc704192573a117a3d92477.


[ROCm/hip commit: e31e0ca12e]
 2019-11-07 13:19:54 +05:30
Alex Voicu 68b4fbd043 Remove native vector support from the GCC case, since it never worked (#1637) 
[ROCm/hip commit: 5530c15cc3]
 2019-11-07 13:19:14 +05:30
Sarbojit2019 fa1e44aa0e [HIP] Fixed hipStreamAddCallback [SWDEV#165185] (#1425) 
Fixed hipStreamAddCallback() as requested in SWDEV#165185
Added unit test to test the behavior


[ROCm/hip commit: 45613311d7]
 2019-11-07 13:18:12 +05:30
ansurya 92dcba11ac Fixed texture 2D mapping for pitched arrays & 3D Texture read (#1415) 
Texture 2D image mapping for pitched arrays:
github issue: Texture Object's Buffer seems to be Misaligned #886
JIRA ticket: SWDEV-199313

SWDEV-151670 : Fixed issue with 3D texture with 4 components
SWDEV-151671 : Issue with 2D layered texture with 4 components

[ROCm/hip commit: e07926ce0f]
 2019-11-07 13:17:46 +05:30
Rahul Garg 6968362d99 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/hip commit: 579a4f36fa]
 2019-11-07 13:17:10 +05:30
foreman d81a4b729f P4 to Git Change 2026174 by eshcherb@evgeny-hip on 2019/11/06 19:37:26 
SWDEV-197289 - tracing callbacks call fix

Affected files ...

... //depot/stg/opencl/drivers/opencl/api/hip/hip_prof_api.h#5 edit


[ROCm/hip commit: 692477f964]
 2019-11-06 19:47:10 -05:00
foreman 23291c1b11 P4 to Git Change 2026152 by cpaquot@cpaquot-ocl-lc-lnx on 2019/11/06 17:50:08 
SWDEV-206239 - [HIP] RCCL: finegrain VRAM does not work
	Implemented fine grained VRAM allocation via ATOMICS.

Affected files ...

... //depot/stg/opencl/drivers/opencl/api/hip/hip_memory.cpp#84 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocdevice.cpp#138 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocdevice.hpp#43 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocmemory.cpp#45 edit


[ROCm/hip commit: 649cb36977]
 2019-11-06 18:00:44 -05:00
Rahul Garg 9248fcd9bc Merge pull request #1630 from ROCm-Developer-Tools/hotfix_volatile_accessors 
__half2 should walk like CUDA and talk like CUDA

[ROCm/hip commit: 2fa45c215a]
 2019-11-06 10:25:03 -08:00
Rahul Garg a48954ef98 Merge pull request #1620 from jeffdaily/hipEventRecord_patch 
fix race condition in hipEventRecord

[ROCm/hip commit: 85446dbd6a]
 2019-11-06 10:23:24 -08:00
Evgeny Mankov 8ddaf844d7 Merge pull request #1636 from emankov/hipify-clang 
[HIPIFY][Win][fix] canCompileHostAndDeviceInOneJob is true only for LLVM >= 10

[ROCm/hip commit: 30c138eda2]
 2019-11-06 19:27:40 +03:00
Evgeny Mankov 282c76c26f [HIPIFY][Win][fix] canCompileHostAndDeviceInOneJob is true only for LLVM >= 10 
[ROCm/hip commit: 9ca4e96641]
 2019-11-06 19:25:42 +03:00
Evgeny Mankov 223897c24c Merge pull request #1635 from emankov/hipify-clang 
[HIPIFY][doc] Update README.md

[ROCm/hip commit: 7875bb789b]
 2019-11-06 19:20:02 +03:00
Evgeny Mankov 7b216ca51c [HIPIFY][doc] Update README.md 
+ Supported versions, testing


[ROCm/hip commit: 96483d0de5]
 2019-11-06 19:18:13 +03:00
Jeff Daily f9ad564380 hipEventRecord only needs one lock; remove locked_eventIsReady 
[ROCm/hip commit: 85080905c0]
 2019-11-06 15:56:32 +00:00
Jeff Daily 8f033af434 remove ihipEvent_t::refreshEventStatus(), new hipEventElapsedTime 
This fixes possible races in hipEventElapsedTime.


[ROCm/hip commit: 7986090d9c]
 2019-11-06 15:46:46 +00:00
Evgeny Mankov b77feedcd9 Merge pull request #1634 from emankov/hipify-clang 
[HIPIFY][format] Apply clang style formatting in LLVMCompat

[ROCm/hip commit: 514180b83c]
 2019-11-06 14:46:45 +03:00
Evgeny Mankov 1b6e4b495a [HIPIFY][format] Apply clang style formatting in LLVMCompat 
[ROCm/hip commit: 3b76fd0b1c]
 2019-11-06 14:43:22 +03:00
Evgeny Mankov 9e3c107549 Merge pull request #1633 from emankov/hipify-clang 
[HIPIFY] Add a compatibility for CharSourceRange if LLVM < 7

[ROCm/hip commit: 89e4330890]
 2019-11-06 14:32:47 +03:00
Evgeny Mankov 1776ff55d3 [HIPIFY] Add a compatibility for CharSourceRange if LLVM < 7 
[ROCm/hip commit: c87ab05fc6]
 2019-11-06 14:30:39 +03:00
Alex Voicu f8506bb669 Remove leftover noise. 
[ROCm/hip commit: b9faa9f8ae]
 2019-11-06 02:46:21 +02:00
Alex Voicu 1baaf44179 __half2 should walk like CUDA and talk like CUDA 
[ROCm/hip commit: e5bd00d06b]
 2019-11-06 02:43:04 +02:00
Rahul Garg 93bd983bbf Merge pull request #1626 from mhbliao/hliao/master/fix.windows.build 
Use portable macro for deprecation message.

[ROCm/hip commit: 32a67c9f14]
 2019-11-05 10:08:43 -08:00
Evgeny Mankov 15406422fe Merge pull request #1595 from emankov/cmake 
[HIP][cmake] Simplify `UNIX` related code (the beginning)

[ROCm/hip commit: 56fc294968]
 2019-11-05 20:30:55 +03:00
Michael LIAO e250f76183 Use portable macro for deprecation message. 
[ROCm/hip commit: a7f311cc14]
 2019-11-05 11:51:00 -05:00
Evgeny Mankov b4a30a0c7a Merge pull request #1624 from emankov/hipify 
[HIPIFY][#1409] Fix for kernel launch macro expansion

[ROCm/hip commit: a601670cb7]
 2019-11-05 14:04:51 +03:00
Evgeny Mankov 5a9c8168c1 [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/hip commit: 976f8e8bf6]
 2019-11-05 14:00:13 +03:00
Rahul Garg 1b8973d6be Deprecate HIP Markers (#1622) 
* Deprecate HIP markers

* Deprecate profiler start/stop


[ROCm/hip commit: 54fab7c35c]
 2019-11-05 12:32:59 +05:30
Aryan Salmanpour 2ad99a6326 [hip][tests] Add two more workgroup sizes for testing hipLaunchCooperativeKernel (#1613) 
[ROCm/hip commit: cf92fae9e6]
 2019-11-05 12:32:46 +05:30
foreman c1400c5234 P4 to Git Change 2024544 by cpaquot@cpaquot-ocl-lc-lnx on 2019/11/04 16:35:14 
SWDEV-145570 - [HIP] Fetched properties from current device and not default 0 one.

Affected files ...

... //depot/stg/opencl/drivers/opencl/api/hip/hip_device_runtime.cpp#21 edit


[ROCm/hip commit: c536429a6b]
 2019-11-04 16:42:31 -05:00
foreman ba23455719 P4 to Git Change 2024543 by cpaquot@cpaquot-ocl-lc-lnx on 2019/11/04 16:32:23 
SWDEV-206239 - [HIP] Return hipErrorMemoryAllocation for fine grained VRAM for now

Affected files ...

... //depot/stg/opencl/drivers/opencl/api/hip/hip_memory.cpp#83 edit


[ROCm/hip commit: 571b8d625d]
 2019-11-04 16:39:35 -05:00