AI/rocm-systems
2
0 Fork 0
Code Issues Pull Requests Actions Packages Projects Releases Wiki Activity
76,333 Commits 3 Branches 0 Tags
develop
Commit Graph
76333 Commits
This Branch
This Branch
All Branches
Author SHA1 Message Date
Rahul Garg 9d078409e3 Merge pull request #1618 from ROCm-Developer-Tools/hotfix_volatile_accessors 
Separate volatile for clarity. Handle assignment.

[ROCm/clr commit: 3b8a5cff2f]
 2019-11-02 13:50:59 -07:00
Rahul Garg 3b8a5cff2f Merge pull request #1618 from ROCm-Developer-Tools/hotfix_volatile_accessors 
Separate volatile for clarity. Handle assignment.
 2019-11-02 13:50:59 -07:00
Rahul Garg dfbbe8119e Merge pull request #1618 from ROCm-Developer-Tools/hotfix_volatile_accessors 
Separate volatile for clarity. Handle assignment.

[ROCm/hip commit: 815a601dcb]
 2019-11-02 13:50:59 -07:00
Rahul Garg 815a601dcb Merge pull request #1618 from ROCm-Developer-Tools/hotfix_volatile_accessors 
Separate volatile for clarity. Handle assignment.
 2019-11-02 13:50:59 -07:00
Alex Voicu 1a3d02fb08 Separate volatile for clarity. Handle assignment. 
[ROCm/clr commit: ed0d6ec51e]
 2019-11-02 22:02:08 +02:00
Alex Voicu ed0d6ec51e Separate volatile for clarity. Handle assignment. 2019-11-02 22:02:08 +02:00
Alex Voicu e87f9b1944 Separate volatile for clarity. Handle assignment. 
[ROCm/hip commit: 99b9d5449f]
 2019-11-02 22:02:08 +02:00
Alex Voicu 99b9d5449f Separate volatile for clarity. Handle assignment. 2019-11-02 22:02:08 +02:00
Evgeny Mankov 8e369f9c7d Merge pull request #1617 from emankov/hipify-clang 
[HIPIFY] Introduce --cuda-gpu-arch as hipify-clang's option

[ROCm/clr commit: 758ab23b8f]
 2019-11-02 14:21:21 +03:00
Evgeny Mankov 758ab23b8f Merge pull request #1617 from emankov/hipify-clang 
[HIPIFY] Introduce --cuda-gpu-arch as hipify-clang's option
 2019-11-02 14:21:21 +03:00
Evgeny Mankov 093d205c24 Merge pull request #1617 from emankov/hipify-clang 
[HIPIFY] Introduce --cuda-gpu-arch as hipify-clang's option

[ROCm/hip commit: 728bd683b1]
 2019-11-02 14:21:21 +03:00
Evgeny Mankov 728bd683b1 Merge pull request #1617 from emankov/hipify-clang 
[HIPIFY] Introduce --cuda-gpu-arch as hipify-clang's option
 2019-11-02 14:21:21 +03:00
Evgeny Mankov bc9690328f [HIPIFY] Introduce --cuda-gpu-arch as hipify-clang's option 
+ Pass it to clang if specified


[ROCm/clr commit: 7142b884ab]
 2019-11-02 14:19:31 +03:00
Evgeny Mankov 7142b884ab [HIPIFY] Introduce --cuda-gpu-arch as hipify-clang's option 
+ Pass it to clang if specified
 2019-11-02 14:19:31 +03:00
Evgeny Mankov 92cd5e4fc1 [HIPIFY] Introduce --cuda-gpu-arch as hipify-clang's option 
+ Pass it to clang if specified


[ROCm/hip commit: 02589264a0]
 2019-11-02 14:19:31 +03:00
Evgeny Mankov 02589264a0 [HIPIFY] Introduce --cuda-gpu-arch as hipify-clang's option 
+ Pass it to clang if specified
 2019-11-02 14:19:31 +03:00
Evgeny d8560ae0b3 enable rocprofiler kernels trace; fixing signal value for proxy signal; fixing scope options in input txt format; 
Change-Id: Ife63c4091e565a2158e292c7acf9718085c709be
 2019-11-01 20:44:02 -05:00
Evgeny 7ac1e3dcd9 enable rocprofiler kernels trace; fixing signal value for proxy signal; fixing scope options in input txt format; 
Change-Id: Ife63c4091e565a2158e292c7acf9718085c709be


[ROCm/rocprofiler commit: d8560ae0b3]
 2019-11-01 20:44:02 -05:00
Wenkai Du 41f6319b33 Check for fine grain support using memory allocation 
[ROCm/rccl commit: 669f1951a4]
 2019-11-01 15:58:49 -07:00
Wenkai Du 669f1951a4 Check for fine grain support using memory allocation 2019-11-01 15:58:49 -07:00
Felix Kuehling 07b8c30ce8 kfdtest: Return address of packet from IndirectBuffer::AddPacket 
This can be used for allocating space in the IB for write-back data
in a NOP-packet with a payload.

Change-Id: I6202b89a455a65326366a15291789004dfdcc0b9
Signed-off-by: Felix Kuehling <Felix.Kuehling@amd.com>
 2019-11-01 18:31:28 -04:00
Felix Kuehling 0e79756932 kfdtest: Return address of packet from IndirectBuffer::AddPacket 
This can be used for allocating space in the IB for write-back data
in a NOP-packet with a payload.

Change-Id: I6202b89a455a65326366a15291789004dfdcc0b9
Signed-off-by: Felix Kuehling <Felix.Kuehling@amd.com>


[ROCm/ROCR-Runtime commit: 07b8c30ce8]
 2019-11-01 18:31:28 -04:00
Felix Kuehling 664bb13bc4 kfdtest: Add PM4 NOP packet payload capability 
Useful for allocating space for write-back data in a queue or IB.

Change-Id: I47bd2dcb8537a91410e9a91413979a8a2c1c5f21
Signed-off-by: Felix Kuehling <Felix.Kuehling@amd.com>
 2019-11-01 18:30:52 -04:00
Felix Kuehling 7b3b7de7b6 kfdtest: Add PM4 NOP packet payload capability 
Useful for allocating space for write-back data in a queue or IB.

Change-Id: I47bd2dcb8537a91410e9a91413979a8a2c1c5f21
Signed-off-by: Felix Kuehling <Felix.Kuehling@amd.com>


[ROCm/ROCR-Runtime commit: 664bb13bc4]
 2019-11-01 18:30:52 -04:00
Felix Kuehling ea7619c929 kfdtest: Re-factor dynamic packet allocation into BasePacket 
Avoids unnecessary and error-prone duplication of dynamic packet
allocation in many packet classes.

Change-Id: Icec981ae2cd7a3d88cdf9213298940d85627f853
Signed-off-by: Felix Kuehling <Felix.Kuehling@amd.com>
 2019-11-01 18:30:52 -04:00
Felix Kuehling 1e6ec31611 kfdtest: Re-factor dynamic packet allocation into BasePacket 
Avoids unnecessary and error-prone duplication of dynamic packet
allocation in many packet classes.

Change-Id: Icec981ae2cd7a3d88cdf9213298940d85627f853
Signed-off-by: Felix Kuehling <Felix.Kuehling@amd.com>


[ROCm/ROCR-Runtime commit: ea7619c929]
 2019-11-01 18:30:52 -04:00
Felix Kuehling 12e4ea94f1 kfdtest: Fix SDMA NOP packet size 
packetSize is used as the size in bytes.

Change-Id: I900f9a4f37b840cbb957184705db04a4c64d1654
Signed-off-by: Felix Kuehling <Felix.Kuehling@amd.com>
 2019-11-01 18:30:52 -04:00
Felix Kuehling b6487541a6 kfdtest: Fix SDMA NOP packet size 
packetSize is used as the size in bytes.

Change-Id: I900f9a4f37b840cbb957184705db04a4c64d1654
Signed-off-by: Felix Kuehling <Felix.Kuehling@amd.com>


[ROCm/ROCR-Runtime commit: 12e4ea94f1]
 2019-11-01 18:30:52 -04:00
Rahul Garg 91832b3b13 Merge pull request #1616 from ROCm-Developer-Tools/hotfix_volatile_accessors 
Accessors should work even when oddly volatile.

[ROCm/clr commit: dc702f5ffe]
 2019-11-01 13:45:54 -07:00
Rahul Garg dc702f5ffe Merge pull request #1616 from ROCm-Developer-Tools/hotfix_volatile_accessors 
Accessors should work even when oddly volatile.
 2019-11-01 13:45:54 -07:00
Rahul Garg d688b66b31 Merge pull request #1616 from ROCm-Developer-Tools/hotfix_volatile_accessors 
Accessors should work even when oddly volatile.

[ROCm/hip commit: 562da597a0]
 2019-11-01 13:45:54 -07:00
Rahul Garg 562da597a0 Merge pull request #1616 from ROCm-Developer-Tools/hotfix_volatile_accessors 
Accessors should work even when oddly volatile.
 2019-11-01 13:45:54 -07:00
Wenkai Du 0d6b476b08 Merge pull request #145 from wenkaidu/prim_test 
rccl-prim-test: use hipExtLaunchMultiKernelMultiDevice and minor cleanup

[ROCm/rccl commit: 90b2921207]
 2019-11-01 13:30:01 -07:00
Wenkai Du 90b2921207 Merge pull request #145 from wenkaidu/prim_test 
rccl-prim-test: use hipExtLaunchMultiKernelMultiDevice and minor cleanup
 2019-11-01 13:30:01 -07:00
Alex Voicu 5c2503f0bd Accessors should work even when oddly volatile. 
[ROCm/clr commit: 2d76dde05b]
 2019-11-01 22:18:01 +02:00
Alex Voicu 2d76dde05b Accessors should work even when oddly volatile. 2019-11-01 22:18:01 +02:00
Alex Voicu b30a42f678 Accessors should work even when oddly volatile. 
[ROCm/hip commit: ee5097f2c2]
 2019-11-01 22:18:01 +02:00
Alex Voicu ee5097f2c2 Accessors should work even when oddly volatile. 2019-11-01 22:18:01 +02:00
gilbertlee-amd f9ef1553aa Single Sync Timing mode (#144) 
* Adding single sync timing mode to emulate timing reported by rccl-prim-test / rccl-tests
* Adding duration / overhead info


[ROCm/rccl commit: 2f9edd2432]
 2019-11-01 10:18:25 -06:00
gilbertlee-amd 2f9edd2432 Single Sync Timing mode (#144) 
* Adding single sync timing mode to emulate timing reported by rccl-prim-test / rccl-tests
* Adding duration / overhead info
 2019-11-01 10:18:25 -06:00
Oak Zeng fa0cb9ebeb Handle IOCTL failure in fmm_release 
FREE_MEMORY_OF_GPU ioctl could fail, e.g., if memory is still mapped
to GPU. Handle this failure by return error in fmm_release/HsaKmtFreeMemory

Change-Id: I5461db39964f733cf97376d50e44906a9b4c0f13
Signed-off-by: Oak Zeng <Oak.Zeng@amd.com>
 2019-11-01 08:59:05 -04:00
Oak Zeng d5d66661f6 Handle IOCTL failure in fmm_release 
FREE_MEMORY_OF_GPU ioctl could fail, e.g., if memory is still mapped
to GPU. Handle this failure by return error in fmm_release/HsaKmtFreeMemory

Change-Id: I5461db39964f733cf97376d50e44906a9b4c0f13
Signed-off-by: Oak Zeng <Oak.Zeng@amd.com>


[ROCm/ROCR-Runtime commit: fa0cb9ebeb]
 2019-11-01 08:59:05 -04:00
Oak Zeng 7593b41575 Unmap memory from GPU before free 
Change-Id: Ic33b17cbaee5de7908d37527254f4f146e6b71e3
Signed-off-by: Oak Zeng <Oak.Zeng@amd.com>
 2019-11-01 08:58:55 -04:00
Oak Zeng 6b094ef4d8 Unmap memory from GPU before free 
Change-Id: Ic33b17cbaee5de7908d37527254f4f146e6b71e3
Signed-off-by: Oak Zeng <Oak.Zeng@amd.com>


[ROCm/ROCR-Runtime commit: 7593b41575]
 2019-11-01 08:58:55 -04:00
Evgeny Mankov 3b84d8e638 Merge pull request #1615 from emankov/hipify 
[HIPIFY][CUB][#1460][perl] Add "cub::" namespace prefix support in hipify-perl as well

[ROCm/clr commit: 48bb6df7e2]
 2019-11-01 14:35:55 +03:00
Evgeny Mankov 48bb6df7e2 Merge pull request #1615 from emankov/hipify 
[HIPIFY][CUB][#1460][perl] Add "cub::" namespace prefix support in hipify-perl as well
 2019-11-01 14:35:55 +03:00
Evgeny Mankov 0e30eb9a31 Merge pull request #1615 from emankov/hipify 
[HIPIFY][CUB][#1460][perl] Add "cub::" namespace prefix support in hipify-perl as well

[ROCm/hip commit: a3f6e0eda4]
 2019-11-01 14:35:55 +03:00
Evgeny Mankov a3f6e0eda4 Merge pull request #1615 from emankov/hipify 
[HIPIFY][CUB][#1460][perl] Add "cub::" namespace prefix support in hipify-perl as well
 2019-11-01 14:35:55 +03:00
Evgeny Mankov 43d286e9ce [HIPIFY][CUB][#1460][perl] Add "cub::" namespace prefix support in hipify-perl as well 
[ROCm/clr commit: c5a2a2daf2]
 2019-11-01 14:34:18 +03:00
Evgeny Mankov c5a2a2daf2 [HIPIFY][CUB][#1460][perl] Add "cub::" namespace prefix support in hipify-perl as well 2019-11-01 14:34:18 +03:00