Commit Graph

141 Commits

Author SHA1 Message Date
Rahul Garg 896c146fef Porting guides update for texture APIs usage
[ROCm/clr commit: 3e9a4cfdd1]
2017-11-24 12:00:55 +05:30
Evgeny Mankov 72215db89e [HIPIFY] CUDA RT Textures and Arrays support update
[ROCm/clr commit: 858315b4cd]
2017-10-05 16:38:36 +03:00
Evgeny Mankov 6043ab0755 [HIPIFY] CUDA RT Textures support update
[ROCm/clr commit: bbaf16b263]
2017-09-18 17:52:50 +03:00
Evgeny Mankov c49d3445b5 [HIPIFY] Fix typo in doc
[ROCm/clr commit: bfa3a0a433]
2017-09-18 17:26:33 +03:00
Sandeep Kumar 695862fdc6 Add more info for inline asm in hip kernel guide and cookbook readme
[ROCm/clr commit: 6eb1d2d52f]
2017-09-13 12:57:37 +05:30
Ben Sander dcd8961a9d Update docs.
- Review unsupported comments and refresh.
- Review experimental tag in API.


[ROCm/clr commit: a6d1778fff]
2017-08-28 15:44:38 -05:00
Rahul Garg 93d30119d0 docs update for memcpytosymbol support
[ROCm/clr commit: a8512b7597]
2017-08-08 09:13:12 +05:30
Evgeny Mankov f9780654b8 Update CUDA_Runtime_API_functions_supported_by_HIP.md
[ROCm/clr commit: 4486f91350]
2017-07-28 01:41:14 +03:00
Evgeny Mankov 4940eea975 Update CUDA_Runtime_API_functions_supported_by_HIP.md
[ROCm/clr commit: 681dd9e14d]
2017-07-28 01:38:50 +03:00
Evgeny Mankov e586926eb7 [HIPIFY] CUDA RT Textures support
[ROCm/clr commit: fa7719b5b5]
2017-07-27 18:39:40 +03:00
Maneesh Gupta 97edbda54d Merge pull request #116 from bensander/enable_coh_host
Make host memory allocations coherent by default.

[ROCm/clr commit: 9086c14936]
2017-07-27 10:45:32 +05:30
Ben Sander 235b60165f Make host memory allocations coherent by default.
Associated change is to optimize event recording so it uses
agent-scope releaes (since it was only using system-scope release
to support non-coherent host mem).

Flags and environment variables exist to obtain previous behavior
if desired.  Options are documented in new performance guide.


[ROCm/clr commit: 6576201ec2]
2017-07-26 19:20:34 -05:00
Evgeny Mankov 7428857399 [HIPIFY] CUDA Stream Callback support
[ROCm/clr commit: af9dadf20a]
2017-07-26 19:29:50 +03:00
Evgeny Mankov 7fab0b5ecc [HIPIFY] Finally finished syncing with CUDA 8.0.61 Driver and Runtime… (#105)
[hipify-clang] Finally finished syncing with CUDA 8.0.61 Driver and Runtime API (including missing data types, D3D, OpenGL, VDPAU and EGL interop).

    + All the Modules are supported now:
	1) 4.1 – 4.31 from CUDA 8.0.61 Driver API
	2) CUDA_Driver_API_functions_supported_by_HIP.md updated accordingly
	3) 4.1 – 4.31 from CUDA 8.0.61 Runtime API
	4) CUDA_Runtime_API_functions_supported_by_HIP.md updated accordingly
    + Typos fixing
    + Annotating

[ROCm/clr commit: 9b10efe419]
2017-07-26 09:38:03 +05:30
Maneesh Gupta 7b011a5996 Update toc in markdown documentation
Change-Id: I6da7053672b306442f3640fff3471efe25593870


[ROCm/clr commit: f907a986a1]
2017-06-28 11:32:25 +05:30
sunway513 9f949c5ec3 Fix docs for HIP_TRACE_API bit masks.
[ROCm/clr commit: c80d906624]
2017-06-26 17:54:30 -05:00
Ben Sander 16b2a0b76e Add docs for launch_bounds.
[ROCm/clr commit: 76c2397281]
2017-06-23 18:05:30 -05:00
Evgeny Mankov 8c20ecdfde [HIPIFY] Sync more CUDA Driver API functions.
+ 4.14. Event Management
+ 4.15. Execution Control

ToDo: 4.16 - 4.31 modules of CUDA Driver API.


[ROCm/clr commit: cbb5c63dd6]
2017-06-22 21:53:32 +03:00
Evgeny Mankov 1912c9f308 [HIPIFY] Sync HIPIFY with HIP by CUDA Driver API functions.
+ 4.12. Unified Addressing
+ 4.13. Stream Management

ToDo: 4.14 - 4.31 modules of CUDA Driver API.


[ROCm/clr commit: 094f1b1f2f]
2017-06-14 19:55:55 +03:00
Evgeny Mankov cfe2dc9fc0 [HIPIFY] Initial sync HIPIFY with HIP by CUDA Driver API functions.
+ CUDA_Driver_API_functions_supported_by_HIP.md update.
+ Initial update of HIPIFY with CUDA driver API functions:
  1.Error Handling, 2.Initialization, 3.Version Management, 5-6.Device Management, 7.Primary Context, 8-9.Context, 10.Module Management, 11.Memory Management.
+ Sync HIP functions against CUDA Driver and Runtime API functions.
+ Typo fixes.

ToDo: 12-30 modules of CUDA Driver API.


[ROCm/clr commit: 82b37fe481]
2017-06-13 20:25:11 +03:00
Ben Sander b4363ffcba Remove HIP_NUM_KERNELS_INFLIGHT. (redundant with HCC controls)
[ROCm/clr commit: 35212632e7]
2017-05-24 01:03:28 -05:00
Evgeny Mankov 052f630bd3 [HIP] [HIPIFY] [FIX] cuModuleLoadDataEx -> hipModuleLoadDataEx
https://github.com/GPUOpen-ProfessionalCompute-Tools/HIP/issues/81

1.	Do not use JIT options on HCC path, call hipModuleLoadData instead.
2.	NVCC path is unchanged, to call cuModuleLoadDataEx with all options.
3.	Get rid of manual hipification, based on #ifdef #else for NVCC/HIP.
4.	Update documentation accordingly.


[ROCm/clr commit: ae9f14ef9c]
2017-05-19 17:22:14 +03:00
Ben Sander b8b6cfe02e Doc update - split hip_debugging.md into separate file.
[ROCm/clr commit: a5a12942b2]
2017-05-16 19:04:25 -05:00
Ben Sander ee05975efa Add HIP_TRACE_API=4. Only display memory allocation/free apis.
[ROCm/clr commit: 7e7ba5027f]
2017-05-16 19:04:25 -05:00
Ben Sander fa1ac559cb Fix some typos, add additional guidance for -BSymbolic
[ROCm/clr commit: 9a026b62a8]
2017-05-05 17:29:04 -05:00
Evgeny Mankov 3ca552c669 [HIPIFY] HIPIFY and HIP sync with CUDA Driver API data types.
+ Update CUDA_Driver_API_functions_supported_by_HIP.md.
+ Final update of HIPIFY with CUDA driver data types.

[TODO] Syncing HIPIFY and HIP by CUDA Driver API functions.


[ROCm/clr commit: 3b40776244]
2017-05-03 21:59:48 +03:00
Evgeny Mankov 8805f2ce66 [HIPIFY] Initial sync HIPIFY with HIP by CUDA Driver API data types.
+ Introduce CUDA_Driver_API_functions_supported_by_HIP.md.
+ Initial update of HIPIFY with CUDA driver data types.
+ Initial sync HIP types against CUDA Driver and Runtime API types.
+ Typo fixes.


[ROCm/clr commit: 342c63d398]
2017-04-21 21:46:30 +03:00
Ben Sander 41b7984cd0 Update bugs - Add CreateKernel, new signature for static kerns.
[ROCm/clr commit: 710c83b73b]
2017-04-16 14:22:48 -05:00
Ben Sander 0d24c155a3 Doc update for Serialization.
Describe workaround for partial specialization


[ROCm/clr commit: 29af40fa76]
2017-04-10 19:45:18 -05:00
Maneesh Gupta 4dcbf609b7 Updated table of contents in markdown documentation
Change-Id: I7347a06f57f9927ca3fcc5590a6c8200bc1bb1f5


[ROCm/clr commit: cfd4620f36]
2017-04-07 15:38:56 +05:30
Ben Sander 2f050e56f8 Update bug workarounds to reflect tool improvements.
[ROCm/clr commit: e8f4f76649]
2017-04-05 21:59:32 -05:00
Ben Sander 251db89f03 Doc cleanup & add bug descript for restrict specifier issue
[ROCm/clr commit: 294ffbb51f]
2017-04-05 19:40:00 -05:00
Ben Sander 2dbc9b1d08 Add bug descrip for "no matching constructor"
[ROCm/clr commit: f345cd6f47]
2017-04-05 17:43:20 -05:00
Sun, Peng 19c64a41a3 hip_debug.md update from Alex, regarding __device__ function restrictions
Change-Id: I5e54fd97fc632d4283f76282e3935396a1aad235


[ROCm/clr commit: bfe499a13b]
2017-04-05 16:23:27 -05:00
Sun, Peng a4901cdcd3 Move current GGL limitations to hip_bugs.md
Change-Id: I77d0eae0a67eccef7dd2bea0f402736642c96554


[ROCm/clr commit: 5826e53644]
2017-04-01 08:21:06 -05:00
Sun, Peng b602d68f95 update hip_faq.md on using GGL as default
Change-Id: I6ce1112eedeac3b377fe55ad8445f3c465c2eed4


[ROCm/clr commit: 67e14da511]
2017-03-30 15:03:09 -05:00
Sun, Peng db4bedeafc revert workaround for square sample and update doc on GGL
Change-Id: I731c68ca4111e7dc2e45bef51c4cad2c23fc81f8


[ROCm/clr commit: 14f8c7cf74]
2017-03-21 10:26:09 -05:00
Sun, Peng 4dbdf4e7eb Add link to GGL document in hip_faq.md
Change-Id: I9f7f0200a06976d580be334c21640c816f812ebb


[ROCm/clr commit: 1fd2e281d0]
2017-03-20 15:50:10 -05:00
Sun, Peng 5c284999b2 Add document for switching to GGL in hip_faq.md
Change-Id: I83d9fd3e76d21ab572949c3a446ac3898acb3ded


[ROCm/clr commit: 3bd73d6280]
2017-03-20 15:44:28 -05:00
Evgeny Mankov 151612e184 [HIP] [DOC] Update hip_porting_driver_api.md
+ Fix typos, formatting, update CUDA Driver API support.


[ROCm/clr commit: c6de5b92b5]
2017-03-16 14:39:28 +03:00
Siu Chi Chan ff4621af4e replace code names with gfx names
Change-Id: I5e0b96a0b474b16cfa92077a30a5b80b7230254b


[ROCm/clr commit: c6efbc1f25]
2017-03-15 12:26:13 -04:00
pensun a49f5c7e1d update porting guide for updated __HIP_DEVICE_COMPILE__
Change-Id: I0f025d354f76e2d728231bf112a77e8c8fcacc8c


[ROCm/clr commit: 1a2844e3a3]
2017-03-10 10:01:12 -06:00
pensun f4e9b51d35 fix typo in hip_porting_guide
Change-Id: I42553d9a4de2901dfdd57384b52a04e8fb22edde


[ROCm/clr commit: 308638c911]
2017-03-08 23:37:50 -06:00
Evgeny Mankov 0d33e087b3 [HIP] [DOC] Update CUDA_Runtime_API_functions_supported_by_HIP
+ update all Cuda 7.5 RT API enum values.


[ROCm/clr commit: b8dc082ffb]
2017-03-03 22:05:23 +03:00
pensun e5bf4ec700 update hip_porting_guide regarding platform depended macros
Change-Id: I3029c6ae6cb280500bba294925ed6e9dc9dcc94d


[ROCm/clr commit: ae1c6ee68a]
2017-02-28 07:33:01 -06:00
Evgeny Mankov 8a25b2e284 [HIP] [DOC] Update CUDA_Runtime_API_functions_supported_by_HIP
cudaDeviceGetPCIBusId -> hipDeviceGetPCIBusId


[ROCm/clr commit: 45f6b10459]
2017-02-20 21:21:47 +03:00
Evgeny Mankov 45846037b1 [HIP] [DOC] Update CUDA_Runtime_API_functions_supported_by_HIP
Section "20. Data types used by CUDA Runtime API and supported by HIP" is added.

+ 44 supported data types are added
- 46 at least to support

All the supported data types are also supported by hipify-clang (synced).


[ROCm/clr commit: 2fb5ef1545]
2017-02-20 18:32:54 +03:00
Evgeny Mankov 6449bad064 [HIP] [DOC] Update CUDA_Runtime_API_functions_supported_by_HIP
Move hipBindTexture and hipUnbindTexture to "18. C++ API Routines" from "13. Texture Reference Management". They are C++, not C.


[ROCm/clr commit: ce245f14e8]
2017-02-17 18:09:08 +03:00
Evgeny Mankov f8f5b51164 [HIP] [DOC] Update CUDA_Runtime_API_functions_supported_by_HIP
+ 21 supported functions
- 99 at least to support

All the supported functions are also supported by hipify-clang (synced).


[ROCm/clr commit: ce664e2418]
2017-02-17 18:06:47 +03:00
pensun b411549397 Add pseudo code example for hip_bugs.md
Change-Id: Ia2af8e6165faeb3fbb81428e20d4dc5b19b2fa9e


[ROCm/clr commit: f2bfc8a405]
2017-02-08 16:20:01 -06:00