Commit Graph

1592 Commits

Author SHA1 Message Date
Ben Sander 3da8e94cbf Tailor pointer info for src/dst before calling HCC copy routines.
HCC sometimes uses the srcPtrInfo or dstPtrInfo to determine the
pointer.  Make sure these use the actual pointer and not the base
of the allocation.
2017-04-24 22:30:54 -05:00
Ben Sander d120b2dd12 Add test for non-page-aligned mem copies. 2017-04-24 22:30:54 -05:00
Ben Sander b44a3eefd1 Add corrected test for offsets 2017-04-24 22:30:54 -05:00
Ben Sander 6b16f56f38 Refactor hipMemcpy test to share mem alloc for multiple copies. 2017-04-24 22:30:54 -05:00
Ben Sander 693e5abc1c Add negative testing for memory full condition. 2017-04-24 22:30:54 -05:00
Ben Sander dfacfbb641 Fix hip debug for case where copyAgent is null (host-to-host) 2017-04-24 22:30:54 -05:00
Ben Sander fb7eee01ff Fix hipMalloc to return error code if allocation fails. 2017-04-24 22:30:54 -05:00
Aditya Atluri 1f532b06f6 fixed build issues with hipPointerGetAttributes
Change-Id: I3f5fbc05bdaef720884ba949075928752a070377
2017-04-24 15:31:07 -05:00
Aditya Atluri 85c189c846 changed arguments for hipPointerGetAttributes
Change-Id: Ia7a7c4722c1f7d0a23f0e5cc3dd6dea6c01c1fd8
2017-04-24 15:24:16 -05:00
Maneesh Gupta c16e0fb088 Updated release notes
Change-Id: Ia98aff420ea9d488924dce8fe9168cec9da301ab
2017-04-24 08:48:35 +05:30
Evgeny Mankov f66780f39b [HIPIFY] [DOC] Readme.md update: Ubuntu 16.04 support 2017-04-22 01:01:31 +03:00
Evgeny Mankov 342c63d398 [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 f1f907cb51 Fix compilation error with nvcc (c++ nullptr) 2017-04-21 09:01:34 -05:00
Sun, Peng c224209200 add support of hipLaunchKernelGGL on NV path
Change-Id: I0aeafd80c2181873be385d985f1d8ed86a98d136
2017-04-19 11:00:25 -05:00
Sun, Peng ee299695a8 fix broken header in NV path
Change-Id: Ia3aff2a89d9ba49547f51ce03a3304dfab58ba25
2017-04-19 10:47:40 -05:00
James Edwards edfefc9aee Fix RPM HIP packages from specifying /opt
Change-Id: Iec3c3b81eef4c8888d425eefc80b12488a8d20a1
2017-04-19 12:35:42 +05:30
Maneesh Gupta 137c04c536 FindHIP: Apply remove_item on non-empty lists only
Change-Id: Ib7fcb992d7e1bb679d4d86676fe3d980ba204815
2017-04-18 10:21:20 +05:30
Ben Sander 710c83b73b Update bugs - Add CreateKernel, new signature for static kerns. 2017-04-16 14:22:48 -05:00
Maneesh Gupta e45ee8c37a FindHIP: Handle remove_item from empty lists
Change-Id: I6adf31b32edeae9e8454b1a2528064cf3985fca1
2017-04-13 14:41:11 +05:30
Maneesh Gupta b3b1ba1e5d Do not rebuild cmake cache by default
Change-Id: Ie21e99beaa3465b54b5a6a77439c455f34de98b3
2017-04-13 12:38:38 +05:30
Maneesh Gupta 6db8c7c69e dtests should ignore HIP_PATH env var
Change-Id: I27b1cdab6e6b799987dad3ce97b56c764b1b8867
2017-04-13 12:12:04 +05:30
Maneesh Gupta 0d4f1c2d0c Add hip-config.cmake to hip_hcc package
Due to the way hip packages are generated, for the purpose of
packaging hip-targets*.cmake are not generated at build time.
However hip-config*.cmake are generated at build time.
This will be fixed in future.

Change-Id: I5d79bc58a4f7a324ae06457130d8372ffe403830
2017-04-13 10:34:33 +05:30
Ben Sander 8bd34535b4 Add integer abs (initial implementation, can be optimized with OCML)
Change-Id: I1f568c8c0e2333af1fda4c313dc48ea0c5b6ab00
2017-04-11 01:16:28 +00:00
Ben Sander 29af40fa76 Doc update for Serialization.
Describe workaround for partial specialization
2017-04-10 19:45:18 -05:00
Sun, Peng 3c04722d10 Fix ifndef guard in hip_fp16.h
Change-Id: I0215556e7aa98a74e8a984e4de3fb6e8cafdfb24
2017-04-10 11:17:05 -05:00
Sun, Peng bfa61eac2c add math.h to cover sqrtf function
Change-Id: Ia37752710cea4ca77e0a4e61f8e69a0355d9488d
2017-04-10 08:53:12 -05:00
Sun, Peng 9884f2e83f Update the define of __global__ for GGL
Change-Id: I563bb2a132403bcbe9e9f279b55406cf0255af7d
2017-04-07 16:39:33 -05:00
Sun, Peng 19987ede22 Add more operator overloading for float2 type, contributed by Aditya
Change-Id: If1ab7fb24d64bb5304142aed0951c9bd5ad47d20
2017-04-07 14:17:41 -05:00
Sun, Peng f699e02715 update GGL to log launched kernel information
Change-Id: Ied0aa6055673c687071b4a579aecd17f0f3f09ce
2017-04-07 14:06:31 -05:00
Maneesh Gupta cfd4620f36 Updated table of contents in markdown documentation
Change-Id: I7347a06f57f9927ca3fcc5590a6c8200bc1bb1f5
2017-04-07 15:38:56 +05:30
Maneesh Gupta cbb7f12b1d Fix build issues with bit_extract sample
Change-Id: I628b3c83a16f7adf0ab8ca60aecde8c073c34fd9
2017-04-07 15:24:10 +05:30
Maneesh Gupta 6877554f5e Fix build issues in hipCommander sample
- Remove -stdlib=libstdc++ from Makefile
- Removed deleted HIP header file fom includes

Change-Id: Ia189396bee19fc52b679259df56c6c6e2bafb6fe
2017-04-07 14:54:03 +05:30
Ben Sander e9eaadd135 Finish adding start/stop event support to hipHccModuleLaunchKernel.
Change interface to use hipEvent_t rather than hipEvent_t*

Change-Id: I259062dc087a13d51dc27f84e1e8861f332a104d
2017-04-06 21:02:50 -05:00
sunway513 f442e975c6 Refactor events and add initial event option for hipHccModuleLaunchKernel
- Change hipEvent_t to a class.
- Move event logic inside the class.
- Add _type to support Independent, StartCommand, StopCommand events.
  StartCommand returns start timestamp from events.

Change-Id: I4ddd694f2645a3ff7170c9111dc1d3e39931ca21
2017-04-06 21:02:50 -05:00
sunway513 fb4e2307f1 Improve documentation for hipModuleLaunch functions.
Change-Id: I0e22621e499775740c3301347b7416d5f98c2414
2017-04-06 21:02:50 -05:00
Aditya Atluri 1358bd8f07 fixed header structure for complex data types
Change-Id: I16bf19005d933f42e8c8603c5d0b2df8ea3ad04f
2017-04-06 16:43:26 -05:00
Sun, Peng 49a38da6e3 GGL update, add while 0 guard for hipLaunchKernel API
Change-Id: Ie48ef8ca2ab5e26a51febfcd92417902c33fbf66
2017-04-06 10:48:11 -05:00
Aditya Atluri 42739c37ef added __host__ for complex functions and corrected memset and memcpy test
Change-Id: I9ffefb7a0025aa111a54d20d2766982df15532e7
2017-04-06 09:29:44 -05:00
Sun, Peng 335e107f5f add extra guard to grid_launch_GGL header
Change-Id: I120619c08ea2d084804fcb1639efbe6c4648dde9
2017-04-05 22:25:41 -05:00
Ben Sander e8f4f76649 Update bug workarounds to reflect tool improvements. 2017-04-05 21:59:32 -05:00
Ben Sander 294ffbb51f Doc cleanup & add bug descript for restrict specifier issue 2017-04-05 19:40:00 -05:00
Ben Sander f345cd6f47 Add bug descrip for "no matching constructor" 2017-04-05 17:43:20 -05:00
Sun, Peng bfe499a13b hip_debug.md update from Alex, regarding __device__ function restrictions
Change-Id: I5e54fd97fc632d4283f76282e3935396a1aad235
2017-04-05 16:23:27 -05:00
Rahul Garg 4906cd5f0d mgpu IPC support fix
Change-Id: I12e4b2fd189c3658efd3b07defa18ece3853b0eb
2017-04-04 15:51:10 +05:30
Maneesh Gupta 714dd99e2d Remove unused packaging scripts
Change-Id: I609391b905810eb24f7fd4ea6d7f27166ca001b3
2017-04-04 08:07:56 +05:30
Maneesh Gupta b54954b09f hip_doc packaging script updates
- Gracefully handle missing doxygen and grip tools

Change-Id: I1a4a653d687c136c6d9237062ab4d02bc6cb3db1
2017-04-04 08:06:09 +05:30
Evgeny Mankov 81415a41b8 [HIPIFY] GGL support
+ hipLaunchKernel -> hipLaunchKernelGGL
+ macro HIP_KERNEL_NAME is no longer used
2017-04-03 22:05:01 +03:00
Evgeny Mankov a9268008ac [HIPIFY] Remove hipLaunchParm in HIP kernel declaration. 2017-04-03 20:32:50 +03:00
Sun, Peng 2ca9eec9fc Add more include header file for GGL, to make it self-compilable
Change-Id: I833cb194784450fb86e7961a7f9fe196ce3c7da5
2017-04-03 11:16:35 -05:00
Maneesh Gupta 3df134971b Force stdlib=libc++ on UB14.04
Change-Id: I7f24d663e57fbbee56afde12a0e61fc8bfc1e9b6
2017-04-03 15:09:31 +05:30