Evgeny Mankov
f40a69409b
[HIPIFY][test] add cuDNN test
...
[ROCm/hip commit: a56b480c5e ]
2018-05-04 12:37:15 +03:00
Evgeny Mankov
61d95e4b42
[HIPIFY][doc] Readme.md update
...
+ supported CUDA version to LLVM version correspondence table is added.
+ Test section is rewritten.
+ Windows support is added.
[ROCm/hip commit: 054c3f71f0 ]
2018-05-04 10:50:18 +03:00
foreman
263a583c01
P4 to Git Change 1550010 by cpaquot@cpaquot-ocl-lc-lnx on 2018/05/03 21:16:06
...
SWDEV-145570 - [HIP] Fixed region initialization
Affected files ...
... //depot/stg/opencl/drivers/opencl/api/hip/hip_memory.cpp#22 edit
[ROCm/hip commit: 0508a4ed37 ]
2018-05-03 21:26:33 -04:00
foreman
0c52fe6234
P4 to Git Change 1549971 by skudchad@skudchad_rocm on 2018/05/03 18:39:37
...
SWDEV-145570 - [HIP] - Fix build
Affected files ...
... //depot/stg/opencl/drivers/opencl/api/hip/hip_memory.cpp#21 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rockernel.hpp#21 edit
[ROCm/hip commit: 99d3444f00 ]
2018-05-03 18:56:01 -04:00
foreman
2f4bfed956
P4 to Git Change 1549965 by skudchad@skudchad_test2_win_opencl on 2018/05/03 18:15:18
...
SWDEV-145570 - [HIP] - Minor fixes. Use coarse grain for hipMallocPitch
ReviewBoardURL = http://ocltc.amd.com/reviews/r/14768/diff/
Affected files ...
... //depot/stg/opencl/drivers/opencl/api/hip/hip_memory.cpp#20 edit
[ROCm/hip commit: 3ad5f2a01b ]
2018-05-03 18:26:45 -04:00
Evgeny Mankov
057b13fc4a
[HIPIFY] Initial cuDNN support
...
- based on https://github.com/ROCmSoftwarePlatform/hipDNN .
- lit testing was supplemented with CUDA_DNN_ROOT_DIR for cuDNN testing.
- single cuDNN test was added.
[ROCm/hip commit: fe421c89b2 ]
2018-05-03 11:33:40 +03:00
Evgeny Mankov
1b652107f7
Merge pull request #417 from emankov/master
...
[HIPIFY] Sync with HIP (Execution Control, Surfaces, Memory)
[ROCm/hip commit: e1d1835798 ]
2018-05-03 10:45:51 +03:00
Lakhan Singh
51dbf4f5ca
Null checks added for hipmallocpitch and hipmemcpy apis
...
[ROCm/hip commit: 6411ca1f6d ]
2018-05-03 09:27:50 +05:30
foreman
7b03ff80d4
P4 to Git Change 1549067 by skudchad@skudchad_rocm on 2018/05/02 17:40:37
...
SWDEV-145570 - [HIP] - Fix build
Affected files ...
... //depot/stg/opencl/drivers/opencl/api/hip/hip_memory.cpp#19 edit
[ROCm/hip commit: a10512c510 ]
2018-05-02 22:25:53 -04:00
foreman
129f0a9d0f
P4 to Git Change 1549060 by skudchad@skudchad_test2_win_opencl on 2018/05/02 17:36:53
...
SWDEV-145570 - [HIP] - Add hipMemcpyDeviceToDevice/hipMemcpyHostToHost/hipMemcpyDefault cases to hipMemcpy/hipMemcpyAsync, hipMemset2DAsync
ReviewBoardURL = http://ocltc.amd.com/reviews/r/14746/diff/
Affected files ...
... //depot/stg/opencl/drivers/opencl/api/hip/hip_memory.cpp#18 edit
[ROCm/hip commit: 445d300d63 ]
2018-05-02 21:08:53 -04:00
foreman
7d6c9d4602
P4 to Git Change 1549012 by lmoriche@lmoriche_opencl_dev2 on 2018/05/02 16:56:02
...
SWDEV-145570 - [HIP] - Add hipMemset2DAsync, fix the HCC triple for device binaries (make sure to update to the latest HCC).
Affected files ...
... //depot/stg/opencl/drivers/opencl/api/hip/hip_hcc.def.in#4 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_hcc.map.in#4 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_memory.cpp#17 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_platform.cpp#10 edit
[ROCm/hip commit: 0ddf288904 ]
2018-05-02 19:14:52 -04:00
Rahul Garg
e687245eb0
Cleaned up
...
[ROCm/hip commit: b4585a2a90 ]
2018-05-02 12:54:17 +05:30
Rahul Garg
ab1dabe61b
Fix texture 3D for HIP/NVCC
...
[ROCm/hip commit: 9de5f23d54 ]
2018-05-02 11:56:37 +05:30
foreman
01296ff827
P4 to Git Change 1548560 by skudchad@skudchad_rocm on 2018/05/01 18:53:54
...
SWDEV-145570 - [HIP] - Fix hipDeviceSynchronize.
Affected files ...
... //depot/stg/opencl/drivers/opencl/api/hip/hip_device_runtime.cpp#8 edit
[ROCm/hip commit: 5f549b62e8 ]
2018-05-01 19:01:10 -04:00
foreman
07cc8f7a6d
P4 to Git Change 1548558 by skudchad@skudchad_test2_win_opencl on 2018/05/01 18:39:58
...
SWDEV-145570 - [HIP] - Implement some of hipMem*Async and hipMemSet2D APIs. Part 4.
ReviewBoardURL = http://ocltc.amd.com/reviews/r/14743/diff/
Affected files ...
... //depot/stg/opencl/drivers/opencl/api/hip/hip_memory.cpp#16 edit
[ROCm/hip commit: 9c7b328101 ]
2018-05-01 18:46:32 -04:00
foreman
0e2eaa1aa1
P4 to Git Change 1548476 by cpaquot@cpaquot-ocl-lc-lnx on 2018/05/01 15:50:51
...
SWDEV-145570 - [HIP]
Added support for null stream avoiding creating/destroying dummy streams.
Added basic event class for hipEvent* support.
Refactored some common functionality: No more direct access to g_context.
Support hipStreamSynchronize(0).
Affected files ...
... //depot/stg/opencl/drivers/opencl/api/hip/hip_context.cpp#9 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_device_runtime.cpp#7 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_event.cpp#3 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_event.hpp#1 add
... //depot/stg/opencl/drivers/opencl/api/hip/hip_internal.hpp#8 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_memory.cpp#15 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_module.cpp#8 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_platform.cpp#9 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_stream.cpp#4 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_texture.cpp#7 edit
[ROCm/hip commit: 61378a359c ]
2018-05-01 18:10:09 -04:00
Maneesh Gupta
c41d423404
Merge pull request #420 from ROCm-Developer-Tools/sunway513-patch-1
...
Update hip_bugs.md
[ROCm/hip commit: 92f1071eb1 ]
2018-05-01 12:43:01 +05:30
Maneesh Gupta
d3d11ff829
Merge pull request #419 from gargrahul/fix_hip_gcc_host_build
...
Fix gcc build issues for host code
[ROCm/hip commit: adcd8553c3 ]
2018-05-01 12:42:50 +05:30
Maneesh Gupta
825c697d32
Merge pull request #414 from aaronenyeshi/patch-1
...
Remove unsupported targets gfx801 and gfx802
[ROCm/hip commit: 539a3df316 ]
2018-05-01 12:38:49 +05:30
Maneesh Gupta
ef13aa3a0b
Merge pull request #415 from deven-amd/master
...
Checkin to fix bugs in math functions.
[ROCm/hip commit: e17ade3afb ]
2018-05-01 12:29:03 +05:30
Maneesh Gupta
b272e57c33
Merge pull request #410 from gargrahul/hipCtx_deprecation_warning
...
Mark hipCtx APIs as deprecated
[ROCm/hip commit: caa13f98ed ]
2018-05-01 12:23:22 +05:30
Maneesh Gupta
b40c05e452
Merge pull request #411 from luckynikki/SWDEV-141024
...
SWDEV-141024
[ROCm/hip commit: d2a51ee651 ]
2018-05-01 09:29:26 +05:30
Maneesh Gupta
93fc0a8312
Merge pull request #406 from gargrahul/fix_tex1D_coordinate_type
...
Resolve tex1D float to int conversion issue
[ROCm/hip commit: 365d155774 ]
2018-05-01 09:18:11 +05:30
foreman
e6c77307b7
P4 to Git Change 1548145 by cpaquot@cpaquot-ocl-lc-lnx on 2018/04/30 21:15:56
...
SWDEV-145570 - [HIP] Handle hStream=nullptr case
Affected files ...
... //depot/stg/opencl/drivers/opencl/api/hip/hip_module.cpp#7 edit
[ROCm/hip commit: dc1497535d ]
2018-04-30 21:20:26 -04:00
foreman
7a594eacaa
P4 to Git Change 1548038 by lmoriche@lmoriche_opencl_dev2 on 2018/04/30 15:55:18
...
SWDEV-145570 - [HIP] Fix kernel disptach for HCC compiled programs.
Affected files ...
... //depot/stg/opencl/drivers/opencl/api/hip/hip_module.cpp#6 edit
[ROCm/hip commit: 213f721318 ]
2018-04-30 20:17:46 -04:00
foreman
cffb35e422
P4 to Git Change 1547830 by skudchad@skudchad_test2_win_opencl on 2018/04/30 12:03:10
...
SWDEV-145570 - [HIP] - Add couple of hip_mem* APIs. Part 3.
ReviewBoardURL = http://ocltc.amd.com/reviews/r/14727/diff/
Affected files ...
... //depot/stg/opencl/drivers/opencl/api/hip/hip_memory.cpp#14 edit
[ROCm/hip commit: 6f7e33cb91 ]
2018-04-30 14:55:41 -04:00
foreman
5695bb3ca8
P4 to Git Change 1547825 by cpaquot@cpaquot-ocl-lc-lnx on 2018/04/30 11:59:32
...
SWDEV-145570 - [HIP] Fixed release build
Affected files ...
... //depot/stg/opencl/drivers/opencl/api/hip/hip_memory.cpp#13 edit
[ROCm/hip commit: 36d2d37804 ]
2018-04-30 13:34:32 -04:00
Peng
919254839a
Update hip_bugs.md
...
Remove several out-date links in hip_bugs.md document
[ROCm/hip commit: 2e76f563cd ]
2018-04-30 09:36:37 -05:00
foreman
9bbba2ee75
P4 to Git Change 1547686 by cpaquot@cpaquot-ocl-lc-lnx on 2018/04/30 00:52:23
...
SWDEV-145570 - [HIP] CreateTexture with hipArray
Affected files ...
... //depot/stg/opencl/drivers/opencl/api/hip/hip_texture.cpp#6 edit
[ROCm/hip commit: 5fc5d098a9 ]
2018-04-30 01:03:06 -04:00
foreman
b51c887a83
P4 to Git Change 1547669 by lmoriche@lmoriche_opencl_dev2 on 2018/04/29 14:53:31
...
SWDEV-145570 - [HIP] Fix kernel disptach for HCC compiled programs.
Affected files ...
... //depot/stg/opencl/drivers/opencl/api/hip/hip_module.cpp#5 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_platform.cpp#8 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rockernel.cpp#34 edit
[ROCm/hip commit: 1cb879968b ]
2018-04-29 15:04:45 -04:00
foreman
c3847507d9
P4 to Git Change 1547563 by lmoriche@lmoriche_opencl_dev2 on 2018/04/27 21:10:47
...
SWDEV-145570 - [HIP] - Add support for HCC compiled binaries.
Affected files ...
... //depot/stg/opencl/drivers/opencl/api/hip/build/Makefile.hip#2 edit
... //depot/stg/opencl/drivers/opencl/api/hip/elfio/elf_types.hpp#1 add
... //depot/stg/opencl/drivers/opencl/api/hip/elfio/elfio.hpp#1 add
... //depot/stg/opencl/drivers/opencl/api/hip/elfio/elfio_dump.hpp#1 add
... //depot/stg/opencl/drivers/opencl/api/hip/elfio/elfio_dynamic.hpp#1 add
... //depot/stg/opencl/drivers/opencl/api/hip/elfio/elfio_header.hpp#1 add
... //depot/stg/opencl/drivers/opencl/api/hip/elfio/elfio_note.hpp#1 add
... //depot/stg/opencl/drivers/opencl/api/hip/elfio/elfio_relocation.hpp#1 add
... //depot/stg/opencl/drivers/opencl/api/hip/elfio/elfio_section.hpp#1 add
... //depot/stg/opencl/drivers/opencl/api/hip/elfio/elfio_segment.hpp#1 add
... //depot/stg/opencl/drivers/opencl/api/hip/elfio/elfio_strings.hpp#1 add
... //depot/stg/opencl/drivers/opencl/api/hip/elfio/elfio_symbols.hpp#1 add
... //depot/stg/opencl/drivers/opencl/api/hip/elfio/elfio_utils.hpp#1 add
... //depot/stg/opencl/drivers/opencl/api/hip/hip_platform.cpp#7 edit
[ROCm/hip commit: 2605d50ce7 ]
2018-04-27 21:21:31 -04:00
Deven Desai
43c2724907
Fixing a copy/paste error in my previous checkin
...
[ROCm/hip commit: 76a7d7e374 ]
2018-04-27 12:59:51 +00:00
Deven Desai
2b3332ac72
Checkin to add unit tests for fixes in my previous commit
...
This change adds unit tests for
1. __hisinf
2. __hisnan
2. abs(long long)
3. lgamma(double)
[ROCm/hip commit: 4be4cf644f ]
2018-04-25 17:53:21 +00:00
foreman
67731a083a
P4 to Git Change 1546224 by skudchad@skudchad_test2_win_opencl on 2018/04/25 12:24:40
...
SWDEV-145570 - [HIP] - Add hipMemcpyTo/FromArray APIs.
ReviewBoardURL = http://ocltc.amd.com/reviews/r/14696/diff/
Affected files ...
... //depot/stg/opencl/drivers/opencl/api/hip/hip_memory.cpp#12 edit
[ROCm/hip commit: 18c7c164c6 ]
2018-04-25 12:32:11 -04:00
Rahul Garg
c1b94eb29f
Fix gcc build issues for host code
...
[ROCm/hip commit: 639001933c ]
2018-04-25 12:30:11 +05:30
foreman
066a072226
P4 to Git Change 1545859 by cpaquot@cpaquot-ocl-lc-lnx on 2018/04/24 16:44:17
...
SWDEV-145570 - [HIP] Get hipCtx_simple to pass
Implemented hipCtxGetDevice
hipCtxCreate must push the created context onto the context stack
hipCtxDestroy must check if the top of the stack is the context being destroy
and not just pop the top of the stack w/o checking.
Affected files ...
... //depot/stg/opencl/drivers/opencl/api/hip/hip_context.cpp#8 edit
[ROCm/hip commit: d2fbde728c ]
2018-04-24 16:49:38 -04:00
Paul
8643ed5ca9
Add host and device targets
...
[ROCm/hip commit: 516d92f4d7 ]
2018-04-24 14:04:24 -05:00
Evgeny Mankov
6b53512635
[HIPIFY] Sync with HIP (Execution Control, Surfaces, Memory)
...
Execution Control [deprecated since 7.0]:
cudaConfigureCall -> hipConfigureCall
cudaLaunch -> hipLaunchByPtr
cudaSetupArgument -> hipSetupArgument
Surfaces (partially):
cudaSurfaceObject_t -> hipSurfaceObject_t
cudaSurfaceBoundaryMode -> hipSurfaceBoundaryMode
cudaCreateSurfaceObject -> hipCreateSurfaceObject
cudaDestroySurfaceObject -> hipDestroySurfaceObject
Memory Management:
cudaMemset2DAsync -> hipMemset2DAsync
[ROCm/hip commit: 6f501f6094 ]
2018-04-24 22:04:04 +03:00
Deven Desai
16d2b986aa
Checkin to fix bugs in math functions.
...
This change fixes the following bugs that were discovered while debuggnig TF unit test failures (cwise_ops_test)
1. __hisinf and __hisnan routines
Both had incorrect implementations.
2. abs
A "long long" (64bit int) version was missing, resulting in the 32bit version being used for 64bit ints (which resulted in incorrect results, when the value passed in was outside the 32bit int range)
3. lgamma
We seemed to have a custom version for the 'double' datatype (which was giving incorrect results). Replaced it with a call to the 'double' version of the underlying 'hc::precision_math::lgamma'
[ROCm/hip commit: af586bbbf2 ]
2018-04-24 18:10:07 +00:00
foreman
f4b08ad496
P4 to Git Change 1545750 by skudchad@skudchad_test2_win_opencl on 2018/04/24 13:55:57
...
SWDEV-145570 - [HIP] - Add some hip_mem* APIs. Part 2.
ReviewBoardURL = http://ocltc.amd.com/reviews/r/14681/diff/
Affected files ...
... //depot/stg/opencl/drivers/opencl/api/hip/hip_memory.cpp#11 edit
[ROCm/hip commit: 13355e5de5 ]
2018-04-24 14:05:20 -04:00
Aaron Enye Shi
583942c3cb
Remove unsupported targets gfx801 and gfx802
...
These architectures are no longer supported. Should not compile for them.
[ROCm/hip commit: 433866eb60 ]
2018-04-23 15:25:35 -04:00
Evgeny Mankov
540fc92b1c
[HIPIFY] undo apply .clangformat to HIPIFY source files
...
[ROCm/hip commit: 8499e79e2b ]
2018-04-23 20:22:15 +03:00
foreman
1cafd8bd20
P4 to Git Change 1544858 by skudchad@skudchad_rocm on 2018/04/22 21:07:25
...
SWDEV-144570 - [HIP] - Fix a few APIs and typos.
Affected files ...
... //depot/stg/opencl/drivers/opencl/api/hip/hip_device_runtime.cpp#6 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_platform.cpp#6 edit
[ROCm/hip commit: 66640b546f ]
2018-04-22 21:17:27 -04:00
Rahul Garg
6538884ebe
Added deprecation note in cuCtx section
...
[ROCm/hip commit: 39b5b07dc3 ]
2018-04-20 22:43:58 +05:30
Rahul Garg
c4df5688c4
Moved deprecated macro to the end
...
[ROCm/hip commit: 19cb6c61ab ]
2018-04-20 21:57:23 +05:30
Lakhan Singh
701de3092b
SWDEV-141024
...
[ROCm/hip commit: 1c2509dc04 ]
2018-04-20 17:40:00 +05:30
Rahul Garg
3b4875ba77
Mark hipCtx APIs as deprecated
...
[ROCm/hip commit: a039dbf2dd ]
2018-04-20 17:34:48 +05:30
foreman
10d96d33ce
P4 to Git Change 1544061 by skudchad@skudchad_test2_win_opencl on 2018/04/19 18:24:45
...
SWDEV-145570 - [HIP] - Add some hip_mem* APIs
ReviewBoardURL = http://ocltc.amd.com/reviews/r/14647/diff/
Affected files ...
... //depot/stg/opencl/drivers/opencl/api/hip/hip_memory.cpp#10 edit
[ROCm/hip commit: 3ce752065a ]
2018-04-19 18:35:00 -04:00
foreman
07285483d9
P4 to Git Change 1543751 by cpaquot@cpaquot-ocl-lc-lnx on 2018/04/19 11:17:02
...
SWDEV-145570 - [HIP] Implemented a bunch of texture APIs
Affected files ...
... //depot/stg/opencl/drivers/opencl/api/hip/hip_texture.cpp#5 edit
[ROCm/hip commit: 63babe9e66 ]
2018-04-19 12:27:09 -04:00
Rahul Garg
80d7e34418
Resolve tex1D float to int conversion issue
...
[ROCm/hip commit: ffe18d1505 ]
2018-04-18 14:15:18 +05:30