bddcbdeeb6
[HIPIFY] Add cudaMallocManaged -> hipMallocManaged
...
+ Add mapping for corresponding data types
+ Add a test
+ Update docs
[ROCm/hip commit: d20ae3b50a
2019-08-13 17:56:06 +03:00
595ce3e048
[HIPIFY][Driver API] Add support for hipFuncGetAttribute() and enum hipFunction_attribute
...
[ROCm/hip commit: 27d101aa76
2019-08-13 16:48:07 +03:00
681ab172b6
[HIPIFY] Add cuMemcpy2DAsync -> hipMemcpyParam2DAsync mapping
...
[ROCm/hip commit: 1390ecf538
2019-08-13 16:31:19 +03:00
3a6d027037
P4 to Git Change 1982056 by kjayapra@3_HIPWS_TXT_ROCM on 2019/08/12 21:16:51
...
SWDEV-199635 - Setting VarInfoCallBack before all program builds.
Affected files ...
... //depot/stg/opencl/drivers/opencl/api/hip/hip_internal.hpp#36 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_module.cpp#33 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/devprogram.cpp#58 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palprogram.cpp#97 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocprogram.cpp#106 edit
[ROCm/hip commit: c2ffca9c1d
2019-08-12 21:22:47 -04:00
0bc4597204
P4 to Git Change 1982034 by cpaquot@cpaquot-ocl-lc-lnx on 2019/08/12 19:08:13
...
SWDEV-199606 - [HIP] hipStreamQuery issue
Don't test against CL_COMMAND_MARKER but 0 instead (user visible=false)
Affected files ...
... //depot/stg/opencl/drivers/opencl/api/hip/hip_event.cpp#15 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_event.hpp#6 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_stream.cpp#22 edit
[ROCm/hip commit: 4e71cb437e
2019-08-12 19:16:30 -04:00
bf883d95e9
[HIPIFY] Cooperative groups support
...
[ROCm/hip commit: aa285d978e
2019-08-12 19:20:13 +03:00
7a63df9aec
P4 to Git Change 1981324 by kjayapra@3_HIPWS_TXT_ROCM on 2019/08/11 18:44:40
...
SWDEV-188177 - Texture API implementation and support for extern variables.
Affected files ...
... //depot/stg/opencl/drivers/opencl/api/hip/hip_hcc.def.in#18 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_hcc.map.in#20 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_internal.hpp#35 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_module.cpp#32 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_platform.cpp#37 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_texture.cpp#14 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/device.hpp#340 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/devprogram.cpp#57 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/devprogram.hpp#31 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/gpu/gpudevice.cpp#608 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/gpu/gpudevice.hpp#172 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/gpu/gpuprogram.cpp#250 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/gpu/gpuprogram.hpp#79 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/paldevice.cpp#152 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/paldevice.hpp#41 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palprogram.cpp#96 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palprogram.hpp#39 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocdevice.cpp#133 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocdevice.hpp#39 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocprogram.cpp#105 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocprogram.hpp#48 edit
... //depot/stg/opencl/drivers/opencl/runtime/platform/program.cpp#102 edit
... //depot/stg/opencl/drivers/opencl/runtime/platform/program.hpp#46 edit
[ROCm/hip commit: 7e6c7a9b8a
2019-08-11 18:53:11 -04:00
250a441899
P4 to Git Change 1981152 by cpaquot@cpaquot-ocl-lc-lnx on 2019/08/09 20:33:32
...
SWDEV-193430 - [HIP] Delay creating HostQueue till commands are enqueued.
Affected files ...
... //depot/stg/opencl/drivers/opencl/api/hip/hip_event.cpp#14 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_event.hpp#5 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_internal.hpp#34 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_memory.cpp#68 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_module.cpp#31 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_stream.cpp#21 edit
[ROCm/hip commit: 92840c805e
2019-08-09 20:41:13 -04:00
3bd691396e
P4 to Git Change 1981065 by cpaquot@cpaquot-ocl-lc-lnx on 2019/08/09 16:31:44
...
SWDEV-198556 - [HIP] Use src/dstMemory->getContext instead of host_context.
Also relax the check for P2P copies in case of hipMemcpy(hostMalloced, hipMalloced(dev1), dev0)
Affected files ...
... //depot/stg/opencl/drivers/opencl/api/hip/hip_memory.cpp#67 edit
[ROCm/hip commit: 867d521a08
2019-08-09 16:34:38 -04:00
f0789e57e6
[HIPIFY][cuRAND][ #1257 ] Fix
...
+ Update CURAND_API_supported_by_HIP.md and test accordingly
[ROCm/hip commit: 3ac3b2800b
2019-08-09 21:27:16 +03:00
5fa2bfab3b
Fix HIP Platform defines
...
Remove extra trailing `_` in platform defines
[ROCm/hip commit: b3322784e4
2019-08-09 09:25:31 -05:00
b58887c33d
Bump HIP version ( #1311 )
...
- Match HIP version with upcoming ROCm version
- Add githash to version string
[ROCm/hip commit: 3ccddcde25
2019-08-09 12:13:29 +00:00
07ee0e825b
[dtests] Fix build issues with hipMemoryAllocateCoherentDriver.cpp on windows ( #1309 )
...
Compilation error being observed due to popen(), pclose() and setenv() linux calls on windows. Replaced with appropriate calls on windows.
[ROCm/hip commit: 9b31d26237
2019-08-09 11:53:16 +00:00
45652a1fba
[dtests] Fix build issue with hipMemcpy_simple.cpp on windows ( #1306 )
...
Compilation error being observed on windows due to aligned_alloc() call. Mapped the call to _aligned_malloc() for windows.
[ROCm/hip commit: 9abae7114c
2019-08-09 11:52:46 +00:00
83e95631cf
[dtests[ Fix build issues with hipEnvVar*.cpp on windows ( #1299 )
...
* replace getopt with clara based command line options
* Removed header getopt.h
[ROCm/hip commit: cbe9f8dc6b
2019-08-09 11:52:10 +00:00
d42844182c
Add hipMemcpyParam2DAsync ( #1296 )
...
* Add hipMemcpyParam2DAsync
* Add NVCC path changes
* Clean up
* Fix build issue
* Fix else use in both sync and async apis
[ROCm/hip commit: 45b73e0961
2019-08-09 11:50:37 +00:00
eacee18c37
[dtests] Fix build issues with hipLaunchParm.cpp on windows ( #1293 )
...
* Removed unwanted #include sys/time.h , gettimeofday() and timeval variables and this also helps avavoid compilation error in windows due to gettimeofday() call equivalent of which is not available in windows
* Changed the Macro name from GPU_PRINT_TIME to MY_LAUNCH_MACRO
[ROCm/hip commit: e94c0592de
2019-08-09 11:50:10 +00:00
2658921cfb
[dtests] Fixed build issues with hipAsynchronousStreams.cpp on windows ( #1292 )
...
Changed the third arg of the functions __hip_as_write_block and __ockl_as_write_block from ulong to uint64_t so as to fix the compilation error in windows
[ROCm/hip commit: d3ffad7c83
2019-08-09 11:49:31 +00:00
fae2466d94
P4 to Git Change 1980493 by cpaquot@cpaquot-ocl-lc-lnx on 2019/08/08 18:57:21
...
SWDEV-198556 - [HIP] Override queue if src/dst's device doesn't match the queue's device.
Affected files ...
... //depot/stg/opencl/drivers/opencl/api/hip/hip_memory.cpp#66 edit
[ROCm/hip commit: 8fdb248e42
2019-08-08 19:03:46 -04:00
f867ab417b
Merge pull request #1300 from amd-lthakur/windows-Single-Double-Precision-Math-Host-fixes
...
Fixed compilation errors being observed on windows
[ROCm/hip commit: 20628bd03f
2019-08-09 00:15:48 +03:00
075790c90b
Add missing hipHostRegister flags to hipify-perl for flags that are defined and supported in hip_runtime_api.h
...
[ROCm/hip commit: 05b685cc6b
2019-08-08 10:46:45 -05:00
83269bea32
Compile HIP runtime with hidden visibility by default ( #1303 )
...
* add default visibility to most APIs in program_state
* remove unwanted C++ headers
* Add symbol visibility pragmas and compiler flags
* Add visibility attribute to APIs in channel_descriptor and hip_hcc
* remove unused headers
* simplify build flags with hcc
* add pragma visibility hidden to functional_grid_launch
* [CMake] add gfx908 back
[ROCm/hip commit: 83af327ef2
2019-08-08 08:33:04 +00:00
227060fada
Merge pull request #1305 from ROCm-Developer-Tools/fix-hip-vdi-include-clang
...
Fix HIP-VDI using incorrect include files
[ROCm/hip commit: ce7469ba20
2019-08-08 08:28:20 +00:00
f4e7f3be33
Merge pull request #1302 from davidrohr/master
...
Treat .cxx files like .cpp files
[ROCm/hip commit: 01c17071cd
2019-08-08 08:28:01 +00:00
d429ba57e1
Add support for hipFuncGetAttribute ( #1279 )
...
* Add support for hipFunGetAttribute
* Support NVCC path
* Test using sample module_api_global
* Try fixing CI build failure due to hip_prof_gen scan
* Fix for CI build issue
* Resolve conflict
* Rebase and resolve conflicts with master
* Fix build error
* Fix NVCC path build error
[ROCm/hip commit: 6ce86f409d
2019-08-08 08:27:41 +00:00
c9ddc379aa
Merge pull request #1290 from emankov/master
...
[HIP][doc] Populate README.md with the supported CUDA APIs links
[ROCm/hip commit: 771820766a
2019-08-08 11:17:50 +03:00
68139db6b8
Resubmitting the fix so as to address the changed format in the last submission
...
[ROCm/hip commit: d18160920e
2019-08-08 11:26:26 +05:30
7272379649
Fix HIP-VDI using incorrect include files
...
When HIP-VDI depends on an llvm-amdgpu package, the include clang directory is not properly assessed.
[ROCm/hip commit: 80a3897f9e
2019-08-07 16:59:17 -04:00
a2e61f597e
Treat .cxx files like .cpp files
...
[ROCm/hip commit: a90310162d
2019-08-07 19:11:35 +02:00
9f77fec459
P4 to Git Change 1979518 by kjayapra@3_HIPWS_TXHDR_ROCM on 2019/08/07 12:40:50
...
SWDEV-198194 - Adding lock in Unregistervar.
Affected files ...
... //depot/stg/opencl/drivers/opencl/api/hip/hip_platform.cpp#36 edit
[ROCm/hip commit: 4092ab0f7a
2019-08-07 12:45:50 -04:00
1a4364558a
P4 to Git Change 1979482 by zukhan@zukhan-ocl-win10 on 2019/08/07 11:30:33
...
SWDEV-196326 - [hipclang-vdi-rocm]: [FBA-80]: Runtime error when all GPUs are hidden by ROCR_VISIBLE_DEVICES
- Adjusted hipGetDeviceCount to return "hipErrorNoDevice".
- This was done to match the same behaviour as HIP-HCC, and API spec for when no devices are found. Rather then return "count = 0" as it did.
ReviewBoardURL = http://ocltc.amd.com/reviews/r/17789/diff/
Affected files ...
... //depot/stg/opencl/drivers/opencl/api/hip/hip_device.cpp#22 edit
[ROCm/hip commit: 7f0373f2e3
2019-08-07 11:44:31 -04:00
32919a1ecb
P4 to Git Change 1979479 by cpaquot@cpaquot-ocl-lc-lnx on 2019/08/07 11:25:59
...
SWDEV-198424 - [HIP] Implemented missing fields for hipGetDeviceAttribute.
Affected files ...
... //depot/stg/opencl/drivers/opencl/api/hip/hip_device.cpp#21 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_device_runtime.cpp#17 edit
[ROCm/hip commit: 042a4c2bb2
2019-08-07 11:30:59 -04:00
b6bbedd924
P4 to Git Change 1979460 by kjayapra@3_HIPWS_TXHDR_ROCM on 2019/08/07 11:05:27
...
SWDEV-145570 - Code changes after header update.
Affected files ...
... //depot/stg/opencl/drivers/opencl/api/hip/hip_texture.cpp#13 edit
[ROCm/hip commit: fa2d5186ba
2019-08-07 11:07:16 -04:00
aeb53881fb
Fixed compilation errors being observed on windows
...
[ROCm/hip commit: 435badcb0e
2019-08-07 15:54:46 +05:30
fe9cfbdd3c
Enable temporarily disabled device properties on HIP/VDI
...
[ROCm/hip commit: 59bda14979
2019-08-06 22:03:19 -04:00
a36e00c36d
P4 to Git Change 1979123 by cpaquot@cpaquot-ocl-lc-lnx on 2019/08/06 17:15:10
...
SWDEV-198556 - [HIP] Gnarly bug due to macros:
HIP_RETURN(ret) duplicates ret twice first by setting the last error
then via LogDebugInfo. So if HIP_RETURN has a function as a parameter,
the function would get called twice. So ihipMalloc and ihipMemcpy were
being called twice (and perhaps more functions).
Also logging the pointer returned by ihipMalloc so we can track memory
in logs more easily.
Affected files ...
... //depot/stg/opencl/drivers/opencl/api/hip/hip_internal.hpp#33 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_memory.cpp#65 edit
[ROCm/hip commit: adf865621c
2019-08-06 17:19:28 -04:00
1429e1c2fb
[HIP][doc] Populate README.md with the supported CUDA APIs links
...
[ROCm/hip commit: cf8ec29fe2
2019-08-05 16:05:39 +03:00
3d8fa99789
[HIPIFY][doc] Update README.md
...
+ cuDNN, Python, and VS supported versions update;
+ testing output update.
[ROCm/hip commit: 739e2df224
2019-08-05 14:49:01 +03:00
e61c6214f4
Merge pull request #1286 from mangupta/swdev-198753
...
Partial revert of 'Add HSA_PATH to hip_Includes in cmake and hipconfig (#1260 )'
[ROCm/hip commit: 63831417ac
2019-08-05 09:52:47 +00:00
4509df8151
Fix hip_throw. ( #1285 )
...
* Fix hip_throw.
* Fix typo
* No, really fix typo
[ROCm/hip commit: fbbed603ff
2019-08-05 09:52:22 +00:00
3a04541b9d
Merge pull request #1280 from ROCm-Developer-Tools/fix_dont_break_hcc_just_because
...
This difference makes absolutely no sense.
[ROCm/hip commit: 4ee600ed5e
2019-08-05 09:51:53 +00:00
b72170d037
Enabled gcc for hip host code ( #1214 )
...
* Enabled gcc for hip host code
* Adding tests for hip code + (gcc & g++), without kernels
* Excluding nvcc platforms for gcc and g++ tests + Addressing review comments
* minor code clean-up
* Add rocm include path
* Added relative path for library
* Hiding non supported functions for gcc
* Incorporating review comments
[ROCm/hip commit: 3bfff0a23d
2019-08-05 09:51:36 +00:00
9b44993343
consolidate thread local storage ( #915 )
...
* all thread local access now through single struct
* clean up old commented-out code, more use of GET_TLS()
* fewer calls to GET_TLS by passing tls as a funtion argument
* revert unnecessary change to printf
* fix failing tests due to TLS change
* fix merge conflicts in ihipOccupancyMaxActiveBlocksPerMultiprocessor
[ROCm/hip commit: 1eb3dbf065
2019-08-05 09:51:02 +00:00
4e771d6097
Partial revert of 'Add HSA_PATH to hip_Includes in cmake and hipconfig ( #1260 )'
...
Change-Id: I35173f2defe446c0d1e5511e582e9c8722841381
[ROCm/hip commit: 0782e79478
2019-08-05 13:32:46 +05:30
cd496a5a90
P4 to Git Change 1978068 by cpaquot@cpaquot-ocl-lc-lnx on 2019/08/03 12:16:57
...
SWDEV-198546 - [HIP] Implemented basic Ctx APIs that are deprecated.
Affected files ...
... //depot/stg/opencl/drivers/opencl/api/hip/hip_context.cpp#20 edit
[ROCm/hip commit: 44813761ba
2019-08-03 12:23:25 -04:00
728b2f5843
[HIPIFY][fix][ #211 ] Taking into account include guard controlling macro
...
...while including HIP main header file, which is inserted now after #indef controlling macro, or after #pragma once, if it's occurred earlier.
+ Add a couple of unit tests.
ToDo: Check backward compatibility on older clang versions.
[ROCm/hip commit: 25075729f9
2019-08-02 16:46:45 +03:00
ba14b149d4
Merge pull request #1278 from gargrahul/fix_hipfuncGetAttribute_logstatus
...
Fix missing logstatus in hipFuncGetAttributes
[ROCm/hip commit: f52245d440
2019-08-02 10:00:38 +00:00
b663dbc5ce
Added CooperativeLaunch and CooperativeMultiDeviceLaunch flag and property for hipDeviceGetAttribute() and hipGetDeviceProperties() ( #1247 )
...
[ROCm/hip commit: aaec4f73a6
2019-08-02 10:00:25 +00:00
b859635575
This difference makes absolutely no sense.
...
[ROCm/hip commit: a85b0fe68e
2019-08-02 12:30:03 +03:00
8b597565c4
Fix missing logstatus in hipFuncGetAttributes
...
[ROCm/hip commit: 474bf0effc
2019-08-02 11:51:34 +05:30
Evgeny Mankov
foreman
Nick Curtis
Maneesh Gupta
amd-lthakur
ansurya
Rahul Garg
Rene van Oostrum
Siu Chi Chan
lthakur
Aaron Enye Shi
David Rohr
Rahul Garg
Alex Voicu
Sarbojit2019
Jeff Daily
wkwchau