Alex Voicu
a45ff026ea
Merge remote-tracking branch 'origin/master' into feature_support_globals_for_module_api
...
[ROCm/hip commit: 0545a49381 ]
2017-10-09 13:28:13 +01:00
Alex Voicu
fbcd3b0aa6
This adds cursory support for globals to the HIP module loading API. The
...
style is purposefully alien so as to signal that HIP experts should turn
it into HIP worthy code as soon as possible.
[ROCm/hip commit: ffffe052b6 ]
2017-10-09 13:27:11 +01:00
Maneesh Gupta
710d095874
Merge pull request #194 from bensander/fix_genco_math_path
...
Fix math ordering for --genco mode.
[ROCm/hip commit: c1803c1951 ]
2017-10-03 16:17:34 +05:30
Ben Sander
d1be93bbd9
Fix math ordering for --genco mode.
...
[ROCm/hip commit: 68c2146dc3 ]
2017-10-02 21:52:16 +00:00
Rahul Garg
be4b7099bb
Fixed review comment
...
[ROCm/hip commit: b8aae66424 ]
2017-10-02 17:29:08 +05:30
Rahul Garg
28b92618b7
Fixed review comments
...
[ROCm/hip commit: 19d574d939 ]
2017-10-02 10:57:25 +05:30
Rahul Garg
71552c63ac
Fixed build issue
...
[ROCm/hip commit: f62254a8d8 ]
2017-10-02 10:40:01 +05:30
Rahul Garg
69508f52cc
Fix texture support on HIP/NVCC path
...
[ROCm/hip commit: 470224cf25 ]
2017-10-02 10:40:01 +05:30
Siu Chi Chan
6884635ae0
ensure the condition is evaluated before applying the negation operator
...
[ROCm/hip commit: 83d9e889a9 ]
2017-09-20 01:38:28 -04:00
Maneesh Gupta
ed0f94c051
Merge pull request #155 from wsttiger/master
...
Modify hip headers such that they are more compatible with strict C compiler
[ROCm/hip commit: 8c92d28ff3 ]
2017-09-15 10:49:55 +05:30
Maneesh Gupta
569ec04d0c
Fix typo in nvcc_detail/hip_runtime_api.h
...
[ROCm/hip commit: c3c94dcd8d ]
2017-09-14 16:19:57 +05:30
Maneesh Gupta
0ba15f6faf
Merge pull request #175 from gargrahul/assert_support
...
Device side assert support
[ROCm/hip commit: c7e5fd24ac ]
2017-09-14 16:08:00 +05:30
sriharikarnam
ba8fd5cbee
Add hipDevice[Get/Set]SharedMemConfig API on nvcc details
...
[ROCm/hip commit: 3e69b2ed5a ]
2017-09-14 16:03:19 +05:30
Rahul Garg
d1425f3cf5
Device side assert support
...
[ROCm/hip commit: 40ff42e555 ]
2017-09-07 20:45:27 +05:30
Ben Sander
a497059d78
Update docs.
...
- Review unsupported comments and refresh.
- Review experimental tag in API.
[ROCm/hip commit: 1a9e588932 ]
2017-08-28 15:44:38 -05:00
wsttiger
09fb0fce42
Modify header such that it's compatible with strict C compiler
...
[ROCm/hip commit: b6a3d8c946 ]
2017-08-15 13:23:09 -05:00
wsttiger
db3ebbcbae
Add missing CUDA tags
...
[ROCm/hip commit: 512214e930 ]
2017-08-15 13:22:20 -05:00
Siu Chi Chan
21c1d69e77
implement __threadfence_system
...
[ROCm/hip commit: 96e79f97e2 ]
2017-08-02 08:50:18 +00:00
Ben Sander
9ec4b0b66f
Merge pull request #100 from weixingzhang/texture
...
HIP Texture Support
[ROCm/hip commit: 4f93b99f23 ]
2017-07-26 19:28:15 -05:00
Maneesh Gupta
9ce8abb1ed
Renable frexp(f) device math function
...
Change-Id: I53c022b8ddf38cd17ddb42eba457b9020db66395
[ROCm/hip commit: 7a446dcbc5 ]
2017-07-20 14:41:30 +05:30
Weixing Zhang
65bec11393
HIP Texture Support
...
[ROCm/hip commit: e671cec367 ]
2017-07-17 15:16:12 -04:00
Wen-Heng (Jack) Chung
f28a1365f8
Remove explicit address spaces declarations
...
[ROCm/hip commit: 30ee797dd4 ]
2017-07-07 12:46:29 -05:00
Ben Sander
042ed2c38f
Add hipdbPrintMem - wrapper for hcc memory tracker.
...
[ROCm/hip commit: 0459f3db72 ]
2017-07-03 15:05:30 -05:00
Rahul Garg
9498754cf6
Fixed build error in hipDeviceGetByPCIBusId
...
Change-Id: I33be362910c4c5dca7435fb9c41f427b54f0e9a7
[ROCm/hip commit: 34fcaa23bb ]
2017-07-01 07:56:30 +05:30
Ben Sander
15527645f1
Refactor hip_hcc.
...
Don't require setting __HIP_PLATFORM_HCC__ ; Instead check if compiler is HCC.
The functions here use HCC-specific functionality so only work with HCC.
ANd they work regardless of the __HIP_PLATFORM_HCC__ setting so don't
require that.
Also remove the "hcc_detail" extra hierarchy level for hip_hcc.h as
it is not necessary. Remove hcc_detail/hip_hcc.h.
[ROCm/hip commit: 9c229f7530 ]
2017-06-30 08:26:15 -05:00
Rahul Garg
83f3ed16de
Fixed hipDeviceGetByPCIBusId
...
Change-Id: Ia36bb9425671ef7659541c9aeedae4098456a31b
[ROCm/hip commit: 65cb024b61 ]
2017-06-30 10:11:41 +05:30
Rahul Garg
9e55cdfa90
Fixed hipDeviceGetPCIBusId for HIP/NVCC
...
Change-Id: I662efa148257a710f09002850b41d57bef00dff3
[ROCm/hip commit: d6db525f51 ]
2017-06-29 00:13:02 +05:30
Rahul Garg
ff48608355
Fixed hipDeviceGetPCIBusId for HIP/HCC
...
Change-Id: I3688fa2476e1baada2d3c5fc3735cec3f15a1e21
[ROCm/hip commit: f4ea3b76c8 ]
2017-06-28 23:48:27 +05:30
Sun, Peng
5a6d4a30c4
Remove some warning debug info and add weak attribute back to GGL __global__ define
...
Change-Id: I2021b107dda697b1262d44fa1506465e94a3916b
[ROCm/hip commit: 1e1654c225 ]
2017-06-27 14:15:16 -05:00
Aditya Atluri
c96e9341f7
fixed default args for symbol memcpy apis
...
Change-Id: Ie0b63f8b9c5535eb3946bd6af3f30fe71a015244
[ROCm/hip commit: 522e059a79 ]
2017-06-23 19:05:44 -05:00
Ben Sander
ed1f242c60
Clean up old USE_* and RELEASE.md notes.
...
[ROCm/hip commit: 7912e61502 ]
2017-06-23 18:05:30 -05:00
Rahul Garg
1678be3d74
Added device side abort function in HIP/NVCC
...
Change-Id: I6ae35a72a8b9c34852619f02da1a046c8d3b2ed3
[ROCm/hip commit: e6e4fe613c ]
2017-06-20 09:38:56 +05:30
Rahul Garg
3cb1061f65
Abort device function in HIP/HCC, need new HCC
...
Change-Id: I4195ab75e9b7b48c8b8128d6925ddc0fa5e9e009
[ROCm/hip commit: 3c73229916 ]
2017-06-18 12:31:31 +05:30
Aditya Atluri
f5dff37b8b
removed bad copy constructor
...
Change-Id: I661991d9d43941a61848b0b8e9879c0bfa811b40
[ROCm/hip commit: 64bb8d154a ]
2017-06-16 09:02:26 -05:00
Sun, Peng
7e9cfda45e
Additional GGL make_kernel_functor_* macros, contributed by Alex
...
Change-Id: I01aabb7d2b5418fcefb1bbf78eb5d1888dbc5c96
[ROCm/hip commit: fd36303c24 ]
2017-06-14 11:10:52 -05:00
Sun, Peng
47921e39d2
Fix error related to undefined reference of __get_dynamicgroupbaseptr().
...
Change-Id: I14951e1725e35dd5f5e53805f81cdb58661f59f2
[ROCm/hip commit: 43df5ba660 ]
2017-06-08 19:24:32 -05:00
Sun, Peng
8b14507650
Add clang version guard so the hip_fp16.h header won't be picked up by gcc
...
Change-Id: Ia21335a455bc93210901b44bc8c76a7f4a385b55
[ROCm/hip commit: 06816fb68b ]
2017-06-08 19:24:32 -05:00
Sun, Peng
3f9b16c397
Improve HIP kernel names, attributes and codegen, contributed by Alex Voicu
...
Change-Id: I2cafbdc5a98e26c7f4fad84739c915e7dc09993c
[ROCm/hip commit: a9808961bd ]
2017-06-05 11:39:00 -05:00
Ben Sander
445042f916
Fix HIP_SYNC_NULL_STREAM=0 mode.
...
- Fix null-stream sync
- hipStreamDestroy of null stream returns hipErrorInvalidResourceHandle
- Update documentation.
- Add tests for null stream sync, hipEventElapsedTime.
- Rename internal enum hipEventStatusRecorded to hipEventStatusComplete
- refactor hipStreamWaitEvent to streamline control-flow
[ROCm/hip commit: 39c18e5e5f ]
2017-06-05 08:50:22 -05:00
Aditya Atluri
47ec040140
added half data type and vector destructors
...
1. Added half data types to hip_fp16.h
2. Added destructor to vector data types
Change-Id: Id5ae76a663bb90a4bde2839ec79c58fbaee5072f
[ROCm/hip commit: cb7c4c423c ]
2017-06-02 11:19:33 -05:00
Evgeny Mankov
7a3befc555
[HIP] [HIPIFY] CUDA Driver API 8.0.44 JIT options support.
...
[ROCm/hip commit: 6e99e388ea ]
2017-05-31 18:55:29 +03:00
Ben Sander
b3e01ed74f
Add event controls for release fences.
...
Env var : HIP_EVENT_SYS_RELEASE
Event allocation flags : hipEventReleaseToDevice, hipEventReleaseToSystem
(remove hipEventDisableSystemRelease)
Update test for new functionality.
[ROCm/hip commit: ec7102f461 ]
2017-05-27 16:02:34 -05:00
Ben Sander
c88190d698
Updates so hip compiles on CUDA.
...
[ROCm/hip commit: be8d0ba644 ]
2017-05-27 15:55:07 -05:00
Ben Sander
5b9ce41633
Add hipHostMallocCoherent, hipHostMallocNonCoherent
...
Provide per-allocation control over coherent/non-coherent mem.
These overrid the default HIP_COHERENT_HOST_ALLOC setting.
[ROCm/hip commit: 75f691ec2f ]
2017-05-24 00:48:10 -05:00
pensun
b19e862dc4
fix GGL helper header file, reorder for C++17
...
Change-Id: I3d9ddfe670bf7e3e8e7bd85e52cc61f48c19c213
[ROCm/hip commit: 6d0f58b939 ]
2017-05-22 08:52:43 -05:00
Evgeny Mankov
042de3e175
[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/hip commit: 270f643c9c ]
2017-05-19 17:22:14 +03:00
Aditya Atluri
721cb0f7db
fixed vector type issues by reverting to old code, changed __half2 to map to vector types in llvm
...
Change-Id: I7317408c25e8c1a0c02a346042c9137e160c8bbd
[ROCm/hip commit: bdc08fcf10 ]
2017-05-18 10:51:07 -05:00
Aditya Atluri
4dbebe0409
changed vector types to make sure it generate proper llvm vector types
...
Change-Id: I6c4616dae137dc4eac35e5827dc5b7f3251e0247
[ROCm/hip commit: 9dceccf136 ]
2017-05-16 21:35:40 -05:00
Ben Sander
a55ce5bee4
Add initial HIP_SYNC_NULL_STREAM=0 mode.
...
This eliminates host-synchronization for null stream. Instead, the
null-stream uses GPU-side events to wait for other streams.
Default is OFF pending additional testing.
Add enhanced null-stream test.
Also refine HIP_TRACE_API.
[ROCm/hip commit: 27877f8854 ]
2017-05-16 19:04:25 -05:00
Rahul Garg
c6a2d65d5e
Added hipMallocPitch on HIP/NVCC path
...
Change-Id: Ie3ba7d3f95acac23805efa919531043b350a3f21
[ROCm/hip commit: 1223612331 ]
2017-05-16 07:15:13 +05:30