normalizing trace comparison mechanism
This commit is contained in:
Evgeny
@@ -41,14 +41,14 @@ def parse_trace_levels(filename):
|
||||
def check_trace_status(tracename):
|
||||
trace2level = parse_trace_levels(trace2level_filename)
|
||||
|
||||
trace = tracename + '.txt'
|
||||
rtrace = tracename + '_r.txt'
|
||||
trace = 'test/' + tracename + '.txt'
|
||||
rtrace = tracename + '.txt'
|
||||
if os.path.basename(tracename) in trace2level:
|
||||
trace_level = trace2level[os.path.basename(tracename)]
|
||||
print 'Trace comparison for ' + os.path.basename(tracename) + ' is at level ' + str(trace_level)
|
||||
else:
|
||||
print 'Trace ' + os.path.basename(tracename) + ' not found in ' + trace2level_filename + ', defaulting to level 0'
|
||||
return 0
|
||||
return 1
|
||||
|
||||
if trace_level == 1:
|
||||
cnt_r = gen_events_info(rtrace,'cnt')
|
||||
|
||||
@@ -853,6 +853,7 @@ static roctracer_status_t roctracer_enable_activity_fun(
|
||||
roctracer::hsa_support::async_copy_callback_enabled = true;
|
||||
} else {
|
||||
const bool init_phase = (roctracer::RocpLoader::GetRef() == NULL);
|
||||
if (roctracer::RocpLoader::GetRef() == NULL) break;
|
||||
if (init_phase == true) {
|
||||
roctracer::RocpLoader::Instance().InitActivityCallback((void*)roctracer::HSA_AsyncActivityCallback,
|
||||
(void*)pool);
|
||||
|
||||
+5
-5
@@ -25,6 +25,7 @@ set ( CMAKE_VERBOSE_MAKEFILE TRUE CACHE BOOL "Verbose Output" FORCE )
|
||||
|
||||
## Path to HSA test
|
||||
set ( HSA_TEST_DIR "${TEST_DIR}/hsa/test" )
|
||||
set ( HSA_REV "5c90a68" )
|
||||
|
||||
## test run script
|
||||
set ( RUN_SCRIPT "${TEST_DIR}/run.sh" )
|
||||
@@ -41,9 +42,8 @@ add_custom_target( mytest
|
||||
COMMAND C_TEST=1 ${TEST_CFLAGS} make -C "${TEST_DIR}/MatrixTranspose_test"
|
||||
COMMAND sh -xc "cp ${TEST_DIR}/MatrixTranspose_test/MatrixTranspose ${PROJECT_BINARY_DIR}/test/MatrixTranspose_ctest"
|
||||
# copy traces
|
||||
COMMAND sh -xc "cp ${TEST_DIR}/MatrixTranspose*/*_trace.txt ${PROJECT_BINARY_DIR}/test/"
|
||||
COMMAND sh -xc "cp ${TEST_DIR}/*_trace.txt ${PROJECT_BINARY_DIR}/test/"
|
||||
COMMAND sh -xc "cp ${TEST_DIR}/tests_trace_cmp_levels.txt ${PROJECT_BINARY_DIR}/test/"
|
||||
COMMAND sh -xc "cp ${TEST_DIR}/golden_traces/*_trace.txt ${PROJECT_BINARY_DIR}/test/"
|
||||
COMMAND sh -xc "cp ${TEST_DIR}/golden_traces/tests_trace_cmp_levels.txt ${PROJECT_BINARY_DIR}/test/"
|
||||
)
|
||||
|
||||
## Util sources
|
||||
@@ -58,9 +58,9 @@ target_link_libraries ( ${TEST_LIB} ${ROCTRACER_TARGET} ${HSA_RUNTIME_LIB} c std
|
||||
|
||||
## Build HSA test
|
||||
execute_process ( COMMAND sh -xc "if [ ! -e ${TEST_DIR}/hsa ] ; then git clone https://github.com/ROCmSoftwarePlatform/hsa-class.git ${TEST_DIR}/hsa; fi" )
|
||||
execute_process ( COMMAND sh -xc "if [ -e ${TEST_DIR}/hsa ] ; then cd ${TEST_DIR}/hsa && git fetch origin && git checkout 777c308; fi" )
|
||||
execute_process ( COMMAND sh -xc "if [ -e ${TEST_DIR}/hsa ] ; then cd ${TEST_DIR}/hsa && git fetch origin && git checkout ${HSA_REV}; fi" )
|
||||
set ( TEST_DIR ${HSA_TEST_DIR} )
|
||||
add_subdirectory ( ${TEST_DIR} ${PROJECT_BINARY_DIR}/test/hsa )
|
||||
|
||||
## copying run script
|
||||
execute_process ( COMMAND sh -xc "cp ${RUN_SCRIPT} ${PROJECT_BINARY_DIR}" )
|
||||
execute_process ( COMMAND sh -xc "cp ${RUN_SCRIPT} ${PROJECT_BINARY_DIR}" )
|
||||
|
||||
@@ -1,466 +0,0 @@
|
||||
tool period test: "ROCP_CTRL_RATE=10:100000:1000000 ./test/MatrixTranspose"
|
||||
ROCTracer (pid=116438):
|
||||
HIP-trace()
|
||||
ROCTracer: trace control: delay(10us), length(100000us), rate(1000000us)
|
||||
Device name Vega 10 XT [Radeon RX Vega 64]
|
||||
## Iteration (99) #################
|
||||
PASSED!
|
||||
## Iteration (98) #################
|
||||
PASSED!
|
||||
## Iteration (97) #################
|
||||
PASSED!
|
||||
## Iteration (96) #################
|
||||
PASSED!
|
||||
## Iteration (95) #################
|
||||
PASSED!
|
||||
## Iteration (94) #################
|
||||
PASSED!
|
||||
## Iteration (93) #################
|
||||
PASSED!
|
||||
## Iteration (92) #################
|
||||
PASSED!
|
||||
## Iteration (91) #################
|
||||
PASSED!
|
||||
## Iteration (90) #################
|
||||
PASSED!
|
||||
## Iteration (89) #################
|
||||
PASSED!
|
||||
## Iteration (88) #################
|
||||
PASSED!
|
||||
## Iteration (87) #################
|
||||
PASSED!
|
||||
## Iteration (86) #################
|
||||
PASSED!
|
||||
## Iteration (85) #################
|
||||
PASSED!
|
||||
## Iteration (84) #################
|
||||
PASSED!
|
||||
## Iteration (83) #################
|
||||
PASSED!
|
||||
## Iteration (82) #################
|
||||
PASSED!
|
||||
## Iteration (81) #################
|
||||
PASSED!
|
||||
## Iteration (80) #################
|
||||
PASSED!
|
||||
## Iteration (79) #################
|
||||
PASSED!
|
||||
## Iteration (78) #################
|
||||
PASSED!
|
||||
## Iteration (77) #################
|
||||
PASSED!
|
||||
## Iteration (76) #################
|
||||
PASSED!
|
||||
## Iteration (75) #################
|
||||
PASSED!
|
||||
## Iteration (74) #################
|
||||
PASSED!
|
||||
## Iteration (73) #################
|
||||
PASSED!
|
||||
## Iteration (72) #################
|
||||
PASSED!
|
||||
## Iteration (71) #################
|
||||
PASSED!
|
||||
## Iteration (70) #################
|
||||
PASSED!
|
||||
## Iteration (69) #################
|
||||
PASSED!
|
||||
## Iteration (68) #################
|
||||
PASSED!
|
||||
## Iteration (67) #################
|
||||
PASSED!
|
||||
## Iteration (66) #################
|
||||
PASSED!
|
||||
## Iteration (65) #################
|
||||
PASSED!
|
||||
## Iteration (64) #################
|
||||
PASSED!
|
||||
## Iteration (63) #################
|
||||
PASSED!
|
||||
## Iteration (62) #################
|
||||
PASSED!
|
||||
## Iteration (61) #################
|
||||
PASSED!
|
||||
## Iteration (60) #################
|
||||
PASSED!
|
||||
## Iteration (59) #################
|
||||
PASSED!
|
||||
## Iteration (58) #################
|
||||
PASSED!
|
||||
## Iteration (57) #################
|
||||
PASSED!
|
||||
## Iteration (56) #################
|
||||
PASSED!
|
||||
## Iteration (55) #################
|
||||
PASSED!
|
||||
## Iteration (54) #################
|
||||
PASSED!
|
||||
## Iteration (53) #################
|
||||
PASSED!
|
||||
## Iteration (52) #################
|
||||
PASSED!
|
||||
## Iteration (51) #################
|
||||
PASSED!
|
||||
## Iteration (50) #################
|
||||
PASSED!
|
||||
## Iteration (49) #################
|
||||
PASSED!
|
||||
## Iteration (48) #################
|
||||
PASSED!
|
||||
## Iteration (47) #################
|
||||
PASSED!
|
||||
## Iteration (46) #################
|
||||
PASSED!
|
||||
## Iteration (45) #################
|
||||
PASSED!
|
||||
## Iteration (44) #################
|
||||
PASSED!
|
||||
## Iteration (43) #################
|
||||
PASSED!
|
||||
## Iteration (42) #################
|
||||
PASSED!
|
||||
## Iteration (41) #################
|
||||
PASSED!
|
||||
## Iteration (40) #################
|
||||
PASSED!
|
||||
## Iteration (39) #################
|
||||
PASSED!
|
||||
## Iteration (38) #################
|
||||
PASSED!
|
||||
## Iteration (37) #################
|
||||
PASSED!
|
||||
## Iteration (36) #################
|
||||
PASSED!
|
||||
## Iteration (35) #################
|
||||
PASSED!
|
||||
## Iteration (34) #################
|
||||
PASSED!
|
||||
## Iteration (33) #################
|
||||
PASSED!
|
||||
## Iteration (32) #################
|
||||
PASSED!
|
||||
## Iteration (31) #################
|
||||
PASSED!
|
||||
## Iteration (30) #################
|
||||
PASSED!
|
||||
## Iteration (29) #################
|
||||
PASSED!
|
||||
## Iteration (28) #################
|
||||
PASSED!
|
||||
## Iteration (27) #################
|
||||
PASSED!
|
||||
## Iteration (26) #################
|
||||
PASSED!
|
||||
## Iteration (25) #################
|
||||
PASSED!
|
||||
## Iteration (24) #################
|
||||
PASSED!
|
||||
## Iteration (23) #################
|
||||
PASSED!
|
||||
## Iteration (22) #################
|
||||
PASSED!
|
||||
## Iteration (21) #################
|
||||
PASSED!
|
||||
## Iteration (20) #################
|
||||
PASSED!
|
||||
## Iteration (19) #################
|
||||
PASSED!
|
||||
## Iteration (18) #################
|
||||
PASSED!
|
||||
## Iteration (17) #################
|
||||
PASSED!
|
||||
## Iteration (16) #################
|
||||
PASSED!
|
||||
## Iteration (15) #################
|
||||
PASSED!
|
||||
## Iteration (14) #################
|
||||
PASSED!
|
||||
## Iteration (13) #################
|
||||
PASSED!
|
||||
## Iteration (12) #################
|
||||
PASSED!
|
||||
## Iteration (11) #################
|
||||
PASSED!
|
||||
## Iteration (10) #################
|
||||
PASSED!
|
||||
## Iteration (9) #################
|
||||
PASSED!
|
||||
## Iteration (8) #################
|
||||
PASSED!
|
||||
## Iteration (7) #################
|
||||
PASSED!
|
||||
## Iteration (6) #################
|
||||
PASSED!
|
||||
## Iteration (5) #################
|
||||
PASSED!
|
||||
## Iteration (4) #################
|
||||
PASSED!
|
||||
## Iteration (3) #################
|
||||
PASSED!
|
||||
## Iteration (2) #################
|
||||
PASSED!
|
||||
## Iteration (1) #################
|
||||
PASSED!
|
||||
## Iteration (0) #################
|
||||
PASSED!
|
||||
1822770162190096:1822770162201236 116438:116438 hipGetDeviceProperties()
|
||||
1822770164732632:1822770164861753 116438:116438 hipMalloc(ptr(0x7fdfe4c00000) size(0x400000))
|
||||
1822770164862903:1822770164922593 116438:116438 hipMalloc(ptr(0x7fdfe4600000) size(0x400000))
|
||||
1822770164934104:1822770173240357 116438:116438 hipMemcpy(dst(0x7fdfe4c00000) src(0x20b7940) size(0x400000) kind(1))
|
||||
1822770173243647:1822770173243648 116438:116438 MARK(name(before HIP LaunchKernel))
|
||||
1822770618561423:1822770618561424 116438:116438 MARK(name(after HIP LaunchKernel))
|
||||
1822770636292136:1822770636292137 116438:116438 MARK(name(before HIP LaunchKernel))
|
||||
1822770636318946:1822770636318947 116438:116438 MARK(name(after HIP LaunchKernel))
|
||||
1822770649027427:1822770649027428 116438:116438 MARK(name(before HIP LaunchKernel))
|
||||
1822770649055147:1822770649055148 116438:116438 MARK(name(after HIP LaunchKernel))
|
||||
1822770661858819:1822770661858820 116438:116438 MARK(name(before HIP LaunchKernel))
|
||||
1822770661886030:1822770661886031 116438:116438 MARK(name(after HIP LaunchKernel))
|
||||
1822770674690761:1822770674690762 116438:116438 MARK(name(before HIP LaunchKernel))
|
||||
1822770674719182:1822770674719183 116438:116438 MARK(name(after HIP LaunchKernel))
|
||||
1822770687446783:1822770687446784 116438:116438 MARK(name(before HIP LaunchKernel))
|
||||
1822770687474763:1822770687474764 116438:116438 MARK(name(after HIP LaunchKernel))
|
||||
1822770700179044:1822770700179045 116438:116438 MARK(name(before HIP LaunchKernel))
|
||||
1822770700207174:1822770700207175 116438:116438 MARK(name(after HIP LaunchKernel))
|
||||
1822770713015755:1822770713015756 116438:116438 MARK(name(before HIP LaunchKernel))
|
||||
1822770713043885:1822770713043886 116438:116438 MARK(name(after HIP LaunchKernel))
|
||||
1822770725806637:1822770725806638 116438:116438 MARK(name(before HIP LaunchKernel))
|
||||
1822770725833717:1822770725833718 116438:116438 MARK(name(after HIP LaunchKernel))
|
||||
1822770738590118:1822770738590119 116438:116438 MARK(name(before HIP LaunchKernel))
|
||||
1822770738618148:1822770738618149 116438:116438 MARK(name(after HIP LaunchKernel))
|
||||
1822770751343939:1822770751343940 116438:116438 MARK(name(before HIP LaunchKernel))
|
||||
1822770751372549:1822770751372550 116438:116438 MARK(name(after HIP LaunchKernel))
|
||||
1822770764097681:1822770764097682 116438:116438 MARK(name(before HIP LaunchKernel))
|
||||
1822770764136631:1822770764136632 116438:116438 MARK(name(after HIP LaunchKernel))
|
||||
1822770776839992:1822770776839993 116438:116438 MARK(name(before HIP LaunchKernel))
|
||||
1822770776867912:1822770776867913 116438:116438 MARK(name(after HIP LaunchKernel))
|
||||
1822770789778774:1822770789778775 116438:116438 MARK(name(before HIP LaunchKernel))
|
||||
1822770789807094:1822770789807095 116438:116438 MARK(name(after HIP LaunchKernel))
|
||||
1822770802678836:1822770802678837 116438:116438 MARK(name(before HIP LaunchKernel))
|
||||
1822770802707166:1822770802707167 116438:116438 MARK(name(after HIP LaunchKernel))
|
||||
1822770815520828:1822770815520829 116438:116438 MARK(name(before HIP LaunchKernel))
|
||||
1822770815548698:1822770815548699 116438:116438 MARK(name(after HIP LaunchKernel))
|
||||
1822770828292289:1822770828292290 116438:116438 MARK(name(before HIP LaunchKernel))
|
||||
1822770828320769:1822770828320770 116438:116438 MARK(name(after HIP LaunchKernel))
|
||||
1822770841038531:1822770841038532 116438:116438 MARK(name(before HIP LaunchKernel))
|
||||
1822770841065971:1822770841065972 116438:116438 MARK(name(after HIP LaunchKernel))
|
||||
1822770853790232:1822770853790233 116438:116438 MARK(name(before HIP LaunchKernel))
|
||||
1822770853820062:1822770853820063 116438:116438 MARK(name(after HIP LaunchKernel))
|
||||
1822770866522263:1822770866522264 116438:116438 MARK(name(before HIP LaunchKernel))
|
||||
1822770866550493:1822770866550494 116438:116438 MARK(name(after HIP LaunchKernel))
|
||||
1822770879265854:1822770879265855 116438:116438 MARK(name(before HIP LaunchKernel))
|
||||
1822770879294035:1822770879294036 116438:116438 MARK(name(after HIP LaunchKernel))
|
||||
1822770892077246:1822770892077247 116438:116438 MARK(name(before HIP LaunchKernel))
|
||||
1822770892105206:1822770892105207 116438:116438 MARK(name(after HIP LaunchKernel))
|
||||
1822770904861617:1822770904861618 116438:116438 MARK(name(before HIP LaunchKernel))
|
||||
1822770904892457:1822770904892458 116438:116438 MARK(name(after HIP LaunchKernel))
|
||||
1822770917627368:1822770917627369 116438:116438 MARK(name(before HIP LaunchKernel))
|
||||
1822770917655519:1822770917655520 116438:116438 MARK(name(after HIP LaunchKernel))
|
||||
1822770930409670:1822770930409671 116438:116438 MARK(name(before HIP LaunchKernel))
|
||||
1822770930438360:1822770930438361 116438:116438 MARK(name(after HIP LaunchKernel))
|
||||
1822770943189151:1822770943189152 116438:116438 MARK(name(before HIP LaunchKernel))
|
||||
1822770943217081:1822770943217082 116438:116438 MARK(name(after HIP LaunchKernel))
|
||||
1822770956024813:1822770956024814 116438:116438 MARK(name(before HIP LaunchKernel))
|
||||
1822770956052314:1822770956052315 116438:116438 MARK(name(after HIP LaunchKernel))
|
||||
1822770968829485:1822770968829486 116438:116438 MARK(name(before HIP LaunchKernel))
|
||||
1822770968857945:1822770968857946 116438:116438 MARK(name(after HIP LaunchKernel))
|
||||
1822770981593826:1822770981593827 116438:116438 MARK(name(before HIP LaunchKernel))
|
||||
1822770981621566:1822770981621567 116438:116438 MARK(name(after HIP LaunchKernel))
|
||||
1822770994423678:1822770994423679 116438:116438 MARK(name(before HIP LaunchKernel))
|
||||
1822770994452568:1822770994452569 116438:116438 MARK(name(after HIP LaunchKernel))
|
||||
1822771007194429:1822771007194430 116438:116438 MARK(name(before HIP LaunchKernel))
|
||||
1822771007221919:1822771007221920 116438:116438 MARK(name(after HIP LaunchKernel))
|
||||
1822771020222042:1822771020222043 116438:116438 MARK(name(before HIP LaunchKernel))
|
||||
1822771020249972:1822771020249973 116438:116438 MARK(name(after HIP LaunchKernel))
|
||||
1822771032985534:1822771032985535 116438:116438 MARK(name(before HIP LaunchKernel))
|
||||
1822771033013724:1822771033013725 116438:116438 MARK(name(after HIP LaunchKernel))
|
||||
1822771045714144:1822771045714145 116438:116438 MARK(name(before HIP LaunchKernel))
|
||||
1822771045741935:1822771045741936 116438:116438 MARK(name(after HIP LaunchKernel))
|
||||
1822771058596217:1822771058596218 116438:116438 MARK(name(before HIP LaunchKernel))
|
||||
1822771058624617:1822771058624618 116438:116438 MARK(name(after HIP LaunchKernel))
|
||||
1822771071441309:1822771071441310 116438:116438 MARK(name(before HIP LaunchKernel))
|
||||
1822771071469609:1822771071469610 116438:116438 MARK(name(after HIP LaunchKernel))
|
||||
1822771084319850:1822771084319851 116438:116438 MARK(name(before HIP LaunchKernel))
|
||||
1822771084348361:1822771084348362 116438:116438 MARK(name(after HIP LaunchKernel))
|
||||
1822771097128132:1822771097128133 116438:116438 MARK(name(before HIP LaunchKernel))
|
||||
1822771097156612:1822771097156613 116438:116438 MARK(name(after HIP LaunchKernel))
|
||||
1822771109883183:1822771109883184 116438:116438 MARK(name(before HIP LaunchKernel))
|
||||
1822771109921563:1822771109921564 116438:116438 MARK(name(after HIP LaunchKernel))
|
||||
1822771122729855:1822771122729856 116438:116438 MARK(name(before HIP LaunchKernel))
|
||||
1822771122757155:1822771122757156 116438:116438 MARK(name(after HIP LaunchKernel))
|
||||
1822771135568637:1822771135568638 116438:116438 MARK(name(before HIP LaunchKernel))
|
||||
1822771135597657:1822771135597658 116438:116438 MARK(name(after HIP LaunchKernel))
|
||||
1822771148375219:1822771148375220 116438:116438 MARK(name(before HIP LaunchKernel))
|
||||
1822771148403629:1822771148403630 116438:116438 MARK(name(after HIP LaunchKernel))
|
||||
1822771159180137:1822771161235110 116438:116438 hipMemcpy(dst(0x7fdfe4c00000) src(0x20b7940) size(0x400000) kind(1))
|
||||
1822771161236660:1822771161236661 116438:116438 MARK(name(before HIP LaunchKernel))
|
||||
1822771161248381:1822771161264431 116438:116438 hipModuleLaunchKernel(kernel(matrixTranspose(float*, float*, int)) stream((nil)))
|
||||
1822771161285751:1822771161285752 116438:116438 MARK(name(after HIP LaunchKernel))
|
||||
1822771161287281:1822771165514938 116438:116438 hipMemcpy(dst(0x24b7950) src(0x7fdfe4600000) size(0x400000) kind(2))
|
||||
1822771171918848:1822771173984782 116438:116438 hipMemcpy(dst(0x7fdfe4c00000) src(0x20b7940) size(0x400000) kind(1))
|
||||
1822771173986152:1822771173986153 116438:116438 MARK(name(before HIP LaunchKernel))
|
||||
1822771173996942:1822771174012792 116438:116438 hipModuleLaunchKernel(kernel(matrixTranspose(float*, float*, int)) stream((nil)))
|
||||
1822771174014272:1822771174014273 116438:116438 MARK(name(after HIP LaunchKernel))
|
||||
1822771174015382:1822771178279619 116438:116438 hipMemcpy(dst(0x24b7950) src(0x7fdfe4600000) size(0x400000) kind(2))
|
||||
1822771184673329:1822771186731413 116438:116438 hipMemcpy(dst(0x7fdfe4c00000) src(0x20b7940) size(0x400000) kind(1))
|
||||
1822771186732863:1822771186732864 116438:116438 MARK(name(before HIP LaunchKernel))
|
||||
1822771186744233:1822771186760743 116438:116438 hipModuleLaunchKernel(kernel(matrixTranspose(float*, float*, int)) stream((nil)))
|
||||
1822771186761783:1822771186761784 116438:116438 MARK(name(after HIP LaunchKernel))
|
||||
1822771186762873:1822771191066460 116438:116438 hipMemcpy(dst(0x24b7950) src(0x7fdfe4600000) size(0x400000) kind(2))
|
||||
1822771197562312:1822771199606165 116438:116438 hipMemcpy(dst(0x7fdfe4c00000) src(0x20b7940) size(0x400000) kind(1))
|
||||
1822771199607685:1822771199607686 116438:116438 MARK(name(before HIP LaunchKernel))
|
||||
1822771199618535:1822771199634505 116438:116438 hipModuleLaunchKernel(kernel(matrixTranspose(float*, float*, int)) stream((nil)))
|
||||
1822771199635835:1822771199635836 116438:116438 MARK(name(after HIP LaunchKernel))
|
||||
1822771199636915:1822771203924882 116438:116438 hipMemcpy(dst(0x24b7950) src(0x7fdfe4600000) size(0x400000) kind(2))
|
||||
1822771210390814:1822771212448587 116438:116438 hipMemcpy(dst(0x7fdfe4c00000) src(0x20b7940) size(0x400000) kind(1))
|
||||
1822771212450127:1822771212450128 116438:116438 MARK(name(before HIP LaunchKernel))
|
||||
1822771212462917:1822771212479457 116438:116438 hipModuleLaunchKernel(kernel(matrixTranspose(float*, float*, int)) stream((nil)))
|
||||
1822771212480477:1822771212480478 116438:116438 MARK(name(after HIP LaunchKernel))
|
||||
1822771212481567:1822771216792744 116438:116438 hipMemcpy(dst(0x24b7950) src(0x7fdfe4600000) size(0x400000) kind(2))
|
||||
1822771223198475:1822771225253498 116438:116438 hipMemcpy(dst(0x7fdfe4c00000) src(0x20b7940) size(0x400000) kind(1))
|
||||
1822771225255288:1822771225255289 116438:116438 MARK(name(before HIP LaunchKernel))
|
||||
1822771225266888:1822771225282819 116438:116438 hipModuleLaunchKernel(kernel(matrixTranspose(float*, float*, int)) stream((nil)))
|
||||
1822771225283809:1822771225283810 116438:116438 MARK(name(after HIP LaunchKernel))
|
||||
1822771225284909:1822771229566596 116438:116438 hipMemcpy(dst(0x24b7950) src(0x7fdfe4600000) size(0x400000) kind(2))
|
||||
1822771236041977:1822771238101610 116438:116438 hipMemcpy(dst(0x7fdfe4c00000) src(0x20b7940) size(0x400000) kind(1))
|
||||
1822771238103080:1822771238103081 116438:116438 MARK(name(before HIP LaunchKernel))
|
||||
1822771238113820:1822771238129850 116438:116438 hipModuleLaunchKernel(kernel(matrixTranspose(float*, float*, int)) stream((nil)))
|
||||
1822771238130840:1822771238130841 116438:116438 MARK(name(after HIP LaunchKernel))
|
||||
1822771238131950:1822771242369628 116438:116438 hipMemcpy(dst(0x24b7950) src(0x7fdfe4600000) size(0x400000) kind(2))
|
||||
1822771248769078:1822771250830021 116438:116438 hipMemcpy(dst(0x7fdfe4c00000) src(0x20b7940) size(0x400000) kind(1))
|
||||
1822771250831601:1822771250831602 116438:116438 MARK(name(before HIP LaunchKernel))
|
||||
1822771250842911:1822771250858631 116438:116438 hipModuleLaunchKernel(kernel(matrixTranspose(float*, float*, int)) stream((nil)))
|
||||
1822771250859621:1822771250859622 116438:116438 MARK(name(after HIP LaunchKernel))
|
||||
1822771250860701:1822771255145869 116438:116438 hipMemcpy(dst(0x24b7950) src(0x7fdfe4600000) size(0x400000) kind(2))
|
||||
1822771263595032:1822771263595033 116438:116438 MARK(name(before HIP LaunchKernel))
|
||||
1822771263622582:1822771263622583 116438:116438 MARK(name(after HIP LaunchKernel))
|
||||
1822771276404694:1822771276404695 116438:116438 MARK(name(before HIP LaunchKernel))
|
||||
1822771276431864:1822771276431865 116438:116438 MARK(name(after HIP LaunchKernel))
|
||||
1822771289132475:1822771289132476 116438:116438 MARK(name(before HIP LaunchKernel))
|
||||
1822771289160596:1822771289160597 116438:116438 MARK(name(after HIP LaunchKernel))
|
||||
1822771301911557:1822771301911558 116438:116438 MARK(name(before HIP LaunchKernel))
|
||||
1822771301950127:1822771301950128 116438:116438 MARK(name(after HIP LaunchKernel))
|
||||
1822771314764229:1822771314764230 116438:116438 MARK(name(before HIP LaunchKernel))
|
||||
1822771314791509:1822771314791510 116438:116438 MARK(name(after HIP LaunchKernel))
|
||||
1822771327616470:1822771327616471 116438:116438 MARK(name(before HIP LaunchKernel))
|
||||
1822771327644471:1822771327644472 116438:116438 MARK(name(after HIP LaunchKernel))
|
||||
1822771340467792:1822771340467793 116438:116438 MARK(name(before HIP LaunchKernel))
|
||||
1822771340495392:1822771340495393 116438:116438 MARK(name(after HIP LaunchKernel))
|
||||
1822771353284764:1822771353284765 116438:116438 MARK(name(before HIP LaunchKernel))
|
||||
1822771353314034:1822771353314035 116438:116438 MARK(name(after HIP LaunchKernel))
|
||||
1822771366027805:1822771366027806 116438:116438 MARK(name(before HIP LaunchKernel))
|
||||
1822771366054975:1822771366054976 116438:116438 MARK(name(after HIP LaunchKernel))
|
||||
1822771378747056:1822771378747057 116438:116438 MARK(name(before HIP LaunchKernel))
|
||||
1822771378775616:1822771378775617 116438:116438 MARK(name(after HIP LaunchKernel))
|
||||
1822771391520358:1822771391520359 116438:116438 MARK(name(before HIP LaunchKernel))
|
||||
1822771391548328:1822771391548329 116438:116438 MARK(name(after HIP LaunchKernel))
|
||||
1822771404259849:1822771404259850 116438:116438 MARK(name(before HIP LaunchKernel))
|
||||
1822771404287629:1822771404287630 116438:116438 MARK(name(after HIP LaunchKernel))
|
||||
1822771417078650:1822771417078651 116438:116438 MARK(name(before HIP LaunchKernel))
|
||||
1822771417105521:1822771417105522 116438:116438 MARK(name(after HIP LaunchKernel))
|
||||
1822771429921622:1822771429921623 116438:116438 MARK(name(before HIP LaunchKernel))
|
||||
1822771429948912:1822771429948913 116438:116438 MARK(name(after HIP LaunchKernel))
|
||||
1822771442703863:1822771442703864 116438:116438 MARK(name(before HIP LaunchKernel))
|
||||
1822771442732114:1822771442732115 116438:116438 MARK(name(after HIP LaunchKernel))
|
||||
1822771455546175:1822771455546176 116438:116438 MARK(name(before HIP LaunchKernel))
|
||||
1822771455574765:1822771455574766 116438:116438 MARK(name(after HIP LaunchKernel))
|
||||
1822771468309596:1822771468309597 116438:116438 MARK(name(before HIP LaunchKernel))
|
||||
1822771468337556:1822771468337557 116438:116438 MARK(name(after HIP LaunchKernel))
|
||||
1822771481124388:1822771481124389 116438:116438 MARK(name(before HIP LaunchKernel))
|
||||
1822771481151899:1822771481151900 116438:116438 MARK(name(after HIP LaunchKernel))
|
||||
1822771493874879:1822771493874880 116438:116438 MARK(name(before HIP LaunchKernel))
|
||||
1822771493904120:1822771493904121 116438:116438 MARK(name(after HIP LaunchKernel))
|
||||
1822771506687371:1822771506687372 116438:116438 MARK(name(before HIP LaunchKernel))
|
||||
1822771506715871:1822771506715872 116438:116438 MARK(name(after HIP LaunchKernel))
|
||||
1822771519464533:1822771519464534 116438:116438 MARK(name(before HIP LaunchKernel))
|
||||
1822771519492293:1822771519492294 116438:116438 MARK(name(after HIP LaunchKernel))
|
||||
1822771532279194:1822771532279195 116438:116438 MARK(name(before HIP LaunchKernel))
|
||||
1822771532307234:1822771532307235 116438:116438 MARK(name(after HIP LaunchKernel))
|
||||
1822771545016015:1822771545016016 116438:116438 MARK(name(before HIP LaunchKernel))
|
||||
1822771545044205:1822771545044206 116438:116438 MARK(name(after HIP LaunchKernel))
|
||||
1822771557801846:1822771557801847 116438:116438 MARK(name(before HIP LaunchKernel))
|
||||
1822771557829627:1822771557829628 116438:116438 MARK(name(after HIP LaunchKernel))
|
||||
1822771570644168:1822771570644169 116438:116438 MARK(name(before HIP LaunchKernel))
|
||||
1822771570672029:1822771570672030 116438:116438 MARK(name(after HIP LaunchKernel))
|
||||
1822771583412800:1822771583412801 116438:116438 MARK(name(before HIP LaunchKernel))
|
||||
1822771583440560:1822771583440561 116438:116438 MARK(name(after HIP LaunchKernel))
|
||||
1822771596207231:1822771596207232 116438:116438 MARK(name(before HIP LaunchKernel))
|
||||
1822771596235072:1822771596235073 116438:116438 MARK(name(after HIP LaunchKernel))
|
||||
1822771609169614:1822771609169615 116438:116438 MARK(name(before HIP LaunchKernel))
|
||||
1822771609198584:1822771609198585 116438:116438 MARK(name(after HIP LaunchKernel))
|
||||
1822771621935145:1822771621935146 116438:116438 MARK(name(before HIP LaunchKernel))
|
||||
1822771621963045:1822771621963046 116438:116438 MARK(name(after HIP LaunchKernel))
|
||||
1822771634755077:1822771634755078 116438:116438 MARK(name(before HIP LaunchKernel))
|
||||
1822771634782347:1822771634782348 116438:116438 MARK(name(after HIP LaunchKernel))
|
||||
1822771647514558:1822771647514559 116438:116438 MARK(name(before HIP LaunchKernel))
|
||||
1822771647554188:1822771647554189 116438:116438 MARK(name(after HIP LaunchKernel))
|
||||
1822771660410781:1822771660410782 116438:116438 MARK(name(before HIP LaunchKernel))
|
||||
1822771660438721:1822771660438722 116438:116438 MARK(name(after HIP LaunchKernel))
|
||||
1822771673205902:1822771673205903 116438:116438 MARK(name(before HIP LaunchKernel))
|
||||
1822771673233972:1822771673233973 116438:116438 MARK(name(after HIP LaunchKernel))
|
||||
1822771686004863:1822771686004864 116438:116438 MARK(name(before HIP LaunchKernel))
|
||||
1822771686032954:1822771686032955 116438:116438 MARK(name(after HIP LaunchKernel))
|
||||
1822771698793305:1822771698793306 116438:116438 MARK(name(before HIP LaunchKernel))
|
||||
1822771698821805:1822771698821806 116438:116438 MARK(name(after HIP LaunchKernel))
|
||||
1822771711576346:1822771711576347 116438:116438 MARK(name(before HIP LaunchKernel))
|
||||
1822771711604186:1822771711604187 116438:116438 MARK(name(after HIP LaunchKernel))
|
||||
1822771724367387:1822771724367388 116438:116438 MARK(name(before HIP LaunchKernel))
|
||||
1822771724394878:1822771724394879 116438:116438 MARK(name(after HIP LaunchKernel))
|
||||
1822771737130739:1822771737130740 116438:116438 MARK(name(before HIP LaunchKernel))
|
||||
1822771737160079:1822771737160080 116438:116438 MARK(name(after HIP LaunchKernel))
|
||||
1822771749894700:1822771749894701 116438:116438 MARK(name(before HIP LaunchKernel))
|
||||
1822771749922980:1822771749922981 116438:116438 MARK(name(after HIP LaunchKernel))
|
||||
1822771762658122:1822771762658123 116438:116438 MARK(name(before HIP LaunchKernel))
|
||||
1822771762686292:1822771762686293 116438:116438 MARK(name(after HIP LaunchKernel))
|
||||
1822771775443853:1822771775443854 116438:116438 MARK(name(before HIP LaunchKernel))
|
||||
1822771775471433:1822771775471434 116438:116438 MARK(name(after HIP LaunchKernel))
|
||||
1822771788218125:1822771788218126 116438:116438 MARK(name(before HIP LaunchKernel))
|
||||
1822771788245825:1822771788245826 116438:116438 MARK(name(after HIP LaunchKernel))
|
||||
1822771801042946:1822771801042947 116438:116438 MARK(name(before HIP LaunchKernel))
|
||||
1822771801071416:1822771801071417 116438:116438 MARK(name(after HIP LaunchKernel))
|
||||
1822771813839688:1822771813839689 116438:116438 MARK(name(before HIP LaunchKernel))
|
||||
1822771813867578:1822771813867579 116438:116438 MARK(name(after HIP LaunchKernel))
|
||||
1822771826878471:1822771826878472 116438:116438 MARK(name(before HIP LaunchKernel))
|
||||
1822771826906261:1822771826906262 116438:116438 MARK(name(after HIP LaunchKernel))
|
||||
1822771839641572:1822771839641573 116438:116438 MARK(name(before HIP LaunchKernel))
|
||||
1822771839669053:1822771839669054 116438:116438 MARK(name(after HIP LaunchKernel))
|
||||
1822771852458764:1822771852458765 116438:116438 MARK(name(before HIP LaunchKernel))
|
||||
1822771852485704:1822771852485705 116438:116438 MARK(name(after HIP LaunchKernel))
|
||||
1822771865247615:1822771865247616 116438:116438 MARK(name(before HIP LaunchKernel))
|
||||
1822771865275756:1822771865275757 116438:116438 MARK(name(after HIP LaunchKernel))
|
||||
1822771878163408:1822771878163409 116438:116438 MARK(name(before HIP LaunchKernel))
|
||||
1822771878191438:1822771878191439 116438:116438 MARK(name(after HIP LaunchKernel))
|
||||
1822771891031999:1822771891032000 116438:116438 MARK(name(before HIP LaunchKernel))
|
||||
1822771891060780:1822771891060781 116438:116438 MARK(name(after HIP LaunchKernel))
|
||||
1822770164959094:1822770173233007 0:0 hcMemcpyHostToDevice:4
|
||||
1822771159196627:1822771161231010 0:0 hcMemcpyHostToDevice:89
|
||||
1822771161271486:1822771162462508 0:0 hcCommandKernel:91
|
||||
1822771162546779:1822771165512668 0:0 hcMemcpyDeviceToHost:93
|
||||
1822771171936428:1822771173981162 0:0 hcMemcpyHostToDevice:94
|
||||
1822771174019952:1822771175216159 0:0 hcCommandKernel:96
|
||||
1822771162467378:1822771162499379 0:0 hcCommandMarker:93
|
||||
1822771175297180:1822771178277099 0:0 hcMemcpyDeviceToHost:98
|
||||
1822771184690200:1822771186728003 0:0 hcMemcpyHostToDevice:99
|
||||
1822771186767974:1822771187965367 0:0 hcCommandKernel:101
|
||||
1822771175221178:1822771175252439 0:0 hcCommandMarker:98
|
||||
1822771188052511:1822771191063960 0:0 hcMemcpyDeviceToHost:103
|
||||
1822771197579732:1822771199602785 0:0 hcMemcpyHostToDevice:104
|
||||
1822771199641385:1822771200839370 0:0 hcCommandKernel:106
|
||||
1822771187970434:1822771188001695 0:0 hcCommandMarker:103
|
||||
1822771200920833:1822771203922192 0:0 hcMemcpyDeviceToHost:108
|
||||
1822771210408554:1822771212444577 0:0 hcMemcpyHostToDevice:109
|
||||
1822771212486611:1822771213670374 0:0 hcCommandKernel:111
|
||||
1822771200844255:1822771200875960 0:0 hcCommandMarker:108
|
||||
1822771213752345:1822771216790154 0:0 hcMemcpyDeviceToHost:113
|
||||
1822771223214605:1822771225250368 0:0 hcMemcpyHostToDevice:114
|
||||
1822771225289765:1822771226493528 0:0 hcCommandKernel:116
|
||||
1822771213675410:1822771213707115 0:0 hcCommandMarker:113
|
||||
1822771226574837:1822771229564026 0:0 hcMemcpyDeviceToHost:118
|
||||
1822771236058777:1822771238097360 0:0 hcMemcpyHostToDevice:119
|
||||
1822771238136777:1822771239325132 0:0 hcCommandKernel:121
|
||||
1822771226498570:1822771226530127 0:0 hcCommandMarker:118
|
||||
1822771239406108:1822771242367398 0:0 hcMemcpyDeviceToHost:123
|
||||
1822771248787248:1822771250826071 0:0 hcMemcpyHostToDevice:124
|
||||
1822771250866138:1822771252059234 0:0 hcCommandKernel:126
|
||||
1822771239330157:1822771239361418 0:0 hcCommandMarker:123
|
||||
1822771252142610:1822771255143279 0:0 hcMemcpyDeviceToHost:128
|
||||
1822771252064420:1822771252095680 0:0 hcCommandMarker:128
|
||||
File diff suppressed because it is too large
Load Diff
File diff suppressed because it is too large
Load Diff
File diff suppressed because it is too large
Load Diff
@@ -20,7 +20,9 @@ OUT OF OR IN CONNECTION WITH THE SOFTWARE OR THE USE OR OTHER DEALINGS IN
|
||||
THE SOFTWARE.
|
||||
*/
|
||||
|
||||
#include <stdarg.h>
|
||||
#include <stdio.h>
|
||||
#include <stdlib.h>
|
||||
|
||||
#ifdef __cplusplus
|
||||
#include <cstdlib>
|
||||
@@ -34,6 +36,28 @@ using namespace std;
|
||||
// roctracer extension API
|
||||
#include <inc/roctracer_ext.h>
|
||||
|
||||
const size_t msg_size = 512;
|
||||
char* msg_buf = NULL;
|
||||
char* message = NULL;
|
||||
void SPRINT(const char* fmt, ...) {
|
||||
if (msg_buf == NULL) {
|
||||
msg_buf = (char*) calloc(msg_size, 1);
|
||||
message = msg_buf;
|
||||
}
|
||||
|
||||
va_list args;
|
||||
va_start(args, fmt);
|
||||
message += vsnprintf(message, msg_size - (message - msg_buf), fmt, args);
|
||||
va_end(args);
|
||||
}
|
||||
void SFLUSH() {
|
||||
if (msg_buf == NULL) abort();
|
||||
message = msg_buf;
|
||||
msg_buf[msg_size - 1] = 0;
|
||||
fprintf(stdout, "%s", msg_buf);
|
||||
fflush(stdout);
|
||||
}
|
||||
|
||||
#if HIP_TEST
|
||||
// hip header file
|
||||
#include <hip/hip_runtime.h>
|
||||
@@ -248,7 +272,7 @@ void api_callback(
|
||||
return;
|
||||
}
|
||||
const hip_api_data_t* data = (const hip_api_data_t*)(callback_data);
|
||||
fprintf(stdout, "<%s id(%u)\tcorrelation_id(%lu) %s> ",
|
||||
SPRINT("<%s id(%u)\tcorrelation_id(%lu) %s> ",
|
||||
roctracer_op_string(ACTIVITY_DOMAIN_HIP_API, cid, 0),
|
||||
cid,
|
||||
data->correlation_id,
|
||||
@@ -256,39 +280,22 @@ void api_callback(
|
||||
if (data->phase == ACTIVITY_API_PHASE_ENTER) {
|
||||
switch (cid) {
|
||||
case HIP_API_ID_hipMemcpy:
|
||||
fprintf(stdout, "<%s id(%u)\tcorrelation_id(%lu) %s>\n dst(%p) src(%p) size(0x%x) kind(%u)\n",
|
||||
roctracer_op_string(ACTIVITY_DOMAIN_HIP_API, cid, 0),
|
||||
cid,
|
||||
data->correlation_id,
|
||||
"on-enter",
|
||||
SPRINT("dst(%p) src(%p) size(0x%x) kind(%u)",
|
||||
data->args.hipMemcpy.dst,
|
||||
data->args.hipMemcpy.src,
|
||||
(uint32_t)(data->args.hipMemcpy.sizeBytes),
|
||||
(uint32_t)(data->args.hipMemcpy.kind));
|
||||
break;
|
||||
case HIP_API_ID_hipMalloc:
|
||||
fprintf(stdout, "<%s id(%u)\tcorrelation_id(%lu) %s>\n ptr(%p) size(0x%x)\n",
|
||||
roctracer_op_string(ACTIVITY_DOMAIN_HIP_API, cid, 0),
|
||||
cid,
|
||||
data->correlation_id,
|
||||
"on-enter",
|
||||
SPRINT("ptr(%p) size(0x%x)",
|
||||
data->args.hipMalloc.ptr,
|
||||
(uint32_t)(data->args.hipMalloc.size));
|
||||
break;
|
||||
case HIP_API_ID_hipFree:
|
||||
fprintf(stdout, "<%s id(%u)\tcorrelation_id(%lu) %s>\n ptr(%p)\n",
|
||||
roctracer_op_string(ACTIVITY_DOMAIN_HIP_API, cid, 0),
|
||||
cid,
|
||||
data->correlation_id,
|
||||
"on-enter",
|
||||
data->args.hipFree.ptr);
|
||||
SPRINT("ptr(%p)", data->args.hipFree.ptr);
|
||||
break;
|
||||
case HIP_API_ID_hipModuleLaunchKernel:
|
||||
fprintf(stdout, "<%s id(%u)\tcorrelation_id(%lu) %s>\n kernel(\"%s\") stream(%p)\n",
|
||||
roctracer_op_string(ACTIVITY_DOMAIN_HIP_API, cid, 0),
|
||||
cid,
|
||||
data->correlation_id,
|
||||
"on-enter",
|
||||
SPRINT("kernel(\"%s\") stream(%p)",
|
||||
hipKernelNameRef(data->args.hipModuleLaunchKernel.f),
|
||||
data->args.hipModuleLaunchKernel.stream);
|
||||
break;
|
||||
@@ -298,60 +305,52 @@ void api_callback(
|
||||
} else {
|
||||
switch (cid) {
|
||||
case HIP_API_ID_hipMalloc:
|
||||
fprintf(stdout, "<%s id(%u)\tcorrelation_id(%lu) %s>\n *ptr(0x%p)\n",
|
||||
roctracer_op_string(ACTIVITY_DOMAIN_HIP_API, cid, 0),
|
||||
cid,
|
||||
data->correlation_id,
|
||||
"on-exit",
|
||||
*(data->args.hipMalloc.ptr));
|
||||
SPRINT("*ptr(0x%p)", *(data->args.hipMalloc.ptr));
|
||||
break;
|
||||
default:
|
||||
break;
|
||||
}
|
||||
}
|
||||
//fprintf(stdout, "\n");
|
||||
fflush(stdout);
|
||||
SPRINT("\n");
|
||||
SFLUSH();
|
||||
}
|
||||
// Activity tracing callback
|
||||
// hipMalloc id(3) correlation_id(1): begin_ns(1525888652762640464) end_ns(1525888652762877067)
|
||||
void activity_callback(const char* begin, const char* end, void* arg) {
|
||||
const roctracer_record_t* record = (const roctracer_record_t*)(begin);
|
||||
const roctracer_record_t* end_record = (const roctracer_record_t*)(end);
|
||||
fprintf(stdout, "\tActivity records:\n"); fflush(stdout);
|
||||
|
||||
SPRINT("\tActivity records:\n");
|
||||
while (record < end_record) {
|
||||
const char * name = roctracer_op_string(record->domain, record->op, record->kind);
|
||||
fprintf(stdout, "\t%s\tcorrelation_id(%lu) time_ns(%lu:%lu)",
|
||||
SPRINT("\t%s\tcorrelation_id(%lu) time_ns(%lu:%lu)",
|
||||
name,
|
||||
record->correlation_id,
|
||||
record->begin_ns,
|
||||
record->end_ns
|
||||
);
|
||||
record->end_ns);
|
||||
if ((record->domain == ACTIVITY_DOMAIN_HIP_API) || (record->domain == ACTIVITY_DOMAIN_KFD_API)) {
|
||||
fprintf(stdout, " process_id(%u) thread_id(%u)",
|
||||
SPRINT(" process_id(%u) thread_id(%u)",
|
||||
record->process_id,
|
||||
record->thread_id
|
||||
);
|
||||
record->thread_id);
|
||||
} else if (record->domain == ACTIVITY_DOMAIN_HCC_OPS) {
|
||||
fprintf(stdout, " device_id(%d) queue_id(%lu)\n",
|
||||
SPRINT(" device_id(%d) queue_id(%lu)",
|
||||
record->device_id,
|
||||
record->queue_id
|
||||
);
|
||||
if (record->op == HIP_OP_ID_COPY) fprintf(stdout, " bytes(0x%zx)", record->bytes);
|
||||
record->queue_id);
|
||||
if (record->op == HIP_OP_ID_COPY) SPRINT(" bytes(0x%zx)", record->bytes);
|
||||
} else if (record->domain == ACTIVITY_DOMAIN_HSA_OPS) {
|
||||
fprintf(stdout, " se(%u) cycle(%lu) pc(%lx)",
|
||||
SPRINT(" se(%u) cycle(%lu) pc(%lx)",
|
||||
record->pc_sample.se,
|
||||
record->pc_sample.cycle,
|
||||
record->pc_sample.pc
|
||||
);
|
||||
record->pc_sample.pc);
|
||||
} else if (record->domain == ACTIVITY_DOMAIN_EXT_API) {
|
||||
fprintf(stdout, " external_id(%lu)\n",
|
||||
record->external_id
|
||||
);
|
||||
SPRINT(" external_id(%lu)", record->external_id);
|
||||
} else {
|
||||
fprintf(stderr, "Bad domain %d\n\n", record->domain);
|
||||
abort();
|
||||
}
|
||||
fflush(stdout);
|
||||
SPRINT("\n");
|
||||
SFLUSH();
|
||||
|
||||
ROCTRACER_CALL(roctracer_next_record(record, &record));
|
||||
}
|
||||
}
|
||||
|
||||
File diff suppressed because it is too large
Load Diff
@@ -1,77 +0,0 @@
|
||||
tool HSA test input: "./test/hsa/ctrl"
|
||||
ROCTracer (pid=116477): input from "input.xml"
|
||||
HSA-trace( hsa_agent_get_info hsa_amd_memory_pool_allocate)
|
||||
HSA-activity-trace()
|
||||
> GPU agents :
|
||||
> agent[0] :
|
||||
>> Name : gfx900
|
||||
>> APU : 0
|
||||
>> HSAIL profile : 0
|
||||
>> Max Wave Size : 64
|
||||
>> Max Queue Size : 131072
|
||||
>> CU number : 64
|
||||
>> Waves per CU : 40
|
||||
>> SIMDs per CU : 4
|
||||
>> SE number : 4
|
||||
>> Shader Arrays per SE : 1
|
||||
TestHsa::Initialize :
|
||||
> Using agent[0] : gfx900
|
||||
TestHsa::setup :
|
||||
Code object filename: gfx9_DummyKernel.hsaco
|
||||
TestHsa::run :
|
||||
> Executing kernel: "DummyKernel"
|
||||
> Waiting on kernel dispatch signal, que_idx=0
|
||||
> DONE, que_idx=0
|
||||
Test : Passed
|
||||
Time taken for Setup by DummyKernel : 0.000853027
|
||||
Time taken for Dispatch by DummyKernel : 2.39258e-05
|
||||
Time taken in Total by DummyKernel : 0.000876953
|
||||
TestHsa::Initialize :
|
||||
> Using agent[0] : gfx900
|
||||
TestHsa::setup :
|
||||
Code object filename: gfx9_SimpleConvolution.hsaco
|
||||
SimpleConvolution::init :
|
||||
> Input[0] :
|
||||
> 15 201 51 89 92 34 96 66 11 225 161 96 81 211 108 124 202 244 182 90 215 92 98 20 44 225 55 247 202 0 45 218 202 97 51 39 131 147 105 143 116 11 239 198 222 92 67 169 81 250 3 40 86 101 60 131 70 116 123 17 117 168 236 64
|
||||
> Mask :
|
||||
> 0 0.2 0
|
||||
> 0.2 0.2 0.2
|
||||
> 0 0.2 0
|
||||
TestHsa::run :
|
||||
> Executing kernel: "SimpleConvolution"
|
||||
> Waiting on kernel dispatch signal, que_idx=1
|
||||
> DONE, que_idx=1
|
||||
> Output[0] :
|
||||
> 45 60 89 75 79 86 45 43 104 82 144 105 99 90 109 124 123 146 149 124 120 87 43 36 88 91 113 103 98 53 68 104 113 106 76 90 90 122 82 92 102 124 95 149 112 102 69 82 146 116 103 62 50 96 99 87 84 110 88 81 61 105 134 71
|
||||
Test : Passed
|
||||
Time taken for Setup by SimpleConvolution : 0.000602051
|
||||
Time taken for Dispatch by SimpleConvolution : 4.00391e-05
|
||||
Time taken in Total by SimpleConvolution : 0.00064209
|
||||
1822810967909998:1822810967921554 async-copy0
|
||||
1822810364769411:1822810364771941 116477:116477 hsa_agent_get_info(<agent 0x8990e0>, 17, 0x7ffeac015fec) = 0
|
||||
1822810364778011:1822810364778611 116477:116477 hsa_agent_get_info(<agent 0x86f770>, 17, 0x7ffeac015fec) = 0
|
||||
1822810364779111:1822810364782691 116477:116477 hsa_agent_get_info(<agent 0x86f770>, 0, 0x8aac04) = 0
|
||||
1822810364784511:1822810364785051 116477:116477 hsa_agent_get_info(<agent 0x86f770>, 6, 0x8aac44) = 0
|
||||
1822810364785491:1822810364785841 116477:116477 hsa_agent_get_info(<agent 0x86f770>, 14, 0x8aac48) = 0
|
||||
1822810364786281:1822810364786611 116477:116477 hsa_agent_get_info(<agent 0x86f770>, 4, 0x8aac4c) = 0
|
||||
1822810364787051:1822810364787401 116477:116477 hsa_agent_get_info(<agent 0x86f770>, 40962, 0x8aac68) = 0
|
||||
1822810364787841:1822810364788181 116477:116477 hsa_agent_get_info(<agent 0x86f770>, 40970, 0x8aac6c) = 0
|
||||
1822810364788621:1822810364788951 116477:116477 hsa_agent_get_info(<agent 0x86f770>, 40971, 0x8aac70) = 0
|
||||
1822810364789381:1822810364789711 116477:116477 hsa_agent_get_info(<agent 0x86f770>, 40972, 0x8aac74) = 0
|
||||
1822810364790151:1822810364790471 116477:116477 hsa_agent_get_info(<agent 0x86f770>, 40973, 0x8aac78) = 0
|
||||
1822810966872900:1822810966889591 116477:116485 hsa_amd_memory_pool_allocate(<amd_memory_pool>, <uint64_t 0x4000>, <uint32_t 0x0>, 0x7fe988df8c68) = 0
|
||||
1822810966960311:1822810966961441 116477:116485 hsa_amd_memory_pool_allocate(<amd_memory_pool>, <uint64_t 0x4000>, <uint32_t 0x0>, 0x7fe988df8c70) = 0
|
||||
1822810966961951:1822810966973001 116477:116485 hsa_amd_memory_pool_allocate(<amd_memory_pool>, <uint64_t 0x1000>, <uint32_t 0x0>, 0x7fe988df8c68) = 0
|
||||
1822810967025981:1822810967035781 116477:116485 hsa_amd_memory_pool_allocate(<amd_memory_pool>, <uint64_t 0x1000>, <uint32_t 0x0>, 0x7fe988df8c68) = 0
|
||||
1822810967298203:1822810967317743 116477:116485 hsa_amd_memory_pool_allocate(<amd_memory_pool>, <uint64_t 0x4000>, <uint32_t 0x0>, 0x7fe988df8c68) = 0
|
||||
1822810967384054:1822810967384814 116477:116485 hsa_agent_get_info(<agent 0x8990e0>, 17, 0x7fe988df87bc) = 0
|
||||
1822810967387674:1822810967388054 116477:116485 hsa_agent_get_info(<agent 0x86f770>, 17, 0x7fe988df87bc) = 0
|
||||
1822810967388514:1822810967391744 116477:116485 hsa_agent_get_info(<agent 0x86f770>, 0, 0x7fe930006e04) = 0
|
||||
1822810967394494:1822810967394794 116477:116485 hsa_agent_get_info(<agent 0x86f770>, 6, 0x7fe930006e44) = 0
|
||||
1822810967395194:1822810967395514 116477:116485 hsa_agent_get_info(<agent 0x86f770>, 14, 0x7fe930006e48) = 0
|
||||
1822810967395924:1822810967396214 116477:116485 hsa_agent_get_info(<agent 0x86f770>, 4, 0x7fe930006e4c) = 0
|
||||
1822810967396604:1822810967396904 116477:116485 hsa_agent_get_info(<agent 0x86f770>, 40962, 0x7fe930006e68) = 0
|
||||
1822810967397294:1822810967397594 116477:116485 hsa_agent_get_info(<agent 0x86f770>, 40970, 0x7fe930006e6c) = 0
|
||||
1822810967397984:1822810967398284 116477:116485 hsa_agent_get_info(<agent 0x86f770>, 40971, 0x7fe930006e70) = 0
|
||||
1822810967398674:1822810967398974 116477:116485 hsa_agent_get_info(<agent 0x86f770>, 40972, 0x7fe930006e74) = 0
|
||||
1822810967399364:1822810967399654 116477:116485 hsa_agent_get_info(<agent 0x86f770>, 40973, 0x7fe930006e78) = 0
|
||||
@@ -1,163 +0,0 @@
|
||||
tool HSA test: "./test/hsa/ctrl"
|
||||
ROCTracer (pid=116451):
|
||||
HSA-trace()
|
||||
HSA-activity-trace()
|
||||
> GPU agents :
|
||||
> agent[0] :
|
||||
>> Name : gfx900
|
||||
>> APU : 0
|
||||
>> HSAIL profile : 0
|
||||
>> Max Wave Size : 64
|
||||
>> Max Queue Size : 131072
|
||||
>> CU number : 64
|
||||
>> Waves per CU : 40
|
||||
>> SIMDs per CU : 4
|
||||
>> SE number : 4
|
||||
>> Shader Arrays per SE : 1
|
||||
TestHsa::Initialize :
|
||||
> Using agent[0] : gfx900
|
||||
TestHsa::setup :
|
||||
Code object filename: gfx9_DummyKernel.hsaco
|
||||
TestHsa::run :
|
||||
> Executing kernel: "DummyKernel"
|
||||
> Waiting on kernel dispatch signal, que_idx=0
|
||||
> DONE, que_idx=0
|
||||
Test : Passed
|
||||
Time taken for Setup by DummyKernel : 0.000803955
|
||||
Time taken for Dispatch by DummyKernel : 2.68555e-05
|
||||
Time taken in Total by DummyKernel : 0.000830811
|
||||
TestHsa::Initialize :
|
||||
> Using agent[0] : gfx900
|
||||
TestHsa::setup :
|
||||
Code object filename: gfx9_SimpleConvolution.hsaco
|
||||
SimpleConvolution::init :
|
||||
> Input[0] :
|
||||
> 15 201 51 89 92 34 96 66 11 225 161 96 81 211 108 124 202 244 182 90 215 92 98 20 44 225 55 247 202 0 45 218 202 97 51 39 131 147 105 143 116 11 239 198 222 92 67 169 81 250 3 40 86 101 60 131 70 116 123 17 117 168 236 64
|
||||
> Mask :
|
||||
> 0 0.2 0
|
||||
> 0.2 0.2 0.2
|
||||
> 0 0.2 0
|
||||
TestHsa::run :
|
||||
> Executing kernel: "SimpleConvolution"
|
||||
> Waiting on kernel dispatch signal, que_idx=1
|
||||
> DONE, que_idx=1
|
||||
> Output[0] :
|
||||
> 45 60 89 75 79 86 45 43 104 82 144 105 99 90 109 124 123 146 149 124 120 87 43 36 88 91 113 103 98 53 68 104 113 106 76 90 90 122 82 92 102 124 95 149 112 102 69 82 146 116 103 62 50 96 99 87 84 110 88 81 61 105 134 71
|
||||
Test : Passed
|
||||
Time taken for Setup by SimpleConvolution : 0.00060498
|
||||
Time taken for Dispatch by SimpleConvolution : 4.29687e-05
|
||||
Time taken in Total by SimpleConvolution : 0.000647949
|
||||
1822787198892285:1822787198903100 async-copy0
|
||||
1822786593183215:1822786593187325 116451:116451 hsa_amd_profiling_async_copy_enable(<bool 0x1>) = 0
|
||||
1822786593205695:1822786593206405 116451:116451 hsa_agent_get_info(<agent 0x14290e0>, 17, 0x7ffd08170f5c) = 0
|
||||
1822786593211235:1822786593212485 116451:116451 hsa_amd_memory_pool_get_info(<amd_memory_pool>, 0, 0x7ffd08170df8) = 0
|
||||
1822786593213335:1822786593213925 116451:116451 hsa_amd_memory_pool_get_info(<amd_memory_pool>, 1, 0x7ffd08170dfc) = 0
|
||||
1822786593214745:1822786593215305 116451:116451 hsa_amd_memory_pool_get_info(<amd_memory_pool>, 0, 0x7ffd08170df8) = 0
|
||||
1822786593216065:1822786593216635 116451:116451 hsa_amd_memory_pool_get_info(<amd_memory_pool>, 1, 0x7ffd08170dfc) = 0
|
||||
1822786593216065:1822786593217435 116451:116451 hsa_amd_agent_iterate_memory_pools(<agent 0x14290e0>, 1, 0x143cfc0) = 1
|
||||
1822786593219035:1822786593219605 116451:116451 hsa_amd_memory_pool_get_info(<amd_memory_pool>, 0, 0x7ffd08170df8) = 0
|
||||
1822786593220385:1822786593220945 116451:116451 hsa_amd_memory_pool_get_info(<amd_memory_pool>, 1, 0x7ffd08170dfc) = 0
|
||||
1822786593220385:1822786593221715 116451:116451 hsa_amd_agent_iterate_memory_pools(<agent 0x14290e0>, 1, 0x143cfd0) = 1
|
||||
1822786593224085:1822786593224895 116451:116451 hsa_agent_get_info(<agent 0x13ff770>, 17, 0x7ffd08170f5c) = 0
|
||||
1822786593225835:1822786593231426 116451:116451 hsa_agent_get_info(<agent 0x13ff770>, 0, 0x143d094) = 0
|
||||
1822786593233936:1822786593234536 116451:116451 hsa_agent_get_info(<agent 0x13ff770>, 6, 0x143d0d4) = 0
|
||||
1822786593235326:1822786593235926 116451:116451 hsa_agent_get_info(<agent 0x13ff770>, 14, 0x143d0d8) = 0
|
||||
1822786593236696:1822786593237276 116451:116451 hsa_agent_get_info(<agent 0x13ff770>, 4, 0x143d0dc) = 0
|
||||
1822786593238046:1822786593238646 116451:116451 hsa_agent_get_info(<agent 0x13ff770>, 40962, 0x143d0f8) = 0
|
||||
1822786593239416:1822786593240136 116451:116451 hsa_agent_get_info(<agent 0x13ff770>, 40970, 0x143d0fc) = 0
|
||||
1822786593240946:1822786593241526 116451:116451 hsa_agent_get_info(<agent 0x13ff770>, 40971, 0x143d100) = 0
|
||||
1822786593242296:1822786593242886 116451:116451 hsa_agent_get_info(<agent 0x13ff770>, 40972, 0x143d104) = 0
|
||||
1822786593243666:1822786593244246 116451:116451 hsa_agent_get_info(<agent 0x13ff770>, 40973, 0x143d108) = 0
|
||||
1822786593245736:1822786593246326 116451:116451 hsa_amd_memory_pool_get_info(<amd_memory_pool>, 0, 0x7ffd08170de8) = 0
|
||||
1822786593247096:1822786593247676 116451:116451 hsa_amd_memory_pool_get_info(<amd_memory_pool>, 1, 0x7ffd08170dec) = 0
|
||||
1822786593247096:1822786593248456 116451:116451 hsa_amd_agent_iterate_memory_pools(<agent 0x13ff770>, 1, 0x143d0e8) = 1
|
||||
1822786593247096:1822786593250036 116451:116451 hsa_iterate_agents(1, 0x13fd320) = 0
|
||||
1822786593251826:1822786593416117 116451:116451 hsa_system_get_extension_table(<uint16_t 0x202>, <uint16_t 0x1>, <uint16_t 0x0>, 0x13fd3b8) = 0
|
||||
1822786593417707:1822786593420377 116451:116451 hsa_system_get_extension_table(<uint16_t 0x201>, <uint16_t 0x1>, <uint16_t 0x0>, 0x13fd408) = 0
|
||||
1822786593422447:1822786593423047 116451:116451 hsa_system_get_info(3, 0x7ffd08171128) = 0
|
||||
1822786593658778:1822786608352362 116451:116459 hsa_queue_create(<agent 0x13ff770>, <uint32_t 0x80>, <uint32_t 0x0>, 0, 0, <uint32_t 0xffffffff>, <uint32_t 0xffffffff>, <queue 0x1102d0e9006a>) = 0
|
||||
1822786902531377:1822786902535757 116451:116459 hsa_signal_create(1, <uint32_t 0x0>, 0, 0x7fa610001f20) = 0
|
||||
1822786902571037:1822786902584537 116451:116459 hsa_code_object_reader_create_from_file(5, 0x7fa665ffcbe0) = 0
|
||||
1822786902586167:1822786902597097 116451:116459 hsa_executable_create_alt(1, 0,
|
||||
1822786902598597:1822786902965610 116451:116459 hsa_executable_load_agent_code_object(<executable>, <agent 0x13ff770>, <code_object_reader>,
|
||||
1822786902967780:1822786903353172 116451:116459 hsa_executable_freeze(<executable>, ) = 0
|
||||
1822786903355162:1822786903356442 116451:116459 hsa_executable_get_symbol(<executable>,
|
||||
1822786903362512:1822786903363052 116451:116459 hsa_executable_symbol_get_info(<executable_symbol>, 13, 0x7fa665ffcc44) = 0
|
||||
1822786903363492:1822786903363782 116451:116459 hsa_executable_symbol_get_info(<executable_symbol>, 14, 0x7fa665ffcc48) = 0
|
||||
1822786903364172:1822786903364492 116451:116459 hsa_executable_symbol_get_info(<executable_symbol>, 22, 0x7fa665ffcc58) = 0
|
||||
1822786903365702:1822786903366022 116451:116459 hsa_signal_store_relaxed(<signal 0x7fa7a2d2cc80>, 1) = void
|
||||
1822786903370912:1822786903371252 116451:116459 hsa_queue_load_write_index_relaxed(0x7fa7a2ce1000) = 0
|
||||
1822786903372632:1822786903372942 116451:116459 hsa_queue_store_write_index_relaxed(0x7fa7a2ce1000, <uint64_t 0x1>) = void
|
||||
1822786903374072:1822786903374512 116451:116459 hsa_queue_load_read_index_relaxed(0x7fa7a2ce1000) = 0
|
||||
1822786903375092:1822786903375562 116451:116459 hsa_signal_store_relaxed(<signal 0x7fa7a2d2cd80>, 0) = void
|
||||
1822786903379112:1822786903393132 116451:116459 hsa_signal_wait_scacquire(<signal 0x7fa7a2d2cc80>, 2, 1, <uint64_t 0xffffffffffffffff>, 0) = 0
|
||||
1822786903425033:1822786903474693 116451:116459 hsa_executable_destroy(<executable>) = 0
|
||||
1822786903475683:1822786903476973 116451:116459 hsa_signal_destroy(<signal 0x7fa7a2d2cc80>) = 0
|
||||
1822787197612807:1822787197613567 116451:116459 hsa_signal_create(1, <uint32_t 0x0>, 0, 0x7fa610007340) = 0
|
||||
1822787197622077:1822787197628137 116451:116459 hsa_code_object_reader_create_from_file(7, 0x7fa665ffcbe0) = 0
|
||||
1822787197628677:1822787197629627 116451:116459 hsa_executable_create_alt(1, 0,
|
||||
1822787197630087:1822787197791048 116451:116459 hsa_executable_load_agent_code_object(<executable>, <agent 0x13ff770>, <code_object_reader>,
|
||||
1822787197792018:1822787197833668 116451:116459 hsa_executable_freeze(<executable>, ) = 0
|
||||
1822787197834218:1822787197839559 116451:116459 hsa_executable_get_symbol(<executable>,
|
||||
1822787197841769:1822787197856699 116451:116459 hsa_amd_memory_pool_allocate(<amd_memory_pool>, <uint64_t 0x4000>, <uint32_t 0x0>, 0x7fa665ffcc68) = 0
|
||||
1822787197858079:1822787197924589 116451:116459 hsa_amd_agents_allow_access(<uint32_t 0x1>, 0x7fa665ffcc70, 0, 0x7fa7a2cc4000) = 0
|
||||
1822787197926269:1822787197927179 116451:116459 hsa_amd_memory_pool_allocate(<amd_memory_pool>, <uint64_t 0x4000>, <uint32_t 0x0>, 0x7fa665ffcc70) = 0
|
||||
1822787197927659:1822787197939219 116451:116459 hsa_amd_memory_pool_allocate(<amd_memory_pool>, <uint64_t 0x1000>, <uint32_t 0x0>, 0x7fa665ffcc68) = 0
|
||||
1822787197939719:1822787197992339 116451:116459 hsa_amd_agents_allow_access(<uint32_t 0x1>, 0x7fa665ffcc70, 0, 0x7fa7a2cd6000) = 0
|
||||
1822787197993039:1822787197993399 116451:116459 hsa_executable_symbol_get_info(<executable_symbol>, 11, 0x7fa665ffcca0) = 0
|
||||
1822787197995009:1822787198005070 116451:116459 hsa_amd_memory_pool_allocate(<amd_memory_pool>, <uint64_t 0x1000>, <uint32_t 0x0>, 0x7fa665ffcc68) = 0
|
||||
1822787198005560:1822787198054310 116451:116459 hsa_amd_agents_allow_access(<uint32_t 0x1>, 0x7fa665ffcc70, 0, 0x7fa7a2cd4000) = 0
|
||||
1822787198222651:1822787198223061 116451:116459 hsa_executable_symbol_get_info(<executable_symbol>, 13, 0x7fa665ffcc44) = 0
|
||||
1822787198223531:1822787198223831 116451:116459 hsa_executable_symbol_get_info(<executable_symbol>, 14, 0x7fa665ffcc48) = 0
|
||||
1822787198224221:1822787198224531 116451:116459 hsa_executable_symbol_get_info(<executable_symbol>, 22, 0x7fa665ffcc58) = 0
|
||||
1822787198224991:1822787198225351 116451:116459 hsa_signal_store_relaxed(<signal 0x7fa7a2d2cc80>, 1) = void
|
||||
1822787198228821:1822787198229191 116451:116459 hsa_queue_load_write_index_relaxed(0x7fa7a2ce1000) = 1
|
||||
1822787198229651:1822787198229961 116451:116459 hsa_queue_store_write_index_relaxed(0x7fa7a2ce1000, <uint64_t 0x2>) = void
|
||||
1822787198230421:1822787198230851 116451:116459 hsa_queue_load_read_index_relaxed(0x7fa7a2ce1000) = 1
|
||||
1822787198231381:1822787198231871 116451:116459 hsa_signal_store_relaxed(<signal 0x7fa7a2d2cd80>, 1) = void
|
||||
1822787198234591:1822787198268311 116451:116459 hsa_signal_wait_scacquire(<signal 0x7fa7a2d2cc80>, 2, 1, <uint64_t 0xffffffffffffffff>, 0) = 0
|
||||
1822787198271101:1822787198289651 116451:116459 hsa_amd_memory_pool_allocate(<amd_memory_pool>, <uint64_t 0x4000>, <uint32_t 0x0>, 0x7fa665ffcc68) = 0
|
||||
1822787198290261:1822787198347092 116451:116459 hsa_amd_agents_allow_access(<uint32_t 0x1>, 0x7fa665ffcc70, 0, 0x7fa7a2c78000) = 0
|
||||
1822787198347792:1822787198349312 116451:116459 hsa_signal_create(1, <uint32_t 0x0>, 0, 0x7fa665ffcc40) = 0
|
||||
1822787198356932:1822787198357642 116451:116459 hsa_agent_get_info(<agent 0x14290e0>, 17, 0x7fa665ffc7bc) = 0
|
||||
1822787198359432:1822787198360132 116451:116459 hsa_amd_memory_pool_get_info(<amd_memory_pool>, 0, 0x7fa665ffc658) = 0
|
||||
1822787198360542:1822787198360842 116451:116459 hsa_amd_memory_pool_get_info(<amd_memory_pool>, 1, 0x7fa665ffc65c) = 0
|
||||
1822787198361262:1822787198361552 116451:116459 hsa_amd_memory_pool_get_info(<amd_memory_pool>, 0, 0x7fa665ffc658) = 0
|
||||
1822787198361942:1822787198362232 116451:116459 hsa_amd_memory_pool_get_info(<amd_memory_pool>, 1, 0x7fa665ffc65c) = 0
|
||||
1822787198361942:1822787198362632 116451:116459 hsa_amd_agent_iterate_memory_pools(<agent 0x14290e0>, 1, 0x7fa610006d60) = 1
|
||||
1822787198363522:1822787198363812 116451:116459 hsa_amd_memory_pool_get_info(<amd_memory_pool>, 0, 0x7fa665ffc658) = 0
|
||||
1822787198364212:1822787198364502 116451:116459 hsa_amd_memory_pool_get_info(<amd_memory_pool>, 1, 0x7fa665ffc65c) = 0
|
||||
1822787198364212:1822787198364892 116451:116459 hsa_amd_agent_iterate_memory_pools(<agent 0x14290e0>, 1, 0x7fa610006d70) = 1
|
||||
1822787198365732:1822787198366072 116451:116459 hsa_agent_get_info(<agent 0x13ff770>, 17, 0x7fa665ffc7bc) = 0
|
||||
1822787198366522:1822787198369532 116451:116459 hsa_agent_get_info(<agent 0x13ff770>, 0, 0x7fa610006e34) = 0
|
||||
1822787198372162:1822787198372472 116451:116459 hsa_agent_get_info(<agent 0x13ff770>, 6, 0x7fa610006e74) = 0
|
||||
1822787198372872:1822787198373172 116451:116459 hsa_agent_get_info(<agent 0x13ff770>, 14, 0x7fa610006e78) = 0
|
||||
1822787198373572:1822787198373862 116451:116459 hsa_agent_get_info(<agent 0x13ff770>, 4, 0x7fa610006e7c) = 0
|
||||
1822787198374262:1822787198374572 116451:116459 hsa_agent_get_info(<agent 0x13ff770>, 40962, 0x7fa610006e98) = 0
|
||||
1822787198375892:1822787198376202 116451:116459 hsa_agent_get_info(<agent 0x13ff770>, 40970, 0x7fa610006e9c) = 0
|
||||
1822787198376692:1822787198376992 116451:116459 hsa_agent_get_info(<agent 0x13ff770>, 40971, 0x7fa610006ea0) = 0
|
||||
1822787198377392:1822787198377692 116451:116459 hsa_agent_get_info(<agent 0x13ff770>, 40972, 0x7fa610006ea4) = 0
|
||||
1822787198378092:1822787198378392 116451:116459 hsa_agent_get_info(<agent 0x13ff770>, 40973, 0x7fa610006ea8) = 0
|
||||
1822787198379162:1822787198379462 116451:116459 hsa_amd_memory_pool_get_info(<amd_memory_pool>, 0, 0x7fa665ffc648) = 0
|
||||
1822787198379852:1822787198380152 116451:116459 hsa_amd_memory_pool_get_info(<amd_memory_pool>, 1, 0x7fa665ffc64c) = 0
|
||||
1822787198379852:1822787198380542 116451:116459 hsa_amd_agent_iterate_memory_pools(<agent 0x13ff770>, 1, 0x7fa610006e88) = 1
|
||||
1822787198379852:1822787198381142 116451:116459 hsa_iterate_agents(1, 0x7fa610006980) = 0
|
||||
1822787198381692:1822787198397632 116451:116459 hsa_system_get_major_extension_table(<uint16_t 0x202>, <uint16_t 0x1>, <uint64_t 0x50>, 0x7fa610006a18) = 0
|
||||
1822787198398112:1822787198398412 116451:116459 hsa_system_get_major_extension_table(<uint16_t 0x201>, <uint16_t 0x1>, <uint64_t 0x18>, 0x7fa610006a68) = 0
|
||||
1822787198399032:1822787198399332 116451:116459 hsa_system_get_info(3, 0x7fa665ffc988) = 0
|
||||
1822787198399782:1822787198400322 116451:116459 hsa_system_get_info(2, 0x7fa665ffc9d0) = 0
|
||||
1822787198400762:1822787198401922 116451:116459 hsa_signal_create(1, <uint32_t 0x0>, 0, 0x7fa68f797050) = 0
|
||||
1822787198402472:1822787198405132 116451:116459 hsa_amd_signal_async_handler(<signal 0x7fa7a2d2cb00>, 2, 1, 1, 0x7fa68f797010) = 0
|
||||
1822787198405752:1822787198837475 116451:116459 hsa_amd_memory_async_copy(0x7fa7a2c78000, <agent 0x14290e0>, 0x7fa688203000, <agent 0x13ff770>, <uint64_t 0x4000>, <uint32_t 0x0>, 0, <signal 0x7fa7a2d2cb00>) = 0
|
||||
1822787198931945:1822787198941165 116451:116454 hsa_amd_profiling_get_async_copy_time(<signal 0x7fa7a2d2cb00>, 0x7fa7a092bc40) = 0
|
||||
1822787198944925:1822787198946035 116451:116454 hsa_system_get_info(2, 0x7fa7a092bc38) = 0
|
||||
1822787198947005:1822787198948155 116451:116454 hsa_signal_load_relaxed(<signal 0x7fa7a2d2cb80>) = 1
|
||||
1822787198838365:1822787198950945 116451:116459 hsa_signal_wait_scacquire(<signal 0x7fa7a2d2cb80>, 2, 1, <uint64_t 0xffffffffffffffff>, 0) = 0
|
||||
1822787198949035:1822787198951965 116451:116454 hsa_signal_store_screlease(<signal 0x7fa7a2d2cb80>, 0) = void
|
||||
1822787198952535:1822787198953995 116451:116459 hsa_signal_destroy(<signal 0x7fa7a2d2cb80>) = 0
|
||||
1822787198953835:1822787198955305 116451:116454 hsa_signal_destroy(<signal 0x7fa7a2d2cb00>) = 0
|
||||
1822787199054396:1822787199072966 116451:116459 hsa_memory_free(0x7fa7a2c78000) = 0
|
||||
1822787199096536:1822787199113536 116451:116459 hsa_executable_destroy(<executable>) = 0
|
||||
1822787199114426:1822787199116066 116451:116459 hsa_signal_destroy(<signal 0x7fa7a2d2cc80>) = 0
|
||||
1822787199118006:1822787200339674 116451:116459 hsa_queue_destroy(<queue 0x7fa7a2ce1000>) = 0
|
||||
|
||||
-1
@@ -1,4 +1,3 @@
|
||||
standalone C test: "LD_PRELOAD=libkfdwrapper64.so ./test/MatrixTranspose_ctest"
|
||||
# INIT #############################
|
||||
# START (99) #############################
|
||||
<rocTX "before hipLaunchKernel">
|
||||
@@ -0,0 +1,412 @@
|
||||
ROCTracer (pid=26066):
|
||||
ROCTracer: trace control flush rate(100000us)
|
||||
HIP-trace()
|
||||
ROCTracer (pid=26066):
|
||||
ROCTracer: trace control flush rate(100000us)
|
||||
HIP-trace()
|
||||
Device name Ellesmere [Radeon RX 470/480/570/570X/580/580X]
|
||||
## Iteration (99) #################
|
||||
43934932418043:43934932456496 26066:26066 hipGetDeviceProperties()
|
||||
43934934626423:43934934675542 26066:26066 hipMalloc(ptr(0x902800000) size(0x400000))
|
||||
43934934677103:43934934698784 26066:26066 hipMalloc(ptr(0x903000000) size(0x400000))
|
||||
43934934708976:43934940336620 26066:26066 hipMemcpy(dst(0x902800000) src(0x1384170) size(0x400000) kind(1))
|
||||
43934940338871:43934940338872 26066:26066 MARK(name(before HIP LaunchKernel))
|
||||
43935225511780:43935227349863 0:0 hcCommandKernel:6
|
||||
43935227358980:43935227395780 0:0 hcCommandMarker:8
|
||||
PASSED!
|
||||
## Iteration (98) #################
|
||||
PASSED!
|
||||
## Iteration (97) #################
|
||||
PASSED!
|
||||
## Iteration (96) #################
|
||||
PASSED!
|
||||
## Iteration (95) #################
|
||||
PASSED!
|
||||
## Iteration (94) #################
|
||||
43935243433550:43935245268113 0:0 hcCommandKernel:11
|
||||
43935245270936:43935245302936 0:0 hcCommandMarker:13
|
||||
43935261086822:43935262934346 0:0 hcCommandKernel:16
|
||||
43935262937310:43935262969310 0:0 hcCommandMarker:18
|
||||
43935278843800:43935280686843 0:0 hcCommandKernel:21
|
||||
43935280690009:43935280722009 0:0 hcCommandMarker:23
|
||||
43935296495925:43935298337528 0:0 hcCommandKernel:26
|
||||
43935298340338:43935298371858 0:0 hcCommandMarker:28
|
||||
43935314291986:43935316140949 0:0 hcCommandKernel:31
|
||||
43935316144062:43935316175422 0:0 hcCommandMarker:33
|
||||
PASSED!
|
||||
## Iteration (93) #################
|
||||
PASSED!
|
||||
## Iteration (92) #################
|
||||
PASSED!
|
||||
## Iteration (91) #################
|
||||
PASSED!
|
||||
## Iteration (90) #################
|
||||
PASSED!
|
||||
## Iteration (89) #################
|
||||
43935332066943:43935333908066 0:0 hcCommandKernel:36
|
||||
43935333911153:43935333942513 0:0 hcCommandMarker:38
|
||||
43935350038934:43935351880697 0:0 hcCommandKernel:41
|
||||
43935351883641:43935351915001 0:0 hcCommandMarker:43
|
||||
43935367793257:43935369638700 0:0 hcCommandKernel:46
|
||||
43935369641744:43935369673104 0:0 hcCommandMarker:48
|
||||
43935385528005:43935387375368 0:0 hcCommandKernel:51
|
||||
43935387378362:43935387409722 0:0 hcCommandMarker:53
|
||||
43935403309412:43935405152295 0:0 hcCommandKernel:56
|
||||
43935405155209:43935405186569 0:0 hcCommandMarker:58
|
||||
PASSED!
|
||||
## Iteration (88) #################
|
||||
43935421119359:43935422961442 0:0 hcCommandKernel:61
|
||||
43935422964474:43935422995834 0:0 hcCommandMarker:63
|
||||
PASSED!
|
||||
## Iteration (87) #################
|
||||
PASSED!
|
||||
## Iteration (86) #################
|
||||
PASSED!
|
||||
## Iteration (85) #################
|
||||
PASSED!
|
||||
## Iteration (84) #################
|
||||
PASSED!
|
||||
## Iteration (83) #################
|
||||
43935438844897:43935440686660 0:0 hcCommandKernel:66
|
||||
43935440689713:43935440721393 0:0 hcCommandMarker:68
|
||||
43935456490502:43935458334505 0:0 hcCommandKernel:71
|
||||
43935458337617:43935458368977 0:0 hcCommandMarker:73
|
||||
43935474147631:43935475986514 0:0 hcCommandKernel:76
|
||||
43935475989587:43935476020947 0:0 hcCommandMarker:78
|
||||
43935491854358:43935492341878 0:0 hcCommandKernel:81
|
||||
43935492345644:43935492352044 0:0 hcCommandMarker:83
|
||||
43935508126004:43935508605044 0:0 hcCommandKernel:86
|
||||
43935508608028:43935508614588 0:0 hcCommandMarker:88
|
||||
PASSED!
|
||||
## Iteration (82) #################
|
||||
43935524418876:43935524907836 0:0 hcCommandKernel:91
|
||||
43935524910557:43935524917117 0:0 hcCommandMarker:93
|
||||
PASSED!
|
||||
## Iteration (81) #################
|
||||
PASSED!
|
||||
## Iteration (80) #################
|
||||
PASSED!
|
||||
## Iteration (79) #################
|
||||
PASSED!
|
||||
## Iteration (78) #################
|
||||
PASSED!
|
||||
## Iteration (77) #################
|
||||
43935540719417:43935541208217 0:0 hcCommandKernel:96
|
||||
43935541211437:43935541217997 0:0 hcCommandMarker:98
|
||||
43935556967811:43935557454211 0:0 hcCommandKernel:101
|
||||
43935557457796:43935557464356 0:0 hcCommandMarker:103
|
||||
43935573251751:43935573737511 0:0 hcCommandKernel:106
|
||||
43935573740418:43935573746978 0:0 hcCommandMarker:108
|
||||
43935589528260:43935590013700 0:0 hcCommandKernel:111
|
||||
43935590017484:43935590024044 0:0 hcCommandMarker:113
|
||||
43935605722549:43935606210549 0:0 hcCommandKernel:116
|
||||
43935606213595:43935606220155 0:0 hcCommandMarker:118
|
||||
PASSED!
|
||||
## Iteration (76) #################
|
||||
43935621981951:43935622472991 0:0 hcCommandKernel:121
|
||||
43935622476644:43935622483204 0:0 hcCommandMarker:123
|
||||
PASSED!
|
||||
## Iteration (75) #################
|
||||
PASSED!
|
||||
## Iteration (74) #################
|
||||
PASSED!
|
||||
## Iteration (73) #################
|
||||
PASSED!
|
||||
## Iteration (72) #################
|
||||
PASSED!
|
||||
## Iteration (71) #################
|
||||
43935638193139:43935638675859 0:0 hcCommandKernel:126
|
||||
43935638678816:43935638685216 0:0 hcCommandMarker:128
|
||||
43935654459215:43935654944496 0:0 hcCommandKernel:131
|
||||
43935654952142:43935654958862 0:0 hcCommandMarker:133
|
||||
43935670702708:43935671183508 0:0 hcCommandKernel:136
|
||||
43935671186548:43935671193108 0:0 hcCommandMarker:138
|
||||
43935686939367:43935687417768 0:0 hcCommandKernel:141
|
||||
43935687425608:43935687432168 0:0 hcCommandMarker:143
|
||||
43935703168285:43935703658045 0:0 hcCommandKernel:146
|
||||
43935703661042:43935703667442 0:0 hcCommandMarker:148
|
||||
PASSED!
|
||||
## Iteration (70) #################
|
||||
43935719453292:43935719944172 0:0 hcCommandKernel:151
|
||||
43935719947859:43935719954419 0:0 hcCommandMarker:153
|
||||
PASSED!
|
||||
## Iteration (69) #################
|
||||
PASSED!
|
||||
## Iteration (68) #################
|
||||
PASSED!
|
||||
## Iteration (67) #################
|
||||
PASSED!
|
||||
## Iteration (66) #################
|
||||
PASSED!
|
||||
## Iteration (65) #################
|
||||
43935735726735:43935736208335 0:0 hcCommandKernel:156
|
||||
43935736212026:43935736218586 0:0 hcCommandMarker:158
|
||||
43935751921190:43935752410790 0:0 hcCommandKernel:161
|
||||
43935752414441:43935752421001 0:0 hcCommandMarker:163
|
||||
43935768118205:43935768606045 0:0 hcCommandKernel:166
|
||||
43935768608995:43935768615555 0:0 hcCommandMarker:168
|
||||
43935784195088:43935784686608 0:0 hcCommandKernel:171
|
||||
43935784689436:43935784695996 0:0 hcCommandMarker:173
|
||||
43935800433600:43935800920160 0:0 hcCommandKernel:176
|
||||
43935800923246:43935800929646 0:0 hcCommandMarker:178
|
||||
PASSED!
|
||||
## Iteration (64) #################
|
||||
43935816699624:43935817182024 0:0 hcCommandKernel:181
|
||||
43935817187808:43935817194368 0:0 hcCommandMarker:183
|
||||
PASSED!
|
||||
## Iteration (63) #################
|
||||
PASSED!
|
||||
## Iteration (62) #################
|
||||
PASSED!
|
||||
## Iteration (61) #################
|
||||
PASSED!
|
||||
## Iteration (60) #################
|
||||
PASSED!
|
||||
## Iteration (59) #################
|
||||
43935832969893:43935833459333 0:0 hcCommandKernel:186
|
||||
43935833462980:43935833469540 0:0 hcCommandMarker:188
|
||||
43935849246062:43935851077905 0:0 hcCommandKernel:191
|
||||
43935851080726:43935851112246 0:0 hcCommandMarker:193
|
||||
43935866982020:43935868823143 0:0 hcCommandKernel:196
|
||||
43935868826123:43935868857483 0:0 hcCommandMarker:198
|
||||
43935884647922:43935886487605 0:0 hcCommandKernel:201
|
||||
43935886490571:43935886521931 0:0 hcCommandMarker:203
|
||||
43935902402549:43935904242232 0:0 hcCommandKernel:206
|
||||
43935904245256:43935904276776 0:0 hcCommandMarker:208
|
||||
PASSED!
|
||||
## Iteration (58) #################
|
||||
43935920062038:43935921897081 0:0 hcCommandKernel:211
|
||||
43935921900164:43935921931524 0:0 hcCommandMarker:213
|
||||
PASSED!
|
||||
## Iteration (57) #################
|
||||
PASSED!
|
||||
## Iteration (56) #################
|
||||
PASSED!
|
||||
## Iteration (55) #################
|
||||
PASSED!
|
||||
## Iteration (54) #################
|
||||
PASSED!
|
||||
## Iteration (53) #################
|
||||
43935937812069:43935939657512 0:0 hcCommandKernel:216
|
||||
43935939660443:43935939691803 0:0 hcCommandMarker:218
|
||||
43935955484682:43935957328525 0:0 hcCommandKernel:221
|
||||
43935957331582:43935957362942 0:0 hcCommandMarker:223
|
||||
43935973218819:43935975058982 0:0 hcCommandKernel:226
|
||||
43935975061799:43935975093159 0:0 hcCommandMarker:228
|
||||
43935990920488:43935992758411 0:0 hcCommandKernel:231
|
||||
43935992761237:43935992792757 0:0 hcCommandMarker:233
|
||||
43936008544679:43936010384682 0:0 hcCommandKernel:236
|
||||
43936010389056:43936010420416 0:0 hcCommandMarker:238
|
||||
PASSED!
|
||||
## Iteration (52) #################
|
||||
43936026228358:43936028068841 0:0 hcCommandKernel:241
|
||||
43936028072005:43936028103685 0:0 hcCommandMarker:243
|
||||
PASSED!
|
||||
## Iteration (51) #################
|
||||
PASSED!
|
||||
## Iteration (50) #################
|
||||
PASSED!
|
||||
## Iteration (49) #################
|
||||
PASSED!
|
||||
## Iteration (48) #################
|
||||
PASSED!
|
||||
## Iteration (47) #################
|
||||
43936043785925:43936045629448 0:0 hcCommandKernel:246
|
||||
43936045632305:43936045663985 0:0 hcCommandMarker:248
|
||||
43936061522848:43936063368291 0:0 hcCommandKernel:251
|
||||
43936063371344:43936063402864 0:0 hcCommandMarker:253
|
||||
43936079184681:43936081031404 0:0 hcCommandKernel:256
|
||||
43936081034470:43936081065830 0:0 hcCommandMarker:258
|
||||
43936096912019:43936098088660 0:0 hcCommandKernel:261
|
||||
43936098091778:43936098098338 0:0 hcCommandMarker:263
|
||||
43936113848983:43936114331063 0:0 hcCommandKernel:266
|
||||
43936114334738:43936114341298 0:0 hcCommandMarker:268
|
||||
PASSED!
|
||||
## Iteration (46) #################
|
||||
43936130207157:43936130701557 0:0 hcCommandKernel:271
|
||||
43936130704352:43936130710912 0:0 hcCommandMarker:273
|
||||
PASSED!
|
||||
## Iteration (45) #################
|
||||
PASSED!
|
||||
## Iteration (44) #################
|
||||
PASSED!
|
||||
## Iteration (43) #################
|
||||
PASSED!
|
||||
## Iteration (42) #################
|
||||
PASSED!
|
||||
## Iteration (41) #################
|
||||
43936146563182:43936147046062 0:0 hcCommandKernel:276
|
||||
43936147049151:43936147055711 0:0 hcCommandMarker:278
|
||||
43936162894728:43936163374888 0:0 hcCommandKernel:281
|
||||
43936163377872:43936163384592 0:0 hcCommandMarker:283
|
||||
43936179200342:43936179687382 0:0 hcCommandKernel:286
|
||||
43936179691196:43936179697756 0:0 hcCommandMarker:288
|
||||
43936195476376:43936195958456 0:0 hcCommandKernel:291
|
||||
43936195961532:43936195968092 0:0 hcCommandMarker:293
|
||||
43936211754702:43936212238862 0:0 hcCommandKernel:296
|
||||
43936212241993:43936212248553 0:0 hcCommandMarker:298
|
||||
PASSED!
|
||||
## Iteration (40) #################
|
||||
43936228051680:43936228530400 0:0 hcCommandKernel:301
|
||||
43936228534046:43936228540606 0:0 hcCommandMarker:303
|
||||
PASSED!
|
||||
## Iteration (39) #################
|
||||
PASSED!
|
||||
## Iteration (38) #################
|
||||
PASSED!
|
||||
## Iteration (37) #################
|
||||
PASSED!
|
||||
## Iteration (36) #################
|
||||
PASSED!
|
||||
## Iteration (35) #################
|
||||
43936244268347:43936244752187 0:0 hcCommandKernel:306
|
||||
43936244759707:43936244766107 0:0 hcCommandMarker:308
|
||||
43936260465746:43936260949906 0:0 hcCommandKernel:311
|
||||
43936260953781:43936260960181 0:0 hcCommandMarker:313
|
||||
43936276704103:43936277186183 0:0 hcCommandKernel:316
|
||||
43936277189819:43936277196379 0:0 hcCommandMarker:318
|
||||
43936292908367:43936293394927 0:0 hcCommandKernel:321
|
||||
43936293398665:43936293405065 0:0 hcCommandMarker:323
|
||||
43936309159941:43936309655781 0:0 hcCommandKernel:326
|
||||
43936309658663:43936309665223 0:0 hcCommandMarker:328
|
||||
PASSED!
|
||||
## Iteration (34) #################
|
||||
43936325491676:43936325977116 0:0 hcCommandKernel:331
|
||||
43936325980102:43936325986662 0:0 hcCommandMarker:333
|
||||
PASSED!
|
||||
## Iteration (33) #################
|
||||
PASSED!
|
||||
## Iteration (32) #################
|
||||
PASSED!
|
||||
## Iteration (31) #################
|
||||
PASSED!
|
||||
## Iteration (30) #################
|
||||
PASSED!
|
||||
## Iteration (29) #################
|
||||
43936341856430:43936342339790 0:0 hcCommandKernel:336
|
||||
43936342342883:43936342349283 0:0 hcCommandMarker:338
|
||||
43936358065666:43936358544706 0:0 hcCommandKernel:341
|
||||
43936358548573:43936358554973 0:0 hcCommandMarker:343
|
||||
43936374226834:43936374711954 0:0 hcCommandKernel:346
|
||||
43936374714957:43936374721517 0:0 hcCommandMarker:348
|
||||
43936390393107:43936390876947 0:0 hcCommandKernel:351
|
||||
43936390879989:43936390886549 0:0 hcCommandMarker:353
|
||||
43936406478567:43936406968327 0:0 hcCommandKernel:356
|
||||
43936406971190:43936406977750 0:0 hcCommandMarker:358
|
||||
PASSED!
|
||||
## Iteration (28) #################
|
||||
43936422759883:43936423242603 0:0 hcCommandKernel:361
|
||||
43936423245282:43936423251842 0:0 hcCommandMarker:363
|
||||
PASSED!
|
||||
## Iteration (27) #################
|
||||
PASSED!
|
||||
## Iteration (26) #################
|
||||
PASSED!
|
||||
## Iteration (25) #################
|
||||
PASSED!
|
||||
## Iteration (24) #################
|
||||
PASSED!
|
||||
## Iteration (23) #################
|
||||
43936439030746:43936439514266 0:0 hcCommandKernel:366
|
||||
43936439518052:43936439524612 0:0 hcCommandMarker:368
|
||||
43936455234140:43936455719900 0:0 hcCommandKernel:371
|
||||
43936455722741:43936455729141 0:0 hcCommandMarker:373
|
||||
43936471535617:43936473377220 0:0 hcCommandKernel:376
|
||||
43936473379982:43936473411502 0:0 hcCommandMarker:378
|
||||
43936489194662:43936491033065 0:0 hcCommandKernel:381
|
||||
43936491035944:43936491067304 0:0 hcCommandMarker:383
|
||||
43936506844418:43936508676581 0:0 hcCommandKernel:386
|
||||
43936508679657:43936508711177 0:0 hcCommandMarker:388
|
||||
PASSED!
|
||||
## Iteration (22) #################
|
||||
43936524587883:43936526420846 0:0 hcCommandKernel:391
|
||||
43936526423835:43936526455195 0:0 hcCommandMarker:393
|
||||
PASSED!
|
||||
## Iteration (21) #################
|
||||
PASSED!
|
||||
## Iteration (20) #################
|
||||
PASSED!
|
||||
## Iteration (19) #################
|
||||
PASSED!
|
||||
## Iteration (18) #################
|
||||
PASSED!
|
||||
## Iteration (17) #################
|
||||
43936542246761:43936544088524 0:0 hcCommandKernel:396
|
||||
43936544091588:43936544123268 0:0 hcCommandMarker:398
|
||||
43936559948159:43936561794402 0:0 hcCommandKernel:401
|
||||
43936561797239:43936561828759 0:0 hcCommandMarker:403
|
||||
43936577605213:43936579448896 0:0 hcCommandKernel:406
|
||||
43936579451894:43936579483254 0:0 hcCommandMarker:408
|
||||
43936595369090:43936597208613 0:0 hcCommandKernel:411
|
||||
43936597211572:43936597242932 0:0 hcCommandMarker:413
|
||||
43936613017192:43936614856075 0:0 hcCommandKernel:416
|
||||
43936614859107:43936614890467 0:0 hcCommandMarker:418
|
||||
PASSED!
|
||||
## Iteration (16) #################
|
||||
43936630770153:43936632618476 0:0 hcCommandKernel:421
|
||||
43936632621411:43936632653091 0:0 hcCommandMarker:423
|
||||
PASSED!
|
||||
## Iteration (15) #################
|
||||
PASSED!
|
||||
## Iteration (14) #################
|
||||
PASSED!
|
||||
## Iteration (13) #################
|
||||
PASSED!
|
||||
## Iteration (12) #################
|
||||
43936648421451:43936650272014 0:0 hcCommandKernel:426
|
||||
43936650274717:43936650306397 0:0 hcCommandMarker:428
|
||||
43936666186176:43936668028259 0:0 hcCommandKernel:431
|
||||
43936668031033:43936668062553 0:0 hcCommandMarker:433
|
||||
43936683847105:43936685694788 0:0 hcCommandKernel:436
|
||||
43936685697850:43936685729530 0:0 hcCommandMarker:438
|
||||
43936701611894:43936703454617 0:0 hcCommandKernel:441
|
||||
43936703457617:43936703488977 0:0 hcCommandMarker:443
|
||||
PASSED!
|
||||
## Iteration (11) #################
|
||||
43936719264608:43936719749728 0:0 hcCommandKernel:446
|
||||
43936719752843:43936719759403 0:0 hcCommandMarker:448
|
||||
PASSED!
|
||||
## Iteration (10) #################
|
||||
PASSED!
|
||||
## Iteration (9) #################
|
||||
PASSED!
|
||||
## Iteration (8) #################
|
||||
PASSED!
|
||||
## Iteration (7) #################
|
||||
PASSED!
|
||||
## Iteration (6) #################
|
||||
PASSED!
|
||||
## Iteration (5) #################
|
||||
43936735528823:43936736005623 0:0 hcCommandKernel:451
|
||||
43936736008904:43936736015464 0:0 hcCommandMarker:453
|
||||
43936751784154:43936752265434 0:0 hcCommandKernel:456
|
||||
43936752268477:43936752274877 0:0 hcCommandMarker:458
|
||||
43936768038508:43936768522508 0:0 hcCommandKernel:461
|
||||
43936768526347:43936768532907 0:0 hcCommandMarker:463
|
||||
43936784289295:43936784779215 0:0 hcCommandKernel:466
|
||||
43936784782982:43936784789542 0:0 hcCommandMarker:468
|
||||
43936800538297:43936801016857 0:0 hcCommandKernel:471
|
||||
43936801019748:43936801026468 0:0 hcCommandMarker:473
|
||||
PASSED!
|
||||
## Iteration (4) #################
|
||||
43936816815614:43936817294654 0:0 hcCommandKernel:476
|
||||
43936817297320:43936817303880 0:0 hcCommandMarker:478
|
||||
PASSED!
|
||||
## Iteration (3) #################
|
||||
PASSED!
|
||||
## Iteration (2) #################
|
||||
PASSED!
|
||||
## Iteration (1) #################
|
||||
PASSED!
|
||||
## Iteration (0) #################
|
||||
43936833089833:43936833579433 0:0 hcCommandKernel:481
|
||||
43936833582286:43936833588846 0:0 hcCommandMarker:483
|
||||
43936849646904:43936850132504 0:0 hcCommandKernel:486
|
||||
43936850135326:43936850141886 0:0 hcCommandMarker:488
|
||||
43936867294430:43936867780350 0:0 hcCommandKernel:491
|
||||
43936867783055:43936867789615 0:0 hcCommandMarker:493
|
||||
43936884613213:43936885103133 0:0 hcCommandKernel:496
|
||||
43936885106028:43936885112748 0:0 hcCommandMarker:498
|
||||
43936901844607:43936902331647 0:0 hcCommandKernel:501
|
||||
43936902334630:43936902341030 0:0 hcCommandMarker:503
|
||||
PASSED!
|
||||
@@ -0,0 +1,443 @@
|
||||
ROCTracer (pid=26055):
|
||||
ROCTracer: trace control: delay(10us), length(100000us), rate(1000000us)
|
||||
HIP-trace()
|
||||
ROCTracer (pid=26055):
|
||||
ROCTracer: trace control: delay(10us), length(100000us), rate(1000000us)
|
||||
HIP-trace()
|
||||
Device name Ellesmere [Radeon RX 470/480/570/570X/580/580X]
|
||||
## Iteration (99) #################
|
||||
PASSED!
|
||||
## Iteration (98) #################
|
||||
PASSED!
|
||||
## Iteration (97) #################
|
||||
PASSED!
|
||||
## Iteration (96) #################
|
||||
PASSED!
|
||||
## Iteration (95) #################
|
||||
PASSED!
|
||||
## Iteration (94) #################
|
||||
PASSED!
|
||||
## Iteration (93) #################
|
||||
PASSED!
|
||||
## Iteration (92) #################
|
||||
PASSED!
|
||||
## Iteration (91) #################
|
||||
PASSED!
|
||||
## Iteration (90) #################
|
||||
PASSED!
|
||||
## Iteration (89) #################
|
||||
PASSED!
|
||||
## Iteration (88) #################
|
||||
PASSED!
|
||||
## Iteration (87) #################
|
||||
PASSED!
|
||||
## Iteration (86) #################
|
||||
PASSED!
|
||||
## Iteration (85) #################
|
||||
PASSED!
|
||||
## Iteration (84) #################
|
||||
PASSED!
|
||||
## Iteration (83) #################
|
||||
PASSED!
|
||||
## Iteration (82) #################
|
||||
PASSED!
|
||||
## Iteration (81) #################
|
||||
PASSED!
|
||||
## Iteration (80) #################
|
||||
PASSED!
|
||||
## Iteration (79) #################
|
||||
PASSED!
|
||||
## Iteration (78) #################
|
||||
PASSED!
|
||||
## Iteration (77) #################
|
||||
PASSED!
|
||||
## Iteration (76) #################
|
||||
PASSED!
|
||||
## Iteration (75) #################
|
||||
PASSED!
|
||||
## Iteration (74) #################
|
||||
PASSED!
|
||||
## Iteration (73) #################
|
||||
PASSED!
|
||||
## Iteration (72) #################
|
||||
PASSED!
|
||||
## Iteration (71) #################
|
||||
PASSED!
|
||||
## Iteration (70) #################
|
||||
PASSED!
|
||||
## Iteration (69) #################
|
||||
PASSED!
|
||||
## Iteration (68) #################
|
||||
PASSED!
|
||||
## Iteration (67) #################
|
||||
PASSED!
|
||||
## Iteration (66) #################
|
||||
PASSED!
|
||||
## Iteration (65) #################
|
||||
PASSED!
|
||||
## Iteration (64) #################
|
||||
PASSED!
|
||||
## Iteration (63) #################
|
||||
PASSED!
|
||||
## Iteration (62) #################
|
||||
PASSED!
|
||||
## Iteration (61) #################
|
||||
PASSED!
|
||||
## Iteration (60) #################
|
||||
PASSED!
|
||||
## Iteration (59) #################
|
||||
PASSED!
|
||||
## Iteration (58) #################
|
||||
PASSED!
|
||||
## Iteration (57) #################
|
||||
PASSED!
|
||||
## Iteration (56) #################
|
||||
PASSED!
|
||||
## Iteration (55) #################
|
||||
PASSED!
|
||||
## Iteration (54) #################
|
||||
PASSED!
|
||||
## Iteration (53) #################
|
||||
PASSED!
|
||||
## Iteration (52) #################
|
||||
PASSED!
|
||||
## Iteration (51) #################
|
||||
PASSED!
|
||||
## Iteration (50) #################
|
||||
PASSED!
|
||||
## Iteration (49) #################
|
||||
PASSED!
|
||||
## Iteration (48) #################
|
||||
PASSED!
|
||||
## Iteration (47) #################
|
||||
PASSED!
|
||||
## Iteration (46) #################
|
||||
PASSED!
|
||||
## Iteration (45) #################
|
||||
PASSED!
|
||||
## Iteration (44) #################
|
||||
PASSED!
|
||||
## Iteration (43) #################
|
||||
PASSED!
|
||||
## Iteration (42) #################
|
||||
PASSED!
|
||||
## Iteration (41) #################
|
||||
PASSED!
|
||||
## Iteration (40) #################
|
||||
PASSED!
|
||||
## Iteration (39) #################
|
||||
PASSED!
|
||||
## Iteration (38) #################
|
||||
PASSED!
|
||||
## Iteration (37) #################
|
||||
PASSED!
|
||||
## Iteration (36) #################
|
||||
PASSED!
|
||||
## Iteration (35) #################
|
||||
PASSED!
|
||||
## Iteration (34) #################
|
||||
PASSED!
|
||||
## Iteration (33) #################
|
||||
PASSED!
|
||||
## Iteration (32) #################
|
||||
PASSED!
|
||||
## Iteration (31) #################
|
||||
PASSED!
|
||||
## Iteration (30) #################
|
||||
PASSED!
|
||||
## Iteration (29) #################
|
||||
PASSED!
|
||||
## Iteration (28) #################
|
||||
PASSED!
|
||||
## Iteration (27) #################
|
||||
PASSED!
|
||||
## Iteration (26) #################
|
||||
PASSED!
|
||||
## Iteration (25) #################
|
||||
PASSED!
|
||||
## Iteration (24) #################
|
||||
PASSED!
|
||||
## Iteration (23) #################
|
||||
PASSED!
|
||||
## Iteration (22) #################
|
||||
PASSED!
|
||||
## Iteration (21) #################
|
||||
PASSED!
|
||||
## Iteration (20) #################
|
||||
PASSED!
|
||||
## Iteration (19) #################
|
||||
PASSED!
|
||||
## Iteration (18) #################
|
||||
PASSED!
|
||||
## Iteration (17) #################
|
||||
PASSED!
|
||||
## Iteration (16) #################
|
||||
PASSED!
|
||||
## Iteration (15) #################
|
||||
PASSED!
|
||||
## Iteration (14) #################
|
||||
PASSED!
|
||||
## Iteration (13) #################
|
||||
PASSED!
|
||||
## Iteration (12) #################
|
||||
PASSED!
|
||||
## Iteration (11) #################
|
||||
PASSED!
|
||||
## Iteration (10) #################
|
||||
PASSED!
|
||||
## Iteration (9) #################
|
||||
PASSED!
|
||||
## Iteration (8) #################
|
||||
PASSED!
|
||||
## Iteration (7) #################
|
||||
PASSED!
|
||||
## Iteration (6) #################
|
||||
PASSED!
|
||||
## Iteration (5) #################
|
||||
PASSED!
|
||||
## Iteration (4) #################
|
||||
PASSED!
|
||||
## Iteration (3) #################
|
||||
PASSED!
|
||||
## Iteration (2) #################
|
||||
PASSED!
|
||||
## Iteration (1) #################
|
||||
PASSED!
|
||||
## Iteration (0) #################
|
||||
PASSED!
|
||||
43932016356046:43932016397500 26055:26055 hipGetDeviceProperties()
|
||||
43932018579649:43932018627633 26055:26055 hipMalloc(ptr(0x903400000) size(0x400000))
|
||||
43932018629101:43932018648692 26055:26055 hipMalloc(ptr(0x903c00000) size(0x400000))
|
||||
43932018657045:43932024206624 26055:26055 hipMemcpy(dst(0x903400000) src(0x25fd170) size(0x400000) kind(1))
|
||||
43932024210084:43932024210085 26055:26055 MARK(name(before HIP LaunchKernel))
|
||||
43932309367516:43932309367517 26055:26055 MARK(name(after HIP LaunchKernel))
|
||||
43932325768070:43932325768071 26055:26055 MARK(name(before HIP LaunchKernel))
|
||||
43932325806211:43932325806212 26055:26055 MARK(name(after HIP LaunchKernel))
|
||||
43932342067435:43932342067436 26055:26055 MARK(name(before HIP LaunchKernel))
|
||||
43932342101677:43932342101678 26055:26055 MARK(name(after HIP LaunchKernel))
|
||||
43932358360160:43932358360161 26055:26055 MARK(name(before HIP LaunchKernel))
|
||||
43932358394862:43932358394863 26055:26055 MARK(name(after HIP LaunchKernel))
|
||||
43932374818865:43932374818866 26055:26055 MARK(name(before HIP LaunchKernel))
|
||||
43932374857099:43932374857100 26055:26055 MARK(name(after HIP LaunchKernel))
|
||||
43932392553937:43932392553938 26055:26055 MARK(name(before HIP LaunchKernel))
|
||||
43932392587074:43932392587075 26055:26055 MARK(name(after HIP LaunchKernel))
|
||||
43932410322278:43932410322279 26055:26055 MARK(name(before HIP LaunchKernel))
|
||||
43932410356222:43932410356223 26055:26055 MARK(name(after HIP LaunchKernel))
|
||||
43932428013622:43932428013623 26055:26055 MARK(name(before HIP LaunchKernel))
|
||||
43932428047370:43932428047371 26055:26055 MARK(name(after HIP LaunchKernel))
|
||||
43932445823875:43932445823876 26055:26055 MARK(name(before HIP LaunchKernel))
|
||||
43932445858364:43932445858365 26055:26055 MARK(name(after HIP LaunchKernel))
|
||||
43932463522521:43932463522522 26055:26055 MARK(name(before HIP LaunchKernel))
|
||||
43932463556106:43932463556107 26055:26055 MARK(name(after HIP LaunchKernel))
|
||||
43932481264157:43932481264158 26055:26055 MARK(name(before HIP LaunchKernel))
|
||||
43932481302264:43932481302265 26055:26055 MARK(name(after HIP LaunchKernel))
|
||||
43932498957147:43932498957148 26055:26055 MARK(name(before HIP LaunchKernel))
|
||||
43932499007307:43932499007308 26055:26055 MARK(name(after HIP LaunchKernel))
|
||||
43932516701532:43932516701533 26055:26055 MARK(name(before HIP LaunchKernel))
|
||||
43932516740634:43932516740635 26055:26055 MARK(name(after HIP LaunchKernel))
|
||||
43932534396161:43932534396162 26055:26055 MARK(name(before HIP LaunchKernel))
|
||||
43932534430109:43932534430110 26055:26055 MARK(name(after HIP LaunchKernel))
|
||||
43932552136507:43932552136508 26055:26055 MARK(name(before HIP LaunchKernel))
|
||||
43932552174955:43932552174956 26055:26055 MARK(name(after HIP LaunchKernel))
|
||||
43932569838372:43932569838373 26055:26055 MARK(name(before HIP LaunchKernel))
|
||||
43932569873357:43932569873358 26055:26055 MARK(name(after HIP LaunchKernel))
|
||||
43932587582936:43932587582937 26055:26055 MARK(name(before HIP LaunchKernel))
|
||||
43932587616530:43932587616531 26055:26055 MARK(name(after HIP LaunchKernel))
|
||||
43932605271897:43932605271898 26055:26055 MARK(name(before HIP LaunchKernel))
|
||||
43932605306872:43932605306873 26055:26055 MARK(name(after HIP LaunchKernel))
|
||||
43932623037986:43932623037987 26055:26055 MARK(name(before HIP LaunchKernel))
|
||||
43932623072073:43932623072074 26055:26055 MARK(name(after HIP LaunchKernel))
|
||||
43932640747873:43932640747874 26055:26055 MARK(name(before HIP LaunchKernel))
|
||||
43932640782515:43932640782516 26055:26055 MARK(name(after HIP LaunchKernel))
|
||||
43932657068887:43932657068888 26055:26055 MARK(name(before HIP LaunchKernel))
|
||||
43932657102762:43932657102763 26055:26055 MARK(name(after HIP LaunchKernel))
|
||||
43932673379533:43932673379534 26055:26055 MARK(name(before HIP LaunchKernel))
|
||||
43932673413702:43932673413703 26055:26055 MARK(name(after HIP LaunchKernel))
|
||||
43932689650275:43932689650276 26055:26055 MARK(name(before HIP LaunchKernel))
|
||||
43932689688120:43932689688121 26055:26055 MARK(name(after HIP LaunchKernel))
|
||||
43932706024306:43932706024307 26055:26055 MARK(name(before HIP LaunchKernel))
|
||||
43932706061892:43932706061893 26055:26055 MARK(name(after HIP LaunchKernel))
|
||||
43932722404114:43932722404115 26055:26055 MARK(name(before HIP LaunchKernel))
|
||||
43932722450953:43932722450954 26055:26055 MARK(name(after HIP LaunchKernel))
|
||||
43932738747072:43932738747073 26055:26055 MARK(name(before HIP LaunchKernel))
|
||||
43932738783895:43932738783896 26055:26055 MARK(name(after HIP LaunchKernel))
|
||||
43932755053911:43932755053912 26055:26055 MARK(name(before HIP LaunchKernel))
|
||||
43932755086752:43932755086753 26055:26055 MARK(name(after HIP LaunchKernel))
|
||||
43932771329207:43932771329208 26055:26055 MARK(name(before HIP LaunchKernel))
|
||||
43932771347101:43932771347102 26055:26055 MARK(name(after HIP LaunchKernel))
|
||||
43932787609603:43932787609604 26055:26055 MARK(name(before HIP LaunchKernel))
|
||||
43932787626372:43932787626373 26055:26055 MARK(name(after HIP LaunchKernel))
|
||||
43932803880283:43932803880284 26055:26055 MARK(name(before HIP LaunchKernel))
|
||||
43932803913740:43932803913741 26055:26055 MARK(name(after HIP LaunchKernel))
|
||||
43932820132122:43932820132123 26055:26055 MARK(name(before HIP LaunchKernel))
|
||||
43932820170233:43932820170234 26055:26055 MARK(name(after HIP LaunchKernel))
|
||||
43932836497613:43932836497614 26055:26055 MARK(name(before HIP LaunchKernel))
|
||||
43932836535605:43932836535606 26055:26055 MARK(name(after HIP LaunchKernel))
|
||||
43932852904822:43932852904823 26055:26055 MARK(name(before HIP LaunchKernel))
|
||||
43932852942407:43932852942408 26055:26055 MARK(name(after HIP LaunchKernel))
|
||||
43932869290524:43932869290525 26055:26055 MARK(name(before HIP LaunchKernel))
|
||||
43932869329866:43932869329867 26055:26055 MARK(name(after HIP LaunchKernel))
|
||||
43932885635307:43932885635308 26055:26055 MARK(name(before HIP LaunchKernel))
|
||||
43932885669256:43932885669257 26055:26055 MARK(name(after HIP LaunchKernel))
|
||||
43932901970155:43932901970156 26055:26055 MARK(name(before HIP LaunchKernel))
|
||||
43932901989697:43932901989698 26055:26055 MARK(name(after HIP LaunchKernel))
|
||||
43932918260839:43932918260840 26055:26055 MARK(name(before HIP LaunchKernel))
|
||||
43932918293762:43932918293763 26055:26055 MARK(name(after HIP LaunchKernel))
|
||||
43932934545610:43932934545611 26055:26055 MARK(name(before HIP LaunchKernel))
|
||||
43932934577595:43932934577596 26055:26055 MARK(name(after HIP LaunchKernel))
|
||||
43932950855037:43932950855038 26055:26055 MARK(name(before HIP LaunchKernel))
|
||||
43932950906554:43932950906555 26055:26055 MARK(name(after HIP LaunchKernel))
|
||||
43932967158140:43932967158141 26055:26055 MARK(name(before HIP LaunchKernel))
|
||||
43932967204959:43932967204960 26055:26055 MARK(name(after HIP LaunchKernel))
|
||||
43932983443711:43932983443712 26055:26055 MARK(name(before HIP LaunchKernel))
|
||||
43932983481045:43932983481046 26055:26055 MARK(name(after HIP LaunchKernel))
|
||||
43932998919789:43932999777243 26055:26055 hipMemcpy(dst(0x903400000) src(0x25fd170) size(0x400000) kind(1))
|
||||
43932999778933:43932999778934 26055:26055 MARK(name(before HIP LaunchKernel))
|
||||
43932999790858:43932999857966 26055:26055 hipModuleLaunchKernel(kernel(matrixTranspose(float*, float*, int)) stream((nil)))
|
||||
43932999869719:43932999869720 26055:26055 MARK(name(after HIP LaunchKernel))
|
||||
43932999871831:43933002727304 26055:26055 hipMemcpy(dst(0x29fd180) src(0x903c00000) size(0x400000) kind(2))
|
||||
43933016724230:43933017583617 26055:26055 hipMemcpy(dst(0x903400000) src(0x25fd170) size(0x400000) kind(1))
|
||||
43933017585152:43933017585153 26055:26055 MARK(name(before HIP LaunchKernel))
|
||||
43933017597371:43933017637628 26055:26055 hipModuleLaunchKernel(kernel(matrixTranspose(float*, float*, int)) stream((nil)))
|
||||
43933017639250:43933017639251 26055:26055 MARK(name(after HIP LaunchKernel))
|
||||
43933017641217:43933020520010 26055:26055 hipMemcpy(dst(0x29fd180) src(0x903c00000) size(0x400000) kind(2))
|
||||
43933034542756:43933035404131 26055:26055 hipMemcpy(dst(0x903400000) src(0x25fd170) size(0x400000) kind(1))
|
||||
43933035405703:43933035405704 26055:26055 MARK(name(before HIP LaunchKernel))
|
||||
43933035417664:43933035457991 26055:26055 hipModuleLaunchKernel(kernel(matrixTranspose(float*, float*, int)) stream((nil)))
|
||||
43933035459677:43933035459678 26055:26055 MARK(name(after HIP LaunchKernel))
|
||||
43933035461554:43933038337624 26055:26055 hipMemcpy(dst(0x29fd180) src(0x903c00000) size(0x400000) kind(2))
|
||||
43933052293417:43933053160408 26055:26055 hipMemcpy(dst(0x903400000) src(0x25fd170) size(0x400000) kind(1))
|
||||
43933053162015:43933053162016 26055:26055 MARK(name(before HIP LaunchKernel))
|
||||
43933053174382:43933053196225 26055:26055 hipModuleLaunchKernel(kernel(matrixTranspose(float*, float*, int)) stream((nil)))
|
||||
43933053198167:43933053198168 26055:26055 MARK(name(after HIP LaunchKernel))
|
||||
43933053200026:43933056101223 26055:26055 hipMemcpy(dst(0x29fd180) src(0x903c00000) size(0x400000) kind(2))
|
||||
43933070121982:43933070978773 26055:26055 hipMemcpy(dst(0x903400000) src(0x25fd170) size(0x400000) kind(1))
|
||||
43933070980262:43933070980263 26055:26055 MARK(name(before HIP LaunchKernel))
|
||||
43933070997704:43933071038037 26055:26055 hipModuleLaunchKernel(kernel(matrixTranspose(float*, float*, int)) stream((nil)))
|
||||
43933071039939:43933071039940 26055:26055 MARK(name(after HIP LaunchKernel))
|
||||
43933071041871:43933073922115 26055:26055 hipMemcpy(dst(0x29fd180) src(0x903c00000) size(0x400000) kind(2))
|
||||
43933087857070:43933088762523 26055:26055 hipMemcpy(dst(0x903400000) src(0x25fd170) size(0x400000) kind(1))
|
||||
43933088764032:43933088764033 26055:26055 MARK(name(before HIP LaunchKernel))
|
||||
43933088775969:43933088816379 26055:26055 hipModuleLaunchKernel(kernel(matrixTranspose(float*, float*, int)) stream((nil)))
|
||||
43933088818233:43933088818234 26055:26055 MARK(name(after HIP LaunchKernel))
|
||||
43933088830023:43933091723027 26055:26055 hipMemcpy(dst(0x29fd180) src(0x903c00000) size(0x400000) kind(2))
|
||||
43933106593182:43933106593183 26055:26055 MARK(name(before HIP LaunchKernel))
|
||||
43933106631182:43933106631183 26055:26055 MARK(name(after HIP LaunchKernel))
|
||||
43933124264790:43933124264791 26055:26055 MARK(name(before HIP LaunchKernel))
|
||||
43933124299416:43933124299417 26055:26055 MARK(name(after HIP LaunchKernel))
|
||||
43933141986334:43933141986335 26055:26055 MARK(name(before HIP LaunchKernel))
|
||||
43933142020652:43933142020653 26055:26055 MARK(name(after HIP LaunchKernel))
|
||||
43933159656263:43933159656264 26055:26055 MARK(name(before HIP LaunchKernel))
|
||||
43933159689392:43933159689393 26055:26055 MARK(name(after HIP LaunchKernel))
|
||||
43933177421632:43933177421633 26055:26055 MARK(name(before HIP LaunchKernel))
|
||||
43933177460424:43933177460425 26055:26055 MARK(name(after HIP LaunchKernel))
|
||||
43933195118213:43933195118214 26055:26055 MARK(name(before HIP LaunchKernel))
|
||||
43933195156305:43933195156306 26055:26055 MARK(name(after HIP LaunchKernel))
|
||||
43933212858769:43933212858770 26055:26055 MARK(name(before HIP LaunchKernel))
|
||||
43933212892428:43933212892429 26055:26055 MARK(name(after HIP LaunchKernel))
|
||||
43933230550599:43933230550600 26055:26055 MARK(name(before HIP LaunchKernel))
|
||||
43933230584794:43933230584795 26055:26055 MARK(name(after HIP LaunchKernel))
|
||||
43933248275723:43933248275724 26055:26055 MARK(name(before HIP LaunchKernel))
|
||||
43933248310176:43933248310177 26055:26055 MARK(name(after HIP LaunchKernel))
|
||||
43933264626153:43933264626154 26055:26055 MARK(name(before HIP LaunchKernel))
|
||||
43933264665629:43933264665630 26055:26055 MARK(name(after HIP LaunchKernel))
|
||||
43933280992560:43933280992561 26055:26055 MARK(name(before HIP LaunchKernel))
|
||||
43933281027422:43933281027423 26055:26055 MARK(name(after HIP LaunchKernel))
|
||||
43933297321505:43933297321506 26055:26055 MARK(name(before HIP LaunchKernel))
|
||||
43933297359452:43933297359453 26055:26055 MARK(name(after HIP LaunchKernel))
|
||||
43933313662994:43933313662995 26055:26055 MARK(name(before HIP LaunchKernel))
|
||||
43933313700705:43933313700706 26055:26055 MARK(name(after HIP LaunchKernel))
|
||||
43933329971419:43933329971420 26055:26055 MARK(name(before HIP LaunchKernel))
|
||||
43933330018417:43933330018418 26055:26055 MARK(name(after HIP LaunchKernel))
|
||||
43933346273054:43933346273055 26055:26055 MARK(name(before HIP LaunchKernel))
|
||||
43933346306837:43933346306838 26055:26055 MARK(name(after HIP LaunchKernel))
|
||||
43933362521760:43933362521761 26055:26055 MARK(name(before HIP LaunchKernel))
|
||||
43933362540391:43933362540392 26055:26055 MARK(name(after HIP LaunchKernel))
|
||||
43933378827233:43933378827234 26055:26055 MARK(name(before HIP LaunchKernel))
|
||||
43933378845241:43933378845242 26055:26055 MARK(name(after HIP LaunchKernel))
|
||||
43933395183216:43933395183217 26055:26055 MARK(name(before HIP LaunchKernel))
|
||||
43933395215386:43933395215387 26055:26055 MARK(name(after HIP LaunchKernel))
|
||||
43933411559286:43933411559287 26055:26055 MARK(name(before HIP LaunchKernel))
|
||||
43933411596821:43933411596822 26055:26055 MARK(name(after HIP LaunchKernel))
|
||||
43933427865512:43933427865513 26055:26055 MARK(name(before HIP LaunchKernel))
|
||||
43933427898752:43933427898753 26055:26055 MARK(name(after HIP LaunchKernel))
|
||||
43933444147624:43933444147625 26055:26055 MARK(name(before HIP LaunchKernel))
|
||||
43933444175808:43933444175809 26055:26055 MARK(name(after HIP LaunchKernel))
|
||||
43933460414293:43933460414294 26055:26055 MARK(name(before HIP LaunchKernel))
|
||||
43933460446208:43933460446209 26055:26055 MARK(name(after HIP LaunchKernel))
|
||||
43933476718044:43933476718045 26055:26055 MARK(name(before HIP LaunchKernel))
|
||||
43933476749715:43933476749716 26055:26055 MARK(name(after HIP LaunchKernel))
|
||||
43933492989969:43933492989970 26055:26055 MARK(name(before HIP LaunchKernel))
|
||||
43933493020764:43933493020765 26055:26055 MARK(name(after HIP LaunchKernel))
|
||||
43933509257931:43933509257932 26055:26055 MARK(name(before HIP LaunchKernel))
|
||||
43933509289509:43933509289510 26055:26055 MARK(name(after HIP LaunchKernel))
|
||||
43933525557224:43933525557225 26055:26055 MARK(name(before HIP LaunchKernel))
|
||||
43933525588932:43933525588933 26055:26055 MARK(name(after HIP LaunchKernel))
|
||||
43933541884683:43933541884684 26055:26055 MARK(name(before HIP LaunchKernel))
|
||||
43933541916037:43933541916038 26055:26055 MARK(name(after HIP LaunchKernel))
|
||||
43933558234802:43933558234803 26055:26055 MARK(name(before HIP LaunchKernel))
|
||||
43933558266471:43933558266472 26055:26055 MARK(name(after HIP LaunchKernel))
|
||||
43933574598996:43933574598997 26055:26055 MARK(name(before HIP LaunchKernel))
|
||||
43933574630471:43933574630472 26055:26055 MARK(name(after HIP LaunchKernel))
|
||||
43933590916499:43933590916500 26055:26055 MARK(name(before HIP LaunchKernel))
|
||||
43933590946901:43933590946902 26055:26055 MARK(name(after HIP LaunchKernel))
|
||||
43933607216207:43933607216208 26055:26055 MARK(name(before HIP LaunchKernel))
|
||||
43933607247236:43933607247237 26055:26055 MARK(name(after HIP LaunchKernel))
|
||||
43933624120350:43933624120351 26055:26055 MARK(name(before HIP LaunchKernel))
|
||||
43933624138017:43933624138018 26055:26055 MARK(name(after HIP LaunchKernel))
|
||||
43933641790135:43933641790136 26055:26055 MARK(name(before HIP LaunchKernel))
|
||||
43933641807143:43933641807144 26055:26055 MARK(name(after HIP LaunchKernel))
|
||||
43933659509173:43933659509174 26055:26055 MARK(name(before HIP LaunchKernel))
|
||||
43933659526749:43933659526750 26055:26055 MARK(name(after HIP LaunchKernel))
|
||||
43933677219727:43933677219728 26055:26055 MARK(name(before HIP LaunchKernel))
|
||||
43933677254061:43933677254062 26055:26055 MARK(name(after HIP LaunchKernel))
|
||||
43933694974650:43933694974651 26055:26055 MARK(name(before HIP LaunchKernel))
|
||||
43933695009347:43933695009348 26055:26055 MARK(name(after HIP LaunchKernel))
|
||||
43933712659673:43933712659674 26055:26055 MARK(name(before HIP LaunchKernel))
|
||||
43933712708655:43933712708656 26055:26055 MARK(name(after HIP LaunchKernel))
|
||||
43933730412868:43933730412869 26055:26055 MARK(name(before HIP LaunchKernel))
|
||||
43933730446931:43933730446932 26055:26055 MARK(name(after HIP LaunchKernel))
|
||||
43933748101862:43933748101863 26055:26055 MARK(name(before HIP LaunchKernel))
|
||||
43933748139940:43933748139941 26055:26055 MARK(name(after HIP LaunchKernel))
|
||||
43933765877856:43933765877857 26055:26055 MARK(name(before HIP LaunchKernel))
|
||||
43933765916382:43933765916383 26055:26055 MARK(name(after HIP LaunchKernel))
|
||||
43933783570361:43933783570362 26055:26055 MARK(name(before HIP LaunchKernel))
|
||||
43933783603616:43933783603617 26055:26055 MARK(name(after HIP LaunchKernel))
|
||||
43933801334338:43933801334339 26055:26055 MARK(name(before HIP LaunchKernel))
|
||||
43933801368467:43933801368468 26055:26055 MARK(name(after HIP LaunchKernel))
|
||||
43933819035225:43933819035226 26055:26055 MARK(name(before HIP LaunchKernel))
|
||||
43933819068314:43933819068315 26055:26055 MARK(name(after HIP LaunchKernel))
|
||||
43933836809157:43933836809158 26055:26055 MARK(name(before HIP LaunchKernel))
|
||||
43933836847860:43933836847861 26055:26055 MARK(name(after HIP LaunchKernel))
|
||||
43933854512746:43933854512747 26055:26055 MARK(name(before HIP LaunchKernel))
|
||||
43933854546024:43933854546025 26055:26055 MARK(name(after HIP LaunchKernel))
|
||||
43933872241982:43933872241983 26055:26055 MARK(name(before HIP LaunchKernel))
|
||||
43933872276613:43933872276614 26055:26055 MARK(name(after HIP LaunchKernel))
|
||||
43933888625718:43933888625719 26055:26055 MARK(name(before HIP LaunchKernel))
|
||||
43933888659297:43933888659298 26055:26055 MARK(name(after HIP LaunchKernel))
|
||||
43933904989760:43933904989761 26055:26055 MARK(name(before HIP LaunchKernel))
|
||||
43933905023554:43933905023555 26055:26055 MARK(name(after HIP LaunchKernel))
|
||||
43933921307079:43933921307080 26055:26055 MARK(name(before HIP LaunchKernel))
|
||||
43933921344505:43933921344506 26055:26055 MARK(name(after HIP LaunchKernel))
|
||||
43933937634499:43933937634500 26055:26055 MARK(name(before HIP LaunchKernel))
|
||||
43933937681958:43933937681959 26055:26055 MARK(name(after HIP LaunchKernel))
|
||||
43933953935834:43933953935835 26055:26055 MARK(name(before HIP LaunchKernel))
|
||||
43933953973608:43933953973609 26055:26055 MARK(name(after HIP LaunchKernel))
|
||||
43933970237558:43933970237559 26055:26055 MARK(name(before HIP LaunchKernel))
|
||||
43933970274704:43933970274705 26055:26055 MARK(name(after HIP LaunchKernel))
|
||||
43933986518798:43933986518799 26055:26055 MARK(name(before HIP LaunchKernel))
|
||||
43933986551047:43933986551048 26055:26055 MARK(name(after HIP LaunchKernel))
|
||||
43934001936907:43934002013320 26055:26055 hipFree(ptr(0x903400000))
|
||||
43934002015215:43934002031122 26055:26055 hipFree(ptr(0x903c00000))
|
||||
43932999861577:43933001699020 0:0 hcCommandKernel:89
|
||||
43933001702044:43933001733884 0:0 hcCommandMarker:91
|
||||
43933017641348:43933019466951 0:0 hcCommandKernel:94
|
||||
43933019470002:43933019501362 0:0 hcCommandMarker:96
|
||||
43933035461722:43933037295325 0:0 hcCommandKernel:99
|
||||
43933037298331:43933037330011 0:0 hcCommandMarker:101
|
||||
43933053199946:43933055040429 0:0 hcCommandKernel:104
|
||||
43933055043394:43933055075234 0:0 hcCommandMarker:106
|
||||
43933071041680:43933072880403 0:0 hcCommandKernel:109
|
||||
43933072883281:43933072915281 0:0 hcCommandMarker:111
|
||||
43933088820348:43933090670751 0:0 hcCommandKernel:114
|
||||
43933090673779:43933090705459 0:0 hcCommandMarker:116
|
||||
File diff suppressed because it is too large
Load Diff
File diff suppressed because it is too large
Load Diff
File diff suppressed because it is too large
Load Diff
File diff suppressed because it is too large
Load Diff
File diff suppressed because it is too large
Load Diff
File diff suppressed because it is too large
Load Diff
@@ -1,8 +1,9 @@
|
||||
ctrl_hsa_input_trace 0
|
||||
ctrl_hsa_trace 1
|
||||
MatrixTranspose_ctest_trace 3
|
||||
MatrixTranspose_hip_trace 1
|
||||
MatrixTranspose_mgpu_trace 1
|
||||
MatrixTranspose_sys_hsa_trace 2
|
||||
MatrixTranspose_sys_trace 1
|
||||
MatrixTranspose_test_trace 1
|
||||
MatrixTranspose_mgpu_trace 1
|
||||
MatrixTranspose_sys_trace 1
|
||||
MatrixTranspose_sys_hsa_trace 2
|
||||
MatrixTranspose_hip_period_trace 1
|
||||
MatrixTranspose_hip_flush_trace 1
|
||||
ctrl_hsa_trace 1
|
||||
ctrl_hsa_input_trace 0
|
||||
+31
-29
@@ -33,16 +33,12 @@ if [ -n "$1" ] ; then
|
||||
test_filter=$1
|
||||
fi
|
||||
|
||||
# debugger
|
||||
debugger=""
|
||||
if [ -n "$3" ] ; then
|
||||
debugger=$3
|
||||
fi
|
||||
|
||||
# test check routin
|
||||
test_status=0
|
||||
test_runnum=0
|
||||
test_number=0
|
||||
failed_tests="Failed tests:"
|
||||
|
||||
xeval_test() {
|
||||
test_number=$test_number
|
||||
}
|
||||
@@ -50,33 +46,36 @@ xeval_test() {
|
||||
eval_test() {
|
||||
label=$1
|
||||
cmdline=$2
|
||||
rtrace="${3}_r.txt"
|
||||
test_name=$3
|
||||
test_trace=$test_name.txt
|
||||
|
||||
if [ $test_filter = -1 -o $test_filter = $test_number ] ; then
|
||||
echo "$label: \"$cmdline\""
|
||||
echo "test $test_number: $test_name \"$label\""
|
||||
echo "CMD: \"$cmdline\""
|
||||
test_runnum=$((test_runnum + 1))
|
||||
eval "$debugger $cmdline" | tee $rtrace
|
||||
if [ $? != 0 ] ; then
|
||||
echo "$label: FAILED"
|
||||
test_status=$(($test_status + 1))
|
||||
eval "$cmdline" | tee $test_trace
|
||||
is_failed=$?
|
||||
if [ $is_failed = 0 ] ; then
|
||||
python ../script/check_trace.py -in $test_name
|
||||
is_failed=$?
|
||||
fi
|
||||
if [ $is_failed = 0 ] ; then
|
||||
echo "$test_name: PASSED"
|
||||
else
|
||||
echo "Comparing traces: ../script/check_trace.py -in $3"
|
||||
eval "../script/check_trace.py -in $3"
|
||||
if [ $? != 0 ] ; then
|
||||
echo "$label: FAILED trace comparison"
|
||||
test_status=$(($test_status + 1))
|
||||
else
|
||||
echo "$label: PASSED trace comparison"
|
||||
fi
|
||||
echo "$test_name: FAILED"
|
||||
failed_tests="$failed_tests\n $test_number: $test_name"
|
||||
test_status=$(($test_status + 1))
|
||||
fi
|
||||
fi
|
||||
|
||||
test_number=$((test_number + 1))
|
||||
}
|
||||
|
||||
# Standalone test
|
||||
# rocTrecer is used explicitely by test
|
||||
eval_test "standalone C test" "LD_PRELOAD=libkfdwrapper64.so ./test/MatrixTranspose_ctest" "test/MatrixTranspose_ctest_trace"
|
||||
eval_test "standalone HIP test" "LD_PRELOAD=libkfdwrapper64.so ./test/MatrixTranspose_test" "test/MatrixTranspose_test_trace"
|
||||
eval_test "standalone HIP MGPU test" "LD_PRELOAD=libkfdwrapper64.so ./test/MatrixTranspose_mgpu" "test/MatrixTranspose_mgpu_trace"
|
||||
eval_test "standalone C test" "LD_PRELOAD=libkfdwrapper64.so ./test/MatrixTranspose_ctest" MatrixTranspose_ctest_trace
|
||||
eval_test "standalone HIP test" "LD_PRELOAD=libkfdwrapper64.so ./test/MatrixTranspose_test" MatrixTranspose_test_trace
|
||||
eval_test "standalone HIP MGPU test" "LD_PRELOAD=libkfdwrapper64.so ./test/MatrixTranspose_mgpu" MatrixTranspose_mgpu_trace
|
||||
|
||||
# Tool test
|
||||
# rocTracer/tool is loaded by HSA runtime
|
||||
@@ -84,13 +83,13 @@ export HSA_TOOLS_LIB="test/libtracer_tool.so"
|
||||
|
||||
# SYS test
|
||||
export ROCTRACER_DOMAIN="sys:roctx"
|
||||
eval_test "tool SYS test" ./test/MatrixTranspose "test/MatrixTranspose_sys_trace"
|
||||
eval_test "tool SYS test" ./test/MatrixTranspose MatrixTranspose_sys_trace
|
||||
export ROCTRACER_DOMAIN="sys:hsa:roctx"
|
||||
eval_test "tool SYS/HSA test" ./test/MatrixTranspose "test/MatrixTranspose_sys_hsa_trace"
|
||||
eval_test "tool SYS/HSA test" ./test/MatrixTranspose MatrixTranspose_sys_hsa_trace
|
||||
# Tracing control <delay:length:rate>
|
||||
export ROCTRACER_DOMAIN="hip"
|
||||
eval_test "tool period test" "ROCP_CTRL_RATE=10:100000:1000000 ./test/MatrixTranspose" "test/MatrixTranspose_hip_trace"
|
||||
eval_test "tool flushing test" "ROCP_FLUSH_RATE=100000 ./test/MatrixTranspose" "test/MatrixTranspose_hip_trace_flush"
|
||||
eval_test "tool period test" "ROCP_CTRL_RATE=10:100000:1000000 ./test/MatrixTranspose" MatrixTranspose_hip_period_trace
|
||||
eval_test "tool flushing test" "ROCP_FLUSH_RATE=100000 ./test/MatrixTranspose" MatrixTranspose_hip_flush_trace
|
||||
|
||||
# HSA test
|
||||
export ROCTRACER_DOMAIN="hsa"
|
||||
@@ -107,15 +106,18 @@ export ROCP_AGENTS=1
|
||||
# each thread creates a queue pre GPU agent
|
||||
export ROCP_THRS=1
|
||||
|
||||
eval_test "tool HSA test" ./test/hsa/ctrl "test/ctrl_hsa_trace"
|
||||
eval_test "tool HSA test" ./test/hsa/ctrl ctrl_hsa_trace
|
||||
|
||||
echo "<trace name=\"HSA\"><parameters api=\"hsa_agent_get_info, hsa_amd_memory_pool_allocate\"></parameters></trace>" > input.xml
|
||||
export ROCP_INPUT=input.xml
|
||||
eval_test "tool HSA test input" ./test/hsa/ctrl "test/ctrl_hsa_input_trace"
|
||||
eval_test "tool HSA test input" ./test/hsa/ctrl ctrl_hsa_input_trace
|
||||
|
||||
#valgrind --leak-check=full $tbin
|
||||
#valgrind --tool=massif $tbin
|
||||
#ms_print massif.out.<N>
|
||||
|
||||
echo "$test_number tests total / $test_runnum tests run / $test_status tests failed"
|
||||
if [ $test_status != 0 ] ; then
|
||||
echo $failed_tests
|
||||
fi
|
||||
exit $test_status
|
||||
|
||||
Reference in New Issue
Block a user