f80bffb4ab
SWDEV-337776 - Fix hipStreamEndCapture API
...
- Return hipErrorInvalidValue when pGraph is nullptr
Change-Id: I8846f4448eb15117f98421632885330f132c4fce
[ROCm/clr commit: e2874d5e22
2022-06-01 00:20:23 -04:00
ea9847c1fd
SWDEV-320640 - Fixes to return right error codes in hipStreamUpdateCaptureDependencies() for negative scenarios
...
Change-Id: I3c4c54f8955fa9bb17eb595544005fe9f0e8a5f0
[ROCm/clr commit: 5a057af564
2022-05-31 14:09:22 -04:00
de626141ee
SWDEV-337703 - nullptr check for hipMallocArray
...
Change-Id: I3b1077e236ccda346d337109014ef7fd2e693ec6
[ROCm/clr commit: 8e28413a9e
2022-05-31 11:19:59 -04:00
48350aea01
SWDEV-336550 - added nullptr check for svm
...
Change-Id: Icfd7dab1c7818958108385261542526d4545721d
[ROCm/clr commit: 2870b7ddd5
2022-05-30 16:58:45 -04:00
9bc0d08679
SWDEV-290384 - Add Linker API support in hiprtc
...
Change-Id: I4621a033a22e4da0201c3804e2b357470a681ab0
[ROCm/clr commit: 84f94fd134
2022-05-24 09:16:14 -04:00
85f42de77c
SWDEV-337119 - Validate width isn't exceeding either dpitch or spitch in
...
ihipMemcpy2D
Change-Id: I8ac68e033762616a42585b26f0b3aa5bbb29ce9c
[ROCm/clr commit: 01a5ddebe6
2022-05-18 23:25:14 +05:30
8e9541dbbd
SWDEV-334908 - Guard the __noinline__ macro as it is also supported as keyword by clang
...
Change-Id: I314b3ac463ea63132a5107f4f24ce769d8112b9b
[ROCm/clr commit: 8dfa7e7f98
2022-05-18 05:51:32 -04:00
b2188142d9
SWDEV-336576 - updated graph check
...
hipGraphExecMemcpyNodeSetParamsFromSymbo was not working in functional
case
Change-Id: I2ad04f6f91519efa075c36fe737a695fa1bc127a
[ROCm/clr commit: bb9e52ab9f
2022-05-17 17:36:10 -04:00
a3c9b7dde6
SWDEV-322620 - Virtual Memory Management
...
Report virtual memory management support.
Change-Id: I448a66c86ab1b2d28f6052e8896ea505e56eb2d2
[ROCm/clr commit: 60656d9fc9
2022-05-17 16:24:53 -04:00
23ba31d7bf
SWDEV-332606 - SWDEV-333585 - Fix hipMemcpySymbol* and hipGetSymbol* APIs
...
This also fixes the QMCPack staging (SWDEV-335826) test failures related
to hipMemcpyToSymbol
Change-Id: Icc3ff04fb1e17999f5bddf12e1a7266e2289032f
[ROCm/clr commit: 8a333a989b
2022-05-16 04:27:02 -04:00
79d6018cd7
SWDEV-319818 - Revert change on hipResourceViewDesc
...
Revert part of
http://gerrit-git.amd.com/c/compute/ec/hipamd/+/675588
Change-Id: Iee9dac9f8c50aa9b6a12ca9d8fd792a51973b8cd
[ROCm/clr commit: 4561a207dd
2022-05-12 12:14:13 -04:00
a206abcaa1
SWDEV-335780 - Address OOM issue with BERT MLPerf
...
Memory free was not happening due to no flush
Change-Id: Iee9d2c9f8c50aa9b6012ca9d8fd792a51973b8c8
[ROCm/clr commit: f6e21144ae
2022-05-11 13:03:32 -04:00
a7d73a753d
SWDEV-311271 - Enable MGPU support for memory pool
...
Change-Id: I36850de282d62139b5cfe342df97bb1204cb7869
[ROCm/clr commit: 8b132beb92
2022-05-11 11:04:24 -04:00
1a9a5f9bfc
SWDEV-319818 - Release restriction on hipResourceViewDesc
...
Let more types support hipResourceViewDesc.
Add missing symbols to fix cuda build failing.
Change-Id: Ife694cc6491427093863252e257e820b0bb4fa0f
[ROCm/clr commit: a19b767e8a
2022-05-10 15:57:31 -04:00
b53cb9e585
SWDEV-336248 - Use public icd header
...
HIP uses icd_dispatch.h, which is not a public header. Using the public
CL/cl_icd.h removes inclusion of the private header.
This allows compiling HIP without relying on OCL ICD source, which makes
distributing a standalone ROCclr easier.
For WIN32, a few other headers are required.
Signed-off-by: Jeremy Newton <Jeremy.Newton@amd.com >
Change-Id: I0cab173b9753c5b0ab3be9222aa8bb0545cdeaab
[ROCm/clr commit: d04938a6ad
2022-05-10 13:46:08 -04:00
1171423bcf
SWDEV-329829 - Fixes to return right error codes for respective negative scenarios
...
Change-Id: Icb615a336bb846df1cf2811316d88a0e88381da8
[ROCm/clr commit: 5fa514fea0
2022-05-10 12:56:20 -04:00
5a9a25fcb6
Revert "SWDEV-332606 - SWDEV-333585 - Fix hipMemcpySymbol* and hipGetSymbol* APIs"
...
This reverts commit 1ab7f2233484c46047e5
2022-05-10 11:20:36 +05:30
b175689cd2
SWDEV-333598 - Use flags field of amd::Memory UserData for hip flags
...
Change-Id: I492c7fe54dba4380fcc53eed1df36bf5ac0af852
[ROCm/clr commit: 4e86d538e5
2022-05-06 13:42:19 +05:30
342d552ba7
SWDEV-333848 - Regression fix
...
Change-Id: I328770d5c51418c7f5bcb73696c81311d8dc3aef
[ROCm/clr commit: 118fad741a
2022-04-29 13:27:46 -04:00
3e667fc98f
200~SWDEV-333583 : hipMallocArray bad channel format
...
- channel format should be consistent accross parameters
Signed-off-by: sdashmiz <shadi.dashmiz@amd.com >
Change-Id: I1e7680ab9262a66e7bea4aaa21f061044b0f7956
[ROCm/clr commit: 8ed471f210
2022-04-29 09:15:41 -04:00
a6f1bde5d7
SWDEV-330667 - SWDEV-333599 - Fix hipHostRegister and hipMallocPitch APIs
...
- hipHostRegister should return hipErrorInvalidValue when size is 0 or
size doesn't match the actual allocated size
- hipMemAllocPitch should return hipErrorInvalidValue when width or height
is 0 and elementSizeBytes should be 4, 8 or 16
Change-Id: I43c9fe4ac1ef0a6ac2f953908d301508a7bc5aa3
[ROCm/clr commit: 06203c251e
2022-04-28 13:07:08 +00:00
c2b3dd7dc5
SWDEV-322620 - Virtual Memory Management
...
Implemented hipMemMap and hipMemUnmap
Change-Id: Idc75e3964d88e375e445733557cfa8e421688f1f
[ROCm/clr commit: 6d73282f25
2022-04-28 02:14:14 -04:00
558467643d
SWDEV-333187 - Support IPC in HIP runtime on Windows
...
enable shared memory based IPC
Change-Id: I2657ef4713240b6f82a34f416d53f222630263ca
[ROCm/clr commit: 59b1ae0a79
2022-04-27 11:14:59 -07:00
0ddbd07e0c
SWDEV-327960, SWDEV-316901 - Adding Graph checks
...
hipGraphExecMemcpyNodeSetParamsToSymbol, fix for functional cases
failing as well
Change-Id: I9f263778f6b24e3ec35a78231a17e01c0d44f23a
[ROCm/clr commit: 63f23ec2b0
2022-04-26 21:04:32 -04:00
12df44b4fc
SWDEV-332522 - ipcEvents Avoid deadlock b/w streamWait & Event
...
Using device write to set 0 to signal while streamWaitEvent is checking
the signal.
Use app in SWDEV-314307 to verify this fix
Requires vdi #668012 change to work
Change-Id: Ie329a29cfaeb5d144b92cda36773646f913ca73d
[ROCm/clr commit: 1abd0d6ecf
2022-04-26 11:59:01 -04:00
1ab7f22334
SWDEV-332606 - SWDEV-333585 - Fix hipMemcpySymbol* and hipGetSymbol* APIs
...
- hipMemcpy[From/To]Symbol APIs to return hipErrorInvalidMemcpyDirection
if the copy kind is incorrect
- hipGetSymbolSize and hipGetSymbolAddress APIs to return hipErrorInvalidValue
if the pointer is null
Change-Id: I32f428045c804b1e4f648e91b507f749f60c09d0
[ROCm/clr commit: f1fb612774
2022-04-25 08:25:29 -04:00
cba04140c0
SWDEV-332603 - Check validity of ihipArrayCreate() first argument
...
Change-Id: Ifd0bdb5708c110da45e4baa9426cccd749732822
[ROCm/clr commit: 8ea74366d7
2022-04-22 11:08:37 +05:30
7a572e0162
SWDEV-332604 - Add nullptr check for argument pitch
...
Change-Id: I6d7aa5356a74b92f21f7a51a7d3e2f8d0b920e07
[ROCm/clr commit: 2613ebf157
2022-04-22 00:13:24 -04:00
1c5b11fd04
SWDEV-322620 - Virtual Memory Management
...
Implement hipMemAddressFree and hipMemAddressReserve
Change-Id: I1b09e433db5c5c6d6b9fe2a7a15fe2c09f1e1874
[ROCm/clr commit: fd17b53ea4
2022-04-21 17:19:10 -04:00
ecb4165943
SWDEV-333607 - Avoid synchronization of all GPU(s)
...
Use the original device from creation to sync before host memory
free.
Change-Id: I510e34afa7accf69e3d01338587bbc817b981cec
[ROCm/clr commit: b4c5a01fbc
2022-04-21 15:36:04 -04:00
a687844e68
SWDEV-332809 - Fix for OpenMp crash
...
Change-Id: I70445edf76261ab8ecf174614f23bd9fb8d60881
[ROCm/clr commit: 71b5235c64
2022-04-19 11:29:19 -04:00
e22f2e1714
SWDEV-323441 - support for default stream per thread
...
Change-Id: I0032da0357f5cffbf5e4ec4a02435d2a128a262b
[ROCm/clr commit: fc1f02bbed
2022-04-18 23:19:55 -04:00
d4991641bd
SWDEV-301667 - Add separate field for event scope
...
Change-Id: I0e6b50d1a34b275ea4f1a4c659430c406d9a5a7e
[ROCm/clr commit: aace42cfab
2022-04-18 15:48:33 -04:00
3de1a9e36c
SWDEV-311271 - Make sure memory pool can accept default stream
...
Add lock protection for access to the pool list.
Remove destroyed stream from the list of the safe streams
Change-Id: I1863b89bd3f5e188c161227cc790c3adaf72cc58
[ROCm/clr commit: 5957ff9f7b
2022-04-18 10:34:21 -04:00
5516c2d12e
SWDEV-308763 - Remove older hiprtc implementation
...
Change-Id: I1f0a1fe9b6590070905348bf71b901ac77b196be
[ROCm/clr commit: b06ee8834d
2022-04-18 05:12:53 -04:00
3db2dd9812
SWDEV-332371 - Address seg fault with hip event tests on Windows
...
Change-Id: I0367f6dbb395b3032c97692c5bde6e99d503c6a9
[ROCm/clr commit: 3b525ad298
2022-04-18 04:19:23 -04:00
9caddbf38a
SWDEV-331301 - Fixes error code mismatch
...
Change-Id: I8dda98609b16ea5c1ce4d9db9471e61e5fb0c12c
[ROCm/clr commit: bd851550bd
2022-04-13 18:51:06 -07:00
50f0103648
SWDEV-276210 - Honor scopes for hipEventRecord
...
Honor hipEventReleaseToDevice and hipEventReleaseToSystem flags.
hipEventRecord would flush caches if no release flags are provided. To
change this behavior set ROC_EVENT_NO_FLUSH=1
Change-Id: I03e41b515b1d0cf963b0c2d5b9901b09e71a0e59
[ROCm/clr commit: f320acb797
2022-04-13 00:35:19 -04:00
3a7351ef9c
SWDEV-330666 - null(default) stream's priority is 0.
...
Change-Id: I115effc2ddaa28dee32967ee28041b9b8da095b9
[ROCm/clr commit: c1503da69b
2022-04-13 00:28:52 -04:00
89ca29819e
SWDEV-329848 - Fixes error code mismatch between CUDA and HIP
...
Change-Id: Ic48de159ca7bdb4b91dadb915972e535518635ae
[ROCm/clr commit: 345e02358c
2022-04-12 15:00:44 -04:00
0d4efc9f0f
SWDEV-328274 - Move DLLMain from VDI layer to HIP/OCL layers
...
Change-Id: Ibd3388f0981672cd209d7370f8a28b2883abdea2
[ROCm/clr commit: cb4aabd285
2022-04-12 11:00:20 -04:00
85f6f2a0c7
SWDEV-331126 - Fix to Cuda return type
...
Change-Id: Iea8e7735ef0c58c1244c92338038d91e61d62c16
[ROCm/clr commit: 8657c40721
2022-04-11 23:35:04 -04:00
013225775c
SWDEV-331095 - Address hipRTC windows test failures
...
Change-Id: I8c1a36ffd362c6f41449092e4dd85f6ec587206a
[ROCm/clr commit: f301bf3962
2022-04-11 09:40:35 +00:00
c6ae81b2f2
SWDEV-322620 - Virtual Memory Management APIs
...
Adding skeletons.
Implemented:
- hipMemGetAllocationGranularity with basic granularity
- hipMemGetAllocationPropertiesFromHandle
- hipMemCreate
Change-Id: I4bd2c75fae45d6a057efcad19d1d3c9715e9ae67
[ROCm/clr commit: cd447a5aaa
2022-04-08 11:38:51 -04:00
583aa7f008
SWDEV-330661 - devicePointer null checking.
...
Change-Id: I3366031954330143109d0a79e86fd0e0ec996f01
[ROCm/clr commit: ff78c439ef
2022-04-08 00:08:37 -04:00
83e2a8a892
SWDEV-326796 - Fix hipMemset crash when the size passed is more than allocated
...
Change-Id: If3b15da0960f3af347fca62beedd8003cb958c2e
[ROCm/clr commit: c0ada4320b
2022-04-07 08:49:54 -04:00
3cec88a755
SWDEV-331152 - Add back HIP_HOST_COHERENT support
...
Change-Id: I1971df55913498df801ad319a20b95380a2c136f
[ROCm/clr commit: b1436f6451
2022-04-06 12:26:01 -04:00
34e1d885a5
SWDEV-326793 - hipStreamGetFlags should query the flags for null stream
...
Change-Id: I1d1b833704c135b5a0c695b244380ac6c5b8438e
[ROCm/clr commit: 0af8904b87
2022-04-06 04:09:17 -04:00
2442d41e31
SWDEV-316292 - adding Graph checks
...
hipGraphExecMemcpyNodeSetParamsFromSymbol negative test cases
Change-Id: I7b6c496a8bca831dc90d1d427273a2a4fea96587
[ROCm/clr commit: 798a304dbd
2022-04-05 13:26:46 -04:00
8a6fd0bd65
SWDEV-316819 - graph check ChildGraphNodeGetGraph
...
Change-Id: Id3a4fb64e6fb5ce37e97f1f3518e09c8bd9a2d0c
[ROCm/clr commit: 8618b1cd07
2022-04-05 01:24:36 -04:00
Rakesh Roy
Sourabh Betigeri
pghafari
kjayapra-amd
Satyanvesh Dittakavi
Christophe Paquot
Tao Sang
German Andryeyev
Jeremy Newton
Jaydeep Patel
sdashmiz
haoyuan2
Ajay
Sarbojit Sarkar
Saleel Kudchadker
Payam