7f62529b1f
Update hip_hcc packaging script
...
Change-Id: I2dc96545c472942bcf2bc8a2e88735f3ba26d1e1
2017-02-09 20:28:28 +05:30
6659eb8d16
Disable failing directed tests
...
- hipTestDeviceSymbol
- hipTestConstant
- hipTestMallocKernel
Change-Id: Ibfe9fc0b8a59882f1de64b42e18777a7bd56ee97
2017-02-09 14:48:22 +05:30
71363810dd
Fix arch specific hcc extra libs env var
...
Change-Id: I7429da2f1cb98750d6a9601e7e5bde844a098487
2017-02-09 14:38:39 +05:30
c6c90f6f5a
added architecture specific macros
...
1. Added __HIP_ARCH_GFXNUM__
2. Usage, -D__HIP_ARCH_GFX803__=1
Change-Id: I68b3a85d62cfab3a45d2b7a70cb3518ab2565236
2017-02-08 19:45:32 -06:00
f2bfc8a405
Add pseudo code example for hip_bugs.md
...
Change-Id: Ia2af8e6165faeb3fbb81428e20d4dc5b19b2fa9e
2017-02-08 16:20:01 -06:00
400d0d4f78
fixed hipcc for new compiler flags
...
Change-Id: I49ec059be20ff26b7482c84d91ab7a43826c6a8d
2017-02-08 14:06:01 -06:00
26b5e57cfd
include arch specific ir on fallback path
...
Change-Id: Ib04996aae2c21eb73ef2a9f6305915e0caccd704
2017-02-08 12:19:06 -06:00
60ec83c683
Fixed Hawaii link issues
...
1. Split hip_ir.ll to hip_hc.ll and hip_hc_gfx803.ll
a. hip_hc.ll contains arch generic ir implementations
b. hip_hc_gfx803.ll contains gfx803 (fiji, polaris) specific ir
2. HIPCC can now parse --amdgpu-target=*.
a. Usage: hipcc --amdgpu-target=gfx803 --amdgpu-target=gfx701
b. TODO: Convert to --amdgpu-target=gfx803,gfx701
3. With LLC in HCC able to generate native f16 isa, removed inline half asm math ops
4. Fixed threadfence and threadfence_block to use functions in rocdl
Change-Id: Ic9a9e3e04139b0d75d2c2a263c030ca77adc1019
2017-02-08 12:04:05 -06:00
cc8a7f3d3e
[HIPIFY] Readme.md update.
2017-02-08 19:50:05 +03:00
b3098091fd
[HIPIFY] Readme.md update.
...
+ Launching example.
+ Delimiter "--" is strongly recommended.
+ "-x cuda" option is mentioned as well.
2017-02-08 19:43:32 +03:00
be6d01ebc3
Fixed HIP for C runtime
...
1. fixed constant memory test
2. added runtime gcc/g++ test
3. added fix for runtime with gcc/g++
Change-Id: Ie14dad6633411b188bdeea044e140b6d5beabe16
2017-02-07 13:15:36 -06:00
6d8007e28c
fixed vector types for c
...
Change-Id: I2330e976060f9a038929cd51be07ae2ee98e81ce
2017-02-07 11:09:54 -06:00
73b56e690f
Command scripts for latency measurements
...
Change-Id: I8c28765a09fb0358447367939de524b12699a317
2017-02-07 15:03:46 +05:30
0bef861f1a
Disable broken test: hipC
...
Change-Id: I061aa125bbdc9f14bc870266ab0735593c861903
2017-02-06 13:00:50 +05:30
f009f3533d
changed __global__ attribute
...
1. Moved around tests and added them to HIT
Change-Id: I5d75280c42a5af852670ebabc7305ee56721ec7b
2017-02-03 10:53:36 -06:00
0d4e6ae60a
fixed symbol memcpy issue
...
Change-Id: I89d7401be51d194bcbf771020ba66e3d3b6a18f8
2017-02-01 17:54:59 -06:00
a5d017e406
removed host math functions from math_functions.h
...
Change-Id: I90d8784e2d6b58c6fade9f0fa12c0db3ee417d3e
2017-01-27 17:38:43 -06:00
eee520def9
changed device code tests to work not to work as one
...
Change-Id: I0eec1eab19dda3b703bc3a0d778a6bbb2802a412
2017-01-27 09:20:14 -06:00
a8c51b822b
fixed arch compiler flag
...
Change-Id: I19f7a0ea513d6b8059f0c10cd0e7a5ead510e246
2017-01-27 08:51:48 -06:00
537dc7597b
fixed threadfence ir
...
Change-Id: Ia3afb54bdb50864e678d849608d72a3c321edba1
2017-01-27 08:42:26 -06:00
33d89d06aa
fixed kernel only compilation for module api
...
Change-Id: I567992fa9b87125318edba41fd82d2f7bc5504a1
2017-01-27 08:41:42 -06:00
125983eed9
hipMallocArray fixes for NV path
...
Change-Id: I1ca43e6bc0cd405998888005c20dfb1ea57003d5
2017-01-27 14:32:08 +05:30
f18efd5d15
more fix on hipmallocarray on NV path
...
Change-Id: I890a36cab10c101f4a112bc4567f765b318d486c
2017-01-26 12:30:52 -06:00
42f22162e0
fix missing semicolon on NV path
...
Change-Id: I3cfecb7bd534578a1f5a07ca9397092dcf01db07
2017-01-26 11:28:15 -06:00
1a24178c78
Add HIP_FAIL_SOC.
...
Fail sub-optimal-copies rather than perform them slowly.
SOC occur on async copy of unpinned memory, or P2P copy between GPUs
that are not peers.
2017-01-25 21:53:17 -06:00
2f7a8ec39c
Read HCC_OPT_FLUSH and optimize dispatch accordingly.
...
If HCC is in this mode, we can use less aggressive flushes in some
cases.
2017-01-25 21:50:52 -06:00
33a3ebad27
added device functions header to hip_runtime.h
...
Change-Id: I635931e1fbe4b7f0f64f3a126c0f1badcd6d234b
2017-01-25 08:14:30 -06:00
a8fcbb2584
Add more hip_bug.md entry, regarding hang after hipLaunchKernel
...
Change-Id: I5800cb627179ec0e913cd36d332fb8c2994ab71e
2017-01-24 22:43:25 -06:00
24d9827688
Initial commit on hip_bugs markdown doc
...
Change-Id: I5a6915337b8664cfed9eaee9443c6e4406348574
2017-01-24 22:30:36 -06:00
73ef364c74
Add debug tip to docs
2017-01-23 22:34:41 -06:00
27447f10c2
Show dynamic shared mem usage not static.
2017-01-23 22:34:41 -06:00
bc809460f5
Move core env var processing to env.cpp
2017-01-23 22:34:41 -06:00
4de3df746c
Add debug tips to docs
2017-01-23 22:34:41 -06:00
fe24996326
Add debug tips to docs
2017-01-23 22:34:41 -06:00
d19c4767b7
Log error with ihipLogError. Cleans up CXL trace display.
2017-01-23 22:34:41 -06:00
df74158d1c
Add HIP_IGNORE_HCC_VERSION.
...
Ignores strict checking of HCC and HIP version.
Can be useful when developing new HCC code.
2017-01-23 22:34:41 -06:00
9952117d64
added ir code sad u8
...
Change-Id: Ie0d454b3bb9a6c9a028c091ad3aa969719b02cc9
2017-01-20 17:21:51 -06:00
97315e8748
added driver_types.h and texture_types.h header files to hip
...
Change-Id: Ic3b2403f07d6767dadf83d6c278fd14e87f6acdb
2017-01-20 17:09:52 -06:00
5b2d4c0e60
fixed hipArray issues
...
1. Fixed build issues produced from previous commit
2. Create new header files to manage data structures better
Change-Id: I704d82c196c1858ed7617d76e40612eb507d2aa0
2017-01-20 16:54:48 -06:00
5f10a69ef7
changes device functions documentation according to the supported apis
...
Change-Id: I47ac6bbde11d54d8265e0d27ec8cd5da4d03eb8e
2017-01-20 14:19:09 -06:00
a7fa600176
added nvcc backend for hipArrays
...
1. Added hip_texture.h to hip_runtime_api.h as cuda does declare array runtime apis inside cuda_runtime_api.h
2. Added nvcc backend for hipArray runtime apis
3. Didn't test on nvidia platform (should work)
Change-Id: I1a14aef41840e4f55e5535132e3443a918b55967
2017-01-20 14:11:45 -06:00
fd2e6ac2f0
added more test coverage for vector data types
...
Change-Id: I9f57a8b597bd2ee4b265eadfd0859531497a6ada
2017-01-20 13:52:02 -06:00
02190736e3
fixed compilation issues for vector types and math functions
...
1. Added math_functions.h to hip_runtime.h
2. Changed operator overloading classifier static to static inline
3. Added vector types test for gpu
4. Seperated __host__ and __device__ for math functions in headers
Change-Id: I499862fad5d7b10da686da9011d7ecefe523f8e2
2017-01-20 09:49:11 -06:00
db3f4889ca
Add HIP_SYNC_HOST_ALLOC, HipReadEnv
2017-01-19 23:55:24 -06:00
6de88d4293
Change ihipDeviceSetState,ihipDevice* so it doesn't log error
...
Cleans up debug trace.
2017-01-19 23:55:24 -06:00
fe5f45caaf
added operator overloading for complex data types
...
Change-Id: Id96d5d000651914169f04497af6ff78ad96d846a
2017-01-19 15:15:25 -06:00
ca1cef4e06
Doc update - describe debug techniques
...
Also tweak sample to remove unneeded HIP_KERNEL_NAME.
Comment update
2017-01-19 12:40:45 -06:00
2ffc9f4e22
Fix debug display for Module launch kernels
2017-01-19 12:40:45 -06:00
aa3f278475
Fixed hipcommander default execution for HCSWAP-106
...
Change-Id: I9fbd10dfaeeb4928b2ec23ceed131b5200a658f9
2017-01-19 15:04:32 +05:30
706a032a29
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
Maneesh Gupta
Aditya Atluri
pensun
Evgeny Mankov
Rahul Garg
Ben Sander