AI/rocm-systems
2
0
Fork 0
Code Issues Pull Requests Actions Packages Projects Releases Wiki Activity
60 Commits 3 Branches 0 Tags
cadb15165e6c4e418f0ccb232ba19f73639b230f
Commit Graph

29 Commits

Author SHA1 Message Date
foreman da7593ae40 P4 to Git Change 1559149 by skudchad@skudchad_test2_win_opencl on 2018/05/24 11:54:02 
SWDEV-145570 - [HIP] - Implement hipMemcpy2DToArray.

	ReviewBoardURL = http://ocltc.amd.com/reviews/r/14953/diff/

Affected files ...

... //depot/stg/opencl/drivers/opencl/api/hip/hip_memory.cpp#29 edit
 2018-05-24 12:01:44 -04:00
foreman 0fe5f87cba P4 to Git Change 1558526 by skudchad@skudchad_test2_win_opencl on 2018/05/23 13:34:33 
SWDEV-145570 - [HIP]  Implement hipPointerGetAttributes.

	ReviewBoardURL = http://ocltc.amd.com/reviews/r/14938/diff/

Affected files ...

... //depot/stg/opencl/drivers/opencl/api/hip/hip_memory.cpp#28 edit
 2018-05-23 13:40:52 -04:00
foreman f165295c66 P4 to Git Change 1557352 by cpaquot@cpaquot-ocl-lc-lnx on 2018/05/21 19:53:00 
SWDEV-145570 - [HIP]  Sync streams in hipFree. hipTestHalf passes now.

Affected files ...

... //depot/stg/opencl/drivers/opencl/api/hip/hip_memory.cpp#27 edit
 2018-05-21 20:02:17 -04:00
foreman b1ab722a25 P4 to Git Change 1555866 by cpaquot@cpaquot-ocl-lc-lnx on 2018/05/16 16:27:00 
SWDEV-145570 - [HIP] Store HIP mem flags inside amd::Buffer's flags
	Use the 16 upper bits of amd::Buffer's flags field instead of adding a new field.

Affected files ...

... //depot/stg/opencl/drivers/opencl/api/hip/hip_memory.cpp#26 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocdevice.cpp#86 edit
 2018-05-16 16:35:53 -04:00
foreman da00b9270a P4 to Git Change 1555193 by cpaquot@cpaquot-ocl-lc-lnx on 2018/05/15 16:19:50 
SWDEV-145570 - [HIP] Implemented events

Affected files ...

... //depot/stg/opencl/drivers/opencl/api/hip/hip_event.cpp#4 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_event.hpp#2 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_memory.cpp#25 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_module.cpp#9 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_stream.cpp#9 edit
 2018-05-15 16:26:16 -04:00
foreman 2df122be02 P4 to Git Change 1552011 by skudchad@skudchad_test2_win_opencl on 2018/05/08 14:48:45 
SWDEV-145570 - [HIP] Fix offset calculation when getting a memory object. Also include case when destination VA may just be a CPU host VA and not nessarily device alloced.
	- Fix hipMemset* to write each byte and now a dword as per the spec

	ReviewBoardURL = http://ocltc.amd.com/reviews/r/14787/diff/

Affected files ...

... //depot/stg/opencl/drivers/opencl/api/hip/hip_memory.cpp#24 edit
 2018-05-08 15:43:13 -04:00
foreman 2c5606ea44 P4 to Git Change 1550648 by skudchad@skudchad_test2_win_opencl on 2018/05/04 20:56:00 
SWDEV-145570 - [HIP]
	- Implement hipMemcpyHtoD/DtoH/DtoD/ and their Async APIs
	- Combine logic for hipMemset/Memcpy/Memset2D/Memcpy2D that can be shared across multiple APIs

	ReviewBoardURL = http://ocltc.amd.com/reviews/r/14782/diff/

Affected files ...

... //depot/stg/opencl/drivers/opencl/api/hip/hip_memory.cpp#23 edit
 2018-05-05 00:34:05 -04:00
foreman 0508a4ed37 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 99d3444f00 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 3ad5f2a01b 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
foreman a10512c510 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 445d300d63 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 0ddf288904 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
foreman 9c7b328101 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 61378a359c 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
foreman 6f7e33cb91 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 36d2d37804 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
foreman 18c7c164c6 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
foreman 13355e5de5 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
foreman 3ce752065a 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 04decb72fc P4 to Git Change 1539198 by skudchad@skudchad_test2_win_opencl on 2018/04/10 17:32:14 
SWDEV-145570 - [HIP] -  Add HIP API skeletons for Peer and memory

	ReviewBoardURL = http://ocltc.amd.com/reviews/r/14596/diff/

Affected files ...

... //depot/stg/opencl/drivers/opencl/api/hip/hip_context.cpp#7 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_memory.cpp#9 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_peer.cpp#1 add
 2018-04-10 17:41:24 -04:00
foreman e7f206d249 P4 to Git Change 1537729 by cpaquot@cpaquot-ocl-lc-lnx on 2018/04/06 17:59:29 
SWDEV-145570 - [HIP] Use Svm path for both hipMalloc and hipHostMalloc
	Make sure hipMemCpy uses SvmBuffer to fetch the cl_mem

Affected files ...

... //depot/stg/opencl/drivers/opencl/api/hip/hip_memory.cpp#8 edit
 2018-04-06 18:08:18 -04:00
foreman 204ecba4b6 P4 to Git Change 1537228 by skudchad@skudchad_test2_win_opencl on 2018/04/05 14:53:31 
SWDEV-145570 - [HIP] -  Add HIP Memory, texture, surface, context api skeletons

	ReviewBoardURL = http://ocltc.amd.com/reviews/r/14565/diff/

Affected files ...

... //depot/stg/opencl/drivers/opencl/api/hip/hip_context.cpp#6 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_device.cpp#9 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_event.cpp#2 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_memory.cpp#7 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_stream.cpp#3 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_surface.cpp#1 add
... //depot/stg/opencl/drivers/opencl/api/hip/hip_texture.cpp#1 add
 2018-04-05 15:02:43 -04:00
foreman 4574e01740 P4 to Git Change 1536698 by skudchad@skudchad_test2_win_opencl on 2018/04/04 13:18:19 
SWDEV-145570 - [HIP] -  Add HIP Memory api skeletons

	ReviewBoardURL = http://ocltc.amd.com/reviews/r/14555/diff/

Affected files ...

... //depot/stg/opencl/drivers/opencl/api/hip/hip_device_runtime.cpp#4 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_memory.cpp#6 edit
 2018-04-04 13:24:15 -04:00
foreman f99db275fe P4 to Git Change 1524135 by cpaquot@cpaquot-ocl-lc-lnx on 2018/03/07 19:52:00 
SWDEV-145570 - [HIP] Hip Rearchitecture
	Implemented hipHostAlloc

Affected files ...

... //depot/stg/opencl/drivers/opencl/api/hip/hip_memory.cpp#5 edit
 2018-03-07 20:03:36 -05:00
foreman d8a344113f P4 to Git Change 1522211 by lmoriche@lmoriche_opencl_dev2 on 2018/03/02 17:41:47 
SWDEV-145570 - [HIP] - Hip Rearchitecture
	- Rename cuda* launch functions -> hip*
	- Add more function prototypes to compile the HIP tests

Affected files ...

... //depot/stg/opencl/drivers/opencl/api/hip/hip_context.cpp#2 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_device.cpp#3 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_hcc.def.in#2 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_hcc.map.in#2 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_memory.cpp#4 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_module.cpp#2 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_platform.cpp#2 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_stream.cpp#1 add
 2018-03-02 17:55:48 -05:00
foreman 73cb309e2b P4 to Git Change 1521675 by lmoriche@lmoriche_opencl_dev2 on 2018/03/01 22:50:06 
SWDEV-145570 - [HIP] - Hip Rearchitecture
	- Add initial prototype implementation

Affected files ...

... //depot/stg/opencl/drivers/opencl/api/Makefile#11 edit
... //depot/stg/opencl/drivers/opencl/api/hip/fixme.cpp#1 add
... //depot/stg/opencl/drivers/opencl/api/hip/hip_context.cpp#1 add
... //depot/stg/opencl/drivers/opencl/api/hip/hip_device.cpp#2 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_error.cpp#1 add
... //depot/stg/opencl/drivers/opencl/api/hip/hip_event.cpp#1 add
... //depot/stg/opencl/drivers/opencl/api/hip/hip_hcc.def.in#1 add
... //depot/stg/opencl/drivers/opencl/api/hip/hip_hcc.map.in#1 add
... //depot/stg/opencl/drivers/opencl/api/hip/hip_hcc.rc#1 add
... //depot/stg/opencl/drivers/opencl/api/hip/hip_internal.hpp#2 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_memory.cpp#3 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_module.cpp#1 add
... //depot/stg/opencl/drivers/opencl/api/hip/hip_platform.cpp#1 add
 2018-03-01 22:57:20 -05:00
foreman 37faef47ba P4 to Git Change 1516173 by skudchad@skudchad_rocm on 2018/02/14 15:02:45 
SWDEV-145570 -  Initial hip api checkin

Affected files ...

... //depot/stg/opencl/drivers/opencl/api/hip/hip_memory.cpp#2 edit
 2018-02-14 15:08:01 -05:00
foreman 2ed585ec08 P4 to Git Change 1515837 by skudchad@skudchad_rocm on 2018/02/13 19:37:06 
SWDEV-145570 -  Initial hip api checkin

Affected files ...

... //depot/stg/opencl/drivers/opencl/api/Makefile#10 edit
... //depot/stg/opencl/drivers/opencl/api/hip/Makefile#1 add
... //depot/stg/opencl/drivers/opencl/api/hip/build/Makefile#1 add
... //depot/stg/opencl/drivers/opencl/api/hip/build/Makefile.hip#1 add
... //depot/stg/opencl/drivers/opencl/api/hip/hip_memory.cpp#1 add
 2018-02-13 19:45:32 -05:00