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
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
ebdd811632
Revert - Changes related to hipMemcpyWithStream ( #1718 )
...
Reverting #1673 , #1697 and #1707 .
Support for hipMemcpyWithStream and memcpy optimizations, will be brought in again once issues seen with these are resolved independently.
[ROCm/hip commit: e53fc316f1
2019-12-06 09:51:53 +05:30
fa87abd58a
Fix hipMemcpyWithStream ( #1707 )
...
* Fix hipMemcpyWithStream
* Add a dtest for the same.
[ROCm/hip commit: 892d2a562e
2019-12-04 11:56:23 +05:30
abe7531676
[hip] refactoring hipExtLaunchMultiKernelMultiDevice API ( #1698 )
...
[Background] it was found that if lazy linking used for a library that calls hipExtLaunchMultiKernelMultiDevice API then this API can get the wrong program_state object for looking up device kernels leading to a "No device code available" error in this API.
To fix this issue, the API was refactored to be inline and get and pass the correct program_state to an internal hip API to request a multi-device kernel launch.
[ROCm/hip commit: 68cc787781
2019-12-04 11:50:51 +05:30
f1544b621d
fix hipMempcy precondition, test for zero size first ( #1697 )
...
[ROCm/hip commit: 299bbe2325
2019-11-25 19:03:03 -08:00
3848cd97ea
fixed directed tests fail when hcc bumped to 3.0 ( #1678 )
...
Handled the HCC version check appropriately as few of the directed tests (SWDEV-212161) were failing when hcc was bumped to 3.0.
[ROCm/hip commit: 6b06911ef1
2019-11-20 21:37:52 +05:30
1baa84eae4
General sync memcpy improvements. Add hipMemcpyWithStream ( #1673 )
...
* General sync memcpy improvements. Add `hipMemcpyWithStream`
* Update hip_memory.cpp
[ROCm/hip commit: 5a1f823739
2019-11-20 21:36:37 +05:30
7e75cf12df
Update error codes for hipGetDevice for doxygen and move up null check ( #1668 )
...
* [docs] Update error codes for hipGetDevice
* Move up out ptr check
[ROCm/hip commit: b3161e9fa0
2019-11-20 21:35:27 +05:30
6679cd3998
Revert [HIP] Fixed hipStreamAddCallback ( #1674 )
...
This reverts commit fa1e44aa0e153a959280
2019-11-20 11:55:46 +05:30
492248ef12
hipStreamSynchronize can skip marker if stream is empty ( #1667 )
...
[ROCm/hip commit: 3a7eb694f5
2019-11-19 09:42:43 -08:00
a4f2c7717f
Added null check in hipEventSynchronize ( #1627 )
...
* Added missing null check in hipEventSynchronize
* Minor correction in the Event API description
[ROCm/hip commit: b865a50e44
2019-11-18 12:18:55 +05:30
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
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
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
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
f9ad564380
hipEventRecord only needs one lock; remove locked_eventIsReady
...
[ROCm/hip commit: 85080905c0
2019-11-06 15:56:32 +00:00
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
cdf59d1de0
fix race condition in hipEventRecord
...
[ROCm/hip commit: 6fcff0118e
2019-11-04 17:45:11 +00:00
3e3cebe614
Merge pull request #1598 from lmoriche/master
...
Fix a code object memory corruption
[ROCm/hip commit: 782cf1c007
2019-10-31 17:12:24 -07:00
75cf902cdb
Add stream
...
[ROCm/hip commit: 85d70086cb
2019-10-31 12:15:56 -04:00
73ca647852
Fix HIP init calls in hipMemcpy2DFromArray
...
[ROCm/hip commit: efe6fa86dc
2019-10-31 12:15:56 -04:00
7e742b1216
Merge pull request #1515 from ansurya/tex_unbind_issue_fix
...
Fix undefined ref to hipUnbindTexture for texture types
[ROCm/hip commit: ba8105e0cd
2019-10-30 17:54:15 -07:00
1056ca35dc
Addressed review comments
...
Change comment "must exceed" to "must be no shorter than"
move the std::string instead of creating a copy
[ROCm/hip commit: 91748f4e6c
2019-10-30 13:14:41 -07:00
70449cfa92
Revert "Fix occupany APIs ( #1560 )"
...
This reverts commit 4f23f9cb18e4a1e44162
2019-10-29 11:41:08 -07:00
86dd262e9b
Fix a code object memory corruption
...
The lifetime of the buffer given to
hsa_code_object_reader_create_from_memory must exceed that of the
code object reader. We need to create a copy of the code object
binary memory (file) that is kept allocated until the code object
reader is destroyed.
[ROCm/hip commit: 7473140a76
2019-10-29 08:23:57 -07:00
5c77b7d19a
Merge branch 'master' into tex_unbind_issue_fix
...
[ROCm/hip commit: 03623cc3f1
2019-10-25 15:54:25 +05:30
196bdea9c0
merge from master
...
[ROCm/hip commit: 5f47e99ffe
2019-10-25 15:52:09 +05:30
c315da2028
Add hipMemcpy2DfromArray ( #1510 )
...
Adds hipMemcpy2DFromArray and hipMemcpy2DFromArrayAsync equivalent to cudaMemcpy2DFromArray and cudaMemcpy2DFromArrayAsync.
[ROCm/hip commit: 356765a223
2019-10-25 15:43:33 +05:30
3007505d30
Merge branch 'master' into tex_unbind_issue_fix
...
[ROCm/hip commit: 259d8b4cdf
2019-10-25 15:36:55 +05:30
4f23f9cb18
Fix occupany APIs ( #1560 )
...
Addresses SWDEV-205006
[ROCm/hip commit: af351d7e1b
2019-10-24 17:44:47 +05:30
4d668d5a52
Improve performance of v2 arg handling ( #1539 )
...
* Improve performance of v2 arg handling
* Missing change to `std::string`
[ROCm/hip commit: c4a51f3679
2019-10-24 17:44:05 +05:30
9ab561dd66
[hip] add support for implicit kernel argument for multi-grid sync ( #1456 )
...
* [hip] add support for implicit kernel argument for multi-grid sync
* modified code for calculating the prev_sum
* change the impCoopArg type to size_t
* add memory clean up
* launch init_gws and main kernels into two separate loops
[ROCm/hip commit: 359dc79101
2019-10-24 17:43:30 +05:30
f82e9cd090
Merge pull request #1544 from vsytch/master
...
QoL changes to the hipMemset family
[ROCm/hip commit: e1aac060da
2019-10-16 18:54:20 -07:00
d2e9718d23
Guard against division by zero for no VGPR usage (e.g., in an empty kernel) ( #1528 )
...
* guard against division by zero for no VGPR usage (e.g., in an empty kernel)
* fix bracket format
* clean up parenthesis
[ROCm/hip commit: 73ca2b0083
2019-10-16 10:49:56 +05:30
370d039d24
Update the declarations of hipMemsetD8, hipMemsetD8Async, hipMemsetD16, hipMemsetD16Async. These functions are type aware and take in as their third argument the number of elements in the buffer, not the buffer size. Change the name of this argument from sizeBytes to count to align with the above description.
...
[ROCm/hip commit: 0b52c1d9d8
2019-10-15 14:18:42 -04:00
04080d4bb1
Fix undefine ref to hipUbindTexture for texture types
...
[ROCm/hip commit: af5f195e46
2019-10-09 16:26:06 +05:30
8c0b43156e
tracing layer unifying with hcc: removing API_ID_ANY
...
[ROCm/hip commit: 4e93833035
2019-10-08 19:09:43 -05:00
4f899d487c
Fix PCI Domain ID query ( #1424 )
...
* Fix PCI Domain ID query
* Update BDF comment
[ROCm/hip commit: 96530cba3b
2019-10-07 14:11:52 +05:30
4b05ebc194
[hip] Add the missing header <sstream>. ( #1498 )
...
[ROCm/hip commit: 4d632166bb
2019-10-04 13:39:29 +05:30
3b9b5fca8d
Add texref get APIs support ( #1471 )
...
Added support for -
hipTexRefGetArray
hipTexRefGetAddressMode
hipTexRefGetAddress
[ROCm/hip commit: bec725dec2
2019-10-04 13:38:45 +05:30
66e94b1b1f
Added new Memory API's ( #1399 )
...
Added new memory API's hipMemAllocPitch, hipMemAllocHost, hipMemsetD16, hipMemsetD16Async, hipMemsetD8Async
Modified to support all scenarios hipMemcpyParam2DAsync, hipMemcpyParam2D.
[ROCm/hip commit: ba9c6e13e4
2019-10-04 13:36:31 +05:30
0f9074b568
fix kernel descriptor bug with code object v3
...
Change-Id: I9306b2baf36d338e36c5ab1226f74373a61a5ae0
[ROCm/hip commit: dcf70ff9a2
2019-10-03 10:56:35 -04:00
bfb64c43a4
Reimplement hipMemGetInfo ( #1447 )
...
Addresses SWDEV-136570. hipMemGetInfo changed to compute free memory based on information from kfd instead of relying on hc::am_tracker.
[ROCm/hip commit: 3d661e4706
2019-10-01 12:40:36 +05:30
dcd73a1a87
hipModuleUnload should remove global variables from memtracker ( #1464 )
...
[ROCm/hip commit: 56f67e5e36
2019-09-30 10:41:20 +05:30
7f7a5a3712
[HIP] Add tccDriver info in hipDeviceProp
...
Fixes #1433 .
[ROCm/hip commit: 0fa42af08c
2019-09-26 13:53:33 +05:30
fe1fae3ec2
Fix checks in hipMemcpy[D/H]to[D/H]() ( #1397 )
...
* SWDEV-202043 hipMemcpyDtoD() issue
[ROCm/hip commit: cfbd0e77fe
2019-09-16 08:32:38 +00:00
b5549f4397
Added new device attributes ( #1377 )
...
* Added new device attributes
* updated comment
* updated with new device attributes supported
[ROCm/hip commit: ceb734b917
2019-09-16 08:31:30 +00:00
9e9a505b39
[hip] add initial support for hipLaunchCooperativeKernelMultiDevice API ( #1368 )
...
* [hip] add initial support for hipLaunchCooperativeKernelMultiDevice API
* fix formatting
[ROCm/hip commit: bac52d3729
2019-09-16 08:31:17 +00:00
saleelk
Alex Voicu
Rahul Garg
Aryan Salmanpour
Jeff Daily
satyanveshd
Sarbojit2019
ansurya
Rahul Garg
Laurent Morichetti
Anusha Godavarthy Surya
searlmc1
Nick Curtis
Vladislav Sytchenko
Evgeny
mhbliao
Siu Chi Chan