27f102b167
SWDEV-323472 - Add hipThreadExchangeStreamCaptureMode
...
Also fix an issue in hip_prof_gen.py with GLenum.
Change-Id: Ib03fe9dae87b850c53b7d8aeb78b8dbdd01f794c
2022-02-24 15:24:22 -05:00
f3f11f4c7d
EXSWCPHIPT-13 - Fix Segfault on Nvidia Platform
...
Change-Id: Ib85bb0b0e91b7703afc4858c4a5ada0115ad68f4
2022-02-19 12:53:46 +00:00
aee5c48848
SWDEV-315981 - make nvidia hiprtc functions static
...
Change-Id: I945426c155ed9ce21c308745f384bbf8669d73c4
2022-02-15 23:38:19 -05:00
e5496b3159
SWDEV-314485 - Remove the older implementation of device-side malloc/free
...
Change-Id: I9ba3c6030a6dd7a5e064073d5c21223041282f61
2022-02-15 07:49:56 -05:00
087c0c25b2
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
2022-02-15 02:03:49 -05:00
f371300933
SWDEV-315017 - Add missing graph error strings
...
Change-Id: I11b5a623756c5bef88cbc93e49c124d0caf62bd1
2022-02-15 01:41:44 -05:00
9c31a738c2
SWDEV-317135 - Fix mapping of hipStreamUpdateCaptureDependencies on cuda path
...
Change-Id: Ibbcf8136fa527a20684a377311bc76182345d17b
2022-02-14 09:10:46 -05:00
7d8c63cc34
SWDEV-294375 - Declares fns() functions static
...
Change-Id: Ife0150b8d6b9531522e61a82df6b88af3282f437
2022-02-13 23:35:46 -05:00
d7beddbfee
SWDEV-316128 - HIP surface API support
...
Change-Id: I5b98f86168e64b36588f5d7efb82191d895e27d7
2022-02-11 11:07:04 -05:00
0759f4ff81
SWDEV-314661 - Add hipGraphInstantiateWithFlags API mapping in nvidia path
...
Change-Id: Ibbf54ef18978448e92571f0535124844154726b6
2022-02-09 00:02:55 -05:00
523e5a007c
SWDEV-294375 - Adding coalesced_groups to ROCm CG
...
Change-Id: I4098e1970ae2c388171fa73deb5bc023ed1b7a68
2022-02-07 11:29:46 -05:00
760f275861
SWDEV-292714 - Added support for hipPointerGetAttribute and
...
hipDrvPointerGetAttributes
Change-Id: I44a0b5c5d9eb5a9a63406b11e8de83e5cb245a59
2022-02-02 05:33:07 -05:00
44e0c246f8
SWDEV-245531 - GLInterop adding register image
...
Change-Id: I075bec49b7ad5f78336586b9d55e259717c4c000
2022-01-23 14:59:18 -05:00
5f9d779324
SWDEV-245531 - GLInterop adding register image
...
Change-Id: Ib16b647e2a1b8f3c578a9689d3987121c984250b
2022-01-14 15:57:24 -05:00
c8103470d5
Fix missing system-scope for CAS in atomic[Min|Max]_system
...
Change-Id: Ieb0ca79eaeba3a0ae56739246e08135a25a8d6dd
2022-01-12 22:53:11 -05:00
0f94653447
SWDEV-315924 - align with CUDA to define vector3 data type
...
Change-Id: I7654fb757b4c387a762f384ccdd3f2c8555d149f
2022-01-06 17:35:56 -05:00
78de8cd672
SWDEV-315590 - Fix texture vector issue
...
Apply mapFrom() to related texture device functions.
Change-Id: Ifed918c87373b784780b2180320ccb746845daff
2022-01-04 19:26:14 -05:00
7de480760b
SWDEV-315590 - Fix texture fetch issue
...
Add mapFrom() to map "float __attribute__((ext_vector_type(4)))"
of output of low-level device function to right vector.
Change-Id: Ifed915c87273b784780b2180320ccb746845dafb
2022-01-04 13:38:57 -05:00
8a8581edf5
SWDEV-316052 - fix HIP_Directed tests build error
...
Change-Id: I782c68859f77934f2cf672ee53378e51b1cb1ddd
2021-12-21 03:21:53 -05:00
a8b30291c3
SWDEV-303956 - add make_int2/3/4 and make_float2/3/4 function support
...
Change-Id: I0260d1a9d2ac66e84dc31a80b0995616ef78b0fe
2021-12-15 14:57:36 -08:00
937415141c
SWDEV-303956 - align with CUDA to define float4 data type
...
Change-Id: I9ad1315e5899a8c0cf1812302b27010d88015f88
2021-12-14 15:22:43 -05:00
f3c5f12d26
SWDEV-311744 - Update floating point max/min atomic implementation
...
Clang builtins doesnt yet support max/min atomics with float/double
parameters, Hence modify atomicMax/Min to use compare and swap
implementation
Change-Id: Ia351f9b136129fe25f0eddcbbb17549553247182
2021-12-07 13:29:44 -05:00
5acc8b5102
SWDEV-303204 - Disable texture/image Apis on some devices
...
If the target device doesn't support image,
compiler will send out unavailable error if device texture apis
are called; and host texture apis will return hipErrorNotSupported.
Remove useless include/hip/amd_detail/texture_functions.h.
Add hipDeviceAttributeImageSupport attribute to check image
support in runtime.
Add __HIP_NO_IMAGE_SUPPORT(=1) macro in device code to indicate
texture apis not supported.
Change-Id: Ia891493e681a61980a2444859a90e046a9ebea39
2021-12-04 08:14:08 -05:00
69117705c8
SWDEV-309292 - add hipPos definition in CUDA path
...
Change-Id: Ia81d5db77d7403cafb583fda8083d0f4dbe33835
2021-12-04 04:40:34 -05:00
5b08779b25
SWDEV-307407 - Add hiprtc's type traits function to match implementation of libcxx
...
Change-Id: I0a10eca329f817bbe31bdc47869b2de104d12d38
2021-12-02 23:32:23 -05:00
e90cb3b07b
SWDEV-305766 - Added new debug APIs to get build information
...
Change-Id: Ibbf0c010cd8f7e6e659f2c4ba932cc8436574431
2021-12-02 12:20:51 -05:00
a6bf18791e
SWDEV-240808 - Added nvidia handling for few graph APIs
...
Change-Id: I8edee87ea75d80152418f76cc8a521b2ba58f139
2021-11-22 07:17:34 -08:00
17cc99c05d
SWDEV-306947 Enable hipAddressModeBorder
...
Enable hipAddressModeBorder.
Fix default of height of hipMallocArray().
Some code improvement.
Change-Id: I57045118e7adf915074c547cbe76349a4cfd72d8
2021-10-27 10:05:53 -04:00
1c51d82dd5
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
2021-10-05 07:44:54 -07:00
1111468b49
SWDEV-240806 - Added few more Graph APIs
...
Change-Id: I028a1fdf30232b0c47443685e03d7ca410d2a0d0
2021-10-05 07:37:11 -04:00
4cd4d2d280
SWDEV-304552 - Add default to return the last error value
...
Change-Id: Ia399033e30aaa454a454067f5afc6f7d1e5ff8dd
2021-10-04 07:23:10 -04:00
70e1fb6a5b
SWDEV-304076 - Fix for Cuda build error
...
Change-Id: Ibca63a08b8d6d1235b51a06c0bc024cd284cee97
2021-09-27 23:55:52 -04:00
7aaad05910
SWDEV-298667 - fix stream operation for Cuda
...
Change-Id: Ida91712e678e324b54293ba48dfca442be390783
2021-09-21 15:07:15 -04:00
673c2deed1
SWDEV-302147 - fix __hip_ds_permutef device function to return float
...
Change-Id: Ie452e90a7f7410401df4a66de468ad850403953c
2021-09-14 02:15:53 -04:00
b25e6d3716
SWDEV-301330 - Remove the hard coded driver version on HIP CUDA platform
...
Change-Id: I0eb10781acc7524174c7ae6fc552c824b7c94b0a
2021-09-02 09:03:04 +00:00
feed2de479
SWDEV-293749 - Add cast before calling the builtin
...
Change-Id: I6224a3693f91a5b4e040bd76918ab04a56a6454b
2021-08-24 10:35:52 -04:00
06e1e4f0de
SWDEV-296918 - Adding unsafe atomic add operation for float and double type
...
Change-Id: I98eabb7412f604733a999bf5e89c2c80b91cfbb1
2021-08-14 12:22:53 +05:30
8a4ca88477
SWDEV-297689 - Moving the vendor specific builtin function calls to hip_cooperative_helper.h header file
...
Change-Id: I797bdde8fbb01285dfda0eac0f960ded260beb8e
2021-08-02 19:14:42 -04:00
ec39f62ee1
SWDEV-297563 - Move surface types
...
Change-Id: Ie2393fb32a30a76c39c81ce17497fa3b131a85b1
2021-08-02 18:48:15 +00:00
3dd9dbb359
SWDEV-297563 - Move declarations to hip
...
Change-Id: Ifdab79945ea2e625e8cef5cd71d638552e9a740b
2021-08-02 11:56:08 -04:00
a71f54d9e9
SWDEV-240806 - Added API hipGraphAddMemcpyNode1D, hipGraphAddEmptyNode, hipGraphExecKernelNodeSetParams
...
Change-Id: I0d7ec8c0ea1abc3fc0f1e10fa7865f355d9cf2ad
2021-07-28 00:09:16 -04:00
c3ca1faee7
SWDEV-292547 - hipStreamPerThread support
...
Change-Id: Id621ce073b0fee9eac03c59ffb78b197fda4ddb5
2021-07-26 20:51:51 -04:00
203c4b9b35
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
2021-07-26 11:30:22 -04:00
cbbf627662
SWDEV-292523 - [hipamd]Change in the signature of streamOperations APIs, particularly 'value' arg to unsigned 'value'
...
Change-Id: I7e31508622865b9986c886c4218ba394ffe9cf9e
2021-07-22 16:24:27 -04:00
9a510f1cf1
SWDEV-281658 - Preserve the callback IDs enum ordering
...
Use continue instead of break to make sure we process the
whole hip_runtime_api.h file.
Change-Id: Ied2a8df69ed9eb1dc04d6b2d0d7b117ce2a2b6b3
2021-07-20 20:12:21 -07:00
a8e0ab621e
SWDEV-282289 - Use preprocessor directive for atomicAdd to support backward compatibility.
...
Change-Id: I73f058040afaa782bf6a491b8761a040fbd5b571
2021-07-19 10:46:01 -04:00
e0ae326f4a
SWDEV-294588 - Enable NV printf DTests
...
Add hipLimitPrintfFifoSize.
Add hipDeviceSetLimit(hipLimit_t limit, size_t value) for NV.
Change-Id: Ife884e0c3081b317bdadc8bec7814d1d7c60153a
2021-07-15 11:02:13 -04:00
ff8c20c092
SWDEV-294395 - HIPRTC add definitions for amd_hip_vector_types.h
...
Add typedefs for int32 and int64. Add templates provided in
system headers such as type_traits used in our HIP header
amd_hip_vector_types.h. Make replacements for clang builtin,
__is_convertible_to.
Change-Id: I4129b3f4f37238e2dda5b64d55e5cffe4d4480c6
2021-07-15 05:41:51 -04:00
e5cbfa8ca9
SWDEV-240807 - Added Implementation for few more graph APIs
...
Change-Id: I76336a22233a208a3f54ff9e90f0c5bf4a1bddb4
2021-07-14 20:56:36 -07:00
4aab5c29ff
SWDEV-278500 - Implement missing atomic APIs and types to match CUDA.
...
Change-Id: I5f5bd94af9b68853bf354c8f90da217434934ddd
2021-07-13 22:15:57 -04:00
Christophe Paquot
Satyanvesh Dittakavi
Sourabh Betigeri
haoyuan2
pghafari
Payam
Nick Curtis
Tao Sang
cjatin
anusha GodavarthySurya
Sarbojit Sarkar
Rahul Garg
kjayapra-amd
Aaron Enye Shi