Граф коммитов

132 Коммитов

Автор SHA1 Сообщение Дата
Evgeny Mankov ffcf5d32a0 [HIPIFY] CUDA RT Textures support 2017-07-27 18:39:40 +03:00
Maneesh Gupta 526fcb1223 Merge pull request #116 from bensander/enable_coh_host
Make host memory allocations coherent by default.
2017-07-27 10:45:32 +05:30
Ben Sander 8b8e97ff28 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.
2017-07-26 19:20:34 -05:00
Evgeny Mankov 368aebc4bc [HIPIFY] CUDA Stream Callback support 2017-07-26 19:29:50 +03:00
Evgeny Mankov 85e6593a1b [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
2017-07-26 09:38:03 +05:30
Maneesh Gupta 91f82ce541 Update toc in markdown documentation
Change-Id: I6da7053672b306442f3640fff3471efe25593870
2017-06-28 11:32:25 +05:30
sunway513 1c3a8b2564 Fix docs for HIP_TRACE_API bit masks. 2017-06-26 17:54:30 -05:00
Ben Sander dff260de7e Add docs for launch_bounds. 2017-06-23 18:05:30 -05:00
Evgeny Mankov b4a39664f0 [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.
2017-06-22 21:53:32 +03:00
Evgeny Mankov 0208fa4e70 [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.
2017-06-14 19:55:55 +03:00
Evgeny Mankov f805bd0c1d [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.
2017-06-13 20:25:11 +03:00
Ben Sander 578d430bb3 Remove HIP_NUM_KERNELS_INFLIGHT. (redundant with HCC controls) 2017-05-24 01:03:28 -05:00
Evgeny Mankov 270f643c9c [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.
2017-05-19 17:22:14 +03:00
Ben Sander 704ba30b32 Doc update - split hip_debugging.md into separate file. 2017-05-16 19:04:25 -05:00
Ben Sander 0edab14139 Add HIP_TRACE_API=4. Only display memory allocation/free apis. 2017-05-16 19:04:25 -05:00
Ben Sander 687809104b Fix some typos, add additional guidance for -BSymbolic 2017-05-05 17:29:04 -05:00
Evgeny Mankov 70c94d7b83 [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.
2017-05-03 21:59:48 +03:00
Evgeny Mankov 3c1dd246d6 [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.
2017-04-21 21:46:30 +03:00
Ben Sander 4f363df159 Update bugs - Add CreateKernel, new signature for static kerns. 2017-04-16 14:22:48 -05:00
Ben Sander 310c130fc6 Doc update for Serialization.
Describe workaround for partial specialization
2017-04-10 19:45:18 -05:00
Maneesh Gupta 16215ea9b2 Updated table of contents in markdown documentation
Change-Id: I7347a06f57f9927ca3fcc5590a6c8200bc1bb1f5
2017-04-07 15:38:56 +05:30
Ben Sander 00bf446d53 Update bug workarounds to reflect tool improvements. 2017-04-05 21:59:32 -05:00
Ben Sander aaadc60264 Doc cleanup & add bug descript for restrict specifier issue 2017-04-05 19:40:00 -05:00
Ben Sander b728637692 Add bug descrip for "no matching constructor" 2017-04-05 17:43:20 -05:00
Sun, Peng a98802f72c hip_debug.md update from Alex, regarding __device__ function restrictions
Change-Id: I5e54fd97fc632d4283f76282e3935396a1aad235
2017-04-05 16:23:27 -05:00
Sun, Peng 15de25b6d2 Move current GGL limitations to hip_bugs.md
Change-Id: I77d0eae0a67eccef7dd2bea0f402736642c96554
2017-04-01 08:21:06 -05:00
Sun, Peng 8ca0d37a67 update hip_faq.md on using GGL as default
Change-Id: I6ce1112eedeac3b377fe55ad8445f3c465c2eed4
2017-03-30 15:03:09 -05:00
Sun, Peng 329e2182d6 revert workaround for square sample and update doc on GGL
Change-Id: I731c68ca4111e7dc2e45bef51c4cad2c23fc81f8
2017-03-21 10:26:09 -05:00
Sun, Peng 384a350f40 Add link to GGL document in hip_faq.md
Change-Id: I9f7f0200a06976d580be334c21640c816f812ebb
2017-03-20 15:50:10 -05:00
Sun, Peng be7466ff67 Add document for switching to GGL in hip_faq.md
Change-Id: I83d9fd3e76d21ab572949c3a446ac3898acb3ded
2017-03-20 15:44:28 -05:00
Evgeny Mankov 76820409a8 [HIP] [DOC] Update hip_porting_driver_api.md
+ Fix typos, formatting, update CUDA Driver API support.
2017-03-16 14:39:28 +03:00
Siu Chi Chan a96821871f replace code names with gfx names
Change-Id: I5e0b96a0b474b16cfa92077a30a5b80b7230254b
2017-03-15 12:26:13 -04:00
pensun 37ed319a20 update porting guide for updated __HIP_DEVICE_COMPILE__
Change-Id: I0f025d354f76e2d728231bf112a77e8c8fcacc8c
2017-03-10 10:01:12 -06:00
pensun 7290cb07ec fix typo in hip_porting_guide
Change-Id: I42553d9a4de2901dfdd57384b52a04e8fb22edde
2017-03-08 23:37:50 -06:00
Evgeny Mankov aa2fc24482 [HIP] [DOC] Update CUDA_Runtime_API_functions_supported_by_HIP
+ update all Cuda 7.5 RT API enum values.
2017-03-03 22:05:23 +03:00
pensun ac4b7e3f91 update hip_porting_guide regarding platform depended macros
Change-Id: I3029c6ae6cb280500bba294925ed6e9dc9dcc94d
2017-02-28 07:33:01 -06:00
Evgeny Mankov bd9b674d3d [HIP] [DOC] Update CUDA_Runtime_API_functions_supported_by_HIP
cudaDeviceGetPCIBusId -> hipDeviceGetPCIBusId
2017-02-20 21:21:47 +03:00
Evgeny Mankov 5c11789358 [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).
2017-02-20 18:32:54 +03:00
Evgeny Mankov ee157678b9 [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.
2017-02-17 18:09:08 +03:00
Evgeny Mankov a35d4b75c5 [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).
2017-02-17 18:06:47 +03:00
pensun 79978182f9 Add pseudo code example for hip_bugs.md
Change-Id: Ia2af8e6165faeb3fbb81428e20d4dc5b19b2fa9e
2017-02-08 16:20:01 -06:00
pensun 95677edabb Add more hip_bug.md entry, regarding hang after hipLaunchKernel
Change-Id: I5800cb627179ec0e913cd36d332fb8c2994ab71e
2017-01-24 22:43:25 -06:00
pensun f3da91de4e Initial commit on hip_bugs markdown doc
Change-Id: I5a6915337b8664cfed9eaee9443c6e4406348574
2017-01-24 22:30:36 -06:00
Ben Sander 9dff0782a4 Add debug tip to docs 2017-01-23 22:34:41 -06:00
Ben Sander 85d41dcd05 Add debug tips to docs 2017-01-23 22:34:41 -06:00
Aditya Atluri 7765469987 changes device functions documentation according to the supported apis
Change-Id: I47ac6bbde11d54d8265e0d27ec8cd5da4d03eb8e
2017-01-20 14:19:09 -06:00
Ben Sander 1f5d16afe7 Doc update - describe debug techniques
Also tweak sample to remove unneeded HIP_KERNEL_NAME.
Comment update
2017-01-19 12:40:45 -06:00
Aditya Atluri 56d73aaee7 moved half device function declarations to top of the file
1. Moved half device functions around so that script can catch the signatures
2. Generated docs for half precision apis

Change-Id: Iee27658e3a639fdb02af135e71841dc6427f15e2
2017-01-18 15:06:18 -06:00
Aditya Atluri db99ac798b more clarification about using device_md_gen.py
Change-Id: I3e207b65683f34d62be3454444ffb32f8814c0aa
2017-01-18 14:49:41 -06:00
Aditya Atluri 91ae5d6bd7 Added script for generating math api docs
1. Commented out unsupported device math functions
2. Moved function signatures to the top of implementation snippets
3. Added script to generate markdown documentation for device math apis
4. Added the generated file from the script which should be present everytime

Change-Id: Ic579dd8b8fdffa6e1b4d4f5f3fd8a803f4dcaac7
2017-01-18 14:40:50 -06:00