41 Commits

Author	SHA1	Message	Date
foreman	0aa24f6d4d	P4 to Git Change 1997981 by cpaquot@cpaquot-ocl-lc-lnx on 2019/09/13 11:17:32 ... SWDEV-203438 - [HIP] AllGather RCCL test issue The test tries to launch a kernel on two devices at once and they need to communicate with each other. For that, it uses a custom stream for each devices. Problem is in getNullStream we used to call syncStreams all the time and it was syncing all the streams even the ones on different devices. So that made the second kernel launch (on 2n dev) to wait for the first kernel to finish which would never occur since the first one was waiting for the second one. The fix is to not call syncStreams from getNullStream because we sync already anyway prior in general. Affected files ... ... //depot/stg/opencl/drivers/opencl/api/hip/hip_context.cpp#21 edit ... //depot/stg/opencl/drivers/opencl/api/hip/hip_event.cpp#16 edit ... //depot/stg/opencl/drivers/opencl/api/hip/hip_internal.hpp#40 edit ... //depot/stg/opencl/drivers/opencl/api/hip/hip_memory.cpp#70 edit ... //depot/stg/opencl/drivers/opencl/api/hip/hip_module.cpp#41 edit ... //depot/stg/opencl/drivers/opencl/api/hip/hip_stream.cpp#24 edit	2019-09-13 11:28:33 -04:00
foreman	b0b5c92469	P4 to Git Change 1997621 by cpaquot@cpaquot-ocl-lc-lnx on 2019/09/12 14:16:09 ... SWDEV-145570 - Fixed some logging issues regarding hip(Ext)ModuleLaunchXXX. Affected files ... ... //depot/stg/opencl/drivers/opencl/api/hip/hip_module.cpp#40 edit	2019-09-12 14:35:36 -04:00
foreman	534727cd01	P4 to Git Change 1990032 by cpaquot@cpaquot-ocl-lc-lnx on 2019/08/27 20:20:36 ... SWDEV-145570 - [HIP] Add missing HIP_INIT_API macros and more debug printf. Affected files ... ... //depot/stg/opencl/drivers/opencl/api/hip/hip_module.cpp#39 edit ... //depot/stg/opencl/drivers/opencl/api/hip/hip_stream.cpp#23 edit	2019-08-27 20:26:25 -04:00
foreman	441eefa78b	P4 to Git Change 1989089 by kjayapra@0_HIPWS_P2P_ROCM on 2019/08/26 14:24:21 ... SWDEV-198194 - Delete vars at __hipUnregisterFatBinary. Affected files ... ... //depot/stg/opencl/drivers/opencl/api/hip/hip_internal.hpp#39 edit ... //depot/stg/opencl/drivers/opencl/api/hip/hip_module.cpp#38 edit ... //depot/stg/opencl/drivers/opencl/api/hip/hip_platform.cpp#40 edit	2019-08-26 14:32:48 -04:00
foreman	d9777f8524	P4 to Git Change 1988234 by kjayapra@3_HIPWS_TXT_ROCM on 2019/08/23 12:12:45 ... SWDEV-201068 - Reverting back CL 1987582. Affected files ... ... //depot/stg/opencl/drivers/opencl/api/hip/hip_module.cpp#37 edit ... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocvirtual.cpp#84 edit ... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocvirtual.hpp#27 edit ... //depot/stg/opencl/drivers/opencl/runtime/platform/command.cpp#98 edit ... //depot/stg/opencl/drivers/opencl/runtime/platform/command.hpp#96 edit	2019-08-23 12:15:29 -04:00
foreman	fb37058725	P4 to Git Change 1987582 by cpaquot@cpaquot-ocl-lc-lnx on 2019/08/22 13:20:28 ... SWDEV-185742 - [HIP] Add a svm path to avoid analyzing the mem objs and just memcpy the kernel args Affected files ... ... //depot/stg/opencl/drivers/opencl/api/hip/hip_module.cpp#36 edit ... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocvirtual.cpp#82 edit ... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocvirtual.hpp#25 edit ... //depot/stg/opencl/drivers/opencl/runtime/platform/command.cpp#96 edit ... //depot/stg/opencl/drivers/opencl/runtime/platform/command.hpp#94 edit	2019-08-22 13:26:57 -04:00
foreman	26a9ba7ba7	P4 to Git Change 1987529 by kjayapra@4_HIPWS_RCCM_ROCM on 2019/08/22 12:32:42 ... SWDEV-200625 - Reverting back CL#1986255. Affected files ... ... //depot/stg/opencl/drivers/opencl/api/hip/hip_internal.hpp#38 edit ... //depot/stg/opencl/drivers/opencl/api/hip/hip_module.cpp#35 edit ... //depot/stg/opencl/drivers/opencl/api/hip/hip_platform.cpp#39 edit	2019-08-22 12:41:42 -04:00
foreman	68402a82c9	P4 to Git Change 1986255 by kjayapra@4_HIPWS_RCCM_ROCM on 2019/08/20 17:06:44 ... SWDEV-198194 - Making some code common between static and dynamically created module handling. Affected files ... ... //depot/stg/opencl/drivers/opencl/api/hip/hip_internal.hpp#37 edit ... //depot/stg/opencl/drivers/opencl/api/hip/hip_module.cpp#34 edit ... //depot/stg/opencl/drivers/opencl/api/hip/hip_platform.cpp#38 edit	2019-08-20 17:11:51 -04:00
foreman	602da8e12d	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	2019-08-12 21:22:47 -04:00
foreman	e51298aee1	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	2019-08-11 18:53:11 -04:00
foreman	3494344c4d	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	2019-08-09 20:41:13 -04:00
foreman	7edcf4b581	P4 to Git Change 1972494 by kjayapra@0_HIPWS_P2P1_ROCM on 2019/07/23 20:01:13 ... SWDEV-144570 - Handling variable register during hipModuleLoad. Affected files ... ... //depot/stg/opencl/drivers/opencl/api/hip/hip_internal.hpp#31 edit ... //depot/stg/opencl/drivers/opencl/api/hip/hip_module.cpp#30 edit ... //depot/stg/opencl/drivers/opencl/api/hip/hip_platform.cpp#34 edit ... //depot/stg/opencl/drivers/opencl/runtime/device/devprogram.cpp#51 edit ... //depot/stg/opencl/drivers/opencl/runtime/device/devprogram.hpp#30 edit	2019-07-23 20:09:59 -04:00
foreman	bca0438b69	P4 to Git Change 1879857 by gandryey@gera-win10 on 2019/06/20 18:06:07 ... SWDEV-184710 - Support hipLaunchCooperativeKernelMultiDevice() - Clean-up the loop for the launch on each device - Add hipExtLaunchMultiKernelMultiDevice() http://ocltc.amd.com/reviews/r/17573/ Affected files ... ... //depot/stg/opencl/drivers/opencl/api/hip/hip_module.cpp#29 edit	2019-06-20 18:13:20 -04:00
foreman	623320cd93	P4 to Git Change 1809277 by gandryey@gera-win10 on 2019/06/11 17:34:13 ... SWDEV-180872 - Runtime support changes for Cooperative Group Features - Initial implementation of the core functionality. Disabled by default. Use GPU_ENABLE_COOP_GROUPS=1 to enable the feature. - Runtime uses device queue for cooperative executions with a synchronization on the launched queue. - The current implementation is pure runtime change and it can work if only one app uses this feature. No ROCr/KFD support was added or tested - Only inline assembler was tested Affected files ... ... //depot/stg/opencl/drivers/opencl/api/hip/hip_device.cpp#20 edit ... //depot/stg/opencl/drivers/opencl/api/hip/hip_device_runtime.cpp#15 edit ... //depot/stg/opencl/drivers/opencl/api/hip/hip_hcc.def.in#15 edit ... //depot/stg/opencl/drivers/opencl/api/hip/hip_hcc.map.in#17 edit ... //depot/stg/opencl/drivers/opencl/api/hip/hip_module.cpp#28 edit ... //depot/stg/opencl/drivers/opencl/api/hip/hip_platform.cpp#32 edit ... //depot/stg/opencl/drivers/opencl/runtime/device/device.hpp#338 edit ... //depot/stg/opencl/drivers/opencl/runtime/device/gpu/gpudevice.cpp#606 edit ... //depot/stg/opencl/drivers/opencl/runtime/device/gpu/gpudevice.hpp#171 edit ... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palblit.cpp#31 edit ... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palblit.hpp#9 edit ... //depot/stg/opencl/drivers/opencl/runtime/device/pal/paldevice.cpp#142 edit ... //depot/stg/opencl/drivers/opencl/runtime/device/pal/paldevice.hpp#39 edit ... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palschedcl.cpp#6 edit ... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palvirtual.cpp#135 edit ... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palvirtual.hpp#61 edit ... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocblit.cpp#32 edit ... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocblit.hpp#12 edit ... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocdevice.cpp#127 edit ... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocdevice.hpp#37 edit ... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocschedcl.cpp#3 edit ... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocvirtual.cpp#75 edit ... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocvirtual.hpp#23 edit ... //depot/stg/opencl/drivers/opencl/runtime/platform/command.cpp#94 edit ... //depot/stg/opencl/drivers/opencl/runtime/platform/command.hpp#92 edit ... //depot/stg/opencl/drivers/opencl/runtime/utils/flags.hpp#311 edit	2019-06-12 10:00:38 -04:00
foreman	bea21af6ad	P4 to Git Change 1787806 by yaxunl@yaxunl-lc10 on 2019/05/27 10:53:56 ... SWDEV-145570 - Support loading fat binary generated through --genco by hipModuleLoad. hip-clang --genco generates fat binary instead of code object. To support that we need to extract code object from fat binary in hipModuleLoadData. This is needed for hipRTC since multiple GPU archs may be passed. Affected files ... ... //depot/stg/opencl/drivers/opencl/api/hip/hip_module.cpp#27 edit ... //depot/stg/opencl/drivers/opencl/api/hip/hip_platform.cpp#31 edit ... //depot/stg/opencl/drivers/opencl/runtime/device/devprogram.cpp#42 edit ... //depot/stg/opencl/drivers/opencl/runtime/utils/flags.hpp#308 edit	2019-05-27 20:11:08 -04:00
foreman	f8d8559328	P4 to Git Change 1781540 by kpyzhov@hip-vdi-pal-win on 2019/05/10 17:10:30 ... SWDEV-188234 - Corrected reading binary module file in hipModuleLoad(). Affected files ... ... //depot/stg/opencl/drivers/opencl/api/hip/hip_module.cpp#26 edit	2019-05-10 19:19:11 -04:00
foreman	9aecfde4a5	P4 to Git Change 1778985 by cpaquot@cpaquot-ocl-lc-lnx on 2019/05/06 17:21:57 ... SWDEV-188668 - [HIP] Implemented hipExtModuleLaunchKernel. Ignoring the flag for now. Affected files ... ... //depot/stg/opencl/drivers/opencl/api/hip/hip_hcc.def.in#14 edit ... //depot/stg/opencl/drivers/opencl/api/hip/hip_hcc.map.in#15 edit ... //depot/stg/opencl/drivers/opencl/api/hip/hip_module.cpp#25 edit	2019-05-06 18:02:54 -04:00
foreman	84d257cf3b	P4 to Git Change 1778971 by cpaquot@cpaquot-ocl-lc-lnx on 2019/05/06 17:03:12 ... SWDEV-187125 - [HIP] Protect hip::Event with lock and add threadId to logs. Affected files ... ... //depot/stg/opencl/drivers/opencl/api/hip/hip_event.cpp#9 edit ... //depot/stg/opencl/drivers/opencl/api/hip/hip_event.hpp#3 edit ... //depot/stg/opencl/drivers/opencl/api/hip/hip_internal.hpp#30 edit ... //depot/stg/opencl/drivers/opencl/api/hip/hip_module.cpp#24 edit ... //depot/stg/opencl/drivers/opencl/api/hip/hip_stream.cpp#18 edit	2019-05-06 17:43:06 -04:00
foreman	33ebadc935	P4 to Git Change 1775366 by kjayapra@99_HIPWS_SLV_CHECKIN on 2019/04/26 14:48:23 ... SWDEV-144570 - hipFuncGetAttributes() API changes. Affected files ... ... //depot/stg/opencl/drivers/opencl/api/hip/hip_internal.hpp#29 edit ... //depot/stg/opencl/drivers/opencl/api/hip/hip_module.cpp#23 edit ... //depot/stg/opencl/drivers/opencl/api/hip/hip_platform.cpp#28 edit	2019-04-26 15:15:48 -04:00
foreman	d0c8e12d00	P4 to Git Change 1766106 by kjayapra@99_HIPWS_SLV_CHECKIN on 2019/04/04 18:07:26 ... SWDEV-144570 - Implementation of hipMemcpyToSymbol and simillar fns for PAL. Affected files ... ... //depot/stg/opencl/drivers/opencl/api/hip/hip_internal.hpp#24 edit ... //depot/stg/opencl/drivers/opencl/api/hip/hip_module.cpp#22 edit ... //depot/stg/opencl/drivers/opencl/api/hip/hip_platform.cpp#26 edit ... //depot/stg/opencl/drivers/opencl/runtime/device/devprogram.hpp#23 edit ... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palprogram.cpp#89 edit ... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palprogram.hpp#37 edit ... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocprogram.cpp#102 edit ... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocprogram.hpp#46 edit ... //depot/stg/opencl/drivers/opencl/runtime/platform/memory.cpp#135 edit	2019-04-04 18:22:40 -04:00
foreman	e432cfb2e9	P4 to Git Change 1757948 by kjayapra@1_HIPWS_SL_IPC on 2019/03/18 18:29:24 ... SWDEV-144570 - Implementation of hipMemcpyToSymbol, hipMemcpyFromSymbol, hipMemcpyToSymbolAsync, hipMemcpyFromSymbolAsync, hipGetSymbolAddress, hipModuleGetGlobal Affected files ... ... //depot/stg/opencl/drivers/opencl/api/hip/hip_hcc.def.in#12 edit ... //depot/stg/opencl/drivers/opencl/api/hip/hip_hcc.map.in#13 edit ... //depot/stg/opencl/drivers/opencl/api/hip/hip_internal.hpp#23 edit ... //depot/stg/opencl/drivers/opencl/api/hip/hip_memory.cpp#45 edit ... //depot/stg/opencl/drivers/opencl/api/hip/hip_module.cpp#21 edit ... //depot/stg/opencl/drivers/opencl/api/hip/hip_platform.cpp#22 edit ... //depot/stg/opencl/drivers/opencl/runtime/device/devprogram.hpp#20 edit ... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocprogram.cpp#101 edit ... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocprogram.hpp#45 edit	2019-03-18 18:44:55 -04:00
foreman	8cdcb7edb5	P4 to Git Change 1746912 by cpaquot@cpaquot-ocl-lc-lnx on 2019/02/21 14:16:35 ... SWDEV-178453 - [HIP] Add extra parameter for sharedMemBytes Affected files ... ... //depot/stg/opencl/drivers/opencl/api/hip/hip_module.cpp#20 edit ... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palvirtual.cpp#129 edit ... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palvirtual.hpp#58 edit ... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocvirtual.cpp#72 edit ... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocvirtual.hpp#21 edit ... //depot/stg/opencl/drivers/opencl/runtime/platform/command.cpp#91 edit ... //depot/stg/opencl/drivers/opencl/runtime/platform/command.hpp#91 edit	2019-02-21 17:42:08 -05:00
foreman	63e7f9255c	P4 to Git Change 1604214 by cpaquot@cpaquot-ocl-lc-lnx on 2018/09/11 12:12:23 ... SWDEV-145570 - [HIP] Added empty hipModuleGetGlobal function. Affected files ... ... //depot/stg/opencl/drivers/opencl/api/hip/hip_module.cpp#19 edit	2018-09-11 12:26:34 -04:00
foreman	556ef9c0d1	P4 to Git Change 1598666 by cpaquot@cpaquot-ocl-lc-lnx on 2018/08/27 18:36:44 ... SWDEV-145570 - [HIP] - Multithreading issues Add a lock per function so kernel parameters don't get overwritten Make execStack_ thread local and remove global lock use for it: The compiler uses the same thread to set it up and launch the function Affected files ... ... //depot/stg/opencl/drivers/opencl/api/hip/hip_internal.hpp#16 edit ... //depot/stg/opencl/drivers/opencl/api/hip/hip_module.cpp#18 edit ... //depot/stg/opencl/drivers/opencl/api/hip/hip_platform.cpp#19 edit	2018-08-27 18:46:34 -04:00
foreman	2ec2cfd3c1	P4 to Git Change 1593706 by skudchad@skudchad_test2_win_opencl on 2018/08/14 18:44:29 ... SWDEV-145570 - [HIP] Implement hipError* ReviewBoardURL = http://ocltc.amd.com/reviews/r/15619/diff/ Affected files ... ... //depot/stg/opencl/drivers/opencl/api/hip/hip_context.cpp#13 edit ... //depot/stg/opencl/drivers/opencl/api/hip/hip_device.cpp#14 edit ... //depot/stg/opencl/drivers/opencl/api/hip/hip_device_runtime.cpp#11 edit ... //depot/stg/opencl/drivers/opencl/api/hip/hip_error.cpp#2 edit ... //depot/stg/opencl/drivers/opencl/api/hip/hip_event.cpp#5 edit ... //depot/stg/opencl/drivers/opencl/api/hip/hip_internal.hpp#13 edit ... //depot/stg/opencl/drivers/opencl/api/hip/hip_memory.cpp#41 edit ... //depot/stg/opencl/drivers/opencl/api/hip/hip_module.cpp#17 edit ... //depot/stg/opencl/drivers/opencl/api/hip/hip_peer.cpp#2 edit ... //depot/stg/opencl/drivers/opencl/api/hip/hip_platform.cpp#17 edit ... //depot/stg/opencl/drivers/opencl/api/hip/hip_profile.cpp#2 edit ... //depot/stg/opencl/drivers/opencl/api/hip/hip_stream.cpp#12 edit ... //depot/stg/opencl/drivers/opencl/api/hip/hip_surface.cpp#2 edit ... //depot/stg/opencl/drivers/opencl/api/hip/hip_texture.cpp#9 edit	2018-08-14 18:54:13 -04:00
foreman	a9a9217b4b	P4 to Git Change 1592348 by cpaquot@cpaquot-ocl-lc-lnx on 2018/08/10 17:00:39 ... SWDEV-145570 - [HIP] Do not multiply block and dims for Hcc/Ext kernel module launch Affected files ... ... //depot/stg/opencl/drivers/opencl/api/hip/hip_module.cpp#16 edit	2018-08-10 17:16:53 -04:00
foreman	b4ccaeffe1	P4 to Git Change 1590010 by skudchad@skudchad_test2_win_opencl on 2018/08/06 21:18:48 ... SWDEV-145570 - [HIP] - Fix some issues in hip runtime - Set stream for event - Free mem needs to be reported in bytes but runtime backends reports in Kb ReviewBoardURL = http://ocltc.amd.com/reviews/r/15586/diff/ Affected files ... ... //depot/stg/opencl/drivers/opencl/api/hip/hip_memory.cpp#40 edit ... //depot/stg/opencl/drivers/opencl/api/hip/hip_module.cpp#15 edit	2018-08-06 21:24:14 -04:00
foreman	678764d113	P4 to Git Change 1589087 by skudchad@skudchad_rocm on 2018/08/02 20:10:02 ... SWDEV-145570 - [HIP] - hipHccModuleLaunchKernel needs to be a c++ sym Affected files ... ... //depot/stg/opencl/drivers/opencl/api/hip/hip_hcc.map.in#9 edit ... //depot/stg/opencl/drivers/opencl/api/hip/hip_module.cpp#14 edit	2018-08-02 20:20:23 -04:00
foreman	e638c1377f	P4 to Git Change 1588556 by skudchad@skudchad_rocm on 2018/08/02 02:04:15 ... SWDEV-145570 - [HIP] - Release eStop if it not a nullptr. Affected files ... ... //depot/stg/opencl/drivers/opencl/api/hip/hip_module.cpp#13 edit	2018-08-02 02:18:57 -04:00
foreman	11a91fbe0b	P4 to Git Change 1588551 by skudchad@skudchad_rocm on 2018/08/02 01:55:45 ... SWDEV-145570 - [HIP] - Refactor ihipModuleLaunchKernel and add hipModuleLaunchKernelExt Affected files ... ... //depot/stg/opencl/drivers/opencl/api/hip/hip_hcc.def.in#8 edit ... //depot/stg/opencl/drivers/opencl/api/hip/hip_hcc.map.in#8 edit ... //depot/stg/opencl/drivers/opencl/api/hip/hip_module.cpp#12 edit	2018-08-02 02:14:04 -04:00
foreman	e51c42ac66	P4 to Git Change 1576872 by skudchad@skudchad_rocm on 2018/07/05 20:20:21 ... SWDEV-145570 - [HIP] - Add hipMalloc3D to linker symtable. - Add structure for hipFuncGetAttributes Affected files ... ... //depot/stg/opencl/drivers/opencl/api/hip/hip_hcc.def.in#6 edit ... //depot/stg/opencl/drivers/opencl/api/hip/hip_hcc.map.in#6 edit ... //depot/stg/opencl/drivers/opencl/api/hip/hip_module.cpp#11 edit	2018-07-05 20:29:27 -04:00
foreman	e9039d398e	P4 to Git Change 1559366 by gandryey@gera-w8 on 2018/05/24 18:06:45 ... SWDEV-79445 - OCL generic changes and code clean-up - Combine validateMemory() and arguments capture() under a single function. Rename validateMemory() in NDRangeKernelCommand class to captureAndValidate() http://ocltc.amd.com/reviews/r/14964/ Affected files ... ... //depot/stg/opencl/drivers/opencl/api/hip/hip_module.cpp#10 edit ... //depot/stg/opencl/drivers/opencl/api/opencl/amdocl/cl_execute.cpp#26 edit ... //depot/stg/opencl/drivers/opencl/runtime/platform/command.cpp#87 edit ... //depot/stg/opencl/drivers/opencl/runtime/platform/command.hpp#90 edit ... //depot/stg/opencl/drivers/opencl/runtime/platform/kernel.cpp#28 edit ... //depot/stg/opencl/drivers/opencl/runtime/platform/kernel.hpp#22 edit	2018-05-24 18:12:49 -04:00
foreman	a896cb9af0	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	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
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	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	9504ce2bc4	P4 to Git Change 1534798 by cpaquot@cpaquot-ocl-lc-lnx on 2018/03/30 00:56:35 ... SWDEV-145570 - [HIP] Implemented hipStream create/destroy Use the provided stream in hipModuleLaunchKernel Affected files ... ... //depot/stg/opencl/drivers/opencl/api/hip/hip_module.cpp#4 edit ... //depot/stg/opencl/drivers/opencl/api/hip/hip_stream.cpp#2 edit	2018-03-30 01:06:00 -04:00
foreman	c531507708	P4 to Git Change 1531138 by cpaquot@cpaquot-ocl-lc-lnx on 2018/03/23 00:10:40 ... SWDEV-145570 - [HIP] Module Check for correct device id in hipDeviceGetAttribute Implement hipModuleLoad Handle kernelParams in hipModuleLaunchKernel Affected files ... ... //depot/stg/opencl/drivers/opencl/api/hip/hip_device.cpp#8 edit ... //depot/stg/opencl/drivers/opencl/api/hip/hip_device_runtime.cpp#3 edit ... //depot/stg/opencl/drivers/opencl/api/hip/hip_internal.hpp#5 edit ... //depot/stg/opencl/drivers/opencl/api/hip/hip_module.cpp#3 edit	2018-03-23 00:19:22 -04:00
foreman	f27e6709eb	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	13f4e897fc	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