AI/rocm-systems
2
0
Форкнуть 0
Код Задачи Запросы на слияние Действия Пакеты Проекты Релизы Вики Активность
5 990 коммитов 3 Ветки 0 Теги
7fc700c34848569fa340f7b72c36db43e49c8a21
Граф коммитов

5276 Коммитов

Автор SHA1 Сообщение Дата
foreman a6c58d73f6 P4 to Git Change 1550486 by cpaquot@cpaquot-ocl-lc-lnx on 2018/05/04 14:00:33 
SWDEV-145570 - [HIP] Fix multithread init
	Make the g_ihipInitialized variable per thread
	And make sure to assign a default g_context

Affected files ...

... //depot/stg/opencl/drivers/opencl/api/hip/hip_context.cpp#10 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_internal.hpp#9 edit
 2018-05-04 14:13:13 -04:00
Evgeny Mankov 0bf8e42caa [HIPIFY][test] add cuDNN test 2018-05-04 12:37:15 +03:00
Evgeny Mankov b6d4c7cfe6 [HIPIFY][doc] Readme.md update 
+ supported CUDA version to LLVM version correspondence table is added.
+ Test section is rewritten.
+ Windows support is added.
 2018-05-04 10:50:18 +03:00
foreman f404808c04 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
 2018-05-03 21:26:33 -04:00
foreman d6ffa28a5f 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
 2018-05-03 18:56:01 -04:00
foreman f1f8ea8266 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
 2018-05-03 18:26:45 -04:00
Evgeny Mankov 4d19bd1da5 [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.
 2018-05-03 11:33:40 +03:00
Evgeny Mankov 0ad4d520ed Merge pull request #417 from emankov/master 
[HIPIFY] Sync with HIP (Execution Control, Surfaces, Memory)
 2018-05-03 10:45:51 +03:00
Lakhan Singh 12d8a47c0c Null checks added for hipmallocpitch and hipmemcpy apis 2018-05-03 09:27:50 +05:30
foreman 16f6cf55e9 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
 2018-05-02 22:25:53 -04:00
foreman ed35f0693f 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
 2018-05-02 21:08:53 -04:00
foreman 57a05ba4d5 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
 2018-05-02 19:14:52 -04:00
Rahul Garg 976b9ed200 Cleaned up 2018-05-02 12:54:17 +05:30
Rahul Garg 1d76c48e3d Fix texture 3D for HIP/NVCC 2018-05-02 11:56:37 +05:30
foreman 6bd6d3d4c1 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
 2018-05-01 19:01:10 -04:00
foreman 4a081cbc2f 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
 2018-05-01 18:46:32 -04:00
foreman c874bb2b90 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
 2018-05-01 18:10:09 -04:00
Maneesh Gupta e1af82d81e Merge pull request #420 from ROCm-Developer-Tools/sunway513-patch-1 
Update hip_bugs.md
 2018-05-01 12:43:01 +05:30
Maneesh Gupta 2e6b46f308 Merge pull request #419 from gargrahul/fix_hip_gcc_host_build 
Fix gcc build issues for host code
 2018-05-01 12:42:50 +05:30
Maneesh Gupta fb82411b23 Merge pull request #414 from aaronenyeshi/patch-1 
Remove unsupported targets gfx801 and gfx802
 2018-05-01 12:38:49 +05:30
Maneesh Gupta af0c227df4 Merge pull request #415 from deven-amd/master 
Checkin to fix bugs in math functions.
 2018-05-01 12:29:03 +05:30
Maneesh Gupta f8431772a8 Merge pull request #410 from gargrahul/hipCtx_deprecation_warning 
Mark hipCtx APIs as deprecated
 2018-05-01 12:23:22 +05:30
Maneesh Gupta 1a5c72885a Merge pull request #411 from luckynikki/SWDEV-141024 
SWDEV-141024
 2018-05-01 09:29:26 +05:30
Maneesh Gupta 885e51e1a5 Merge pull request #406 from gargrahul/fix_tex1D_coordinate_type 
Resolve tex1D float to int conversion issue
 2018-05-01 09:18:11 +05:30
foreman 7e5c7954b9 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
 2018-04-30 21:20:26 -04:00
foreman 12c490ff1d 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
 2018-04-30 20:17:46 -04:00
foreman 88f8260277 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
 2018-04-30 14:55:41 -04:00
foreman bc34be99d2 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
 2018-04-30 13:34:32 -04:00
Peng ac591da0dd Update hip_bugs.md 
Remove several out-date links in hip_bugs.md document
 2018-04-30 09:36:37 -05:00
foreman ad390dbe6d 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
 2018-04-30 01:03:06 -04:00
foreman 9f4d0049aa 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
 2018-04-29 15:04:45 -04:00
foreman c323c0b74d 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
 2018-04-27 21:21:31 -04:00
Deven Desai 30f0c19cf1 Fixing a copy/paste error in my previous checkin 2018-04-27 12:59:51 +00:00
Deven Desai 76e808304c 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)
 2018-04-25 17:53:21 +00:00
foreman 9aef0311c1 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
 2018-04-25 12:32:11 -04:00
Rahul Garg 720e209366 Fix gcc build issues for host code 2018-04-25 12:30:11 +05:30
foreman 894f01c206 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
 2018-04-24 16:49:38 -04:00
Paul 56734306ed Add host and device targets 2018-04-24 14:04:24 -05:00
Evgeny Mankov bfee03f95b [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
 2018-04-24 22:04:04 +03:00
Deven Desai 65a90c55e7 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'
 2018-04-24 18:10:07 +00:00
foreman 5eace16718 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
 2018-04-24 14:05:20 -04:00
Aaron Enye Shi 1149f88413 Remove unsupported targets gfx801 and gfx802 
These architectures are no longer supported. Should not compile for them.
 2018-04-23 15:25:35 -04:00
Evgeny Mankov ad28f72ca9 [HIPIFY] undo apply .clangformat to HIPIFY source files 2018-04-23 20:22:15 +03:00
foreman db522a2fbc 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
 2018-04-22 21:17:27 -04:00
Rahul Garg a68b9b6bf6 Added deprecation note in cuCtx section 2018-04-20 22:43:58 +05:30
Rahul Garg bc61260168 Moved deprecated macro to the end 2018-04-20 21:57:23 +05:30
Lakhan Singh 74faa61d52 SWDEV-141024 2018-04-20 17:40:00 +05:30
Rahul Garg 89674c54a7 Mark hipCtx APIs as deprecated 2018-04-20 17:34:48 +05:30
foreman 22439e8644 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
 2018-04-19 18:35:00 -04:00
foreman d532cc2b66 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
 2018-04-19 12:27:09 -04:00