Commit Graph

80 Commits

Author SHA1 Message Date
Sandeep Kumar e41aa1483a Add more apps to 2_Cookbook
Change-Id: Iafe462df9726a32f450bd240a2de3eaa73a10057


[ROCm/clr commit: d025ed980b]
2016-10-19 12:58:16 -04:00
Maneesh Gupta dbfd285aae samples: Updated copyright header
Change-Id: I821f514ced5e34d492cb167b65d7273e26ed7b84


[ROCm/clr commit: 945a09c241]
2016-10-15 23:05:04 +05:30
Ben Sander 5fb10e5742 Refactor module API test.
- Add PASSED/FAIL indication.
- Set args using struct rather than void* array.

Change-Id: Ic924f88c49cc46979b12b7fef8650081e3b5f58c


[ROCm/clr commit: 4668a08783]
2016-10-14 23:19:25 -05:00
Aditya Atluri 0a5761a1de indent correction for square.cu
Change-Id: I2ca008e260b920ac3a503ad2a4bb28cd32300c98


[ROCm/clr commit: d8c0954e13]
2016-10-12 19:26:59 -05:00
Aditya Atluri 18a7a5ce5d added copyright to module sample kernel file
Change-Id: If57e0761df63c902e1677084ff85106ec49df5de


[ROCm/clr commit: cb734a5b1b]
2016-10-12 19:23:48 -05:00
Maneesh Gupta 99d47a0850 clang-hipify -> hipify-clang in documentation
Change-Id: I86ebc8112477db0d3e09f240beb3f9222d909ee6


[ROCm/clr commit: eb1fce0d77]
2016-10-05 23:07:14 +05:30
Maneesh Gupta 19b9ab32b2 samples: Updated to use new hip include path
Change-Id: I53a1385a17f13a997ea21d14315f15a3ad851dab


[ROCm/clr commit: ead394ec09]
2016-10-04 22:21:10 +05:30
Ben Sander 2606f22c7f small typo fix
Change-Id: I01906b330be8e6ec149bcdfe82def73e15931c89


[ROCm/clr commit: e413869271]
2016-10-02 05:57:02 -05:00
sandeep kumar ae352f60d8 Add 2_Cookbook
Change-Id: I10bbbd4bcb80a5900fe6af466c8f4c94ea5efe9a


[ROCm/clr commit: 67c7f0ab5a]
2016-09-30 12:52:06 +05:30
Ben Sander d10d1425f3 Small tool, doc, sample enhancements.
- Expand message when HIP version mismatch detected.
- Doc touchup.
- change sorting of hipBusBandwidth so byte results shown at top.
-

Change-Id: Ifb4e44a5fdfb65d59c4994b11e5f13385705f7e0


[ROCm/clr commit: 061bcc6a5c]
2016-09-26 16:36:01 -05:00
Ben Sander 681f560fe1 Sample improvements.
- Enable -O3 for hipDispatchLatency.
- Use nearly-null kernel to prevent it from being optimized away.
- Formatting for hipDispatchLatency.
- Formatting for hipInfo.


[ROCm/clr commit: e8beacbfb1]
2016-09-22 13:05:47 -05:00
Aditya Atluri 891d5efd18 added vimrc for current project
1. Added vimrc config file for HIP
2. Corrected square sample indent

Change-Id: I3e1d92403571148fe6825db6ad63ad925ae69519


[ROCm/clr commit: 8faf2ed7e3]
2016-09-15 11:40:17 -05:00
Maneesh Gupta f963d347ff module_api/Makefile: Update as per newer hipgenisa.sh
Change-Id: I479c74eae00d7521434f2740ce5930e326ea05cf


[ROCm/clr commit: 66232eb610]
2016-09-06 17:47:10 +05:30
Maneesh Gupta de5701b678 module_api sample: Remove unnecessary platform checks
Change-Id: I1d531264d51ff952a3a68d554672b6d293e23379


[ROCm/clr commit: 40a392800a]
2016-09-04 21:25:14 +05:30
Rahul Garg d95642b85c Removed NVCC check for hipCtxXXX functions in module_api/runKernel.cpp
Change-Id: I2bdd4fadf41063ec60626f1850e16f8307ebe6b5


[ROCm/clr commit: bb5f15e199]
2016-09-04 20:37:29 +05:30
Maneesh Gupta cdfbacb907 module_api: HCC path no longer needs mangled kernel name
Change-Id: I4c1cb218bfdd05c9fba57276167e3e4205b93614


[ROCm/clr commit: 34a3766ae3]
2016-09-04 16:26:16 +05:30
Maneesh Gupta b3779207c3 module_api sample: no longer need EXTERN_C workaround
Change-Id: Ida087d832df8e1f3620b38f920ec2853aad641c8


[ROCm/clr commit: 257774f8f0]
2016-09-04 13:49:43 +05:30
Maneesh Gupta 7974137a91 module_api: workaround to use vcpy_kernel.cpp for NV path
Change-Id: Ib4868bf02c64070e846c19427c39289609909466


[ROCm/clr commit: fa85974c47]
2016-09-04 12:35:08 +05:30
pensun dd92a59939 For module_api sample, use vcpy_kernel.cu to generate ptx file for NV path.
Change-Id: Id0033678834288c4eaa56b12e7d447119be99deb


[ROCm/clr commit: 793dc2bce0]
2016-09-03 21:06:58 -05:00
Aditya Atluri d864a28183 corrected offline kernel compilation on hipcc path
1. hipgenisa.sh now adds int main(){} during kernel compilation. User does not have to put it there
2. Renamed vcpy_isa.cpp to vcpy_kernel.cpp
3. Removed vcpy_isa.cu as the kernel code should be common for both paths
4. Changed Makefile and runkernel.cpp to work with above changes

Change-Id: I9f8c84706b44bb500bc493a68e959762b55a0142


[ROCm/clr commit: 8f536d8580]
2016-09-02 13:17:17 -05:00
Ben Sander f3da27cd5a Fix double-lock of stream on hipModuleLaunchKernel
Change-Id: I4ca164971c25f4eb8fbcca11d6258367bb3d2ab4


[ROCm/clr commit: 0fdb5bf517]
2016-09-02 12:47:49 -05:00
Ben Sander f575ad7396 Fix av::copy in dialects to use capture-by-value
Change-Id: Ibce1488a1326f66b92b4d5b351230666b691ed31


[ROCm/clr commit: 43e9932196]
2016-09-02 09:46:59 -05:00
Ben Sander 61a5a53512 enable hc_am example in hcc_ddialects example
Change-Id: Iec2f9eb05f95cb025c157fee8fd284aab844d1a2


[ROCm/clr commit: 27b3706a72]
2016-09-02 09:46:59 -05:00
Aditya Atluri 8bbd449f9f Fixed offline kernel compilation
1. Removed vcpy_isa.ptx as it should be generated during make
2. Made argument padding specific to hcc path
3. Renamed --gencodeobject to --genco
4. Changed Makefile to work on both nvcc and hcc path

Change-Id: Ifd053d541085d9ce4fd37bc21b07674786c7163e


[ROCm/clr commit: f22fda1291]
2016-09-01 10:39:14 -05:00
Maneesh Gupta 11f6cc4c4a Fixed module_api/Makefile to set flags based on HIP_PLATFORM
Change-Id: I2fa9a556e0c4f25f4963ecef1d25eb922f9af1b9


[ROCm/clr commit: b7b78d3b86]
2016-09-01 15:11:12 +05:30
Maneesh Gupta 291db23ec2 module_api/Makefile: Use gencodeobject instead of genisa
Change-Id: I7e3523810f5603ad727b1fda7ff2d0dc53ec72d7


[ROCm/clr commit: 7c24b08284]
2016-09-01 12:10:31 +05:30
Aditya Atluri 3011696544 added sample for how-to-use pre-compiled kernels1. Corrected the exit output of kernel compilation by hipcc
2. Added sample which loads/run kernel binary during runtime?

Change-Id: I26ccaca1f844fee317592e26c9e654ce548b96a8


[ROCm/clr commit: 667ec7cbe2]
2016-08-31 13:56:07 -05:00
Maneesh Gupta 21b1245c9b Rename 2_Advanced to 7_Advanced
Change-Id: I51e5fa7f4c1dbf467f2d7182ec69d12d5fe548d0


[ROCm/clr commit: 7b8f091f0b]
2016-08-18 12:40:30 +05:30
Maneesh Gupta 07262c48ba Add simple hipblas saxpy sample
Change-Id: I67ae83e1e5397d5191a3c644aba068f06ff97830


[ROCm/clr commit: 7c03a0604a]
2016-08-12 13:50:22 +05:30
Maneesh Gupta c59f486109 hipDispatchLatency: reduce iterations to 5120
Change-Id: I94ae4993ff5058cf15f9487a5a528fc24c1ad5fa


[ROCm/clr commit: 3d4bbc4224]
2016-06-13 14:23:51 +05:30
Maneesh Gupta 5ecd546ea5 Fix bit_extract sample
Change-Id: I933f932bac26d9a9469d5d069973af166e11cbcd

[ROCm/clr commit: af65f415f0]
2016-05-20 01:06:08 -04:00
Maneesh Gupta 6dda3ebbfb Fix square.cu to use cudaError_t instead of hipError_t
Change-Id: If3314910d1c03122741d3e0a45e14a4412c473b3


[ROCm/clr commit: 349b92f2a8]
2016-05-12 10:13:07 +05:30
Maneesh Gupta bd3692dd12 hcc_dialects report PASSED when passed
[ROCm/clr commit: c2c54aa299]
2016-05-03 14:32:59 +05:30
Maneesh Gupta 3ce3e64493 bit_extract reports PASSED when passed
[ROCm/clr commit: ab671b729d]
2016-05-03 14:19:25 +05:30
Maneesh Gupta 0445c95661 Fix makefiles in samples
[ROCm/clr commit: 273f4b4cbe]
2016-04-18 10:15:35 +05:30
Maneesh Gupta 1293709fc0 Replace /opt/hcc -> /opt/rocm/hcc and /opt/hsa -> /opt/rocm/hsa
[ROCm/clr commit: cf4c3b0913]
2016-04-15 12:56:31 +05:30
Ben Sander 70c75c0eed Fix HIP_PATH, CHECK macro in samples.
[ROCm/clr commit: 830527bfdc]
2016-04-13 17:37:39 -05:00
Ben Sander b2237cb953 add hcc dialects sample
[ROCm/clr commit: 8736d77818]
2016-04-13 17:32:38 -05:00
Ben Sander 39cccf94ef fix peer query order
[ROCm/clr commit: a894ca3abb]
2016-04-11 07:58:59 -05:00
Ben Sander 025938b1de P2p checkpoint.
- set USE_PEER_TO_PEER=3 (requires HCC "am_memtracker_update_peers")
- when enabling peer, turn it on for previously allocated memory.
- hipDeviceCanAccessPeer is no longer self-ware (self does not qualify
  as a peer)
- device peerlist always includes self, so when we call allow_access
  we never remove self access.
- hipDeviceReset() removes old peer mappings.


[ROCm/clr commit: 9e7efd7c65]
2016-04-11 07:58:59 -05:00
Ben Sander 20d06df651 Remove stray debug msgs, hipInfo don't print self as peer.
[ROCm/clr commit: a4d97c3172]
2016-04-11 07:58:58 -05:00
Ben Sander eb7b1fa1db Use HIP_PATH if set else use relative ../...
[ROCm/clr commit: 034bf3d31c]
2016-04-11 07:58:58 -05:00
Ben Sander df576efeb4 Print peers in hipConfig.
Also include peer APIs in vim hilighting.


[ROCm/clr commit: 23dbffb207]
2016-04-11 07:58:58 -05:00
Maneesh Gupta c5f7a869a1 Remove deprecated KERNELBEGIN and KERNELEND from bit_extract sample
[ROCm/clr commit: 00be8a1300]
2016-04-04 14:47:02 +05:30
streamhsa 73e7a4a166 change makefile for samples
[ROCm/clr commit: a629d4975f]
2016-03-29 16:02:09 +08:00
Aditya Atluri 3becf113bd Logging dispatch latency through database util
[ROCm/clr commit: 867554c423]
2016-03-23 11:39:57 -05:00
Ben Sander f70dc3c245 Only include activity logger if CodeXL installed.
Fix hipHostMalloc in hipBusBandwidth.


[ROCm/clr commit: 004b4ada93]
2016-03-22 09:27:10 -05:00
Ben Sander 37a02661a6 hipHostRegister and hipHostMalloc refactor.
Note hipHostMalloc (not hipHostAlloc or hipMallocHost).
 -  the hipHost* is used for all HIP APIs dealing with Host memory.
    (including hipHostMalloc, hipHostFree, hipHostRegister,
hipHostUnregister, hipHostGetFlags, hipHostGetDevicePointer).
  - hipMallocHost is consistent with "hipMalloc" for allocating device
    memory.  Enumerations hipHostMalloc* also used as optional
    flags parm to hipHostMalloc.


[ROCm/clr commit: 2d0fade1f7]
2016-03-22 02:30:10 -05:00
Ben Sander 3305c49949 Merge branch 'privatestaging' of https://github.com/AMDComputeLibraries/HIP-privatestaging into privatestaging
Conflicts:
	src/hip_hcc.cpp


[ROCm/clr commit: 90ad8ddc5d]
2016-03-19 03:22:09 -05:00
Ben Sander d207f3bc26 Add beastperiteration and onesize for testing.
onesize allows running tests at one specific size.


[ROCm/clr commit: 5197cf250d]
2016-03-19 02:43:04 -05:00