Граф коммитов

1372 Коммитов

Автор SHA1 Сообщение Дата
Aaron En Ye Shi c9f19b9d26 SWDEV-283266 - Workaround RTC macro in vector types
Temporarily disable __HIPCC_RTC__ in hip_vector_types.h
while the upstream clang headers are outdated on mainline.
Once upstream patch has landed in mainline, revert this
change. This is a workaround for hiprtc testing.

Change-Id: Ib2cf6023b71431bbfbe3c699076caa4f90f7170c


[ROCm/clr commit: 414c80644b]
2021-05-21 15:53:59 +00:00
Tao Sang fad72a437f SWDEV-282588 - Improve clock64()
Let clock64() read s_memtime to prevent rolling over
Add wall_clock64() to read s_memrealtime

Change-Id: I706387355add75852c570be2656131ef99e8968f


[ROCm/clr commit: 26235f49e6]
2021-05-17 13:19:04 -04:00
Aaron En Ye Shi 3a23df8893 SWDEV-263959 - Fix device decl with long and llong
Windows may expect long and ulong to be 4 bytes, while
Linux expects 8 bytes. Instead, use uint64_t for
unsigned long, and unsigned long long, and use int64_t
for long and long long to be consistent.

Change-Id: I6ed1cdde43721bcaaab0245644d607b1adbf9884


[ROCm/clr commit: dd643ec517]
2021-05-14 11:59:27 -04:00
pghafari f0e63eb72f SWDEV-245532 - HIP - Vulkan interop semaphores
Change-Id: I89be5ee84d4728d76e1987d5016c944c0dbc9a96


[ROCm/clr commit: ccff5216f0]
2021-05-11 11:44:59 -04:00
Aaron En Ye Shi 3d40b92eeb SWDEV-283266 - __HIPCC_RTC__ macro added to HIP headers
For hipRTC on Windows, add macro __HIPCC_RTC__ to allow
online compilation of with device functions excluding standard
C/C++ headers, system headers, and host HIP APIs.

Change-Id: I1d91f042baf1359856ec83ab7030dc58785e0334


[ROCm/clr commit: 688693e9fd]
2021-05-10 17:28:07 +00:00
Anusha Godavarthy Surya 1fe1fe9361 SWDEV-240806 - Initial commit for hipGraph and stream capture infrastructure
On StreamBegincapture captures the parameters passed to APIs and respective node will be created and added to graph
All parameters are passed to STREAM_CAPTURE macro, it checks if stream in capture mode and redirects the call to the capture function and returns
Updated hipStream and hipEvent with capture parameters
Added handling for hipStreamBeginCapture & hipStreamEndCapture

Change-Id: Ic8926a7b4336c2cc81f0b3a9a224aa392c474134


[ROCm/clr commit: 8cc0e04239]
2021-05-07 17:38:16 -04:00
Anusha GodavarthySurya 766c6fbdcb SWDEV-271978 - Function __byte_perm to match CUDA behavior
Selector indices are as follows (the upper 16-bits of the selector are not used): selector[0] = s<2:0> selector[1] = s<6:4> selector[2] = s<10:8> selector[3] = s<14:12>

Change-Id: Ibf76c6ec2374f1f5b9bba8bd9dbd73660f830eea


[ROCm/clr commit: e9cc056d25]
2021-05-05 03:00:32 -04:00
kjayapra-amd d3ff861a37 SWDEV-245533 - Implementing Mipmap array APIs
Change-Id: I222c8d0fcbd50cdefd702462e689463bb36366d2


[ROCm/clr commit: 31d412c292]
2021-04-30 16:33:43 -04:00
Satyanvesh Dittakavi 9e4b7ff5bb SWDEV-283388 - Fix hipMemRangeGetAttributes on Nvidia Platform
Change-Id: I5daeacd9dd5c6ce7f914d6e6e45dd41fb2a675a5
hipMemRangeGetAttributes was returning hipErrorInvalidValue due to improper
mapping of the arguments to cudaMemRangeGetAttributes.


[ROCm/clr commit: cc39ceab25]
2021-04-29 06:06:03 -04:00
Satyanvesh Dittakavi 59c118bb57 SWDEV-281789 - Add missing HMM attributes on CUDA path
Change-Id: I11167eea006301e01a1f91708bf6d0ac832d8b7f


[ROCm/clr commit: 120436423c]
2021-04-26 13:54:01 -04:00
Yaxun (Sam) Liu e04783afe7 SWDEV-255234 - remove workaround for warpSize after clang fix is released
The workaround is no longer needed as the compiler emits the macro itself.

Change-Id: I6a06e73353628bcea71f6bd23503ab6d8e42a29d


[ROCm/clr commit: 37b90c2f64]
2021-04-26 08:49:15 -04:00
Anusha GodavarthySurya dcad465a22 SWDEV-282361 - HIP support for NVRTC
Change-Id: I82869af8194b595f9a2fb64ad034630786189335


[ROCm/clr commit: c23586440b]
2021-04-20 09:28:58 -07:00
Tao Sang fe7d103d56 SWDEV-279657 - Fix hipMallocManaged-N256M failure
Add concurrentManagedAccess detection in hipMallocManaged test.
Skip test when device doesn't support concurrentManagedAccess.

Change-Id: Ie54046feef3baba857a7068972ec1fc1a60c2dfd


[ROCm/clr commit: 20fd6b8a66]
2021-04-20 09:07:31 -04:00
Sourabh Betigeri eedde26cc9 SWDEV-256723 - Added group partitioning feature in ROCm CG.
Change-Id: Ie54046feef3baba857a7068972ec1fc0a60c2df9


[ROCm/clr commit: 0a0b026304]
2021-04-19 18:53:17 -04:00
Julia Jiang e103d4f31d SWDEV-270961 - Update hip_programming_guide.md for event handling
Change-Id: Ieadac9972e5ee13c05ccb42a679866f494f96f47


[ROCm/clr commit: cb22874ebd]
2021-04-16 12:14:25 -04:00
Satyanvesh Dittakavi 74cf3b8795 SWDEV-281504 - Rename structure names to use reserved names in HIP headers
HIP headers use few structure names as X, Y, and Z. This causes
compilation issues when the apps use similar names as macros.
Renamed the struct names to use reserved names such as
__X, __Y and __Z

Change-Id: I59416c3734f274e853c87d4856b7e616f6cee5f5


[ROCm/clr commit: 009543ec7a]
2021-04-15 09:52:58 -04:00
Tao Sang 73df8d8dd9 SWDEV-273138 - Rearrange device attributes
Change-Id: Iab5902c9a2702456fbe437fdefc40541c48abb74


[ROCm/clr commit: 2c0b63059b]
2021-04-12 17:05:27 -04:00
kjayapra-amd 693c5653c5 SWDEV-274276 - Implement system scope atomics to _system builtins. Default atomics will map to agent.
Change-Id: I63b13063274418e96d4be0159c779127b166bea5
(cherry picked from commit 7c4ae8ca1daac0b75ac36c4e4a45b8d13f219d14)


[ROCm/clr commit: 61d1eaa522]
2021-04-09 10:23:32 -04:00
Sarbojit Sarkar 9d490550c5 SWDEV-260454 - Fix for idenfying bad streams
Change-Id: I122ff6f47535c3c76ab56ba49ab1450ef886b15f


[ROCm/clr commit: daf0cbca3c]
2021-04-07 12:13:30 -04:00
Sarbojit Sarkar 4e5bf6268b SWDEV-280131 - Fix __half2 member access bug
Change-Id: Ic11750d18e4ba47446a7e494c3089a19cb4df783


[ROCm/clr commit: 9cbb283771]
2021-04-07 12:12:02 -04:00
pghafari 4578277e13 SWDEV-245532 - HIP - Vulkan interop
Change-Id: Iba1ef8112e318b4f099da5a4a4602e0dae7de9e3


[ROCm/clr commit: a9304f6111]
2021-03-31 10:23:31 -04:00
Sarbojit Sarkar 47a6267c7c SWDEV-277926 - Updated deprecated APIs in Cuda
Change-Id: I9ff655af227b245067eb760325c395bb562696ee


[ROCm/clr commit: b7a03695c3]
2021-03-29 01:19:19 -04:00
Satyanvesh Dittakavi 85ca63f256 SWDEV-277152 - Add hipMemcpy2DToArrayAsync API in headers
Also, address few scenarios for hipMemcpy2DToArray/Async to return
proper error types

Change-Id: Idbadf666a5e7bebc0f3ea8b7048b79208e04cf6b


[ROCm/clr commit: 68abfb4aff]
2021-03-27 13:50:38 -04:00
jujiang 88c0959afb SWDEV-277423 - Correct hipStreamWaitValue doxygen format
Change-Id: I8914c14cb7a05d5d0bdfa054af14765c872c70a6


[ROCm/clr commit: cc69e95c1a]
2021-03-19 14:10:41 -04:00
Tao Sang 2e89139b49 SWDEV-273138 - Update canUseStreamWaitValue retrieving
Remove canUseStreamWaitValue from hipDeviceProp_t.
Update canUseStreamWaitValue retrieving in hipDeviceGetAttribute().

Change-Id: I275bd42d8b03e141caaf9f1bc6b714e51ca72dfb


[ROCm/clr commit: 08625144b3]
2021-03-18 22:42:35 -04:00
cjatin 48f0ba9cee SWDEV-272811 - Using OCML functions for conversion of fp to int
Change-Id: Id0c02bf6a2e0553d522035b078a9db4cd3fad215


[ROCm/clr commit: 06fa63df04]
2021-03-18 11:43:30 -04:00
Ravi C Akkenapally 212cc49ed6 SWDEV-276827 - Stream Operations: match API with CUDA
Change-Id: Ia79a950561e97df3b2229f76f5512dede2babf98


[ROCm/clr commit: 397bac37a3]
2021-03-18 07:52:29 -07:00
Tao Sang e212e1a947 SWDEV-273943 - Enable runtimeApi.event dtest
Add device_id_ in hip::event to match cuda behaviour in
hipEventQuery() and hipEventRecord().
Enable hipEventElapsedTime test on AMD platform.
Workarround sporadic crash of hipEventIpc test due to
some bug of event ipc.
Add missing hipEventDestroy() in some event tests.
Fix some logic code errors.
Fix typo in comment.

Change-Id: I9ec74c475161b3e31df48d193449023e921f2924


[ROCm/clr commit: 629ea5fe19]
2021-03-16 17:12:08 -04:00
jujiang 7020872b45 SWDEV-270961 - Add doxygen for Texture APIs
Change-Id: I4038320a638292440d9ca8c23ffcabffcd9a48c2


[ROCm/clr commit: 3126196cca]
2021-03-09 16:23:56 -05:00
Satyanvesh Dittakavi c8e84cbf02 SWDEV-275317 - Fix hipMemcpy2DFromArray to return proper error types
Change-Id: Id722865d81460bfd2fa6ad7a198b6e3c2a08265a


[ROCm/clr commit: daafd303ec]
2021-03-09 05:22:23 -05:00
Satyanvesh Dittakavi 6531614a23 SWDEV-274404 - Add hipDrvMemcpy3D* and hipMemcpy2DFromArray* APIs on HIP CUDA
Change-Id: I4aba2bff60a7bae6b01b6e471968227b0df8e192


[ROCm/clr commit: 37d4677aba]
2021-03-08 13:14:25 -05:00
Arya.Rafii 3d6667ccb7 SWDEV-269246 - Implementation of hipDrvMemcpy2DUnaligned
Change-Id: I86fdd3b930cbd74c45cd31944f0ea52c0ff65a59


[ROCm/clr commit: 8cb232ddef]
2021-03-04 14:38:06 -05:00
Arya.Rafii cd4aec747f SWDEV-269246 - Added missing exports for hipArrayDestroy
Change-Id: I730814720bb618e895efbe2f412e437110bed8bc


[ROCm/clr commit: 9f142f988d]
2021-03-04 14:29:16 -05:00
Ravi C Akkenapally 4cf7a5799a SWDEV-179105 - Stream Operations: Add swqupport for Wait and Write
Change-Id: I9d6d0665d12b62fe705ce1569a0e8264a4f23ab7


[ROCm/clr commit: fd0f49503f]
2021-03-02 12:15:46 -08:00
Vladislav Sytchenko 610611edd1 SWDEV-232428 - Enable device printf for Windows
Change-Id: Id72cfc34cfcfcbcb459bd8d84979637eaf7947dd


[ROCm/clr commit: 1f8bdcaf20]
2021-02-26 11:46:38 -05:00
Satyanvesh Dittakavi 936d760a58 SWDEV-271491 - Fix flags for hipSetDeviceFlags on HIP-CUDA path
Change-Id: I29446d5cc5a26a4b83fa45175ccdf1d8f3a9ea40


[ROCm/clr commit: c2a767a66e]
2021-02-25 12:06:33 -05:00
Jatin Chaudhary 75e91e9073 SWDEV-272811 - hipCabs returns a double and uses sqrtf, which maps to f32 operation. sqrt should be used instead
Change-Id: I4f74ee8853113fcebfa508bea9308ae93c7ad13b


[ROCm/clr commit: 474493b929]
2021-02-25 08:47:19 -05:00
Jatin Chaudhary 3c08aece90 SWDEV-268531 - Fixing shadow variable warning in vector_types
Change-Id: Ic57e22853529a953582c9194d09133a5aab989aa


[ROCm/clr commit: 3f6bf4c260]
2021-02-16 06:51:37 -05:00
Maneesh Gupta 60f4dcc336 SWDEV-271416 - Keep HIP_DYNAMIC_SHARED macro for compat with existing HIP apps
Change-Id: I536e0c65d6e8696cbc369082350834abd710abca


[ROCm/clr commit: 42ab466904]
2021-02-16 00:09:48 -05:00
Maneesh Gupta 125de2dbe6 SWDEV-269351 - Revert "Implement assert() using the new fprintf_stderr facility"
This reverts commit 10af608c66.

Reverting since this is dependent on a device libs change which is not yet in mainline.

Change-Id: I094781b868f39995d1eecb41488c1a1a0147b787


[ROCm/clr commit: 18234e1d24]
2021-02-12 03:46:17 -05:00
cjatin 5fe210011e SWDEV-268531 - Fixing shadow varible warning seen with hip vector usage
Change-Id: I9e20a41e74e473b328cc173f2c27b06352128c88


[ROCm/clr commit: 9a2e762ccb]
2021-02-09 13:33:12 -05:00
Julia Jiang 0e20fbfbec SWDEV-271416 - Remove HIP_DYNAMIC_SHARED macro in hip
Change-Id: I12f39ea8438eb7ce76d8ffb2151b4faa93689048


[ROCm/clr commit: e4fdbfcf5b]
2021-02-08 13:17:46 -05:00
Sarbojit Sarkar 962dff6a61 SWDEV-265469 - added constexpr constructor for dim3
Change-Id: I2e23a403f272d1ff0ade24fec11190d2f3244e5f


[ROCm/clr commit: cee3e1aa37]
2021-01-28 13:23:51 -05:00
Satyanvesh Dittakavi 14be9b54a2 SWDEV-269784 - managed memory support for HIP CUDA
Change-Id: I01f9fc64573f402031eceab24395e5cbd93007f9


[ROCm/clr commit: 0074429d05]
2021-01-28 07:51:52 -05:00
Tao Sang 1b1b7bffb6 SWDEV-268757 - Disable deprecation warning
Disable it as it will fail rocgdb test

Change-Id: Ibf34c780d5bd4278adcedba1d6e057639c258483


[ROCm/clr commit: a0c8c30ae5]
2021-01-21 15:35:32 -05:00
Satyanvesh Dittakavi fb51766fcb SWDEV-268989 - Modify atomicAdd double to use clang builtin
Change-Id: If9d40046df2f3f5af7cc1bd6c935fbe7d686e7d8


[ROCm/clr commit: 8da9f4d432]
2021-01-20 02:39:15 -05:00
Sameer Sahasrabuddhe 10af608c66 Implement assert() using the new fprintf_stderr facility
The device library now provides functions to specify the host stderr
stream in a hostcall printf message. This change implements an
assert() macro which can construct such a message. The end result is
that assertions on the device are now correctly printed on the host
stderr instead of stdout.

Change-Id: I85ab8f7848bcf28303cb8dbb8a798bc6aece7d75


[ROCm/clr commit: 2cac768a07]
2021-01-17 23:54:46 -05:00
Satyanvesh Dittakavi 7b8972f41e device property __HIP_ARCH_HAS_SHARED_INT64_ATOMICS__ set to 1 as it has compiler support
Change-Id: Ic91c4955d4f2d52d844471f81e6f0d19418018f5


[ROCm/clr commit: 84cda7f9c2]
2021-01-15 11:40:09 -05:00
Tao Sang 52954de0eb Fix building mathlibs failure
Add back
__HIP_PLATFORM_HCC__
__HIP_PLATFORM_NVCC__

Change-Id: I1ae48678eafd849d6c25bcb204c1724b026be22f


[ROCm/clr commit: 8fc1ff7d4f]
2021-01-14 14:03:15 -05:00
Tao Sang ef480eb242 Workarround for rocThrust building failure
Define the following for workarround of rocThrust building failure,
HIP_INCLUDE_HIP_HCC_DETAIL_DRIVER_TYPES_H
HIP_INCLUDE_HIP_HCC_DETAIL_HOST_DEFINES_H

Change-Id: I1ae48677eafd749d6c25bca204c1724b026be22f


[ROCm/clr commit: 149254f7f8]
2021-01-12 11:31:06 -05:00