AI/rocm-systems
2
0
派生 0
代码 工单 合并请求 工作流 软件包 项目 发布 百科 活动
58 提交 3 分支 0 Git 标签
5e4c00c4fbfdc083d65ddd7d39c5227d5eecffbb
提交图

58 次代码提交

作者 SHA1 备注 提交日期
sdashmiz 5e4c00c4fb SWDEV-346448 - fix the missing defines 
for nvdi compile

Signed-off-by: sdashmiz <shadi.dashmiz@amd.com>
Change-Id: Ifd0e50a6f8636609fa61680cc719a2f82fb1320c


[ROCm/hipother commit: b875936c5d]
 2022-07-20 11:31:50 -04:00
Brian Sumner a369b4730b SWDEV-333033 - add safe and unsafe atomic min and max including gfx940 and add missing nvidia support 
Change-Id: I829a0a5fd49c510e77eabbcb92d1a415ef6b5a4c


[ROCm/hipother commit: 13d1a1b0e4]
 2022-07-14 10:22:42 -04:00
sdashmiz d163746f0c SWDEV-321698 - add new enum entries to match cuda 
Signed-off-by: sdashmiz <shadi.dashmiz@amd.com>
Change-Id: If0a17b3234fd90b1f553a075e02280258000d36a


[ROCm/hipother commit: e7f7073e96]
 2022-07-13 10:22:06 -04:00
Sarbojit Sarkar 0dbbf52d8e SWDEV-341174 - Fixed typo 
Change-Id: Ib605390bd17d014539d57488f0633db44d7c1fad


[ROCm/hipother commit: 038114c098]
 2022-07-11 12:24:18 -04:00
Sarbojit Sarkar 1dfcc22d96 SWDEV-345723 - Fixed test build issue 
Change-Id: Id9545c9523bfad6b5afefcdc1f705d6043094ae4


[ROCm/hipother commit: 36e047814b]
 2022-07-11 12:23:34 -04:00
Sarbojit Sarkar e0ec532c31 SWDEV-341174 - fixed warning on cuda 
Change-Id: I5d017bcc154a2985e23893c0d933438bf0fc1958


[ROCm/hipother commit: 3289950436]
 2022-06-27 04:49:53 -04:00
Maneesh Gupta 97b4b0506e SWDEV-340918 - make hip_runtime.h work with g++ 
Change-Id: Ief3e6dc075837dfccae3defad7da696130ed05bd


[ROCm/hipother commit: 95e6e11bf0]
 2022-06-20 23:32:58 -04:00
jaypatel 77d84b36e8 SWDEV-322688 - Added hip math constants header. 
Change-Id: I9363f82159a53c6822e943c4950fc7f6c350b326


[ROCm/hipother commit: 53190b0a65]
 2022-06-16 23:56:45 -04:00
Satyanvesh Dittakavi e6e86b0789 SWDEV-336532 - Convert Managed Memory in hipPointerGetAttributes on Nvidia platform 
Change-Id: I3bc6180040b6ad48f06ffdc7d01ca6fd9fe32c0e


[ROCm/hipother commit: 70c90e5975]
 2022-06-16 00:43:15 -04:00
Jaydeep Patel d1e003b718 SWDEV-338376 - Added hipMemGetAllocationGranularity, hipMemCreate and hipMemRelease for CUDA 
Change-Id: If8c6a00958bb39752eb202c30a7960d13de225ae


[ROCm/hipother commit: cb53be08fc]
 2022-06-15 23:59:56 -04:00
sdashmiz c6d10a3bf0 SWDEV-325711 - add Graph memory APIs skeleton 
- hipDeviceGet/SetGraphMemAttr

- hipDeviceGraphMemTrim

- there is no memory pool for graphs currently

Signed-off-by: sdashmiz <shadi.dashmiz@amd.com>
Change-Id: I11db76ea7ea1c7732175fc93264448052357e8dc


[ROCm/hipother commit: 9e3c65ccbd]
 2022-06-15 14:47:16 -04:00
sdashmiz 92423493b1 SWDEV-321698 - remove Memcpy1D type 
- Memcpy1D node type is not complying with cuda

Signed-off-by: sdashmiz <shadi.dashmiz@amd.com>
Change-Id: If8113f5e699de0c62d98effc4580a2e0fee9a950


[ROCm/hipother commit: 9583567388]
 2022-06-13 08:31:02 -04:00
sdashmiz b0d323fe42 SWDEV-318833 - Get and Set attribute for kernel nodes 
Signed-off-by: sdashmiz <shadi.dashmiz@amd.com>
Change-Id: Ie51aa4b56661cbb8c5b4eb1dbaad327377084ffb
Signed-off-by: sdashmiz <shadi.dashmiz@amd.com>


[ROCm/hipother commit: f874762659]
 2022-06-09 09:47:05 -04:00
Tao Sang a87da88ec3 SWDEV-319818 - Release restriction on hipResourceViewDesc 
Let more types support hipResourceViewDesc.
Add missing symbols to fix cuda build failing.

Change-Id: Ife694cc6491427093863252e257e820b0bb4fa0f


[ROCm/hipother commit: 3fc1dca59f]
 2022-05-10 15:57:31 -04:00
Joseph Greathouse de06c6e4b2 SWDEV-332811 - Clean up and extend HIP unsafe atomic add 
Update HIP's unsafeAtomicAdd to:
 - Compile properly even when not compiling for gfx90a
 - Fall back to safe atomic add on non-gfx90a architectures
 - use flat atomic add for FP64 on gfx90a, instead of dynamically
   checking memory spaces.

In addition, when the compiler is passed -munsafe-fp-atomics, it
will define __AMDGCN_UNSAFE_FP_ATOMICS__. When this happens, the
compiler is requesting that the HIP headers force all HIP
atomicAdd() calls on floats or doubles to use their unsafe versions.

This patch thus causes unsafeAtomicAdd() calls when that define
is seen. This call to unsafeAtomicAdd() is also done for atomicSub(),
since that calls atomicAdd underneath. This is not done for
system-scope atomicAdd because, on gfx90a, system-scope atomic FP
add instructions would need to target fine-grained memory, which is
always unsafe.

This patch also creates safeAtomicAdd() functions for float and double.
These functions will create a standalone safe atomic, even when the
application is compiled with -munsafe-fp-atomics.

Finally, this patch adds wrappers in the Nvidia path of HIP so that
these HIP functions call through to atomicAdd there as well.

Change-Id: I8af0621d3d28ea30c9278bfeea7393d03bbdac6d


[ROCm/hipother commit: b712a51e74]
 2022-04-29 07:19:58 -04:00
Rakesh Roy c010936428 SWDEV-326789 - Mark texture reference APIs as deprecated 
Change-Id: I7a39cc1f036cd185ac3aab6c5f44730f16225f69


[ROCm/hipother commit: 0f378ffc09]
 2022-04-05 00:04:34 -04:00
German Andryeyev 681471c584 SWDEV-311271 - Initial mempool implementation 
HIP_MEM_POOL_SUPPORT controls memory pool support in runtime.
Currently it's disabled by default. The initial change doesn't
include: IPC, MGPU, virtual memory alloc, suballoc, defragmentation,
internal dependencies.

Change-Id: Ibed8528ebec698b045ebb247e49c0ecd6e587ed7


[ROCm/hipother commit: 3b89440eb1]
 2022-03-31 09:21:37 -04:00
Rakesh Roy 6536ccbf3d SWDEV-326789 - Add Missing HIP API Functions For Nvidia Platform 
Change-Id: I828028c5d893ca1487f33017a6902c3b7f786762


[ROCm/hipother commit: d5be2bb91d]
 2022-03-25 01:34:57 -04:00
Satyanvesh Dittakavi 3054e52da0 SWDEV-317716 - Add hipDeviceGetUuid API 
Change-Id: I320c7bc11ddd7617e0246f6faf19135ad7363e73


[ROCm/hipother commit: 3eca517625]
 2022-03-16 00:23:44 -04:00
Satyanvesh Dittakavi 5916834034 SWDEV-315118 - Add version check for hipGraphInstantiateWithFlags on nvidia path 
Change-Id: I672b4a5287348bddf6eb8955decc9cce786275a2


[ROCm/hipother commit: af18c3144f]
 2022-03-09 02:10:08 -05:00
Shadi Dashmiz 5fbcf29038 Revert "SWDEV-321698 - hipGraphNodeTypeMemcpy1D NVDIA build failure" 
This reverts commit 09432f798b.

Reason for revert: hip changes not in yet

Change-Id: I89e35d171cf01fb82d361279998efcc90e54ef33


[ROCm/hipother commit: 16dbf85da0]
 2022-03-08 15:08:31 -05:00
sdashmiz 09432f798b SWDEV-321698 - hipGraphNodeTypeMemcpy1D NVDIA build failure 
Signed-off-by: sdashmiz <shadi.dashmiz@amd.com>
Change-Id: I7aea11bf14adbeb7fea68eb862df74fcf6f13d75


[ROCm/hipother commit: d557ade2ad]
 2022-03-07 16:26:11 -05:00
Satyanvesh Dittakavi 8c40dd5606 EXSWCPHIPT-13 - Fix Segfault on Nvidia Platform 
Change-Id: Ib85bb0b0e91b7703afc4858c4a5ada0115ad68f4


[ROCm/hipother commit: 974138cfd5]
 2022-02-19 12:53:46 +00:00
Satyanvesh Dittakavi 859d9065cf SWDEV-315981 - make nvidia hiprtc functions static 
Change-Id: I945426c155ed9ce21c308745f384bbf8669d73c4


[ROCm/hipother commit: e3aafb9636]
 2022-02-15 23:38:19 -05:00
Satyanvesh Dittakavi ccf84797ff SWDEV-315118 - Add version checks for few graph APIs on Nvidia path 
HIP apps running on CUDA 11.0 are failing due to some graph APIs/enums
added only in CUDA 11.1 or CUDA 11.3

Change-Id: I0d32b412cb76c42c7b3a9c612d750990f9e89908


[ROCm/hipother commit: f607f01311]
 2022-02-15 02:03:49 -05:00
Satyanvesh Dittakavi bbc8f30c5c SWDEV-315017 - Add missing graph error strings 
Change-Id: I11b5a623756c5bef88cbc93e49c124d0caf62bd1


[ROCm/hipother commit: c4dcd3398c]
 2022-02-15 01:41:44 -05:00
Satyanvesh Dittakavi 0882ced947 SWDEV-317135 - Fix mapping of hipStreamUpdateCaptureDependencies on cuda path 
Change-Id: Ibbcf8136fa527a20684a377311bc76182345d17b


[ROCm/hipother commit: 334f3c6449]
 2022-02-14 09:10:46 -05:00
Satyanvesh Dittakavi c128131a6e SWDEV-314661 - Add hipGraphInstantiateWithFlags API mapping in nvidia path 
Change-Id: Ibbf54ef18978448e92571f0535124844154726b6


[ROCm/hipother commit: d64b750aec]
 2022-02-09 00:02:55 -05:00
Satyanvesh Dittakavi 2a9d0ec7ef SWDEV-292714 - Added support for hipPointerGetAttribute and 
hipDrvPointerGetAttributes

Change-Id: I44a0b5c5d9eb5a9a63406b11e8de83e5cb245a59


[ROCm/hipother commit: 1a017b591e]
 2022-02-02 05:33:07 -05:00
haoyuan2 5344fabb49 SWDEV-309292 - add hipPos definition in CUDA path 
Change-Id: Ia81d5db77d7403cafb583fda8083d0f4dbe33835


[ROCm/hipother commit: 5a4305c05a]
 2021-12-04 04:40:34 -05:00
anusha GodavarthySurya 5dbc956998 SWDEV-240808 - Added nvidia handling for few graph APIs 
Change-Id: I8edee87ea75d80152418f76cc8a521b2ba58f139


[ROCm/hipother commit: 198ad718a5]
 2021-11-22 07:17:34 -08:00
Tao Sang e530fb9388 SWDEV-306947 Enable hipAddressModeBorder 
Enable hipAddressModeBorder.
Fix default of height of hipMallocArray().
Some code improvement.

Change-Id: I57045118e7adf915074c547cbe76349a4cfd72d8


[ROCm/hipother commit: 910fa7e2fa]
 2021-10-27 10:05:53 -04:00
anusha GodavarthySurya 2a9a8703a4 SWDEV-240806 - Added few Graph API Implementation 
hipGraph APIs clone, childGraph, RemoveDependencies, GetEdges,GetDependencies, GetDependentNodes, GetType and DestroyNode
hipStream APIs GetCaptureInfo, GetCaptureInfo_v2, UpdateCaptureDependencies.

Change-Id: Ib0f4cb8ea335698eecdd6d744ffab1e954153673


[ROCm/hipother commit: 6f942ccdd4]
 2021-10-05 07:44:54 -07:00
Jatin Chaudhary 57177d4f4f SWDEV-304552 - Add default to return the last error value 
Change-Id: Ia399033e30aaa454a454067f5afc6f7d1e5ff8dd


[ROCm/hipother commit: c457f5cd12]
 2021-10-04 07:23:10 -04:00
Sarbojit Sarkar e6c4953026 SWDEV-304076 - Fix for Cuda build error 
Change-Id: Ibca63a08b8d6d1235b51a06c0bc024cd284cee97


[ROCm/hipother commit: 7134d7bb00]
 2021-09-27 23:55:52 -04:00
Sarbojit Sarkar 65590e8191 SWDEV-298667 - fix stream operation for Cuda 
Change-Id: Ida91712e678e324b54293ba48dfca442be390783


[ROCm/hipother commit: e24e026f37]
 2021-09-21 15:07:15 -04:00
Satyanvesh Dittakavi f81f6d80c0 SWDEV-301330 - Remove the hard coded driver version on HIP CUDA platform 
Change-Id: I0eb10781acc7524174c7ae6fc552c824b7c94b0a


[ROCm/hipother commit: 6e7072b980]
 2021-09-02 09:03:04 +00:00
Anusha GodavarthySurya 726949569e SWDEV-240806 - Added API hipGraphAddMemcpyNode1D, hipGraphAddEmptyNode, hipGraphExecKernelNodeSetParams 
Change-Id: I0d7ec8c0ea1abc3fc0f1e10fa7865f355d9cf2ad


[ROCm/hipother commit: a2716fa1af]
 2021-07-28 00:09:16 -04:00
Sarbojit Sarkar 9679384d86 SWDEV-292547 - hipStreamPerThread support 
Change-Id: Id621ce073b0fee9eac03c59ffb78b197fda4ddb5


[ROCm/hipother commit: ce3a40699c]
 2021-07-26 20:51:51 -04:00
Tao Sang 3772d58b55 SWDEV-294594 - Fix hipPointerGetAttributes test on NV 
Replace return value of hipPointerGetAttributes() on NV from
hipErrorUnknown to hipErrorInvalidValue if memory has been freed.

Change-Id: I3fe6dbc35a7a14aa9109df297b7885df83d28149


[ROCm/hipother commit: 3efa0aa254]
 2021-07-26 11:30:22 -04:00
Tao Sang 771b220e8a SWDEV-294588 - Enable NV printf DTests 
Add hipLimitPrintfFifoSize.
Add hipDeviceSetLimit(hipLimit_t limit, size_t value) for NV.

Change-Id: Ife884e0c3081b317bdadc8bec7814d1d7c60153a


[ROCm/hipother commit: b0bd8d6859]
 2021-07-15 11:02:13 -04:00
Anusha GodavarthySurya bd45c7c32f SWDEV-240807 - Added Implementation for few more graph APIs 
Change-Id: I76336a22233a208a3f54ff9e90f0c5bf4a1bddb4


[ROCm/hipother commit: 8b809eb24e]
 2021-07-14 20:56:36 -07:00
agunashe f12034df79 SWDEV-293742 - Update copyrights end year for hipamd 
Change-Id: I08f620f84563a9214b59f1b943ed091b67229eab


[ROCm/hipother commit: 171f5d5869]
 2021-07-09 12:08:39 -04:00
Anusha GodavarthySurya 9602cf2349 SWDEV-240806 - hipGraph support for nvidia path 
Change-Id: Idb51b3ed7ca65474afac0dc714c9097294d46bd2


[ROCm/hipother commit: d931c0eff9]
 2021-07-07 06:51:21 -04:00
Jatin 4bcfffbfcf SWDEV-245414 - fix nvcc CI breakage 
Change-Id: I34ff533f34cfc2f60abefc0d8f6c6d8266d30f61


[ROCm/hipother commit: c0a0999d1a]
 2021-06-26 13:31:10 +05:30
Sarbojit Sarkar 0ff075e785 SWDEV-284435 - StreamOps mapping with cuda drv API 
Change-Id: I6ed9196cfe59d9004338206f6dd8d6fb367b3ffa


[ROCm/hipother commit: ef4d479169]
 2021-06-25 12:20:40 -04:00
Rahul Garg 62a54a9ad5 ROCMOPS-1956 - Push restructured code to hipamd 
hipamd will have AMD's ROCCLR based HIP backend implementation

Change-Id: Id7de9634519b4ce46fca71a1b61f3d5b1e3fc459


[ROCm/hipother commit: b2f4e62135]
 2021-06-07 21:42:44 +00:00
Rahul Garg 7d8b728f8c SWDEV-288707 - Merge HIP refactored code to staging 
These changes move-
- rocclr based implementation inside src/hipamd/src
- platform specific (both nvidia and amd) headers inside
src/hipamd/include/hip

Change-Id: Ia29791a727244952591fe1d813dcef0303b73a9e


[ROCm/hipother commit: 358b6fe5c4]
 2021-06-07 00:07:24 +00:00
Satyanvesh Dittakavi 4871d8275e SWDEV-283388 - Fix hipMemRangeGetAttributes on Nvidia Platform 
Change-Id: I5daeacd9dd5c6ce7f914d6e6e45dd41fb2a675a5
hipMemRangeGetAttributes was returning hipErrorInvalidValue due to improper
mapping of the arguments to cudaMemRangeGetAttributes.


[ROCm/hipother commit: 5165e3650a]
 2021-04-29 06:06:03 -04:00
Satyanvesh Dittakavi d801edf316 SWDEV-281789 - Add missing HMM attributes on CUDA path 
Change-Id: I11167eea006301e01a1f91708bf6d0ac832d8b7f


[ROCm/hipother commit: 49f81037f3]
 2021-04-26 13:54:01 -04:00