mirror/tracy
1
0
Fork 0
mirror of https://github.com/wolfpld/tracy.git synced 2024-11-14 04:01:48 +00:00
Code Issues Packages Projects Releases Wiki Activity
aa2757526a
tracy/server/TracySourceView.cpp

3621 lines
132 KiB
C++
Raw Normal View History

Add C++ tokenizer.
2020-04-24 21:48:18 +00:00
#include <ctype.h>
Display instruction pointer counts in source view.
2020-03-25 00:09:02 +00:00
#include <inttypes.h>
Replace source file viewer with one that actually works. This is much simpler, custom implementation of a text file viewer. It is able to perform these two tasks as intended: - center source view on the selected line, - highlight that line.
2020-03-22 19:53:59 +00:00
#include <stdio.h>
Disassemble symbol code fragments.
2020-03-25 21:37:34 +00:00
#include <capstone/capstone.h>
Replace source file viewer with one that actually works. This is much simpler, custom implementation of a text file viewer. It is able to perform these two tasks as intended: - center source view on the selected line, - highlight that line.
2020-03-22 19:53:59 +00:00
#include "../imgui/imgui.h"
Add C++ tokenizer.
2020-04-24 21:48:18 +00:00
#include "TracyCharUtil.hpp"
Display source locations in assembly view.
2020-04-01 23:32:23 +00:00
#include "TracyColor.hpp"
Don't try to open invalid files.
2020-03-28 14:06:36 +00:00
#include "TracyFilesystem.hpp"
Replace source file viewer with one that actually works. This is much simpler, custom implementation of a text file viewer. It is able to perform these two tasks as intended: - center source view on the selected line, - highlight that line.
2020-03-22 19:53:59 +00:00
#include "TracyImGui.hpp"
Add micro architecture tooltips.
2020-04-26 20:26:17 +00:00
#include "TracyMicroArchitecture.hpp"
Replace source file viewer with one that actually works. This is much simpler, custom implementation of a text file viewer. It is able to perform these two tasks as intended: - center source view on the selected line, - highlight that line.
2020-03-22 19:53:59 +00:00
#include "TracyPrint.hpp"
Calculate jump table.
2020-04-04 00:25:12 +00:00
#include "TracySort.hpp"
Replace source file viewer with one that actually works. This is much simpler, custom implementation of a text file viewer. It is able to perform these two tasks as intended: - center source view on the selected line, - highlight that line.
2020-03-22 19:53:59 +00:00
#include "TracySourceView.hpp"
Substitute source file names in source view.
2020-04-17 17:17:47 +00:00
#include "TracyView.hpp"
Display instruction pointer counts in source view.
2020-03-25 00:09:02 +00:00
#include "TracyWorker.hpp"
Replace source file viewer with one that actually works. This is much simpler, custom implementation of a text file viewer. It is able to perform these two tasks as intended: - center source view on the selected line, - highlight that line.
2020-03-22 19:53:59 +00:00
Remove support for non-extended font builds.
2020-03-26 22:04:44 +00:00
#include "IconsFontAwesome5.h"
Display disassembly.
2020-03-25 21:53:05 +00:00
Implement saving disassembly to a file.
2020-05-09 00:37:18 +00:00
#ifndef TRACY_NO_FILESELECTOR
# include "../nfd/nfd.h"
#endif
Replace source file viewer with one that actually works. This is much simpler, custom implementation of a text file viewer. It is able to perform these two tasks as intended: - center source view on the selected line, - highlight that line.
2020-03-22 19:53:59 +00:00
namespace tracy
{
Add uarch selection UI.
2020-04-26 12:52:18 +00:00
struct MicroArchUx
{
const char* uArch;
const char* cpuName;
const char* moniker;
};
static constexpr MicroArchUx s_uArchUx[] = {
{ "Conroe", "Core 2 Duo E6750", "CON" },
{ "Wolfdale", "Core 2 Duo E8400", "WOL" },
{ "Nehalem", "Core i5-750", "NHM" },
{ "Westmere", "Core i5-650", "WSM" },
{ "Sandy Bridge", "Core i7-2600", "SNB" },
{ "Ivy Bridge", "Core i5-3470", "IVB" },
{ "Haswell", "Xeon E3-1225 v3", "HSW" },
{ "Broadwell", "Core i5-5200U", "BDW" },
{ "Skylake", "Core i7-6500U", "SKL" },
{ "Skylake-X", "Core i9-7900X", "SKX" },
{ "Kaby Lake", "Core i7-7700", "KBL" },
{ "Coffee Lake", "Core i7-8700K", "CFL" },
{ "Cannon Lake", "Core i3-8121U", "CNL" },
{ "Ice Lake", "Core i5-1035G1", "ICL" },
{ "AMD Zen+", "Ryzen 5 2600", "ZEN+" },
{ "AMD Zen 2", "Ryzen 7 3700X", "ZEN2" },
};
Display list of read and write registers.
2020-05-01 11:20:19 +00:00
static constexpr const char* s_regNameX86[] = {
Include flags register.
2020-05-01 14:14:27 +00:00
"invalid", "rflags",
Display list of read and write registers.
2020-05-01 11:20:19 +00:00
"rax", "rbx", "rcx", "rdx", "rsi", "rdi", "rbp", "rsp", "r8", "r9", "r10", "r11", "r12", "r13", "r14", "r15",
"mm0", "mm1", "mm2", "mm3", "mm4", "mm5", "mm6", "mm7",
"xmm0", "xmm1", "xmm2", "xmm3", "xmm4", "xmm5", "xmm6", "xmm7", "xmm8", "xmm9",
"xmm10", "xmm11", "xmm12", "xmm13", "xmm14", "xmm15", "xmm16", "xmm17", "xmm18", "xmm19",
"xmm20", "xmm21", "xmm22", "xmm23", "xmm24", "xmm25", "xmm26", "xmm27", "xmm28", "xmm29",
"xmm30", "xmm31", "k0", "k1", "k2", "k3", "k4", "k5", "k6", "k7"
};
static_assert( sizeof( s_regNameX86 ) / sizeof( *s_regNameX86 ) == (size_t)SourceView::RegsX86::NUMBER_OF_ENTRIES, "Invalid x86 register name table" );
Create x86 common register mapping table.
2020-05-01 00:39:17 +00:00
static SourceView::RegsX86 s_regMapX86[X86_REG_ENDING];
Add uarch selection UI.
2020-04-26 12:52:18 +00:00
Draw jumps in assembly view.
2020-04-04 01:34:54 +00:00
enum { JumpSeparation = 6 };
Adapt to DPI scaling.
2020-04-04 12:19:23 +00:00
enum { JumpArrowBase = 9 };
Draw jumps in assembly view.
2020-04-04 01:34:54 +00:00
Set owner of file dialogs on windows.
2020-06-09 23:52:17 +00:00
SourceView::SourceView( ImFont* font, GetWindowCallback gwcb )
Replace source file viewer with one that actually works. This is much simpler, custom implementation of a text file viewer. It is able to perform these two tasks as intended: - center source view on the selected line, - highlight that line.
2020-03-22 19:53:59 +00:00
: m_font( font )
, m_file( nullptr )
Retrieve file name string idx in source view.
2020-04-02 00:15:10 +00:00
, m_fileStringIdx( 0 )
Pass symbol address to source view.
2020-03-24 23:07:31 +00:00
, m_symAddr( 0 )
Fix init order.
2020-03-27 22:57:23 +00:00
, m_targetAddr( 0 )
Replace source file viewer with one that actually works. This is much simpler, custom implementation of a text file viewer. It is able to perform these two tasks as intended: - center source view on the selected line, - highlight that line.
2020-03-22 19:53:59 +00:00
, m_data( nullptr )
Use cached source files.
2020-05-23 13:14:57 +00:00
, m_dataBuf( nullptr )
Replace source file viewer with one that actually works. This is much simpler, custom implementation of a text file viewer. It is able to perform these two tasks as intended: - center source view on the selected line, - highlight that line.
2020-03-22 19:53:59 +00:00
, m_dataSize( 0 )
, m_targetLine( 0 )
, m_selectedLine( 0 )
Register line selection.
2020-05-01 14:33:24 +00:00
, m_asmSelected( -1 )
Highlight source line corresponding to hovered asm line.
2020-04-09 20:02:06 +00:00
, m_hoveredLine( 0 )
, m_hoveredSource( 0 )
Display code size in source file view window.
2020-03-26 01:23:09 +00:00
, m_codeLen( 0 )
Display jump/call target address.
2020-03-28 00:22:27 +00:00
, m_highlightAddr( 0 )
Allow enumerating asm lines from a given base instruction.
2020-05-11 11:35:49 +00:00
, m_asmCountBase( -1 )
Assembly addresses can be displayed relative to symbol.
2020-03-28 13:33:35 +00:00
, m_asmRelative( false )
Allow displaying machine code bytes in disassembly.
2020-04-19 14:06:45 +00:00
, m_asmBytes( false )
Make source location display optional.
2020-04-01 23:37:56 +00:00
, m_asmShowSourceLocation( true )
Allow showing sample data for whole symbol.
2020-04-09 20:23:57 +00:00
, m_calcInlineStats( true )
Allow switching between Intel and AT&T assembly syntax.
2020-05-09 10:58:09 +00:00
, m_atnt( false )
Draw jumps in assembly view.
2020-04-04 01:34:54 +00:00
, m_showJumps( true )
Store CPU architecture.
2020-04-26 12:23:16 +00:00
, m_cpuArch( CpuArchUnknown )
Optional visualization of uarch latency.
2020-04-27 14:10:47 +00:00
, m_showLatency( false )
Set owner of file dialogs on windows.
2020-06-09 23:52:17 +00:00
, m_gwcb( gwcb )
Replace source file viewer with one that actually works. This is much simpler, custom implementation of a text file viewer. It is able to perform these two tasks as intended: - center source view on the selected line, - highlight that line.
2020-03-22 19:53:59 +00:00
{
Add micro architecture tooltips.
2020-04-26 20:26:17 +00:00
m_microArchOpMap.reserve( OpsNum );
for( int i=0; i<OpsNum; i++ )
{
m_microArchOpMap.emplace( OpsList[i], i );
}
Create x86 common register mapping table.
2020-05-01 00:39:17 +00:00
memset( s_regMapX86, 0, sizeof( s_regMapX86 ) );
Include flags register.
2020-05-01 14:14:27 +00:00
s_regMapX86[X86_REG_EFLAGS] = RegsX86::flags;
Create x86 common register mapping table.
2020-05-01 00:39:17 +00:00
s_regMapX86[X86_REG_AH] = RegsX86::rax;
s_regMapX86[X86_REG_AL] = RegsX86::rax;
s_regMapX86[X86_REG_AX] = RegsX86::rax;
s_regMapX86[X86_REG_EAX] = RegsX86::rax;
s_regMapX86[X86_REG_RAX] = RegsX86::rax;
s_regMapX86[X86_REG_BH] = RegsX86::rbx;
s_regMapX86[X86_REG_BL] = RegsX86::rbx;
s_regMapX86[X86_REG_BX] = RegsX86::rbx;
s_regMapX86[X86_REG_EBX] = RegsX86::rbx;
s_regMapX86[X86_REG_RBX] = RegsX86::rbx;
s_regMapX86[X86_REG_CH] = RegsX86::rcx;
s_regMapX86[X86_REG_CL] = RegsX86::rcx;
s_regMapX86[X86_REG_CX] = RegsX86::rcx;
s_regMapX86[X86_REG_ECX] = RegsX86::rcx;
s_regMapX86[X86_REG_RCX] = RegsX86::rcx;
s_regMapX86[X86_REG_DH] = RegsX86::rdx;
s_regMapX86[X86_REG_DL] = RegsX86::rdx;
s_regMapX86[X86_REG_DX] = RegsX86::rdx;
s_regMapX86[X86_REG_EDX] = RegsX86::rdx;
s_regMapX86[X86_REG_RDX] = RegsX86::rdx;
s_regMapX86[X86_REG_SIL] = RegsX86::rsi;
s_regMapX86[X86_REG_SI] = RegsX86::rsi;
s_regMapX86[X86_REG_ESI] = RegsX86::rsi;
s_regMapX86[X86_REG_RSI] = RegsX86::rsi;
s_regMapX86[X86_REG_DIL] = RegsX86::rdi;
s_regMapX86[X86_REG_DI] = RegsX86::rdi;
s_regMapX86[X86_REG_EDI] = RegsX86::rdi;
s_regMapX86[X86_REG_RDI] = RegsX86::rdi;
s_regMapX86[X86_REG_BP] = RegsX86::rbp;
s_regMapX86[X86_REG_BP] = RegsX86::rbp;
s_regMapX86[X86_REG_EBP] = RegsX86::rbp;
s_regMapX86[X86_REG_RBP] = RegsX86::rbp;
s_regMapX86[X86_REG_SPL] = RegsX86::rsp;
s_regMapX86[X86_REG_SP] = RegsX86::rsp;
s_regMapX86[X86_REG_ESP] = RegsX86::rsp;
s_regMapX86[X86_REG_RSP] = RegsX86::rsp;
s_regMapX86[X86_REG_R8B] = RegsX86::r8;
s_regMapX86[X86_REG_R8W] = RegsX86::r8;
s_regMapX86[X86_REG_R8D] = RegsX86::r8;
s_regMapX86[X86_REG_R8] = RegsX86::r8;
s_regMapX86[X86_REG_R9B] = RegsX86::r9;
s_regMapX86[X86_REG_R9W] = RegsX86::r9;
s_regMapX86[X86_REG_R9D] = RegsX86::r9;
s_regMapX86[X86_REG_R9] = RegsX86::r9;
s_regMapX86[X86_REG_R10B] = RegsX86::r10;
s_regMapX86[X86_REG_R10W] = RegsX86::r10;
s_regMapX86[X86_REG_R10D] = RegsX86::r10;
s_regMapX86[X86_REG_R10] = RegsX86::r10;
s_regMapX86[X86_REG_R11B] = RegsX86::r11;
s_regMapX86[X86_REG_R11W] = RegsX86::r11;
s_regMapX86[X86_REG_R11D] = RegsX86::r11;
s_regMapX86[X86_REG_R11] = RegsX86::r11;
s_regMapX86[X86_REG_R12B] = RegsX86::r12;
s_regMapX86[X86_REG_R12W] = RegsX86::r12;
s_regMapX86[X86_REG_R12D] = RegsX86::r12;
s_regMapX86[X86_REG_R12] = RegsX86::r12;
s_regMapX86[X86_REG_R13B] = RegsX86::r13;
s_regMapX86[X86_REG_R13W] = RegsX86::r13;
s_regMapX86[X86_REG_R13D] = RegsX86::r13;
s_regMapX86[X86_REG_R13] = RegsX86::r13;
s_regMapX86[X86_REG_R14B] = RegsX86::r14;
s_regMapX86[X86_REG_R14W] = RegsX86::r14;
s_regMapX86[X86_REG_R14D] = RegsX86::r14;
s_regMapX86[X86_REG_R14] = RegsX86::r14;
s_regMapX86[X86_REG_R15B] = RegsX86::r15;
s_regMapX86[X86_REG_R15W] = RegsX86::r15;
s_regMapX86[X86_REG_R15D] = RegsX86::r15;
s_regMapX86[X86_REG_R15] = RegsX86::r15;
s_regMapX86[X86_REG_MM0] = RegsX86::mm0;
s_regMapX86[X86_REG_MM1] = RegsX86::mm1;
s_regMapX86[X86_REG_MM2] = RegsX86::mm2;
s_regMapX86[X86_REG_MM3] = RegsX86::mm3;
s_regMapX86[X86_REG_MM4] = RegsX86::mm4;
s_regMapX86[X86_REG_MM5] = RegsX86::mm5;
s_regMapX86[X86_REG_MM6] = RegsX86::mm6;
s_regMapX86[X86_REG_MM7] = RegsX86::mm7;
s_regMapX86[X86_REG_ST0] = RegsX86::mm0;
s_regMapX86[X86_REG_ST1] = RegsX86::mm1;
s_regMapX86[X86_REG_ST2] = RegsX86::mm2;
s_regMapX86[X86_REG_ST3] = RegsX86::mm3;
s_regMapX86[X86_REG_ST4] = RegsX86::mm4;
s_regMapX86[X86_REG_ST5] = RegsX86::mm5;
s_regMapX86[X86_REG_ST6] = RegsX86::mm6;
s_regMapX86[X86_REG_ST7] = RegsX86::mm7;
s_regMapX86[X86_REG_XMM0] = RegsX86::xmm0;
s_regMapX86[X86_REG_YMM0] = RegsX86::xmm0;
s_regMapX86[X86_REG_ZMM0] = RegsX86::xmm0;
s_regMapX86[X86_REG_XMM1] = RegsX86::xmm1;
s_regMapX86[X86_REG_YMM1] = RegsX86::xmm1;
s_regMapX86[X86_REG_ZMM1] = RegsX86::xmm1;
s_regMapX86[X86_REG_XMM2] = RegsX86::xmm2;
s_regMapX86[X86_REG_YMM2] = RegsX86::xmm2;
s_regMapX86[X86_REG_ZMM2] = RegsX86::xmm2;
s_regMapX86[X86_REG_XMM3] = RegsX86::xmm3;
s_regMapX86[X86_REG_YMM3] = RegsX86::xmm3;
s_regMapX86[X86_REG_ZMM3] = RegsX86::xmm3;
s_regMapX86[X86_REG_XMM4] = RegsX86::xmm4;
s_regMapX86[X86_REG_YMM4] = RegsX86::xmm4;
s_regMapX86[X86_REG_ZMM4] = RegsX86::xmm4;
s_regMapX86[X86_REG_XMM5] = RegsX86::xmm5;
s_regMapX86[X86_REG_YMM5] = RegsX86::xmm5;
s_regMapX86[X86_REG_ZMM5] = RegsX86::xmm5;
s_regMapX86[X86_REG_XMM6] = RegsX86::xmm6;
s_regMapX86[X86_REG_YMM6] = RegsX86::xmm6;
s_regMapX86[X86_REG_ZMM6] = RegsX86::xmm6;
s_regMapX86[X86_REG_XMM7] = RegsX86::xmm7;
s_regMapX86[X86_REG_YMM7] = RegsX86::xmm7;
s_regMapX86[X86_REG_ZMM7] = RegsX86::xmm7;
s_regMapX86[X86_REG_XMM8] = RegsX86::xmm8;
s_regMapX86[X86_REG_YMM8] = RegsX86::xmm8;
s_regMapX86[X86_REG_ZMM8] = RegsX86::xmm8;
s_regMapX86[X86_REG_XMM9] = RegsX86::xmm9;
s_regMapX86[X86_REG_YMM9] = RegsX86::xmm9;
s_regMapX86[X86_REG_ZMM9] = RegsX86::xmm9;
s_regMapX86[X86_REG_XMM10] = RegsX86::xmm10;
s_regMapX86[X86_REG_YMM10] = RegsX86::xmm10;
s_regMapX86[X86_REG_ZMM10] = RegsX86::xmm10;
s_regMapX86[X86_REG_XMM11] = RegsX86::xmm11;
s_regMapX86[X86_REG_YMM11] = RegsX86::xmm11;
s_regMapX86[X86_REG_ZMM11] = RegsX86::xmm11;
s_regMapX86[X86_REG_XMM12] = RegsX86::xmm12;
s_regMapX86[X86_REG_YMM12] = RegsX86::xmm12;
s_regMapX86[X86_REG_ZMM12] = RegsX86::xmm12;
s_regMapX86[X86_REG_XMM13] = RegsX86::xmm13;
s_regMapX86[X86_REG_YMM13] = RegsX86::xmm13;
s_regMapX86[X86_REG_ZMM13] = RegsX86::xmm13;
s_regMapX86[X86_REG_XMM14] = RegsX86::xmm14;
s_regMapX86[X86_REG_YMM14] = RegsX86::xmm14;
s_regMapX86[X86_REG_ZMM14] = RegsX86::xmm14;
s_regMapX86[X86_REG_XMM15] = RegsX86::xmm15;
s_regMapX86[X86_REG_YMM15] = RegsX86::xmm15;
s_regMapX86[X86_REG_ZMM15] = RegsX86::xmm15;
s_regMapX86[X86_REG_XMM16] = RegsX86::xmm16;
s_regMapX86[X86_REG_YMM16] = RegsX86::xmm16;
s_regMapX86[X86_REG_ZMM16] = RegsX86::xmm16;
s_regMapX86[X86_REG_XMM17] = RegsX86::xmm17;
s_regMapX86[X86_REG_YMM17] = RegsX86::xmm17;
s_regMapX86[X86_REG_ZMM17] = RegsX86::xmm17;
s_regMapX86[X86_REG_XMM18] = RegsX86::xmm18;
s_regMapX86[X86_REG_YMM18] = RegsX86::xmm18;
s_regMapX86[X86_REG_ZMM18] = RegsX86::xmm18;
s_regMapX86[X86_REG_XMM19] = RegsX86::xmm19;
s_regMapX86[X86_REG_YMM19] = RegsX86::xmm19;
s_regMapX86[X86_REG_ZMM19] = RegsX86::xmm19;
s_regMapX86[X86_REG_XMM20] = RegsX86::xmm20;
s_regMapX86[X86_REG_YMM20] = RegsX86::xmm20;
s_regMapX86[X86_REG_ZMM20] = RegsX86::xmm20;
s_regMapX86[X86_REG_XMM21] = RegsX86::xmm21;
s_regMapX86[X86_REG_YMM21] = RegsX86::xmm21;
s_regMapX86[X86_REG_ZMM21] = RegsX86::xmm21;
s_regMapX86[X86_REG_XMM22] = RegsX86::xmm22;
s_regMapX86[X86_REG_YMM22] = RegsX86::xmm22;
s_regMapX86[X86_REG_ZMM22] = RegsX86::xmm22;
s_regMapX86[X86_REG_XMM23] = RegsX86::xmm23;
s_regMapX86[X86_REG_YMM23] = RegsX86::xmm23;
s_regMapX86[X86_REG_ZMM23] = RegsX86::xmm23;
s_regMapX86[X86_REG_XMM24] = RegsX86::xmm24;
s_regMapX86[X86_REG_YMM24] = RegsX86::xmm24;
s_regMapX86[X86_REG_ZMM24] = RegsX86::xmm24;
s_regMapX86[X86_REG_XMM25] = RegsX86::xmm25;
s_regMapX86[X86_REG_YMM25] = RegsX86::xmm25;
s_regMapX86[X86_REG_ZMM25] = RegsX86::xmm25;
s_regMapX86[X86_REG_XMM26] = RegsX86::xmm26;
s_regMapX86[X86_REG_YMM26] = RegsX86::xmm26;
s_regMapX86[X86_REG_ZMM26] = RegsX86::xmm26;
s_regMapX86[X86_REG_XMM27] = RegsX86::xmm27;
s_regMapX86[X86_REG_YMM27] = RegsX86::xmm27;
s_regMapX86[X86_REG_ZMM27] = RegsX86::xmm27;
s_regMapX86[X86_REG_XMM28] = RegsX86::xmm28;
s_regMapX86[X86_REG_YMM28] = RegsX86::xmm28;
s_regMapX86[X86_REG_ZMM28] = RegsX86::xmm28;
s_regMapX86[X86_REG_XMM29] = RegsX86::xmm29;
s_regMapX86[X86_REG_YMM29] = RegsX86::xmm29;
s_regMapX86[X86_REG_ZMM29] = RegsX86::xmm29;
s_regMapX86[X86_REG_XMM30] = RegsX86::xmm30;
s_regMapX86[X86_REG_YMM30] = RegsX86::xmm30;
s_regMapX86[X86_REG_ZMM30] = RegsX86::xmm30;
s_regMapX86[X86_REG_XMM31] = RegsX86::xmm31;
s_regMapX86[X86_REG_YMM31] = RegsX86::xmm31;
s_regMapX86[X86_REG_ZMM31] = RegsX86::xmm31;
s_regMapX86[X86_REG_K0] = RegsX86::k0;
s_regMapX86[X86_REG_K1] = RegsX86::k1;
s_regMapX86[X86_REG_K2] = RegsX86::k2;
s_regMapX86[X86_REG_K3] = RegsX86::k3;
s_regMapX86[X86_REG_K4] = RegsX86::k4;
s_regMapX86[X86_REG_K5] = RegsX86::k5;
s_regMapX86[X86_REG_K6] = RegsX86::k6;
s_regMapX86[X86_REG_K7] = RegsX86::k7;
Replace source file viewer with one that actually works. This is much simpler, custom implementation of a text file viewer. It is able to perform these two tasks as intended: - center source view on the selected line, - highlight that line.
2020-03-22 19:53:59 +00:00
}
SourceView::~SourceView()
{
Use cached source files.
2020-05-23 13:14:57 +00:00
delete[] m_dataBuf;
Replace source file viewer with one that actually works. This is much simpler, custom implementation of a text file viewer. It is able to perform these two tasks as intended: - center source view on the selected line, - highlight that line.
2020-03-22 19:53:59 +00:00
}
Select microarchitecture basing on cpuid.
2020-05-06 22:53:31 +00:00
static constexpr uint32_t PackCpuInfo( uint32_t cpuid )
{
return ( cpuid & 0xFFF ) | ( ( cpuid & 0xFFF0000 ) >> 4 );
}
struct CpuIdMap
{
uint32_t cpuInfo;
const char* moniker;
};
// .------ extended family id
// |.----- extended model id
// || .--- family id
// || |.-- model
// || ||.- stepping
// || |||
static constexpr CpuIdMap s_cpuIdMap[] = {
{ PackCpuInfo( 0x810F81 ), "ZEN+" },
{ PackCpuInfo( 0x800F82 ), "ZEN+" },
{ PackCpuInfo( 0x870F10 ), "ZEN2" },
{ PackCpuInfo( 0x830F10 ), "ZEN2" },
{ PackCpuInfo( 0x860F01 ), "ZEN2" },
{ PackCpuInfo( 0x0706E5 ), "ICL" },
{ PackCpuInfo( 0x060663 ), "CNL" },
{ PackCpuInfo( 0x0906EA ), "CFL" },
{ PackCpuInfo( 0x0906EB ), "CFL" },
{ PackCpuInfo( 0x0906EC ), "CFL" },
{ PackCpuInfo( 0x0906ED ), "CFL" },
{ PackCpuInfo( 0x0806E9 ), "KBL" },
{ PackCpuInfo( 0x0806EA ), "KBL" },
{ PackCpuInfo( 0x0906E9 ), "KBL" },
{ PackCpuInfo( 0x050654 ), "SKX" },
{ PackCpuInfo( 0x0406E3 ), "SKL" },
{ PackCpuInfo( 0x0506E0 ), "SKL" },
{ PackCpuInfo( 0x0506E3 ), "SKL" },
{ PackCpuInfo( 0x0306D4 ), "BDW" },
{ PackCpuInfo( 0x040671 ), "BDW" },
{ PackCpuInfo( 0x0406F1 ), "BDW" },
{ PackCpuInfo( 0x0306C3 ), "HSW" },
{ PackCpuInfo( 0x0306F2 ), "HSW" },
{ PackCpuInfo( 0x040651 ), "HSW" },
{ PackCpuInfo( 0x0306A9 ), "IVB" },
{ PackCpuInfo( 0x0306E3 ), "IVB" },
{ PackCpuInfo( 0x0306E4 ), "IVB" },
{ PackCpuInfo( 0x0206A2 ), "SNB" },
{ PackCpuInfo( 0x0206A7 ), "SNB" },
{ PackCpuInfo( 0x0206D5 ), "SNB" },
{ PackCpuInfo( 0x0206D6 ), "SNB" },
{ PackCpuInfo( 0x0206D7 ), "SNB" },
{ PackCpuInfo( 0x0206F2 ), "WSM" },
{ PackCpuInfo( 0x0206C0 ), "WSM" },
{ PackCpuInfo( 0x0206C1 ), "WSM" },
{ PackCpuInfo( 0x0206C2 ), "WSM" },
{ PackCpuInfo( 0x020652 ), "WSM" },
{ PackCpuInfo( 0x020655 ), "WSM" },
{ PackCpuInfo( 0x0206E6 ), "NHM" },
{ PackCpuInfo( 0x0106A1 ), "NHM" },
{ PackCpuInfo( 0x0106A2 ), "NHM" },
{ PackCpuInfo( 0x0106A4 ), "NHM" },
{ PackCpuInfo( 0x0106A5 ), "NHM" },
{ PackCpuInfo( 0x0106E4 ), "NHM" },
{ PackCpuInfo( 0x0106E5 ), "NHM" },
{ PackCpuInfo( 0x010676 ), "WOL" },
{ PackCpuInfo( 0x01067A ), "WOL" },
{ PackCpuInfo( 0x0006F2 ), "CON" },
{ PackCpuInfo( 0x0006F4 ), "CON" },
{ PackCpuInfo( 0x0006F6 ), "CON" },
{ PackCpuInfo( 0x0006FB ), "CON" },
{ PackCpuInfo( 0x0006FD ), "CON" },
{ 0, 0 }
};
void SourceView::SetCpuId( uint32_t cpuId )
{
auto ptr = s_cpuIdMap;
while( ptr->cpuInfo )
{
if( cpuId == ptr->cpuInfo )
{
SelectMicroArchitecture( ptr->moniker );
return;
}
ptr++;
}
SelectMicroArchitecture( "ZEN2" );
}
Use cached source files.
2020-05-23 13:14:57 +00:00
void SourceView::OpenSource( const char* fileName, int line, const View& view, const Worker& worker )
Separate opening source and symbol views.
2020-04-08 00:11:58 +00:00
{
m_targetLine = line;
m_selectedLine = line;
m_targetAddr = 0;
m_baseAddr = 0;
m_symAddr = 0;
Build list of symbol source files.
2020-04-08 20:18:00 +00:00
m_sourceFiles.clear();
Clear asm data when opening just source view.
2020-06-04 17:20:24 +00:00
m_asm.clear();
Separate opening source and symbol views.
2020-04-08 00:11:58 +00:00
Use cached source files.
2020-05-23 13:14:57 +00:00
ParseSource( fileName, worker, view );
Separate opening source and symbol views.
2020-04-08 00:11:58 +00:00
assert( !m_lines.empty() );
}
Substitute source file names in source view.
2020-04-17 17:17:47 +00:00
void SourceView::OpenSymbol( const char* fileName, int line, uint64_t baseAddr, uint64_t symAddr, const Worker& worker, const View& view )
Replace source file viewer with one that actually works. This is much simpler, custom implementation of a text file viewer. It is able to perform these two tasks as intended: - center source view on the selected line, - highlight that line.
2020-03-22 19:53:59 +00:00
{
m_targetLine = line;
Display disassembly.
2020-03-25 21:53:05 +00:00
m_targetAddr = symAddr;
Revert "Base address is not needed." This reverts commit 058369bc7a25ea0027916b1dda350d75201b6068.
2020-03-27 23:57:41 +00:00
m_baseAddr = baseAddr;
Pass symbol address to source view.
2020-03-24 23:07:31 +00:00
m_symAddr = symAddr;
Build list of symbol source files.
2020-04-08 20:18:00 +00:00
m_sourceFiles.clear();
Match source and assembly selection.
2020-04-08 20:57:42 +00:00
m_selectedAddresses.clear();
m_selectedAddresses.emplace( symAddr );
Replace source file viewer with one that actually works. This is much simpler, custom implementation of a text file viewer. It is able to perform these two tasks as intended: - center source view on the selected line, - highlight that line.
2020-03-22 19:53:59 +00:00
Use cached source files.
2020-05-23 13:14:57 +00:00
ParseSource( fileName, worker, view );
Mixed source/assembly symbol view.
2020-04-08 20:04:00 +00:00
Disassemble( baseAddr, worker );
Only change assembly target line when necessary.
2020-04-08 21:30:42 +00:00
SelectLine( line, &worker, true, symAddr );
Separate opening source and symbol views.
2020-04-08 00:11:58 +00:00
Mixed source/assembly symbol view.
2020-04-08 20:04:00 +00:00
if( !m_lines.empty() )
{
if( !m_asm.empty() )
{
m_displayMode = DisplayMixed;
}
else
{
m_displayMode = DisplaySource;
}
}
else
{
assert( !m_asm.empty() );
m_displayMode = DisplayAsm;
}
Separate opening source and symbol views.
2020-04-08 00:11:58 +00:00
}
Use cached source files.
2020-05-23 13:14:57 +00:00
void SourceView::ParseSource( const char* fileName, const Worker& worker, const View& view )
Separate opening source and symbol views.
2020-04-08 00:11:58 +00:00
{
Replace source file viewer with one that actually works. This is much simpler, custom implementation of a text file viewer. It is able to perform these two tasks as intended: - center source view on the selected line, - highlight that line.
2020-03-22 19:53:59 +00:00
if( m_file != fileName )
{
Set source view content width to max value, regardless of clipping.
2020-06-06 10:31:47 +00:00
m_srcWidth = 0;
Replace source file viewer with one that actually works. This is much simpler, custom implementation of a text file viewer. It is able to perform these two tasks as intended: - center source view on the selected line, - highlight that line.
2020-03-22 19:53:59 +00:00
m_file = fileName;
Use cached source files.
2020-05-23 13:14:57 +00:00
m_fileStringIdx = worker.FindStringIdx( fileName );
Replace source file viewer with one that actually works. This is much simpler, custom implementation of a text file viewer. It is able to perform these two tasks as intended: - center source view on the selected line, - highlight that line.
2020-03-22 19:53:59 +00:00
m_lines.clear();
Allow viewing assembly without corresponding source code.
2020-03-27 00:47:06 +00:00
if( fileName )
Replace source file viewer with one that actually works. This is much simpler, custom implementation of a text file viewer. It is able to perform these two tasks as intended: - center source view on the selected line, - highlight that line.
2020-03-22 19:53:59 +00:00
{
Use cached source files.
2020-05-23 13:14:57 +00:00
uint32_t sz;
const auto srcCache = worker.GetSourceFileFromCache( fileName );
if( srcCache.data != nullptr )
Replace source file viewer with one that actually works. This is much simpler, custom implementation of a text file viewer. It is able to perform these two tasks as intended: - center source view on the selected line, - highlight that line.
2020-03-22 19:53:59 +00:00
{
Use cached source files.
2020-05-23 13:14:57 +00:00
m_data = srcCache.data;
sz = srcCache.len;
}
else
{
FILE* f = fopen( view.SourceSubstitution( fileName ), "rb" );
assert( f );
fseek( f, 0, SEEK_END );
sz = ftell( f );
fseek( f, 0, SEEK_SET );
if( sz > m_dataSize )
{
delete[] m_dataBuf;
Don't depend on zero-termination of source code.
2020-05-23 15:07:23 +00:00
m_dataBuf = new char[sz];
Use cached source files.
2020-05-23 13:14:57 +00:00
m_dataSize = sz;
}
fread( m_dataBuf, 1, sz, f );
m_data = m_dataBuf;
fclose( f );
Replace source file viewer with one that actually works. This is much simpler, custom implementation of a text file viewer. It is able to perform these two tasks as intended: - center source view on the selected line, - highlight that line.
2020-03-22 19:53:59 +00:00
}
Allow viewing assembly without corresponding source code.
2020-03-27 00:47:06 +00:00
Add C++ tokenizer.
2020-04-24 21:48:18 +00:00
m_tokenizer.Reset();
Allow viewing assembly without corresponding source code.
2020-03-27 00:47:06 +00:00
auto txt = m_data;
for(;;)
Replace source file viewer with one that actually works. This is much simpler, custom implementation of a text file viewer. It is able to perform these two tasks as intended: - center source view on the selected line, - highlight that line.
2020-03-22 19:53:59 +00:00
{
Allow viewing assembly without corresponding source code.
2020-03-27 00:47:06 +00:00
auto end = txt;
while( *end != '\n' && *end != '\r' && end - m_data < sz ) end++;
Add C++ tokenizer.
2020-04-24 21:48:18 +00:00
m_lines.emplace_back( Line { txt, end, Tokenize( txt, end ) } );
Allow viewing assembly without corresponding source code.
2020-03-27 00:47:06 +00:00
if( *end == '\n' )
{
end++;
Don't read beyond buffer end.
2020-06-04 00:46:46 +00:00
if( end - m_data < sz && *end == '\r' ) end++;
Allow viewing assembly without corresponding source code.
2020-03-27 00:47:06 +00:00
}
else if( *end == '\r' )
{
end++;
Don't read beyond buffer end.
2020-06-04 00:46:46 +00:00
if( end - m_data < sz && *end == '\n' ) end++;
Allow viewing assembly without corresponding source code.
2020-03-27 00:47:06 +00:00
}
Don't depend on zero-termination of source code.
2020-05-23 15:07:23 +00:00
if( end - m_data == sz ) break;
Allow viewing assembly without corresponding source code.
2020-03-27 00:47:06 +00:00
txt = end;
Replace source file viewer with one that actually works. This is much simpler, custom implementation of a text file viewer. It is able to perform these two tasks as intended: - center source view on the selected line, - highlight that line.
2020-03-22 19:53:59 +00:00
}
}
}
Display disassembly.
2020-03-25 21:53:05 +00:00
}
Disassemble symbol code fragments.
2020-03-25 21:37:34 +00:00
Detect conditional jumps.
2020-05-01 18:09:21 +00:00
static bool IsJumpConditionalX86( const char* op )
{
static constexpr const char* branchX86[] = {
"je", "jne", "jg", "jge", "ja", "jae", "jl", "jle", "jb", "jbe", "jo", "jno", "jz", "jnz", "js", "jns", "jcxz", "jecxz", "jrcxz", "loop", "loope",
"loopne", "loopnz", "loopz", "jnle", "jnl", "jnge", "jng", "jnbe", "jnb", "jnae", "jna", "jc", "jnc", "jp", "jpe", "jnp", "jpo", nullptr
};
auto ptr = branchX86;
while( *ptr ) if( strcmp( *ptr++, op ) == 0 ) return true;
return false;
}
Display disassembly.
2020-03-25 21:53:05 +00:00
bool SourceView::Disassemble( uint64_t symAddr, const Worker& worker )
{
Disassemble symbol code fragments.
2020-03-25 21:37:34 +00:00
m_asm.clear();
Construct location table during disassembly.
2020-05-09 12:58:06 +00:00
m_locMap.clear();
Calculate jump table.
2020-04-04 00:25:12 +00:00
m_jumpTable.clear();
Collect jumps outside symbol.
2020-04-04 11:51:55 +00:00
m_jumpOut.clear();
Calculate jump table.
2020-04-04 00:25:12 +00:00
m_maxJumpLevel = 0;
Invalidate asm line selection when disassembly is performed.
2020-05-01 18:59:08 +00:00
m_asmSelected = -1;
Allow enumerating asm lines from a given base instruction.
2020-05-11 11:35:49 +00:00
m_asmCountBase = -1;
Set source view content width to max value, regardless of clipping.
2020-06-06 10:31:47 +00:00
m_asmWidth = 0;
Display disassembly.
2020-03-25 21:53:05 +00:00
if( symAddr == 0 ) return false;
Store CPU architecture.
2020-04-26 12:23:16 +00:00
m_cpuArch = worker.GetCpuArch();
if( m_cpuArch == CpuArchUnknown ) return false;
Disassemble symbol code fragments.
2020-03-25 21:37:34 +00:00
uint32_t len;
auto code = worker.GetSymbolCode( symAddr, len );
Display disassembly.
2020-03-25 21:53:05 +00:00
if( !code ) return false;
Detect disassembly failures.
2020-04-19 12:40:36 +00:00
m_disasmFail = -1;
Disassemble symbol code fragments.
2020-03-25 21:37:34 +00:00
csh handle;
Initialize variable.
2020-03-27 22:58:49 +00:00
cs_err rval = CS_ERR_ARCH;
Store CPU architecture.
2020-04-26 12:23:16 +00:00
switch( m_cpuArch )
Disassemble symbol code fragments.
2020-03-25 21:37:34 +00:00
{
case CpuArchX86:
rval = cs_open( CS_ARCH_X86, CS_MODE_32, &handle );
break;
case CpuArchX64:
rval = cs_open( CS_ARCH_X86, CS_MODE_64, &handle );
break;
case CpuArchArm32:
rval = cs_open( CS_ARCH_ARM, CS_MODE_ARM, &handle );
break;
case CpuArchArm64:
rval = cs_open( CS_ARCH_ARM64, CS_MODE_ARM, &handle );
break;
default:
assert( false );
break;
}
Display disassembly.
2020-03-25 21:53:05 +00:00
if( rval != CS_ERR_OK ) return false;
Decode jump/call addresses.
2020-03-27 23:53:48 +00:00
cs_option( handle, CS_OPT_DETAIL, CS_OPT_ON );
Allow switching between Intel and AT&T assembly syntax.
2020-05-09 10:58:09 +00:00
cs_option( handle, CS_OPT_SYNTAX, m_atnt ? CS_OPT_SYNTAX_ATT : CS_OPT_SYNTAX_INTEL );
Disassemble symbol code fragments.
2020-03-25 21:37:34 +00:00
cs_insn* insn;
size_t cnt = cs_disasm( handle, (const uint8_t*)code, len, symAddr, 0, &insn );
if( cnt > 0 )
{
Detect disassembly failures.
2020-04-19 12:40:36 +00:00
if( insn[cnt-1].address - symAddr + insn[cnt-1].size < len ) m_disasmFail = insn[cnt-1].address - symAddr;
Allow displaying machine code bytes in disassembly.
2020-04-19 14:06:45 +00:00
int bytesMax = 0;
Tighten mnemonic display.
2020-04-08 23:45:38 +00:00
int mLenMax = 0;
Disassemble symbol code fragments.
2020-03-25 21:37:34 +00:00
m_asm.reserve( cnt );
for( size_t i=0; i<cnt; i++ )
{
Decode jump/call addresses.
2020-03-27 23:53:48 +00:00
const auto& op = insn[i];
const auto& detail = *op.detail;
bool hasJump = false;
Detect conditional jumps.
2020-05-01 18:09:21 +00:00
bool jumpConditional = false;
Use generic group categories.
2020-03-28 13:00:21 +00:00
for( auto j=0; j<detail.groups_count; j++ )
Decode jump/call addresses.
2020-03-27 23:53:48 +00:00
{
Include return instructions in jump out list.
2020-04-04 12:30:31 +00:00
if( detail.groups[j] == CS_GRP_JUMP || detail.groups[j] == CS_GRP_CALL || detail.groups[j] == CS_GRP_RET )
Decode jump/call addresses.
2020-03-27 23:53:48 +00:00
{
Use generic group categories.
2020-03-28 13:00:21 +00:00
hasJump = true;
break;
Decode jump/call addresses.
2020-03-27 23:53:48 +00:00
}
}
uint64_t jumpAddr = 0;
if( hasJump )
{
Store CPU architecture.
2020-04-26 12:23:16 +00:00
switch( m_cpuArch )
Decode jump/call addresses.
2020-03-27 23:53:48 +00:00
{
case CpuArchX86:
case CpuArchX64:
if( detail.x86.op_count == 1 && detail.x86.operands[0].type == X86_OP_IMM )
{
jumpAddr = (uint64_t)detail.x86.operands[0].imm;
}
Detect conditional jumps.
2020-05-01 18:09:21 +00:00
jumpConditional = IsJumpConditionalX86( op.mnemonic );
Decode jump/call addresses.
2020-03-27 23:53:48 +00:00
break;
case CpuArchArm32:
if( detail.arm.op_count == 1 && detail.arm.operands[0].type == ARM_OP_IMM )
{
jumpAddr = (uint64_t)detail.arm.operands[0].imm;
}
break;
case CpuArchArm64:
if( detail.arm64.op_count == 1 && detail.arm64.operands[0].type == ARM64_OP_IMM )
{
jumpAddr = (uint64_t)detail.arm64.operands[0].imm;
}
break;
default:
assert( false );
break;
}
Ignore out-of-symbol jumps.
2020-04-04 01:13:21 +00:00
if( jumpAddr >= symAddr && jumpAddr < symAddr + len )
Calculate jump table.
2020-04-04 00:25:12 +00:00
{
Filter invalid jumps.
2020-04-19 13:45:19 +00:00
auto fit = std::lower_bound( insn, insn+cnt, jumpAddr, []( const auto& l, const auto& r ) { return l.address < r; } );
if( fit != insn+cnt && fit->address == jumpAddr )
Calculate jump table.
2020-04-04 00:25:12 +00:00
{
Filter invalid jumps.
2020-04-19 13:45:19 +00:00
const auto min = std::min( jumpAddr, op.address );
const auto max = std::max( jumpAddr, op.address );
auto it = m_jumpTable.find( jumpAddr );
if( it == m_jumpTable.end() )
{
m_jumpTable.emplace( jumpAddr, JumpData { min, max, 0, { op.address } } );
}
else
{
if( it->second.min > min ) it->second.min = min;
else if( it->second.max < max ) it->second.max = max;
it->second.source.emplace_back( op.address );
}
Calculate jump table.
2020-04-04 00:25:12 +00:00
}
else
{
Filter invalid jumps.
2020-04-19 13:45:19 +00:00
jumpAddr = 0;
Calculate jump table.
2020-04-04 00:25:12 +00:00
}
}
Collect jumps outside symbol.
2020-04-04 11:51:55 +00:00
else
{
m_jumpOut.emplace( op.address );
}
Decode jump/call addresses.
2020-03-27 23:53:48 +00:00
}
Add micro architecture tooltips.
2020-04-26 20:26:17 +00:00
std::vector<AsmOpParams> params;
switch( m_cpuArch )
{
case CpuArchX86:
case CpuArchX64:
for( uint8_t i=0; i<detail.x86.op_count; i++ )
{
uint8_t type = 0;
switch( detail.x86.operands[i].type )
{
case X86_OP_IMM:
type = 0;
break;
case X86_OP_REG:
type = 1;
break;
case X86_OP_MEM:
type = 2;
break;
default:
assert( false );
break;
}
params.emplace_back( AsmOpParams { type, uint16_t( detail.x86.operands[i].size * 8 ) } );
}
break;
case CpuArchArm32:
for( uint8_t i=0; i<detail.arm.op_count; i++ )
{
uint8_t type = 0;
switch( detail.arm.operands[i].type )
{
case ARM_OP_IMM:
type = 0;
break;
case ARM_OP_REG:
type = 1;
break;
case ARM_OP_MEM:
type = 2;
break;
default:
type = 255;
break;
}
params.emplace_back( AsmOpParams { type, 0 } );
}
break;
case CpuArchArm64:
for( uint8_t i=0; i<detail.arm64.op_count; i++ )
{
uint8_t type = 0;
switch( detail.arm64.operands[i].type )
{
case ARM64_OP_IMM:
type = 0;
break;
case ARM64_OP_REG:
type = 1;
break;
case ARM64_OP_MEM:
type = 2;
break;
default:
type = 255;
break;
}
params.emplace_back( AsmOpParams { type, 0 } );
}
break;
default:
assert( false );
break;
}
Hackish support for LEA variants.
2020-04-26 22:49:37 +00:00
LeaData leaData = LeaData::none;
if( ( m_cpuArch == CpuArchX64 || m_cpuArch == CpuArchX86 ) && op.id == X86_INS_LEA )
{
assert( op.detail->x86.op_count == 2 );
Select proper operand for LEA processing in AT&T mode.
2020-05-14 23:37:08 +00:00
const auto opidx = m_atnt ? 0 : 1;
assert( op.detail->x86.operands[opidx].type == X86_OP_MEM );
auto& mem = op.detail->x86.operands[opidx].mem;
Hackish support for LEA variants.
2020-04-26 22:49:37 +00:00
if( mem.base == X86_REG_INVALID )
{
if( mem.index == X86_REG_INVALID )
{
leaData = LeaData::d;
}
else
{
leaData = mem.disp == 0 ? LeaData::i : LeaData::id;
}
}
else if( mem.base == X86_REG_RIP )
{
leaData = mem.disp == 0 ? LeaData::r : LeaData::rd;
}
else
{
if( mem.index == X86_REG_INVALID )
{
leaData = mem.disp == 0 ? LeaData::b : LeaData::bd;
}
else
{
leaData = mem.disp == 0 ? LeaData::bi : LeaData::bid;
}
}
}
Detect conditional jumps.
2020-05-01 18:09:21 +00:00
m_asm.emplace_back( AsmLine { op.address, jumpAddr, op.mnemonic, op.op_str, (uint8_t)op.size, leaData, jumpConditional, std::move( params ) } );
Store list of read and write registers for each asm instruction.
2020-05-01 11:01:19 +00:00
Register usage is only available in capstone 4.x.
2020-05-02 01:09:16 +00:00
#if CS_API_MAJOR >= 4
Store list of read and write registers for each asm instruction.
2020-05-01 11:01:19 +00:00
auto& entry = m_asm.back();
cs_regs read, write;
uint8_t rcnt, wcnt;
cs_regs_access( handle, &op, read, &rcnt, write, &wcnt );
int idx;
switch( m_cpuArch )
{
case CpuArchX86:
case CpuArchX64:
assert( rcnt < sizeof( entry.readX86 ) );
assert( wcnt < sizeof( entry.writeX86 ) );
idx = 0;
for( int i=0; i<rcnt; i++ )
{
if( s_regMapX86[read[i]] != RegsX86::invalid ) entry.readX86[idx++] = s_regMapX86[read[i]];
entry.readX86[idx] = RegsX86::invalid;
}
idx = 0;
for( int i=0; i<wcnt; i++ )
{
if( s_regMapX86[write[i]] != RegsX86::invalid ) entry.writeX86[idx++] = s_regMapX86[write[i]];
entry.writeX86[idx] = RegsX86::invalid;
}
break;
default:
break;
}
Register usage is only available in capstone 4.x.
2020-05-02 01:09:16 +00:00
#endif
Store list of read and write registers for each asm instruction.
2020-05-01 11:01:19 +00:00
Tighten mnemonic display.
2020-04-08 23:45:38 +00:00
const auto mLen = strlen( op.mnemonic );
if( mLen > mLenMax ) mLenMax = mLen;
Allow displaying machine code bytes in disassembly.
2020-04-19 14:06:45 +00:00
if( op.size > bytesMax ) bytesMax = op.size;
Build list of symbol source files.
2020-04-08 20:18:00 +00:00
Tighten assembly source location display.
2020-04-08 23:52:22 +00:00
uint32_t mLineMax = 0;
Build list of symbol source files.
2020-04-08 20:18:00 +00:00
uint32_t srcline;
const auto srcidx = worker.GetLocationForAddress( op.address, srcline );
if( srcline != 0 )
{
Tighten assembly source location display.
2020-04-08 23:52:22 +00:00
if( srcline > mLineMax ) mLineMax = srcline;
Build list of symbol source files.
2020-04-08 20:18:00 +00:00
const auto idx = srcidx.Idx();
auto sit = m_sourceFiles.find( idx );
if( sit == m_sourceFiles.end() )
{
Symbol file selector.
2020-04-08 20:25:36 +00:00
m_sourceFiles.emplace( idx, srcline );
Build list of symbol source files.
2020-04-08 20:18:00 +00:00
}
}
Tighten assembly source location display.
2020-04-08 23:52:22 +00:00
char tmp[16];
sprintf( tmp, "%" PRIu32, mLineMax );
m_maxLine = strlen( tmp ) + 1;
Disassemble symbol code fragments.
2020-03-25 21:37:34 +00:00
}
cs_free( insn, cnt );
Tighten mnemonic display.
2020-04-08 23:45:38 +00:00
m_maxMnemonicLen = mLenMax + 2;
Allow displaying machine code bytes in disassembly.
2020-04-19 14:06:45 +00:00
m_maxAsmBytes = bytesMax;
Calculate jump table.
2020-04-04 00:25:12 +00:00
if( !m_jumpTable.empty() )
{
struct JumpRange
{
uint64_t target;
uint64_t len;
};
std::vector<JumpRange> jumpRange;
jumpRange.reserve( m_jumpTable.size() );
for( auto& v : m_jumpTable )
{
pdqsort_branchless( v.second.source.begin(), v.second.source.end() );
jumpRange.emplace_back( JumpRange { v.first, v.second.max - v.second.min } );
}
pdqsort_branchless( jumpRange.begin(), jumpRange.end(), []( const auto& l, const auto& r ) { return l.len < r.len; } );
std::vector<std::vector<std::pair<uint64_t, uint64_t>>> levelRanges;
for( auto& v : jumpRange )
{
auto it = m_jumpTable.find( v.target );
assert( it != m_jumpTable.end() );
int level = 0;
for(;;)
{
assert( levelRanges.size() >= level );
if( levelRanges.size() == level )
{
it->second.level = level;
levelRanges.push_back( { { it->second.min, it->second.max } } );
break;
}
else
{
bool validFit = true;
auto& lr = levelRanges[level];
for( auto& range : lr )
{
assert( !( it->second.min >= range.first && it->second.max <= range.second ) );
if( it->second.min <= range.second && it->second.max >= range.first )
{
validFit = false;
break;
}
}
if( validFit )
{
it->second.level = level;
lr.emplace_back( it->second.min, it->second.max );
break;
}
level++;
}
}
if( level > m_maxJumpLevel ) m_maxJumpLevel = level;
}
Construct location table during disassembly.
2020-05-09 12:58:06 +00:00
uint32_t locNum = 0;
for( auto& v : m_asm )
{
if( m_jumpTable.find( v.addr ) != m_jumpTable.end() )
{
m_locMap.emplace( v.addr, locNum++ );
}
}
Calculate jump table.
2020-04-04 00:25:12 +00:00
}
Disassemble symbol code fragments.
2020-03-25 21:37:34 +00:00
}
cs_close( &handle );
Display code size in source file view window.
2020-03-26 01:23:09 +00:00
m_codeLen = len;
Add space for register data in each asm line.
2020-05-01 14:33:09 +00:00
ResetAsm();
Display disassembly.
2020-03-25 21:53:05 +00:00
return true;
Replace source file viewer with one that actually works. This is much simpler, custom implementation of a text file viewer. It is able to perform these two tasks as intended: - center source view on the selected line, - highlight that line.
2020-03-22 19:53:59 +00:00
}
Add ability to show callstack to an asm line.
2020-05-10 14:56:38 +00:00
void SourceView::Render( const Worker& worker, View& view )
Replace source file viewer with one that actually works. This is much simpler, custom implementation of a text file viewer. It is able to perform these two tasks as intended: - center source view on the selected line, - highlight that line.
2020-03-22 19:53:59 +00:00
{
Display jump/call target address.
2020-03-28 00:22:27 +00:00
m_highlightAddr.Decay( 0 );
Highlight source line corresponding to hovered asm line.
2020-04-09 20:02:06 +00:00
m_hoveredLine.Decay( 0 );
m_hoveredSource.Decay( 0 );
Display jump/call target address.
2020-03-28 00:22:27 +00:00
Split source and symbol views in SourceView.
2020-04-07 23:58:23 +00:00
if( m_symAddr == 0 )
{
Sprinkle some icons.
2020-04-09 00:33:02 +00:00
if( m_file ) TextFocused( ICON_FA_FILE " File:", m_file );
Add notification when source file is loaded from cache.
2020-05-23 13:27:00 +00:00
if( m_data == m_dataBuf )
{
TextColoredUnformatted( ImVec4( 1.f, 1.f, 0.2f, 1.f ), ICON_FA_EXCLAMATION_TRIANGLE );
ImGui::SameLine();
TextColoredUnformatted( ImVec4( 1.f, 0.3f, 0.3f, 1.f ), "The source file contents might not reflect the actual profiled code!" );
ImGui::SameLine();
TextColoredUnformatted( ImVec4( 1.f, 1.f, 0.2f, 1.f ), ICON_FA_EXCLAMATION_TRIANGLE );
}
else
{
TextColoredUnformatted( ImVec4( 0.4f, 0.8f, 0.4f, 1.f ), ICON_FA_DATABASE );
ImGui::SameLine();
ImGui::TextUnformatted( "Source file cached during profiling run" );
}
Split source and symbol views in SourceView.
2020-04-07 23:58:23 +00:00
RenderSimpleSourceView();
}
else
{
Perform source file name substitution.
2020-04-17 17:09:13 +00:00
RenderSymbolView( worker, view );
Split source and symbol views in SourceView.
2020-04-07 23:58:23 +00:00
}
}
void SourceView::RenderSimpleSourceView()
{
Set source view content width to max value, regardless of clipping.
2020-06-06 10:31:47 +00:00
ImGui::SetNextWindowContentSize( ImVec2( m_srcWidth, 0 ) );
Enable horizontal scrollbar in source view.
2020-06-05 17:04:12 +00:00
ImGui::BeginChild( "##sourceView", ImVec2( 0, 0 ), true, ImGuiWindowFlags_HorizontalScrollbar );
Split source and symbol views in SourceView.
2020-04-07 23:58:23 +00:00
if( m_font ) ImGui::PushFont( m_font );
Draw a line indicating zeroth column of source code.
2020-04-25 11:52:21 +00:00
auto draw = ImGui::GetWindowDrawList();
const auto wpos = ImGui::GetWindowPos();
const auto wh = ImGui::GetWindowHeight();
const auto ty = ImGui::GetFontSize();
const auto ts = ImGui::CalcTextSize( " " ).x;
const auto lineCount = m_lines.size();
const auto tmp = RealToString( lineCount );
const auto maxLine = strlen( tmp );
const auto lx = ts * maxLine + ty + round( ts*0.4f );
draw->AddLine( wpos + ImVec2( lx, 0 ), wpos + ImVec2( lx, wh ), 0x08FFFFFF );
Split source and symbol views in SourceView.
2020-04-07 23:58:23 +00:00
if( m_targetLine != 0 )
{
int lineNum = 1;
for( auto& line : m_lines )
{
if( m_targetLine == lineNum )
{
m_targetLine = 0;
ImGui::SetScrollHereY();
}
Draw hotness markers next to sample percentage counts.
2020-04-10 23:59:15 +00:00
RenderLine( line, lineNum++, 0, 0, 0, nullptr );
Split source and symbol views in SourceView.
2020-04-07 23:58:23 +00:00
}
Don't mark windows as write-modified when only reading data.
2020-06-06 18:46:46 +00:00
const auto win = ImGui::GetCurrentWindowRead();
Set source view content width to max value, regardless of clipping.
2020-06-06 10:31:47 +00:00
m_srcWidth = win->DC.CursorMaxPos.x - win->DC.CursorStartPos.x;
Split source and symbol views in SourceView.
2020-04-07 23:58:23 +00:00
}
else
{
ImGuiListClipper clipper( (int)m_lines.size() );
while( clipper.Step() )
{
for( auto i=clipper.DisplayStart; i<clipper.DisplayEnd; i++ )
{
Draw hotness markers next to sample percentage counts.
2020-04-10 23:59:15 +00:00
RenderLine( m_lines[i], i+1, 0, 0, 0, nullptr );
Split source and symbol views in SourceView.
2020-04-07 23:58:23 +00:00
}
}
}
if( m_font ) ImGui::PopFont();
ImGui::EndChild();
}
Add ability to show callstack to an asm line.
2020-05-10 14:56:38 +00:00
void SourceView::RenderSymbolView( const Worker& worker, View& view )
Split source and symbol views in SourceView.
2020-04-07 23:58:23 +00:00
{
assert( m_symAddr != 0 );
Don't show invalid contents warning for disassembly.
2020-03-27 16:14:46 +00:00
Mixed source/assembly symbol view.
2020-04-08 20:04:00 +00:00
auto sym = worker.GetSymbolData( m_symAddr );
assert( sym );
if( sym->isInline )
Display instruction pointer counts in source view.
2020-03-25 00:09:02 +00:00
{
Mixed source/assembly symbol view.
2020-04-08 20:04:00 +00:00
auto parent = worker.GetSymbolData( m_baseAddr );
if( parent )
Display instruction pointer counts in source view.
2020-03-25 00:09:02 +00:00
{
Sprinkle some icons.
2020-04-09 00:33:02 +00:00
TextFocused( ICON_FA_PUZZLE_PIECE " Symbol:", worker.GetString( parent->name ) );
Mixed source/assembly symbol view.
2020-04-08 20:04:00 +00:00
}
else
{
char tmp[16];
Use correct print format specifier.
2020-04-14 00:03:19 +00:00
sprintf( tmp, "0x%" PRIx64, m_baseAddr );
Sprinkle some icons.
2020-04-09 00:33:02 +00:00
TextFocused( ICON_FA_PUZZLE_PIECE " Symbol:", tmp );
Display disassembly.
2020-03-25 21:53:05 +00:00
}
Allow viewing assembly without corresponding source code.
2020-03-27 00:47:06 +00:00
}
Mixed source/assembly symbol view.
2020-04-08 20:04:00 +00:00
else
{
Sprinkle some icons.
2020-04-09 00:33:02 +00:00
TextFocused( ICON_FA_PUZZLE_PIECE " Symbol:", worker.GetString( sym->name ) );
Mixed source/assembly symbol view.
2020-04-08 20:04:00 +00:00
}
Show image name next to symbol name.
2020-07-14 15:23:04 +00:00
ImGui::SameLine();
TextDisabledUnformatted( worker.GetString( sym->imageName ) );
Mixed source/assembly symbol view.
2020-04-08 20:04:00 +00:00
Selection of inlined function within symbol.
2020-04-08 20:04:33 +00:00
auto inlineList = worker.GetInlineSymbolList( m_baseAddr, m_codeLen );
if( inlineList )
{
Allow showing sample data for whole symbol.
2020-04-09 20:23:57 +00:00
SmallCheckbox( ICON_FA_SITEMAP " Function:", &m_calcInlineStats );
Selection of inlined function within symbol.
2020-04-08 20:04:33 +00:00
ImGui::SameLine();
ImGui::SetNextItemWidth( -1 );
ImGui::PushStyleVar( ImGuiStyleVar_FramePadding, ImVec2( 0, 0 ) );
Display base function is symbol as '[ - self - ]'.
2020-05-25 19:37:17 +00:00
const auto currSymName = m_symAddr == m_baseAddr ? "[ - self - ]" : worker.GetString( sym->name );
if( ImGui::BeginCombo( "##functionList", currSymName, ImGuiComboFlags_HeightLarge ) )
Selection of inlined function within symbol.
2020-04-08 20:04:33 +00:00
{
Display percentage numbers of sample composition times.
2020-04-17 15:45:20 +00:00
uint32_t totalSamples = 0;
Merge building inline symbol list with stats collection.
2020-04-12 14:11:24 +00:00
const auto& symStat = worker.GetSymbolStats();
Don't build inline symbols list, if not needed.
2020-04-12 14:05:49 +00:00
const auto symEnd = m_baseAddr + m_codeLen;
Merge building inline symbol list with stats collection.
2020-04-12 14:11:24 +00:00
Vector<std::pair<uint64_t, uint32_t>> symInline;
auto baseStatIt = symStat.find( m_baseAddr );
if( baseStatIt == symStat.end() || baseStatIt->second.excl == 0 )
{
symInline.push_back( std::make_pair( m_baseAddr, 0 ) );
}
else
{
symInline.push_back( std::make_pair( m_baseAddr, baseStatIt->second.excl ) );
Display percentage numbers of sample composition times.
2020-04-17 15:45:20 +00:00
totalSamples += baseStatIt->second.excl;
Merge building inline symbol list with stats collection.
2020-04-12 14:11:24 +00:00
}
Don't build inline symbols list, if not needed.
2020-04-12 14:05:49 +00:00
while( *inlineList < symEnd )
{
if( *inlineList != m_baseAddr )
{
Merge building inline symbol list with stats collection.
2020-04-12 14:11:24 +00:00
auto statIt = symStat.find( *inlineList );
if( statIt == symStat.end() || statIt->second.excl == 0 )
{
symInline.push_back_non_empty( std::make_pair( *inlineList, 0 ) );
}
else
{
symInline.push_back_non_empty( std::make_pair( *inlineList, statIt->second.excl ) );
Display percentage numbers of sample composition times.
2020-04-17 15:45:20 +00:00
totalSamples += statIt->second.excl;
Merge building inline symbol list with stats collection.
2020-04-12 14:11:24 +00:00
}
Don't build inline symbols list, if not needed.
2020-04-12 14:05:49 +00:00
}
inlineList++;
}
Sort inline functions list by time spent in function.
2020-04-12 14:13:39 +00:00
pdqsort_branchless( symInline.begin(), symInline.end(), []( const auto& l, const auto& r ) { return l.second == r.second ? l.first < r.first : l.second > r.second; } );
Don't build inline symbols list, if not needed.
2020-04-12 14:05:49 +00:00
Display sample percentage columns only if there's data.
2020-04-23 22:49:38 +00:00
if( totalSamples == 0 )
Display inline functions time composition in symbol.
2020-04-12 14:05:01 +00:00
{
Display sample percentage columns only if there's data.
2020-04-23 22:49:38 +00:00
ImGui::Columns( 2 );
static bool widthSet = false;
if( !widthSet )
{
widthSet = true;
const auto w = ImGui::GetWindowWidth();
const auto c1 = ImGui::CalcTextSize( "0xeeeeeeeeeeeeee" ).x;
ImGui::SetColumnWidth( 0, w - c1 );
ImGui::SetColumnWidth( 1, c1 );
}
}
else
{
ImGui::Columns( 3 );
static bool widthSet = false;
if( !widthSet )
{
widthSet = true;
const auto w = ImGui::GetWindowWidth();
const auto c0 = ImGui::CalcTextSize( "12345678901234567890" ).x;
const auto c2 = ImGui::CalcTextSize( "0xeeeeeeeeeeeeee" ).x;
ImGui::SetColumnWidth( 0, c0 );
ImGui::SetColumnWidth( 1, w - c0 - c2 );
ImGui::SetColumnWidth( 2, c2 );
}
Display inline functions time composition in symbol.
2020-04-12 14:05:01 +00:00
}
Selection of inlined function within symbol.
2020-04-08 20:04:33 +00:00
for( auto& v : symInline )
{
Display sample percentage columns only if there's data.
2020-04-23 22:49:38 +00:00
if( totalSamples != 0 )
Display inline functions time composition in symbol.
2020-04-12 14:05:01 +00:00
{
Display sample percentage columns only if there's data.
2020-04-23 22:49:38 +00:00
if( v.second != 0 )
Display inline functions time composition in symbol.
2020-04-12 14:05:01 +00:00
{
Display sample percentage columns only if there's data.
2020-04-23 22:49:38 +00:00
ImGui::TextUnformatted( TimeToString( v.second * worker.GetSamplingPeriod() ) );
ImGui::SameLine();
ImGui::TextDisabled( "(%.2f%%)", 100.f * v.second / totalSamples );
if( ImGui::IsItemHovered() )
{
ImGui::BeginTooltip();
TextFocused( "Sample count:", RealToString( v.second ) );
ImGui::EndTooltip();
}
Display inline functions time composition in symbol.
2020-04-12 14:05:01 +00:00
}
Display sample percentage columns only if there's data.
2020-04-23 22:49:38 +00:00
ImGui::NextColumn();
Display inline functions time composition in symbol.
2020-04-12 14:05:01 +00:00
}
Merge building inline symbol list with stats collection.
2020-04-12 14:11:24 +00:00
auto isym = worker.GetSymbolData( v.first );
Selection of inlined function within symbol.
2020-04-08 20:04:33 +00:00
assert( isym );
Merge building inline symbol list with stats collection.
2020-04-12 14:11:24 +00:00
ImGui::PushID( v.first );
Display base function is symbol as '[ - self - ]'.
2020-05-25 19:37:17 +00:00
const auto symName = v.first == m_baseAddr ? "[ - self - ]" : worker.GetString( isym->name );
if( ImGui::Selectable( symName, v.first == m_symAddr, ImGuiSelectableFlags_SpanAllColumns ) )
Selection of inlined function within symbol.
2020-04-08 20:04:33 +00:00
{
Merge building inline symbol list with stats collection.
2020-04-12 14:11:24 +00:00
m_symAddr = v.first;
Selection of inlined function within symbol.
2020-04-08 20:04:33 +00:00
}
ImGui::PopID();
Display inline functions time composition in symbol.
2020-04-12 14:05:01 +00:00
ImGui::NextColumn();
Merge building inline symbol list with stats collection.
2020-04-12 14:11:24 +00:00
ImGui::TextDisabled( "0x%" PRIx64, v.first );
Display inline functions time composition in symbol.
2020-04-12 14:05:01 +00:00
ImGui::NextColumn();
Selection of inlined function within symbol.
2020-04-08 20:04:33 +00:00
}
Display inline functions time composition in symbol.
2020-04-12 14:05:01 +00:00
ImGui::EndColumns();
Selection of inlined function within symbol.
2020-04-08 20:04:33 +00:00
ImGui::EndCombo();
}
ImGui::PopStyleVar();
}
Mixed source/assembly symbol view.
2020-04-08 20:04:00 +00:00
TextDisabledUnformatted( "Mode:" );
ImGui::SameLine();
ImGui::PushStyleVar( ImGuiStyleVar_FramePadding, ImVec2( 0, 0 ) );
if( !m_lines.empty() )
Allow viewing assembly without corresponding source code.
2020-03-27 00:47:06 +00:00
{
Mixed source/assembly symbol view.
2020-04-08 20:04:00 +00:00
ImGui::RadioButton( "Source", &m_displayMode, DisplaySource );
if( !m_asm.empty() )
Allow viewing assembly without corresponding source code.
2020-03-27 00:47:06 +00:00
{
ImGui::SameLine();
Mixed source/assembly symbol view.
2020-04-08 20:04:00 +00:00
ImGui::RadioButton( "Assembly", &m_displayMode, DisplayAsm );
Allow viewing assembly without corresponding source code.
2020-03-27 00:47:06 +00:00
ImGui::SameLine();
Sprinkle some icons.
2020-04-09 00:33:02 +00:00
ImGui::RadioButton( "Combined", &m_displayMode, DisplayMixed );
Allow viewing assembly without corresponding source code.
2020-03-27 00:47:06 +00:00
}
Mixed source/assembly symbol view.
2020-04-08 20:04:00 +00:00
}
else
{
ImGui::RadioButton( "Assembly", &m_displayMode, DisplayAsm );
}
ImGui::PopStyleVar();
if( !m_asm.empty() )
{
ImGui::SameLine();
ImGui::Spacing();
ImGui::SameLine();
Sprinkle some icons.
2020-04-09 00:33:02 +00:00
TextFocused( ICON_FA_WEIGHT_HANGING " Code size:", MemSizeToString( m_codeLen ) );
Assembly display is not dependant on sample data.
2020-03-27 00:24:50 +00:00
}
Mixed source/assembly symbol view.
2020-04-08 20:04:00 +00:00
uint32_t iptotalSrc = 0, iptotalAsm = 0;
Calculate max sample counts during ip map creation.
2020-04-10 23:34:44 +00:00
uint32_t ipmaxSrc = 0, ipmaxAsm = 0;
Mixed source/assembly symbol view.
2020-04-08 20:04:00 +00:00
unordered_flat_map<uint64_t, uint32_t> ipcountSrc, ipcountAsm;
Allow showing sample data for whole symbol.
2020-04-09 20:23:57 +00:00
if( m_calcInlineStats )
Assembly display is not dependant on sample data.
2020-03-27 00:24:50 +00:00
{
Calculate max sample counts during ip map creation.
2020-04-10 23:34:44 +00:00
GatherIpStats( m_symAddr, iptotalSrc, iptotalAsm, ipcountSrc, ipcountAsm, ipmaxSrc, ipmaxAsm, worker );
Allow showing sample data for whole symbol.
2020-04-09 20:23:57 +00:00
}
else
{
Calculate max sample counts during ip map creation.
2020-04-10 23:34:44 +00:00
GatherIpStats( m_baseAddr, iptotalSrc, iptotalAsm, ipcountSrc, ipcountAsm, ipmaxSrc, ipmaxAsm, worker );
Allow showing sample data for whole symbol.
2020-04-09 20:23:57 +00:00
auto iptr = worker.GetInlineSymbolList( m_baseAddr, m_codeLen );
if( iptr )
Display disassembly.
2020-03-25 21:53:05 +00:00
{
Allow showing sample data for whole symbol.
2020-04-09 20:23:57 +00:00
const auto symEnd = m_baseAddr + m_codeLen;
while( *iptr < symEnd )
Display disassembly.
2020-03-25 21:53:05 +00:00
{
Calculate max sample counts during ip map creation.
2020-04-10 23:34:44 +00:00
GatherIpStats( *iptr, iptotalSrc, iptotalAsm, ipcountSrc, ipcountAsm, ipmaxSrc, ipmaxAsm, worker );
Allow showing sample data for whole symbol.
2020-04-09 20:23:57 +00:00
iptr++;
Display instruction pointer counts in source view.
2020-03-25 00:09:02 +00:00
}
}
Proper scaling of instruction pointer counts.
2020-04-09 20:52:44 +00:00
iptotalSrc = iptotalAsm;
Display instruction pointer counts in source view.
2020-03-25 00:09:02 +00:00
}
Allow showing sample data for whole symbol.
2020-04-09 20:23:57 +00:00
if( iptotalAsm > 0 )
{
Display wall time in addition to sample counts.
2020-04-11 20:14:56 +00:00
ImGui::SameLine();
ImGui::Spacing();
ImGui::SameLine();
TextFocused( ICON_FA_STOPWATCH " Time:", TimeToString( iptotalAsm * worker.GetSamplingPeriod() ) );
Allow showing sample data for whole symbol.
2020-04-09 20:23:57 +00:00
ImGui::SameLine();
ImGui::Spacing();
ImGui::SameLine();
TextFocused( ICON_FA_EYE_DROPPER " Samples:", RealToString( iptotalAsm ) );
}
Display instruction pointer counts in source view.
2020-03-25 00:09:02 +00:00
Mixed source/assembly symbol view.
2020-04-08 20:04:00 +00:00
ImGui::Separator();
uint64_t jumpOut = 0;
switch( m_displayMode )
Assembly display is not dependant on sample data.
2020-03-27 00:24:50 +00:00
{
Mixed source/assembly symbol view.
2020-04-08 20:04:00 +00:00
case DisplaySource:
Perform source file name substitution.
2020-04-17 17:09:13 +00:00
RenderSymbolSourceView( iptotalSrc, ipcountSrc, ipcountAsm, ipmaxSrc, worker, view );
Mixed source/assembly symbol view.
2020-04-08 20:04:00 +00:00
break;
case DisplayAsm:
Perform source file name substitution.
2020-04-17 17:09:13 +00:00
jumpOut = RenderSymbolAsmView( iptotalAsm, ipcountAsm, ipmaxAsm, worker, view );
Mixed source/assembly symbol view.
2020-04-08 20:04:00 +00:00
break;
case DisplayMixed:
ImGui::Columns( 2 );
Perform source file name substitution.
2020-04-17 17:09:13 +00:00
RenderSymbolSourceView( iptotalSrc, ipcountSrc, ipcountAsm, ipmaxSrc, worker, view );
Mixed source/assembly symbol view.
2020-04-08 20:04:00 +00:00
ImGui::NextColumn();
Perform source file name substitution.
2020-04-17 17:09:13 +00:00
jumpOut = RenderSymbolAsmView( iptotalAsm, ipcountAsm, ipmaxAsm, worker, view );
Mixed source/assembly symbol view.
2020-04-08 20:04:00 +00:00
ImGui::EndColumns();
break;
default:
assert( false );
break;
}
if( jumpOut != 0 )
{
auto sym = worker.GetSymbolData( jumpOut );
if( sym )
Display parent symbol for inline symbols in source view.
2020-03-30 00:46:29 +00:00
{
Mixed source/assembly symbol view.
2020-04-08 20:04:00 +00:00
auto line = sym->line;
auto file = line == 0 ? nullptr : worker.GetString( sym->file );
Use cached source files.
2020-05-23 13:14:57 +00:00
if( file && !SourceFileValid( file, worker.GetCaptureTime(), view, worker ) )
Display parent symbol for inline symbols in source view.
2020-03-30 00:46:29 +00:00
{
Mixed source/assembly symbol view.
2020-04-08 20:04:00 +00:00
file = nullptr;
line = 0;
}
if( line > 0 || sym->size.Val() > 0 )
{
Substitute source file names in source view.
2020-04-17 17:17:47 +00:00
OpenSymbol( file, line, jumpOut, jumpOut, worker, view );
Display parent symbol for inline symbols in source view.
2020-03-30 00:46:29 +00:00
}
}
Assembly display is not dependant on sample data.
2020-03-27 00:24:50 +00:00
}
Mixed source/assembly symbol view.
2020-04-08 20:04:00 +00:00
}
Assembly display is not dependant on sample data.
2020-03-27 00:24:50 +00:00
More code deduplication.
2020-04-10 21:13:51 +00:00
static uint32_t GetHotnessColor( uint32_t ipSum, uint32_t maxIpCount )
{
const auto ipPercent = float( ipSum ) / maxIpCount;
if( ipPercent <= 0.5f )
{
const auto a = int( ( ipPercent * 1.5f + 0.25f ) * 255 );
return 0x000000FF | ( a << 24 );
}
else if( ipPercent <= 1.f )
{
const auto g = int( ( ipPercent - 0.5f ) * 511 );
return 0xFF0000FF | ( g << 8 );
}
else if( ipPercent <= 2.f )
{
const auto b = int( ( ipPercent - 1.f ) * 255 );
return 0xFF00FFFF | ( b << 16 );
}
else
{
return 0xFFFFFFFF;
}
}
Perform source file name substitution.
2020-04-17 17:09:13 +00:00
void SourceView::RenderSymbolSourceView( uint32_t iptotal, unordered_flat_map<uint64_t, uint32_t> ipcount, unordered_flat_map<uint64_t, uint32_t> ipcountAsm, uint32_t ipmax, const Worker& worker, const View& view )
Mixed source/assembly symbol view.
2020-04-08 20:04:00 +00:00
{
Symbol file selector.
2020-04-08 20:25:36 +00:00
if( m_sourceFiles.empty() )
{
Add notification when source file is loaded from cache.
2020-05-23 13:27:00 +00:00
if( m_data == m_dataBuf )
Symbol file selector.
2020-04-08 20:25:36 +00:00
{
TextColoredUnformatted( ImVec4( 1.f, 1.f, 0.2f, 1.f ), ICON_FA_EXCLAMATION_TRIANGLE );
ImGui::SameLine();
TextColoredUnformatted( ImVec4( 1.f, 0.3f, 0.3f, 1.f ), "The source file contents might not reflect the actual profiled code!" );
ImGui::SameLine();
TextColoredUnformatted( ImVec4( 1.f, 1.f, 0.2f, 1.f ), ICON_FA_EXCLAMATION_TRIANGLE );
Add notification when source file is loaded from cache.
2020-05-23 13:27:00 +00:00
}
else
{
TextColoredUnformatted( ImVec4( 0.4f, 0.8f, 0.4f, 1.f ), ICON_FA_DATABASE );
ImGui::SameLine();
ImGui::TextUnformatted( "Source file cached during profiling run" );
}
}
else
{
if( m_data == m_dataBuf )
{
TextColoredUnformatted( ImVec4( 1.f, 1.f, 0.2f, 1.f ), ICON_FA_EXCLAMATION_TRIANGLE );
if( ImGui::IsItemHovered() )
{
ImGui::BeginTooltip();
TextColoredUnformatted( ImVec4( 1.f, 1.f, 0.2f, 1.f ), ICON_FA_EXCLAMATION_TRIANGLE );
ImGui::SameLine();
TextColoredUnformatted( ImVec4( 1.f, 0.3f, 0.3f, 1.f ), "The source file contents might not reflect the actual profiled code!" );
ImGui::SameLine();
TextColoredUnformatted( ImVec4( 1.f, 1.f, 0.2f, 1.f ), ICON_FA_EXCLAMATION_TRIANGLE );
ImGui::EndTooltip();
}
}
else
{
TextColoredUnformatted( ImVec4( 0.4f, 0.8f, 0.4f, 1.f ), ICON_FA_DATABASE );
if( ImGui::IsItemHovered() )
{
ImGui::BeginTooltip();
ImGui::TextUnformatted( "Source file cached during profiling run" );
ImGui::EndTooltip();
}
Symbol file selector.
2020-04-08 20:25:36 +00:00
}
ImGui::SameLine();
Sprinkle some icons.
2020-04-09 00:33:02 +00:00
TextDisabledUnformatted( ICON_FA_FILE " File:" );
Symbol file selector.
2020-04-08 20:25:36 +00:00
ImGui::SameLine();
Add color boxes to file selection.
2020-04-08 21:01:44 +00:00
const auto fileColor = GetHsvColor( m_fileStringIdx, 0 );
SmallColorBox( fileColor );
ImGui::SameLine();
Symbol file selector.
2020-04-08 20:25:36 +00:00
ImGui::SetNextItemWidth( -1 );
ImGui::PushStyleVar( ImGuiStyleVar_FramePadding, ImVec2( 0, 0 ) );
Set sensible combo box heights.
2020-04-09 00:09:54 +00:00
if( ImGui::BeginCombo( "##fileList", m_file, ImGuiComboFlags_HeightLarge ) )
Symbol file selector.
2020-04-08 20:25:36 +00:00
{
Display source files time composition in selected function/symbol.
2020-04-12 15:08:58 +00:00
if( m_asm.empty() )
Symbol file selector.
2020-04-08 20:25:36 +00:00
{
Display source files time composition in selected function/symbol.
2020-04-12 15:08:58 +00:00
for( auto& v : m_sourceFiles )
Symbol file selector.
2020-04-08 20:25:36 +00:00
{
Display source files time composition in selected function/symbol.
2020-04-12 15:08:58 +00:00
const auto color = GetHsvColor( v.first, 0 );
SmallColorBox( color );
ImGui::SameLine();
auto fstr = worker.GetString( StringIdx( v.first ) );
Use cached source files.
2020-05-23 13:14:57 +00:00
if( SourceFileValid( fstr, worker.GetCaptureTime(), view, worker ) )
Prevent opening obsolete source files.
2020-04-08 21:07:59 +00:00
{
Display source files time composition in selected function/symbol.
2020-04-12 15:08:58 +00:00
ImGui::PushID( v.first );
if( ImGui::Selectable( fstr, fstr == m_file ) )
{
Use cached source files.
2020-05-23 13:14:57 +00:00
ParseSource( fstr, worker, view );
Display source files time composition in selected function/symbol.
2020-04-12 15:08:58 +00:00
m_targetLine = v.second;
SelectLine( v.second, &worker );
}
Fix handling of ImGui ID stack.
2020-04-17 17:28:10 +00:00
ImGui::PopID();
Display source files time composition in selected function/symbol.
2020-04-12 15:08:58 +00:00
}
else
{
TextDisabledUnformatted( fstr );
Prevent opening obsolete source files.
2020-04-08 21:07:59 +00:00
}
}
Display source files time composition in selected function/symbol.
2020-04-12 15:08:58 +00:00
}
else
{
Display percentage numbers of sample composition times.
2020-04-17 15:45:20 +00:00
uint32_t totalSamples = 0;
Display source files time composition in selected function/symbol.
2020-04-12 15:08:58 +00:00
unordered_flat_map<uint32_t, uint32_t> fileCounts;
for( auto& v : m_asm )
Prevent opening obsolete source files.
2020-04-08 21:07:59 +00:00
{
Display source files time composition in selected function/symbol.
2020-04-12 15:08:58 +00:00
uint32_t srcline;
const auto srcidx = worker.GetLocationForAddress( v.addr, srcline );
if( srcline != 0 )
{
uint32_t cnt = 0;
auto ait = ipcountAsm.find( v.addr );
if( ait != ipcountAsm.end() ) cnt = ait->second;
auto fit = fileCounts.find( srcidx.Idx() );
if( fit == fileCounts.end() )
{
fileCounts.emplace( srcidx.Idx(), cnt );
}
else if( cnt != 0 )
{
fit->second += cnt;
}
Display percentage numbers of sample composition times.
2020-04-17 15:45:20 +00:00
totalSamples += cnt;
Display source files time composition in selected function/symbol.
2020-04-12 15:08:58 +00:00
}
Symbol file selector.
2020-04-08 20:25:36 +00:00
}
Display source files time composition in selected function/symbol.
2020-04-12 15:08:58 +00:00
std::vector<std::pair<uint32_t, uint32_t>> fileCountsVec;
fileCountsVec.reserve( fileCounts.size() );
for( auto& v : fileCounts ) fileCountsVec.emplace_back( v.first, v.second );
pdqsort_branchless( fileCountsVec.begin(), fileCountsVec.end(), [&worker] (const auto& l, const auto& r ) { return l.second == r.second ? strcmp( worker.GetString( l.first ), worker.GetString( r.first ) ) < 0 : l.second > r.second; } );
Display sample percentage columns only if there's data.
2020-04-23 22:49:38 +00:00
if( totalSamples != 0 )
Display source files time composition in selected function/symbol.
2020-04-12 15:08:58 +00:00
{
Display sample percentage columns only if there's data.
2020-04-23 22:49:38 +00:00
ImGui::Columns( 2 );
static bool widthSet = false;
if( !widthSet )
{
widthSet = true;
const auto w = ImGui::GetWindowWidth();
const auto c0 = ImGui::CalcTextSize( "12345678901234567890" ).x;
ImGui::SetColumnWidth( 0, c0 );
ImGui::SetColumnWidth( 1, w - c0 );
}
Display source files time composition in selected function/symbol.
2020-04-12 15:08:58 +00:00
}
for( auto& v : fileCountsVec )
{
Display sample percentage columns only if there's data.
2020-04-23 22:49:38 +00:00
if( totalSamples != 0 )
Display source files time composition in selected function/symbol.
2020-04-12 15:08:58 +00:00
{
Display sample percentage columns only if there's data.
2020-04-23 22:49:38 +00:00
auto fit = fileCounts.find( v.first );
assert( fit != fileCounts.end() );
if( fit->second != 0 )
Display source files time composition in selected function/symbol.
2020-04-12 15:08:58 +00:00
{
Display sample percentage columns only if there's data.
2020-04-23 22:49:38 +00:00
ImGui::TextUnformatted( TimeToString( fit->second * worker.GetSamplingPeriod() ) );
ImGui::SameLine();
ImGui::TextDisabled( "(%.2f%%)", 100.f * fit->second / totalSamples );
if( ImGui::IsItemHovered() )
{
ImGui::BeginTooltip();
TextFocused( "Sample count:", RealToString( fit->second ) );
ImGui::EndTooltip();
}
Display source files time composition in selected function/symbol.
2020-04-12 15:08:58 +00:00
}
Display sample percentage columns only if there's data.
2020-04-23 22:49:38 +00:00
ImGui::NextColumn();
Display source files time composition in selected function/symbol.
2020-04-12 15:08:58 +00:00
}
const auto color = GetHsvColor( v.first, 0 );
SmallColorBox( color );
ImGui::SameLine();
auto fstr = worker.GetString( StringIdx( v.first ) );
Use cached source files.
2020-05-23 13:14:57 +00:00
if( SourceFileValid( fstr, worker.GetCaptureTime(), view, worker ) )
Display source files time composition in selected function/symbol.
2020-04-12 15:08:58 +00:00
{
ImGui::PushID( v.first );
if( ImGui::Selectable( fstr, fstr == m_file, ImGuiSelectableFlags_SpanAllColumns ) )
{
uint32_t line = 0;
for( auto& file : m_sourceFiles )
{
if( file.first == v.first )
{
line = file.second;
break;
}
}
Use cached source files.
2020-05-23 13:14:57 +00:00
ParseSource( fstr, worker, view );
Display source files time composition in selected function/symbol.
2020-04-12 15:08:58 +00:00
m_targetLine = line;
SelectLine( line, &worker );
}
Fix handling of ImGui ID stack.
2020-04-17 17:28:10 +00:00
ImGui::PopID();
Display source files time composition in selected function/symbol.
2020-04-12 15:08:58 +00:00
}
else
{
TextDisabledUnformatted( fstr );
}
Display sample percentage columns only if there's data.
2020-04-23 22:49:38 +00:00
if( totalSamples != 0 ) ImGui::NextColumn();
Display source files time composition in selected function/symbol.
2020-04-12 15:08:58 +00:00
}
Display sample percentage columns only if there's data.
2020-04-23 22:49:38 +00:00
if( totalSamples != 0 ) ImGui::EndColumns();
Symbol file selector.
2020-04-08 20:25:36 +00:00
}
ImGui::EndCombo();
}
ImGui::PopStyleVar();
}
Don't show invalid contents warning for disassembly.
2020-03-27 16:14:46 +00:00
Implement display of grouped instruction pointer statistics.
2020-05-07 00:33:37 +00:00
const float bottom = m_srcSampleSelect.empty() ? 0 : ImGui::GetFrameHeight();
Set source view content width to max value, regardless of clipping.
2020-06-06 10:31:47 +00:00
ImGui::SetNextWindowContentSize( ImVec2( m_srcWidth, 0 ) );
Enable horizontal scrollbar in source view.
2020-06-05 17:04:12 +00:00
ImGui::BeginChild( "##sourceView", ImVec2( 0, -bottom ), true, ImGuiWindowFlags_NoMove | ImGuiWindowFlags_HorizontalScrollbar );
Replace source file viewer with one that actually works. This is much simpler, custom implementation of a text file viewer. It is able to perform these two tasks as intended: - center source view on the selected line, - highlight that line.
2020-03-22 19:53:59 +00:00
if( m_font ) ImGui::PushFont( m_font );
Mixed source/assembly symbol view.
2020-04-08 20:04:00 +00:00
Draw a line indicating zeroth column of source code.
2020-04-25 11:52:21 +00:00
auto draw = ImGui::GetWindowDrawList();
Fix position of source separator line.
2020-06-06 18:50:24 +00:00
const auto wpos = ImGui::GetWindowPos() - ImVec2( ImGui::GetCurrentWindowRead()->Scroll.x, 0 );
Draw a line indicating zeroth column of source code.
2020-04-25 11:52:21 +00:00
const auto wh = ImGui::GetWindowHeight();
const auto ty = ImGui::GetFontSize();
const auto ts = ImGui::CalcTextSize( " " ).x;
const auto lineCount = m_lines.size();
const auto tmp = RealToString( lineCount );
const auto maxLine = strlen( tmp );
auto lx = ts * maxLine + ty + round( ts*0.4f );
if( iptotal != 0 ) lx += ts * 7 + ty;
if( !m_asm.empty() )
{
const auto tmp = RealToString( m_asm.size() );
const auto maxAsm = strlen( tmp ) + 1;
lx += ts * maxAsm + ty;
}
draw->AddLine( wpos + ImVec2( lx, 0 ), wpos + ImVec2( lx, wh ), 0x08FFFFFF );
Highlight asm lines for hovered source line.
2020-04-09 19:57:28 +00:00
m_selectedAddressesHover.clear();
Mixed source/assembly symbol view.
2020-04-08 20:04:00 +00:00
if( m_targetLine != 0 )
Replace source file viewer with one that actually works. This is much simpler, custom implementation of a text file viewer. It is able to perform these two tasks as intended: - center source view on the selected line, - highlight that line.
2020-03-22 19:53:59 +00:00
{
Mixed source/assembly symbol view.
2020-04-08 20:04:00 +00:00
int lineNum = 1;
for( auto& line : m_lines )
Replace source file viewer with one that actually works. This is much simpler, custom implementation of a text file viewer. It is able to perform these two tasks as intended: - center source view on the selected line, - highlight that line.
2020-03-22 19:53:59 +00:00
{
Mixed source/assembly symbol view.
2020-04-08 20:04:00 +00:00
if( m_targetLine == lineNum )
Use clipper to render source view.
2020-03-24 17:10:56 +00:00
{
Mixed source/assembly symbol view.
2020-04-08 20:04:00 +00:00
m_targetLine = 0;
ImGui::SetScrollHereY();
Display disassembly.
2020-03-25 21:53:05 +00:00
}
Draw hotness markers next to sample percentage counts.
2020-04-10 23:59:15 +00:00
RenderLine( line, lineNum++, 0, iptotal, ipmax, &worker );
Display disassembly.
2020-03-25 21:53:05 +00:00
}
Don't mark windows as write-modified when only reading data.
2020-06-06 18:46:46 +00:00
const auto win = ImGui::GetCurrentWindowRead();
Set source view content width to max value, regardless of clipping.
2020-06-06 10:31:47 +00:00
m_srcWidth = win->DC.CursorMaxPos.x - win->DC.CursorStartPos.x;
Mixed source/assembly symbol view.
2020-04-08 20:04:00 +00:00
}
else
{
ImGuiListClipper clipper( (int)m_lines.size() );
while( clipper.Step() )
Display disassembly.
2020-03-25 21:53:05 +00:00
{
Mixed source/assembly symbol view.
2020-04-08 20:04:00 +00:00
if( iptotal == 0 )
Display disassembly.
2020-03-25 21:53:05 +00:00
{
Mixed source/assembly symbol view.
2020-04-08 20:04:00 +00:00
for( auto i=clipper.DisplayStart; i<clipper.DisplayEnd; i++ )
Display disassembly.
2020-03-25 21:53:05 +00:00
{
Draw hotness markers next to sample percentage counts.
2020-04-10 23:59:15 +00:00
RenderLine( m_lines[i], i+1, 0, 0, 0, &worker );
Draw jumps in assembly view.
2020-04-04 01:34:54 +00:00
}
Mixed source/assembly symbol view.
2020-04-08 20:04:00 +00:00
}
else
{
for( auto i=clipper.DisplayStart; i<clipper.DisplayEnd; i++ )
Draw jumps in assembly view.
2020-04-04 01:34:54 +00:00
{
Mixed source/assembly symbol view.
2020-04-08 20:04:00 +00:00
auto it = ipcount.find( i+1 );
const auto ipcnt = it == ipcount.end() ? 0 : it->second;
Draw hotness markers next to sample percentage counts.
2020-04-10 23:59:15 +00:00
RenderLine( m_lines[i], i+1, ipcnt, iptotal, ipmax, &worker );
Display disassembly.
2020-03-25 21:53:05 +00:00
}
Use clipper to render source view.
2020-03-24 17:10:56 +00:00
}
}
}
Mixed source/assembly symbol view.
2020-04-08 20:04:00 +00:00
Don't mark windows as write-modified when only reading data.
2020-06-06 18:46:46 +00:00
const auto win = ImGui::GetCurrentWindowRead();
Decorate source scroll bar with selected and highlighted line.
2020-04-10 14:08:06 +00:00
if( win->ScrollbarY )
{
auto draw = ImGui::GetWindowDrawList();
auto rect = ImGui::GetWindowScrollbarRect( win, ImGuiAxis_Y );
ImGui::PushClipRect( rect.Min, rect.Max, false );
if( m_selectedLine != 0 )
{
const auto ly = round( rect.Min.y + ( m_selectedLine - 0.5f ) / m_lines.size() * rect.GetHeight() );
draw->AddLine( ImVec2( rect.Min.x, ly ), ImVec2( rect.Max.x, ly ), 0x8899994C, 3 );
}
if( m_fileStringIdx == m_hoveredSource && m_hoveredLine != 0 )
{
const auto ly = round( rect.Min.y + ( m_hoveredLine - 0.5f ) / m_lines.size() * rect.GetHeight() );
draw->AddLine( ImVec2( rect.Min.x, ly ), ImVec2( rect.Max.x, ly ), 0x88888888, 3 );
}
Decorate source scroll bar with line hotness.
2020-04-10 14:56:31 +00:00
std::vector<std::pair<uint64_t, uint32_t>> ipData;
ipData.reserve( ipcount.size() );
Calculate max sample counts during ip map creation.
2020-04-10 23:34:44 +00:00
for( auto& v : ipcount ) ipData.emplace_back( v.first, v.second );
Mark source lines which generated assembly.
2020-04-13 15:47:41 +00:00
for( uint32_t lineNum = 1; lineNum <= m_lines.size(); lineNum++ )
{
if( ipcount.find( lineNum ) == ipcount.end() )
{
auto addresses = worker.GetAddressesForLocation( m_fileStringIdx, lineNum );
if( addresses )
{
for( auto& addr : *addresses )
{
if( addr >= m_baseAddr && addr < m_baseAddr + m_codeLen )
{
ipData.emplace_back( lineNum, 0 );
break;
}
}
}
}
}
Decorate source scroll bar with line hotness.
2020-04-10 14:56:31 +00:00
pdqsort_branchless( ipData.begin(), ipData.end(), []( const auto& l, const auto& r ) { return l.first < r.first; } );
const auto step = uint32_t( m_lines.size() * 2 / rect.GetHeight() );
const auto x14 = round( rect.Min.x + rect.GetWidth() * 0.4f );
const auto x34 = round( rect.Min.x + rect.GetWidth() * 0.6f );
auto it = ipData.begin();
while( it != ipData.end() )
{
const auto firstLine = it->first;
More code deduplication.
2020-04-10 21:13:51 +00:00
uint32_t ipSum = 0;
Decorate source scroll bar with line hotness.
2020-04-10 14:56:31 +00:00
while( it != ipData.end() && it->first <= firstLine + step )
{
ipSum += it->second;
++it;
}
const auto ly = round( rect.Min.y + float( firstLine ) / m_lines.size() * rect.GetHeight() );
Mark source lines which generated assembly.
2020-04-13 15:47:41 +00:00
const uint32_t color = ipSum == 0 ? 0x22FFFFFF : GetHotnessColor( ipSum, ipmax );
Less code duplication.
2020-04-10 21:07:52 +00:00
draw->AddRectFilled( ImVec2( x14, ly ), ImVec2( x34, ly+3 ), color );
Decorate source scroll bar with line hotness.
2020-04-10 14:56:31 +00:00
}
Decorate source scroll bar with selected and highlighted line.
2020-04-10 14:08:06 +00:00
ImGui::PopClipRect();
}
Mixed source/assembly symbol view.
2020-04-08 20:04:00 +00:00
if( m_font ) ImGui::PopFont();
ImGui::EndChild();
Implement display of grouped instruction pointer statistics.
2020-05-07 00:33:37 +00:00
if( !m_srcSampleSelect.empty() )
{
uint32_t count = 0;
Display number of selected lines.
2020-05-09 11:53:11 +00:00
uint32_t numLines = 0;
Implement display of grouped instruction pointer statistics.
2020-05-07 00:33:37 +00:00
for( auto& idx : m_srcSampleSelect )
{
auto it = ipcount.find( idx );
Display number of selected lines.
2020-05-09 11:53:11 +00:00
if( it != ipcount.end() )
{
count += it->second;
numLines++;
}
Implement display of grouped instruction pointer statistics.
2020-05-07 00:33:37 +00:00
}
ImGui::BeginChild( "##srcSelect" );
if( ImGui::SmallButton( ICON_FA_TIMES ) )
{
m_srcSampleSelect.clear();
m_srcGroupSelect = -1;
}
ImGui::SameLine();
char buf[16];
auto end = PrintFloat( buf, buf+16, 100.f * count / iptotal, 2 );
memcpy( end, "%", 2 );
TextFocused( "Selected:", buf );
ImGui::SameLine();
ImGui::Spacing();
ImGui::SameLine();
TextFocused( "Time:", TimeToString( count * worker.GetSamplingPeriod() ) );
ImGui::SameLine();
ImGui::Spacing();
ImGui::SameLine();
TextFocused( "Sample count:", RealToString( count ) );
Display number of selected lines.
2020-05-09 11:53:11 +00:00
ImGui::SameLine();
ImGui::Spacing();
ImGui::SameLine();
TextFocused( "Lines:", RealToString( numLines ) );
Implement display of grouped instruction pointer statistics.
2020-05-07 00:33:37 +00:00
ImGui::EndChild();
}
Mixed source/assembly symbol view.
2020-04-08 20:04:00 +00:00
}
Display disassembly failure notification.
2020-04-19 13:40:42 +00:00
static int PrintHexBytes( char* buf, const uint8_t* bytes, size_t len )
{
static constexpr char HexPrint[] = { '0', '1', '2', '3', '4', '5', '6', '7', '8', '9', 'A', 'B', 'C', 'D', 'E', 'F' };
const auto start = buf;
for( size_t i=0; i<len; i++ )
{
const auto byte = bytes[i];
*buf++ = HexPrint[byte >> 4];
*buf++ = HexPrint[byte & 0xF];
*buf++ = ' ';
}
*--buf = '\0';
return buf - start;
}
Add ability to show callstack to an asm line.
2020-05-10 14:56:38 +00:00
uint64_t SourceView::RenderSymbolAsmView( uint32_t iptotal, unordered_flat_map<uint64_t, uint32_t> ipcount, uint32_t ipmax, const Worker& worker, View& view )
Mixed source/assembly symbol view.
2020-04-08 20:04:00 +00:00
{
Display disassembly failure notification.
2020-04-19 13:40:42 +00:00
if( m_disasmFail >= 0 )
{
TextColoredUnformatted( ImVec4( 1.f, 1.f, 0.2f, 1.f ), ICON_FA_EXCLAMATION_TRIANGLE );
if( ImGui::IsItemHovered() )
{
const bool clicked = ImGui::IsItemClicked();
ImGui::BeginTooltip();
TextColoredUnformatted( ImVec4( 1, 0, 0, 1 ), "Disassembly failure." );
ImGui::TextUnformatted( "Some instructions weren't properly decoded. Possible reasons:" );
ImGui::TextUnformatted( " 1. Old version of capstone library doesn't support some instructions." );
ImGui::TextUnformatted( " 2. Trying to decode data part of the symbol (e.g. jump arrays, etc.)" );
TextFocused( "Code size:", RealToString( m_codeLen ) );
TextFocused( "Disassembled bytes:", RealToString( m_disasmFail ) );
char tmp[64];
auto bytesLeft = std::min( 16u, m_codeLen - m_disasmFail );
Use correct symbol address.
2020-05-26 00:08:30 +00:00
auto code = worker.GetSymbolCode( m_baseAddr, m_codeLen );
Display disassembly failure notification.
2020-04-19 13:40:42 +00:00
assert( code );
PrintHexBytes( tmp, (const uint8_t*)code, bytesLeft );
TextFocused( "Failure bytes:", tmp );
TextDisabledUnformatted( "Click to copy to clipboard." );
ImGui::EndTooltip();
if( clicked ) ImGui::SetClipboardText( tmp );
}
ImGui::SameLine();
}
Allow switching between Intel and AT&T assembly syntax.
2020-05-09 10:58:09 +00:00
SmallCheckbox( ICON_FA_SEARCH_LOCATION " Relative loc.", &m_asmRelative );
Don't display source files, if none available.
2020-04-12 21:26:02 +00:00
if( !m_sourceFiles.empty() )
{
ImGui::SameLine();
ImGui::Spacing();
ImGui::SameLine();
Allow switching between Intel and AT&T assembly syntax.
2020-05-09 10:58:09 +00:00
SmallCheckbox( ICON_FA_FILE_IMPORT " Source loc.", &m_asmShowSourceLocation );
Don't display source files, if none available.
2020-04-12 21:26:02 +00:00
}
Mixed source/assembly symbol view.
2020-04-08 20:04:00 +00:00
ImGui::SameLine();
ImGui::Spacing();
ImGui::SameLine();
Shorten labels.
2020-04-27 15:56:28 +00:00
SmallCheckbox( ICON_FA_COGS " Machine code", &m_asmBytes );
Allow displaying machine code bytes in disassembly.
2020-04-19 14:06:45 +00:00
ImGui::SameLine();
ImGui::Spacing();
ImGui::SameLine();
Shorten labels.
2020-04-27 15:56:28 +00:00
SmallCheckbox( ICON_FA_SHARE " Jumps", &m_showJumps );
Mixed source/assembly symbol view.
2020-04-08 20:04:00 +00:00
Add uarch selection UI.
2020-04-26 12:52:18 +00:00
if( m_cpuArch == CpuArchX64 || m_cpuArch == CpuArchX86 )
{
ImGui::SameLine();
ImGui::Spacing();
ImGui::SameLine();
Show only relevant options in asm view.
2020-06-04 17:59:13 +00:00
if( SmallCheckbox( "AT&T", &m_atnt ) ) Disassemble( m_baseAddr, worker );
if( !m_atnt )
Add uarch selection UI.
2020-04-26 12:52:18 +00:00
{
Show only relevant options in asm view.
2020-06-04 17:59:13 +00:00
ImGui::SameLine();
ImGui::Spacing();
ImGui::SameLine();
float mw = 0;
Add uarch selection UI.
2020-04-26 12:52:18 +00:00
for( auto& v : s_uArchUx )
{
Show only relevant options in asm view.
2020-06-04 17:59:13 +00:00
const auto w = ImGui::CalcTextSize( v.uArch ).x;
if( w > mw ) mw = w;
Add uarch selection UI.
2020-04-26 12:52:18 +00:00
}
Show only relevant options in asm view.
2020-06-04 17:59:13 +00:00
ImGui::TextUnformatted( ICON_FA_MICROCHIP " \xce\xbc""arch:" );
ImGui::SameLine();
ImGui::SetNextItemWidth( mw + ImGui::GetFontSize() );
ImGui::PushStyleVar( ImGuiStyleVar_FramePadding, ImVec2( 0, 0 ) );
if( ImGui::BeginCombo( "##uarch", s_uArchUx[m_selMicroArch].uArch, ImGuiComboFlags_HeightLarge ) )
{
int idx = 0;
for( auto& v : s_uArchUx )
{
if( ImGui::Selectable( v.uArch, idx == m_selMicroArch ) ) SelectMicroArchitecture( v.moniker );
ImGui::SameLine();
TextDisabledUnformatted( v.cpuName );
idx++;
}
ImGui::EndCombo();
}
ImGui::PopStyleVar();
Optional visualization of uarch latency.
2020-04-27 14:10:47 +00:00
Show only relevant options in asm view.
2020-06-04 17:59:13 +00:00
ImGui::SameLine();
ImGui::Spacing();
ImGui::SameLine();
SmallCheckbox( ICON_FA_TRUCK_LOADING " Latency", &m_showLatency );
}
Add uarch selection UI.
2020-04-26 12:52:18 +00:00
}
Implement saving disassembly to a file.
2020-05-09 00:37:18 +00:00
#ifndef TRACY_NO_FILESELECTOR
ImGui::SameLine();
ImGui::Spacing();
ImGui::SameLine();
if( ImGui::SmallButton( ICON_FA_FILE_IMPORT " Save" ) )
{
Extract asm saving to a separate function.
2020-05-11 19:08:50 +00:00
Save( worker );
Implement saving disassembly to a file.
2020-05-09 00:37:18 +00:00
}
#endif
Implement display of grouped instruction pointer statistics.
2020-05-07 00:33:37 +00:00
const float bottom = m_asmSampleSelect.empty() ? 0 : ImGui::GetFrameHeight();
Set source view content width to max value, regardless of clipping.
2020-06-06 10:31:47 +00:00
ImGui::SetNextWindowContentSize( ImVec2( m_asmWidth, 0 ) );
Enable horizontal scrollbar in source view.
2020-06-05 17:04:12 +00:00
ImGui::BeginChild( "##asmView", ImVec2( 0, -bottom ), true, ImGuiWindowFlags_NoMove | ImGuiWindowFlags_HorizontalScrollbar );
Mixed source/assembly symbol view.
2020-04-08 20:04:00 +00:00
if( m_font ) ImGui::PushFont( m_font );
Tighter assembly address display.
2020-04-08 23:31:27 +00:00
int maxAddrLen;
{
char tmp[32];
sprintf( tmp, "%" PRIx64, m_baseAddr + m_codeLen );
maxAddrLen = strlen( tmp );
}
Draw jump range and target on scroll bar, when highlighted.
2020-04-10 21:31:25 +00:00
uint64_t selJumpStart = 0;
uint64_t selJumpEnd;
uint64_t selJumpTarget;
Mixed source/assembly symbol view.
2020-04-08 20:04:00 +00:00
uint64_t jumpOut = 0;
Draw jump range and target on scroll bar, when highlighted.
2020-04-10 21:31:25 +00:00
Mixed source/assembly symbol view.
2020-04-08 20:04:00 +00:00
if( m_targetAddr != 0 )
{
for( auto& line : m_asm )
{
if( m_targetAddr == line.addr )
{
m_targetAddr = 0;
ImGui::SetScrollHereY();
}
Perform source file name substitution.
2020-04-17 17:09:13 +00:00
RenderAsmLine( line, 0, iptotal, ipmax, worker, jumpOut, maxAddrLen, view );
Mixed source/assembly symbol view.
2020-04-08 20:04:00 +00:00
}
Don't mark windows as write-modified when only reading data.
2020-06-06 18:46:46 +00:00
const auto win = ImGui::GetCurrentWindowRead();
Set source view content width to max value, regardless of clipping.
2020-06-06 10:31:47 +00:00
m_asmWidth = win->DC.CursorMaxPos.x - win->DC.CursorStartPos.x;
Mixed source/assembly symbol view.
2020-04-08 20:04:00 +00:00
}
Use clipper to render source view.
2020-03-24 17:10:56 +00:00
else
{
Mixed source/assembly symbol view.
2020-04-08 20:04:00 +00:00
const auto th = (int)ImGui::GetTextLineHeightWithSpacing();
ImGuiListClipper clipper( (int)m_asm.size(), th );
while( clipper.Step() )
Use clipper to render source view.
2020-03-24 17:10:56 +00:00
{
Mixed source/assembly symbol view.
2020-04-08 20:04:00 +00:00
assert( clipper.StepNo == 3 );
const auto wpos = ImGui::GetCursorScreenPos();
static std::vector<uint64_t> insList;
insList.clear();
if( iptotal == 0 )
Use clipper to render source view.
2020-03-24 17:10:56 +00:00
{
Mixed source/assembly symbol view.
2020-04-08 20:04:00 +00:00
for( auto i=clipper.DisplayStart; i<clipper.DisplayEnd; i++ )
Display instruction pointer counts in source view.
2020-03-25 00:09:02 +00:00
{
Perform source file name substitution.
2020-04-17 17:09:13 +00:00
RenderAsmLine( m_asm[i], 0, 0, 0, worker, jumpOut, maxAddrLen, view );
Mixed source/assembly symbol view.
2020-04-08 20:04:00 +00:00
insList.emplace_back( m_asm[i].addr );
Display instruction pointer counts in source view.
2020-03-25 00:09:02 +00:00
}
}
Mixed source/assembly symbol view.
2020-04-08 20:04:00 +00:00
else
Display instruction pointer counts in source view.
2020-03-25 00:09:02 +00:00
{
Mixed source/assembly symbol view.
2020-04-08 20:04:00 +00:00
for( auto i=clipper.DisplayStart; i<clipper.DisplayEnd; i++ )
Display disassembly.
2020-03-25 21:53:05 +00:00
{
Mixed source/assembly symbol view.
2020-04-08 20:04:00 +00:00
auto& line = m_asm[i];
auto it = ipcount.find( line.addr );
const auto ipcnt = it == ipcount.end() ? 0 : it->second;
Perform source file name substitution.
2020-04-17 17:09:13 +00:00
RenderAsmLine( line, ipcnt, iptotal, ipmax, worker, jumpOut, maxAddrLen, view );
Mixed source/assembly symbol view.
2020-04-08 20:04:00 +00:00
insList.emplace_back( line.addr );
Display disassembly.
2020-03-25 21:53:05 +00:00
}
Mixed source/assembly symbol view.
2020-04-08 20:04:00 +00:00
}
if( m_showJumps && !m_jumpTable.empty() )
{
auto draw = ImGui::GetWindowDrawList();
const auto ts = ImGui::CalcTextSize( " " );
const auto th2 = floor( ts.y / 2 );
const auto th4 = floor( ts.y / 4 );
Allow displaying machine code bytes in disassembly.
2020-04-19 14:06:45 +00:00
const auto xoff = ( iptotal == 0 ? 0 : ( 7 * ts.x + ts.y ) ) + (3+maxAddrLen) * ts.x + ( ( m_asmShowSourceLocation && !m_sourceFiles.empty() ) ? 36 * ts.x : 0 ) + ( m_asmBytes ? m_maxAsmBytes*3 * ts.x : 0 );
Mixed source/assembly symbol view.
2020-04-08 20:04:00 +00:00
const auto minAddr = m_asm[clipper.DisplayStart].addr;
const auto maxAddr = m_asm[clipper.DisplayEnd-1].addr;
const auto mjl = m_maxJumpLevel;
const auto JumpArrow = JumpArrowBase * ts.y / 15;
int i = -1;
for( auto& v : m_jumpTable )
Display instruction pointer counts in source view.
2020-03-25 00:09:02 +00:00
{
Mixed source/assembly symbol view.
2020-04-08 20:04:00 +00:00
i++;
if( v.second.min > maxAddr || v.second.max < minAddr ) continue;
const auto col = GetHsvColor( i, 0 );
Add jump arrows tooltip.
2020-04-08 23:09:57 +00:00
auto it0 = std::lower_bound( insList.begin(), insList.end(), v.second.min );
auto it1 = std::lower_bound( insList.begin(), insList.end(), v.second.max );
const auto y0 = ( it0 == insList.end() || *it0 != v.second.min ) ? -th : ( it0 - insList.begin() ) * th;
const auto y1 = it1 == insList.end() ? ( insList.size() + 1 ) * th : ( it1 - insList.begin() ) * th;
float thickness = 1;
Fix jump arrow mouse hover detection.
2020-04-19 12:28:59 +00:00
if( ImGui::IsWindowHovered() && ImGui::IsMouseHoveringRect( wpos + ImVec2( xoff + JumpSeparation * ( mjl - v.second.level ) - JumpSeparation / 2, y0 + th2 ), wpos + ImVec2( xoff + JumpSeparation * ( mjl - v.second.level ) + JumpSeparation / 2, y1 + th2 ) ) )
Add jump arrows tooltip.
2020-04-08 23:09:57 +00:00
{
thickness = 2;
if( m_font ) ImGui::PopFont();
ImGui::BeginTooltip();
char tmp[32];
sprintf( tmp, "+%" PRIu64, v.first - m_baseAddr );
TextFocused( "Jump target:", tmp );
ImGui::SameLine();
sprintf( tmp, "(0x%" PRIx64 ")", v.first );
TextDisabledUnformatted( tmp );
Display jump labels in the UI.
2020-05-09 13:14:33 +00:00
auto lit = m_locMap.find( v.first );
assert( lit != m_locMap.end() );
sprintf( tmp, ".L%" PRIu32, lit->second );
TextFocused( "Jump label:", tmp );
Add jump arrows tooltip.
2020-04-08 23:09:57 +00:00
uint32_t srcline;
const auto srcidx = worker.GetLocationForAddress( v.first, srcline );
if( srcline != 0 )
{
const auto fileName = worker.GetString( srcidx );
const auto fileColor = GetHsvColor( srcidx.Idx(), 0 );
Cosmetics.
2020-04-19 12:10:26 +00:00
TextDisabledUnformatted( "Target location:" );
Add jump arrows tooltip.
2020-04-08 23:09:57 +00:00
ImGui::SameLine();
SmallColorBox( fileColor );
ImGui::SameLine();
ImGui::Text( "%s:%i", fileName, srcline );
}
TextFocused( "Jump range:", MemSizeToString( v.second.max - v.second.min ) );
TextFocused( "Jump sources:", RealToString( v.second.source.size() ) );
ImGui::EndTooltip();
if( m_font ) ImGui::PushFont( m_font );
Follow jump by clicking on jump arrows.
2020-04-09 00:02:06 +00:00
if( ImGui::IsMouseClicked( 0 ) )
{
m_targetAddr = v.first;
m_selectedAddresses.clear();
m_selectedAddresses.emplace( v.first );
}
No saving if there's no file selector.
2020-05-11 20:13:07 +00:00
#ifndef TRACY_NO_FILESELECTOR
Allow saving only lines within jump range.
2020-05-11 19:59:45 +00:00
else if( ImGui::IsMouseClicked( 1 ) )
{
ImGui::OpenPopup( "jumpPopup" );
m_jumpPopupAddr = v.first;
}
No saving if there's no file selector.
2020-05-11 20:13:07 +00:00
#endif
Draw jump range and target on scroll bar, when highlighted.
2020-04-10 21:31:25 +00:00
selJumpStart = v.second.min;
selJumpEnd = v.second.max;
selJumpTarget = v.first;
Add jump arrows tooltip.
2020-04-08 23:09:57 +00:00
}
draw->AddLine( wpos + ImVec2( xoff + JumpSeparation * ( mjl - v.second.level ), y0 + th2 ), wpos + ImVec2( xoff + JumpSeparation * ( mjl - v.second.level ), y1 + th2 ), col, thickness );
Mixed source/assembly symbol view.
2020-04-08 20:04:00 +00:00
if( v.first >= minAddr && v.first <= maxAddr )
Display disassembly.
2020-03-25 21:53:05 +00:00
{
Mixed source/assembly symbol view.
2020-04-08 20:04:00 +00:00
auto iit = std::lower_bound( insList.begin(), insList.end(), v.first );
assert( iit != insList.end() );
const auto y = ( iit - insList.begin() ) * th;
Add jump arrows tooltip.
2020-04-08 23:09:57 +00:00
draw->AddLine( wpos + ImVec2( xoff + JumpSeparation * ( mjl - v.second.level ), y + th2 ), wpos + ImVec2( xoff + JumpSeparation * mjl + JumpArrow + 1, y + th2 ), col, thickness );
draw->AddLine( wpos + ImVec2( xoff + JumpSeparation * mjl + JumpArrow, y + th2 ), wpos + ImVec2( xoff + JumpSeparation * mjl + JumpArrow - th4, y + th2 - th4 ), col, thickness );
draw->AddLine( wpos + ImVec2( xoff + JumpSeparation * mjl + JumpArrow, y + th2 ), wpos + ImVec2( xoff + JumpSeparation * mjl + JumpArrow - th4, y + th2 + th4 ), col, thickness );
Display disassembly.
2020-03-25 21:53:05 +00:00
}
Mixed source/assembly symbol view.
2020-04-08 20:04:00 +00:00
for( auto& s : v.second.source )
{
if( s >= minAddr && s <= maxAddr )
{
auto iit = std::lower_bound( insList.begin(), insList.end(), s );
assert( iit != insList.end() );
const auto y = ( iit - insList.begin() ) * th;
Add jump arrows tooltip.
2020-04-08 23:09:57 +00:00
draw->AddLine( wpos + ImVec2( xoff + JumpSeparation * ( mjl - v.second.level ), y + th2 ), wpos + ImVec2( xoff + JumpSeparation * mjl + JumpArrow, y + th2 ), col, thickness );
Mixed source/assembly symbol view.
2020-04-08 20:04:00 +00:00
}
}
Display instruction pointer counts in source view.
2020-03-25 00:09:02 +00:00
}
Use clipper to render source view.
2020-03-24 17:10:56 +00:00
}
Replace source file viewer with one that actually works. This is much simpler, custom implementation of a text file viewer. It is able to perform these two tasks as intended: - center source view on the selected line, - highlight that line.
2020-03-22 19:53:59 +00:00
}
Allow saving only lines within jump range.
2020-05-11 19:59:45 +00:00
No saving if there's no file selector.
2020-05-11 20:13:07 +00:00
#ifndef TRACY_NO_FILESELECTOR
Allow saving only lines within jump range.
2020-05-11 19:59:45 +00:00
if( m_font ) ImGui::PopFont();
if( ImGui::BeginPopup( "jumpPopup" ) )
{
if( ImGui::Button( ICON_FA_FILE_IMPORT " Save jump range" ) )
{
auto it = m_jumpTable.find( m_jumpPopupAddr );
assert( it != m_jumpTable.end() );
size_t minIdx = 0, maxIdx = 0;
size_t i;
for( i=0; i<m_asm.size(); i++ )
{
Fix typo.
2020-05-13 16:37:37 +00:00
if( m_asm[i].addr == it->second.min )
Allow saving only lines within jump range.
2020-05-11 19:59:45 +00:00
{
minIdx = i++;
break;
}
}
assert( i != m_asm.size() );
for( ; i<m_asm.size(); i++ )
{
if( m_asm[i].addr == it->second.max )
{
maxIdx = i+1;
break;
}
}
assert( i != m_asm.size() );
Save( worker, minIdx, maxIdx );
ImGui::CloseCurrentPopup();
}
ImGui::EndPopup();
}
if( m_font ) ImGui::PushFont( m_font );
No saving if there's no file selector.
2020-05-11 20:13:07 +00:00
#endif
Replace source file viewer with one that actually works. This is much simpler, custom implementation of a text file viewer. It is able to perform these two tasks as intended: - center source view on the selected line, - highlight that line.
2020-03-22 19:53:59 +00:00
}
Mixed source/assembly symbol view.
2020-04-08 20:04:00 +00:00
Don't mark windows as write-modified when only reading data.
2020-06-06 18:46:46 +00:00
const auto win = ImGui::GetCurrentWindowRead();
Scroll bar decorations for asm lines.
2020-04-10 15:13:21 +00:00
if( win->ScrollbarY )
{
auto draw = ImGui::GetWindowDrawList();
auto rect = ImGui::GetWindowScrollbarRect( win, ImGuiAxis_Y );
ImGui::PushClipRect( rect.Min, rect.Max, false );
std::vector<uint32_t> lineOff;
lineOff.reserve( std::max( m_selectedAddresses.size(), m_selectedAddressesHover.size() ) );
if( !m_selectedAddresses.empty() )
{
for( size_t i=0; i<m_asm.size(); i++ )
{
if( m_selectedAddresses.find( m_asm[i].addr ) != m_selectedAddresses.end() )
{
lineOff.push_back( uint32_t( i ) );
}
}
float lastLine = 0;
for( auto& v : lineOff )
{
const auto ly = round( rect.Min.y + ( v - 0.5f ) / m_asm.size() * rect.GetHeight() );
if( ly > lastLine )
{
lastLine = ly;
draw->AddLine( ImVec2( rect.Min.x, ly ), ImVec2( rect.Max.x, ly ), 0x8899994C, 1 );
}
}
}
if( !m_selectedAddressesHover.empty() )
{
lineOff.clear();
for( size_t i=0; i<m_asm.size(); i++ )
{
if( m_selectedAddressesHover.find( m_asm[i].addr ) != m_selectedAddressesHover.end() )
{
lineOff.push_back( uint32_t( i ) );
}
}
float lastLine = 0;
for( auto& v : lineOff )
{
const auto ly = round( rect.Min.y + ( v - 0.5f ) / m_asm.size() * rect.GetHeight() );
if( ly > lastLine )
{
lastLine = ly;
draw->AddLine( ImVec2( rect.Min.x, ly ), ImVec2( rect.Max.x, ly ), 0x88888888, 1 );
}
}
}
Draw asm line hotness.
2020-04-10 15:27:29 +00:00
Draw jump range and target on scroll bar, when highlighted.
2020-04-10 21:31:25 +00:00
uint32_t selJumpLineStart, selJumpLineEnd, selJumpLineTarget;
Draw asm line hotness.
2020-04-10 15:27:29 +00:00
std::vector<std::pair<uint64_t, uint32_t>> ipData;
ipData.reserve( ipcount.size() );
Draw jump range and target on scroll bar, when highlighted.
2020-04-10 21:31:25 +00:00
if( selJumpStart == 0 )
{
for( size_t i=0; i<m_asm.size(); i++ )
{
auto it = ipcount.find( m_asm[i].addr );
if( it == ipcount.end() ) continue;
ipData.emplace_back( i, it->second );
}
}
else
Draw asm line hotness.
2020-04-10 15:27:29 +00:00
{
Draw jump range and target on scroll bar, when highlighted.
2020-04-10 21:31:25 +00:00
for( size_t i=0; i<m_asm.size(); i++ )
{
if( selJumpStart == m_asm[i].addr ) selJumpLineStart = i;
if( selJumpEnd == m_asm[i].addr ) selJumpLineEnd = i;
if( selJumpTarget == m_asm[i].addr ) selJumpLineTarget = i;
auto it = ipcount.find( m_asm[i].addr );
if( it == ipcount.end() ) continue;
ipData.emplace_back( i, it->second );
}
Draw asm line hotness.
2020-04-10 15:27:29 +00:00
}
pdqsort_branchless( ipData.begin(), ipData.end(), []( const auto& l, const auto& r ) { return l.first < r.first; } );
const auto step = uint32_t( m_asm.size() * 2 / rect.GetHeight() );
Draw jump range and target on scroll bar, when highlighted.
2020-04-10 21:31:25 +00:00
const auto x40 = round( rect.Min.x + rect.GetWidth() * 0.4f );
const auto x60 = round( rect.Min.x + rect.GetWidth() * 0.6f );
Draw asm line hotness.
2020-04-10 15:27:29 +00:00
auto it = ipData.begin();
while( it != ipData.end() )
{
const auto firstLine = it->first;
More code deduplication.
2020-04-10 21:13:51 +00:00
uint32_t ipSum = 0;
Draw asm line hotness.
2020-04-10 15:27:29 +00:00
while( it != ipData.end() && it->first <= firstLine + step )
{
ipSum += it->second;
++it;
}
const auto ly = round( rect.Min.y + float( firstLine ) / m_asm.size() * rect.GetHeight() );
Calculate max sample counts during ip map creation.
2020-04-10 23:34:44 +00:00
const uint32_t color = GetHotnessColor( ipSum, ipmax );
Draw jump range and target on scroll bar, when highlighted.
2020-04-10 21:31:25 +00:00
draw->AddRectFilled( ImVec2( x40, ly ), ImVec2( x60, ly+3 ), color );
}
if( selJumpStart != 0 )
{
const auto yStart = rect.Min.y + float( selJumpLineStart ) / m_asm.size() * rect.GetHeight();
const auto yEnd = rect.Min.y + float( selJumpLineEnd ) / m_asm.size() * rect.GetHeight();
const auto yTarget = rect.Min.y + float( selJumpLineTarget ) / m_asm.size() * rect.GetHeight();
const auto x50 = round( rect.Min.x + rect.GetWidth() * 0.5f ) - 1;
const auto x25 = round( rect.Min.x + rect.GetWidth() * 0.25f );
const auto x75 = round( rect.Min.x + rect.GetWidth() * 0.75f );
draw->AddLine( ImVec2( x50, yStart ), ImVec2( x50, yEnd ), 0xFF00FF00 );
draw->AddLine( ImVec2( x25, yTarget ), ImVec2( x75, yTarget ), 0xFF00FF00 );
Draw asm line hotness.
2020-04-10 15:27:29 +00:00
}
Draw register dependency decorations on scroll bar.
2020-05-01 22:05:58 +00:00
if( m_asmSelected >= 0 )
{
const auto x0 = rect.Min.x;
const auto x1 = rect.Min.x + rect.GetWidth() * 0.2f;
float sy;
for( size_t i=0; i<m_asm.size(); i++ )
{
if( i == m_asmSelected )
{
sy = round( rect.Min.y + ( i - 0.5f ) / m_asm.size() * rect.GetHeight() );
}
else if( m_asm[i].regData[0] != 0 )
{
int flags = 0;
int idx = 0;
for(;;)
{
const auto& v = m_asm[i].regData[idx++];
if( v == 0 ) break;
flags |= v & FlagMask;
}
uint32_t col = 0;
if( ( flags & ( WriteBit | ReadBit ) ) == ( WriteBit | ReadBit ) ) col = 0xFF00FFFF;
else if( flags & WriteBit ) col = 0xFF0000FF;
else if( flags & ReadBit ) col = 0xFF00FF00;
if( col != 0 )
{
const auto ly = round( rect.Min.y + ( i - 0.5f ) / m_asm.size() * rect.GetHeight() );
draw->AddLine( ImVec2( x0, ly ), ImVec2( x1, ly ), col, 3 );
}
}
}
draw->AddLine( ImVec2( x0, sy ), ImVec2( x1, sy ), 0xFFFF9900, 3 );
}
Scroll bar decorations for asm lines.
2020-04-10 15:13:21 +00:00
}
Replace source file viewer with one that actually works. This is much simpler, custom implementation of a text file viewer. It is able to perform these two tasks as intended: - center source view on the selected line, - highlight that line.
2020-03-22 19:53:59 +00:00
if( m_font ) ImGui::PopFont();
ImGui::EndChild();
Implement cross-symbol jumping.
2020-03-28 13:27:29 +00:00
Implement display of grouped instruction pointer statistics.
2020-05-07 00:33:37 +00:00
if( !m_asmSampleSelect.empty() )
{
uint32_t count = 0;
Display number of selected lines.
2020-05-09 11:53:11 +00:00
uint32_t numLines = 0;
Implement display of grouped instruction pointer statistics.
2020-05-07 00:33:37 +00:00
for( auto& idx : m_asmSampleSelect )
{
auto it = ipcount.find( m_asm[idx].addr );
Display number of selected lines.
2020-05-09 11:53:11 +00:00
if( it != ipcount.end() )
{
count += it->second;
numLines++;
}
Implement display of grouped instruction pointer statistics.
2020-05-07 00:33:37 +00:00
}
ImGui::BeginChild( "##asmSelect" );
if( ImGui::SmallButton( ICON_FA_TIMES ) )
{
m_asmSampleSelect.clear();
m_asmGroupSelect = -1;
}
ImGui::SameLine();
char buf[16];
auto end = PrintFloat( buf, buf+16, 100.f * count / iptotal, 2 );
memcpy( end, "%", 2 );
TextFocused( "Selected:", buf );
ImGui::SameLine();
ImGui::Spacing();
ImGui::SameLine();
TextFocused( "Time:", TimeToString( count * worker.GetSamplingPeriod() ) );
ImGui::SameLine();
ImGui::Spacing();
ImGui::SameLine();
TextFocused( "Sample count:", RealToString( count ) );
Display number of selected lines.
2020-05-09 11:53:11 +00:00
ImGui::SameLine();
ImGui::Spacing();
ImGui::SameLine();
TextFocused( "Lines:", RealToString( numLines ) );
Implement display of grouped instruction pointer statistics.
2020-05-07 00:33:37 +00:00
ImGui::EndChild();
}
Mixed source/assembly symbol view.
2020-04-08 20:04:00 +00:00
return jumpOut;
Replace source file viewer with one that actually works. This is much simpler, custom implementation of a text file viewer. It is able to perform these two tasks as intended: - center source view on the selected line, - highlight that line.
2020-03-22 19:53:59 +00:00
}
Implement display of grouped instruction pointer statistics.
2020-05-07 00:33:37 +00:00
static bool PrintPercentage( float val, uint32_t col = 0xFFFFFFFF )
Common percentage printing function.
2020-03-30 20:26:45 +00:00
{
Display graphical representation of line percentage.
2020-03-30 20:49:06 +00:00
const auto ty = ImGui::GetFontSize();
auto draw = ImGui::GetWindowDrawList();
const auto wpos = ImGui::GetCursorScreenPos();
const auto stw = ImGui::CalcTextSize( " " ).x;
const auto htw = stw / 2;
const auto tw = stw * 8;
Common percentage printing function.
2020-03-30 20:26:45 +00:00
char tmp[16];
auto end = PrintFloat( tmp, tmp+16, val, 2 );
memcpy( end, "%", 2 );
end++;
const auto sz = end - tmp;
char buf[16];
memset( buf, ' ', 7-sz );
memcpy( buf + 7 - sz, tmp, sz+1 );
Display graphical representation of line percentage.
2020-03-30 20:49:06 +00:00
draw->AddRectFilled( wpos, wpos + ImVec2( val * tw / 100, ty+1 ), 0xFF444444 );
Implement display of grouped instruction pointer statistics.
2020-05-07 00:33:37 +00:00
DrawTextContrast( draw, wpos + ImVec2( htw, 0 ), col, buf );
Display graphical representation of line percentage.
2020-03-30 20:49:06 +00:00
ImGui::ItemSize( ImVec2( stw * 7, ty ), 0 );
Display tooltip for sample percentage.
2020-04-10 21:03:47 +00:00
return ImGui::IsWindowHovered() && ImGui::IsMouseHoveringRect( wpos, wpos + ImVec2( stw * 7, ty ) );
Common percentage printing function.
2020-03-30 20:26:45 +00:00
}
Enable syntax highlighting.
2020-04-24 22:10:53 +00:00
static const ImVec4 SyntaxColors[] = {
{ 0.7f, 0.7f, 0.7f, 1 }, // default
{ 0.45f, 0.68f, 0.32f, 1 }, // comment
{ 0.72f, 0.37f, 0.12f, 1 }, // preprocessor
{ 0.64f, 0.64f, 1, 1 }, // string
{ 0.64f, 0.82f, 1, 1 }, // char literal
{ 1, 0.91f, 0.53f, 1 }, // keyword
Separate coloring for types and special values.
2020-04-24 22:49:51 +00:00
{ 0.81f, 0.6f, 0.91f, 1 }, // number
Enable syntax highlighting.
2020-04-24 22:10:53 +00:00
{ 0.9f, 0.9f, 0.9f, 1 }, // punctuation
Separate coloring for types and special values.
2020-04-24 22:49:51 +00:00
{ 0.78f, 0.46f, 0.75f, 1 }, // type
{ 0.21f, 0.69f, 0.89f, 1 }, // special
Enable syntax highlighting.
2020-04-24 22:10:53 +00:00
};
Draw hotness markers next to sample percentage counts.
2020-04-10 23:59:15 +00:00
void SourceView::RenderLine( const Line& line, int lineNum, uint32_t ipcnt, uint32_t iptotal, uint32_t ipmax, const Worker* worker )
Replace source file viewer with one that actually works. This is much simpler, custom implementation of a text file viewer. It is able to perform these two tasks as intended: - center source view on the selected line, - highlight that line.
2020-03-22 19:53:59 +00:00
{
const auto ty = ImGui::GetFontSize();
auto draw = ImGui::GetWindowDrawList();
Fix determination of line width.
2020-06-08 12:02:11 +00:00
const auto w = std::max( m_srcWidth, ImGui::GetWindowWidth() );
Replace source file viewer with one that actually works. This is much simpler, custom implementation of a text file viewer. It is able to perform these two tasks as intended: - center source view on the selected line, - highlight that line.
2020-03-22 19:53:59 +00:00
const auto wpos = ImGui::GetCursorScreenPos();
Highlight source line corresponding to hovered asm line.
2020-04-09 20:02:06 +00:00
if( m_fileStringIdx == m_hoveredSource && lineNum == m_hoveredLine )
{
draw->AddRectFilled( wpos, wpos + ImVec2( w, ty+1 ), 0x22FFFFFF );
}
else if( lineNum == m_selectedLine )
Replace source file viewer with one that actually works. This is much simpler, custom implementation of a text file viewer. It is able to perform these two tasks as intended: - center source view on the selected line, - highlight that line.
2020-03-22 19:53:59 +00:00
{
draw->AddRectFilled( wpos, wpos + ImVec2( w, ty+1 ), 0xFF333322 );
}
Implement display of grouped instruction pointer statistics.
2020-05-07 00:33:37 +00:00
bool mouseHandled = false;
Display instruction pointer counts in source view.
2020-03-25 00:09:02 +00:00
if( iptotal != 0 )
{
if( ipcnt == 0 )
{
Don't print empty text, just advance cursor.
2020-04-04 00:45:01 +00:00
const auto ts = ImGui::CalcTextSize( " " );
ImGui::ItemSize( ImVec2( 7 * ts.x, ts.y ) );
Display instruction pointer counts in source view.
2020-03-25 00:09:02 +00:00
}
else
{
Implement display of grouped instruction pointer statistics.
2020-05-07 00:33:37 +00:00
auto sit = m_srcSampleSelect.find( lineNum );
if( PrintPercentage( 100.f * ipcnt / iptotal, sit == m_srcSampleSelect.end() ? 0xFFFFFFFF : 0xFF8888FF ) )
Display tooltip for sample percentage.
2020-04-10 21:03:47 +00:00
{
if( m_font ) ImGui::PopFont();
ImGui::BeginTooltip();
if( worker ) TextFocused( "Time:", TimeToString( ipcnt * worker->GetSamplingPeriod() ) );
TextFocused( "Sample count:", RealToString( ipcnt ) );
ImGui::EndTooltip();
if( m_font ) ImGui::PushFont( m_font );
Implement display of grouped instruction pointer statistics.
2020-05-07 00:33:37 +00:00
if( ImGui::IsMouseClicked( 0 ) )
{
mouseHandled = true;
auto& io = ImGui::GetIO();
if( io.KeyCtrl )
{
m_srcGroupSelect = lineNum;
if( sit == m_srcSampleSelect.end() )
{
m_srcSampleSelect.emplace( lineNum );
}
else
{
m_srcSampleSelect.erase( sit );
}
}
else if( io.KeyShift )
{
m_srcSampleSelect.clear();
if( m_srcGroupSelect == -1 )
{
m_srcGroupSelect = lineNum;
m_srcSampleSelect.insert( lineNum );
}
else
{
if( lineNum < m_srcGroupSelect )
{
for( int i=lineNum; i<=m_srcGroupSelect; i++ )
{
m_srcSampleSelect.insert( i );
}
}
else
{
for( int i=m_srcGroupSelect; i<=lineNum; i++ )
{
m_srcSampleSelect.insert( i );
}
}
}
}
else
{
m_srcSampleSelect.clear();
m_srcSampleSelect.insert( lineNum );
m_srcGroupSelect = lineNum;
}
}
else if( ImGui::IsMouseClicked( 1 ) )
{
mouseHandled = true;
m_srcSampleSelect.clear();
m_srcGroupSelect = -1;
}
Display tooltip for sample percentage.
2020-04-10 21:03:47 +00:00
}
Draw hotness markers next to sample percentage counts.
2020-04-10 23:59:15 +00:00
draw->AddLine( wpos + ImVec2( 0, 1 ), wpos + ImVec2( 0, ty-2 ), GetHotnessColor( ipcnt, ipmax ) );
Display instruction pointer counts in source view.
2020-03-25 00:09:02 +00:00
}
ImGui::SameLine( 0, ty );
}
Tighten line numbers in source view.
2020-04-09 22:37:46 +00:00
const auto lineCount = m_lines.size();
const auto tmp = RealToString( lineCount );
const auto maxLine = strlen( tmp );
Replace source file viewer with one that actually works. This is much simpler, custom implementation of a text file viewer. It is able to perform these two tasks as intended: - center source view on the selected line, - highlight that line.
2020-03-22 19:53:59 +00:00
const auto lineString = RealToString( lineNum );
const auto linesz = strlen( lineString );
char buf[16];
Tighten line numbers in source view.
2020-04-09 22:37:46 +00:00
memset( buf, ' ', maxLine - linesz );
memcpy( buf + maxLine - linesz, lineString, linesz+1 );
Replace source file viewer with one that actually works. This is much simpler, custom implementation of a text file viewer. It is able to perform these two tasks as intended: - center source view on the selected line, - highlight that line.
2020-03-22 19:53:59 +00:00
TextDisabledUnformatted( buf );
Display number of assembly instructions for each line.
2020-04-02 00:35:41 +00:00
ImGui::SameLine( 0, ty );
Match source and assembly selection.
2020-04-08 20:57:42 +00:00
uint32_t match = 0;
Don't display asm counts if no asm available.
2020-04-25 11:51:58 +00:00
if( !m_asm.empty() )
Display number of assembly instructions for each line.
2020-04-02 00:35:41 +00:00
{
Split source and symbol views in SourceView.
2020-04-07 23:58:23 +00:00
assert( worker );
Don't try to display assembly line counts if no symbol is selected.
2020-04-07 23:48:22 +00:00
const auto stw = ImGui::CalcTextSize( " " ).x;
Split source and symbol views in SourceView.
2020-04-07 23:58:23 +00:00
auto addresses = worker->GetAddressesForLocation( m_fileStringIdx, lineNum );
Don't try to display assembly line counts if no symbol is selected.
2020-04-07 23:48:22 +00:00
if( addresses )
Display number of assembly instructions for each line.
2020-04-02 00:35:41 +00:00
{
Don't try to display assembly line counts if no symbol is selected.
2020-04-07 23:48:22 +00:00
for( auto& addr : *addresses )
{
Use correct address range.
2020-04-09 20:21:21 +00:00
match += ( addr >= m_baseAddr && addr < m_baseAddr + m_codeLen );
Don't try to display assembly line counts if no symbol is selected.
2020-04-07 23:48:22 +00:00
}
Display number of assembly instructions for each line.
2020-04-02 00:35:41 +00:00
}
Tighten assembly counts in source view.
2020-04-09 22:40:31 +00:00
const auto tmp = RealToString( m_asm.size() );
const auto maxAsm = strlen( tmp ) + 1;
Don't try to display assembly line counts if no symbol is selected.
2020-04-07 23:48:22 +00:00
if( match > 0 )
Going from source location to assembly line.
2020-04-02 11:10:18 +00:00
{
Don't try to display assembly line counts if no symbol is selected.
2020-04-07 23:48:22 +00:00
const auto asmString = RealToString( match );
sprintf( buf, "@%s", asmString );
const auto asmsz = strlen( buf );
TextDisabledUnformatted( buf );
ImGui::SameLine( 0, 0 );
Tighten assembly counts in source view.
2020-04-09 22:40:31 +00:00
ImGui::ItemSize( ImVec2( stw * ( maxAsm - asmsz ), ty ), 0 );
Don't try to display assembly line counts if no symbol is selected.
2020-04-07 23:48:22 +00:00
}
else
{
Tighten assembly counts in source view.
2020-04-09 22:40:31 +00:00
ImGui::ItemSize( ImVec2( stw * maxAsm, ty ), 0 );
Going from source location to assembly line.
2020-04-02 11:10:18 +00:00
}
Display number of assembly instructions for each line.
2020-04-02 00:35:41 +00:00
}
Replace source file viewer with one that actually works. This is much simpler, custom implementation of a text file viewer. It is able to perform these two tasks as intended: - center source view on the selected line, - highlight that line.
2020-03-22 19:53:59 +00:00
ImGui::SameLine( 0, ty );
Enable syntax highlighting.
2020-04-24 22:10:53 +00:00
auto ptr = line.begin;
auto it = line.tokens.begin();
while( ptr < line.end )
{
if( it == line.tokens.end() )
{
ImGui::TextUnformatted( ptr, line.end );
ImGui::SameLine( 0, 0 );
break;
}
if( ptr < it->begin )
{
ImGui::TextUnformatted( ptr, it->begin );
ImGui::SameLine( 0, 0 );
}
TextColoredUnformatted( SyntaxColors[(int)it->color], it->begin, it->end );
ImGui::SameLine( 0, 0 );
ptr = it->end;
++it;
}
ImGui::ItemSize( ImVec2( 0, 0 ), 0 );
Replace source file viewer with one that actually works. This is much simpler, custom implementation of a text file viewer. It is able to perform these two tasks as intended: - center source view on the selected line, - highlight that line.
2020-03-22 19:53:59 +00:00
Fix detection of hovering over source lines.
2020-04-12 14:21:03 +00:00
if( match > 0 && ImGui::IsWindowHovered() && ImGui::IsMouseHoveringRect( wpos, wpos + ImVec2( w, ty+1 ) ) )
Match source and assembly selection.
2020-04-08 20:57:42 +00:00
{
draw->AddRectFilled( wpos, wpos + ImVec2( w, ty+1 ), 0x11FFFFFF );
Implement display of grouped instruction pointer statistics.
2020-05-07 00:33:37 +00:00
if( !mouseHandled && ( ImGui::IsMouseClicked( 0 ) || ImGui::IsMouseClicked( 1 ) ) )
Match source and assembly selection.
2020-04-08 20:57:42 +00:00
{
m_displayMode = DisplayMixed;
Use left and right mouse buttons for asm navigation. Left click on source line just selects the line and the corresponding asm lines. Right click does the above and focuses asm view on the first selected line.
2020-04-09 21:12:17 +00:00
SelectLine( lineNum, worker, ImGui::IsMouseClicked( 1 ) );
Match source and assembly selection.
2020-04-08 20:57:42 +00:00
}
Highlight asm lines for hovered source line.
2020-04-09 19:57:28 +00:00
else
{
SelectAsmLinesHover( m_fileStringIdx, lineNum, *worker );
}
Match source and assembly selection.
2020-04-08 20:57:42 +00:00
}
Replace source file viewer with one that actually works. This is much simpler, custom implementation of a text file viewer. It is able to perform these two tasks as intended: - center source view on the selected line, - highlight that line.
2020-03-22 19:53:59 +00:00
draw->AddLine( wpos + ImVec2( 0, ty+2 ), wpos + ImVec2( w, ty+2 ), 0x08FFFFFF );
}
Add ability to show callstack to an asm line.
2020-05-10 14:56:38 +00:00
void SourceView::RenderAsmLine( AsmLine& line, uint32_t ipcnt, uint32_t iptotal, uint32_t ipmax, const Worker& worker, uint64_t& jumpOut, int maxAddrLen, View& view )
Display disassembly.
2020-03-25 21:53:05 +00:00
{
const auto ty = ImGui::GetFontSize();
auto draw = ImGui::GetWindowDrawList();
Fix determination of line width.
2020-06-08 12:02:11 +00:00
const auto w = std::max( m_asmWidth, ImGui::GetWindowWidth() );
Display disassembly.
2020-03-25 21:53:05 +00:00
const auto wpos = ImGui::GetCursorScreenPos();
Highlight asm lines for hovered source line.
2020-04-09 19:57:28 +00:00
if( m_selectedAddressesHover.find( line.addr ) != m_selectedAddressesHover.end() )
{
draw->AddRectFilled( wpos, wpos + ImVec2( w, ty+1 ), 0x22FFFFFF );
}
else if( m_selectedAddresses.find( line.addr ) != m_selectedAddresses.end() )
Display disassembly.
2020-03-25 21:53:05 +00:00
{
draw->AddRectFilled( wpos, wpos + ImVec2( w, ty+1 ), 0xFF333322 );
}
Display jump/call target address.
2020-03-28 00:22:27 +00:00
if( line.addr == m_highlightAddr )
{
draw->AddRectFilled( wpos, wpos + ImVec2( w, ty+1 ), 0xFF222233 );
}
Display disassembly.
2020-03-25 21:53:05 +00:00
Allow enumerating asm lines from a given base instruction.
2020-05-11 11:35:49 +00:00
const auto asmIdx = &line - m_asm.data();
Display disassembly.
2020-03-25 21:53:05 +00:00
if( iptotal != 0 )
{
if( ipcnt == 0 )
{
Don't print empty text, just advance cursor.
2020-04-04 00:45:01 +00:00
const auto ts = ImGui::CalcTextSize( " " );
ImGui::ItemSize( ImVec2( 7 * ts.x, ts.y ) );
Display disassembly.
2020-03-25 21:53:05 +00:00
}
else
{
Implement display of grouped instruction pointer statistics.
2020-05-07 00:33:37 +00:00
const auto idx = &line - m_asm.data();
auto sit = m_asmSampleSelect.find( idx );
if( PrintPercentage( 100.f * ipcnt / iptotal, sit == m_asmSampleSelect.end() ? 0xFFFFFFFF : 0xFF8888FF ) )
Display tooltip for sample percentage.
2020-04-10 21:03:47 +00:00
{
if( m_font ) ImGui::PopFont();
ImGui::BeginTooltip();
TextFocused( "Time:", TimeToString( ipcnt * worker.GetSamplingPeriod() ) );
TextFocused( "Sample count:", RealToString( ipcnt ) );
ImGui::EndTooltip();
if( m_font ) ImGui::PushFont( m_font );
Implement display of grouped instruction pointer statistics.
2020-05-07 00:33:37 +00:00
if( ImGui::IsMouseClicked( 0 ) )
{
auto& io = ImGui::GetIO();
if( io.KeyCtrl )
{
m_asmGroupSelect = idx;
if( sit == m_asmSampleSelect.end() )
{
m_asmSampleSelect.emplace( idx );
}
else
{
m_asmSampleSelect.erase( sit );
}
}
else if( io.KeyShift )
{
m_asmSampleSelect.clear();
if( m_asmGroupSelect == -1 )
{
m_asmGroupSelect = idx;
m_asmSampleSelect.insert( idx );
}
else
{
if( idx < m_asmGroupSelect )
{
for( int i=idx; i<=m_asmGroupSelect; i++ )
{
m_asmSampleSelect.insert( i );
}
}
else
{
for( int i=m_asmGroupSelect; i<=idx; i++ )
{
m_asmSampleSelect.insert( i );
}
}
}
}
else
{
m_asmSampleSelect.clear();
m_asmSampleSelect.insert( idx );
m_asmGroupSelect = idx;
}
}
else if( ImGui::IsMouseClicked( 1 ) )
{
m_asmSampleSelect.clear();
m_asmGroupSelect = -1;
}
Add ability to show callstack to an asm line.
2020-05-10 14:56:38 +00:00
else if( ImGui::IsMouseClicked( 2 ) )
{
const auto cfi = worker.PackPointer( line.addr );
const auto& symStat = worker.GetSymbolStats();
auto inlineList = worker.GetInlineSymbolList( m_baseAddr, m_codeLen );
if( inlineList )
{
bool found = false;
const auto symEnd = m_baseAddr + m_codeLen;
while( *inlineList < symEnd )
{
auto ipmap = worker.GetSymbolInstructionPointers( *inlineList );
if( ipmap )
{
if( ipmap->find( cfi ) != ipmap->end() )
{
view.ShowSampleParents( *inlineList );
found = true;
break;
}
}
inlineList++;
}
if( !found )
{
view.ShowSampleParents( m_baseAddr );
}
}
else
{
view.ShowSampleParents( m_baseAddr );
}
}
Display tooltip for sample percentage.
2020-04-10 21:03:47 +00:00
}
Draw hotness markers next to sample percentage counts.
2020-04-10 23:59:15 +00:00
draw->AddLine( wpos + ImVec2( 0, 1 ), wpos + ImVec2( 0, ty-2 ), GetHotnessColor( ipcnt, ipmax ) );
Display disassembly.
2020-03-25 21:53:05 +00:00
}
ImGui::SameLine( 0, ty );
}
char buf[256];
Allow enumerating asm lines from a given base instruction.
2020-05-11 11:35:49 +00:00
if( m_asmCountBase >= 0 )
{
Cast to correct type.
2020-05-13 16:38:40 +00:00
sprintf( buf, "[%i]", int( asmIdx - m_asmCountBase ) );
Allow enumerating asm lines from a given base instruction.
2020-05-11 11:35:49 +00:00
}
else if( m_asmRelative )
Assembly addresses can be displayed relative to symbol.
2020-03-28 13:33:35 +00:00
{
sprintf( buf, "+%" PRIu64, line.addr - m_baseAddr );
}
else
{
sprintf( buf, "%" PRIx64, line.addr );
}
Display disassembly.
2020-03-25 21:53:05 +00:00
const auto asz = strlen( buf );
Tighter assembly address display.
2020-04-08 23:31:27 +00:00
memset( buf+asz, ' ', maxAddrLen-asz );
buf[maxAddrLen] = '\0';
Allow enumerating asm lines from a given base instruction.
2020-05-11 11:35:49 +00:00
if( m_asmCountBase >= 0 )
{
TextColoredUnformatted( asmIdx - m_asmCountBase < 0 ? 0xFFBB6666 : 0xFF66BBBB, buf );
}
else
{
TextDisabledUnformatted( buf );
}
if( ImGui::IsItemClicked( 0 ) )
{
m_asmCountBase = asmIdx;
}
else if( ImGui::IsItemClicked( 1 ) )
{
m_asmCountBase = -1;
}
Display source locations in assembly view.
2020-04-01 23:32:23 +00:00
Allow displaying machine code bytes in disassembly.
2020-04-19 14:06:45 +00:00
const auto stw = ImGui::CalcTextSize( " " ).x;
Match source and assembly selection.
2020-04-08 20:57:42 +00:00
bool lineHovered = false;
Don't display source files, if none available.
2020-04-12 21:26:02 +00:00
if( m_asmShowSourceLocation && !m_sourceFiles.empty() )
Add source file location tooltip for assembly instructions. This has bad UX, better solution is needed.
2020-04-01 22:39:17 +00:00
{
Display source locations in assembly view.
2020-04-01 23:32:23 +00:00
ImGui::SameLine();
Make source location display optional.
2020-04-01 23:37:56 +00:00
uint32_t srcline;
const auto srcidx = worker.GetLocationForAddress( line.addr, srcline );
if( srcline != 0 )
Display source locations in assembly view.
2020-04-01 23:32:23 +00:00
{
Make source location display optional.
2020-04-01 23:37:56 +00:00
const auto fileName = worker.GetString( srcidx );
const auto fileColor = GetHsvColor( srcidx.Idx(), 0 );
SmallColorBox( fileColor );
ImGui::SameLine();
const auto lineString = RealToString( srcline );
const auto linesz = strlen( lineString );
Increase buffer size.
2020-06-04 17:54:11 +00:00
char buf[64];
Make source location display optional.
2020-04-01 23:37:56 +00:00
const auto fnsz = strlen( fileName );
Tighten assembly source location display.
2020-04-08 23:52:22 +00:00
if( fnsz < 30 - m_maxLine )
Make source location display optional.
2020-04-01 23:37:56 +00:00
{
sprintf( buf, "%s:%i", fileName, srcline );
}
else
{
Tighten assembly source location display.
2020-04-08 23:52:22 +00:00
sprintf( buf, "...%s:%i", fileName+fnsz-(30-3-1-m_maxLine), srcline );
Make source location display optional.
2020-04-01 23:37:56 +00:00
}
const auto bufsz = strlen( buf );
TextDisabledUnformatted( buf );
if( ImGui::IsItemHovered() )
{
Match source and assembly selection.
2020-04-08 20:57:42 +00:00
lineHovered = true;
Make source location display optional.
2020-04-01 23:37:56 +00:00
if( m_font ) ImGui::PopFont();
ImGui::BeginTooltip();
Improve source file tooltip.
2020-05-14 23:39:14 +00:00
TextFocused( "File:", fileName );
TextFocused( "Line:", RealToString( srcline ) );
Make source location display optional.
2020-04-01 23:37:56 +00:00
ImGui::EndTooltip();
if( m_font ) ImGui::PushFont( m_font );
Ditto for source navigation.
2020-04-09 21:28:51 +00:00
if( ImGui::IsItemClicked( 0 ) || ImGui::IsItemClicked( 1 ) )
Make source location display optional.
2020-04-01 23:37:56 +00:00
{
Switching between source files from asm view.
2020-04-08 20:10:58 +00:00
if( m_file == fileName )
{
Ditto for source navigation.
2020-04-09 21:28:51 +00:00
if( ImGui::IsMouseClicked( 1 ) ) m_targetLine = srcline;
Only change assembly target line when necessary.
2020-04-08 21:30:42 +00:00
SelectLine( srcline, &worker, false );
Switching between source files from asm view.
2020-04-08 20:10:58 +00:00
m_displayMode = DisplayMixed;
}
Use cached source files.
2020-05-23 13:14:57 +00:00
else if( SourceFileValid( fileName, worker.GetCaptureTime(), view, worker ) )
Switching between source files from asm view.
2020-04-08 20:10:58 +00:00
{
Use cached source files.
2020-05-23 13:14:57 +00:00
ParseSource( fileName, worker, view );
Switching between source files from asm view.
2020-04-08 20:10:58 +00:00
m_targetLine = srcline;
Only change assembly target line when necessary.
2020-04-08 21:30:42 +00:00
SelectLine( srcline, &worker, false );
Switching between source files from asm view.
2020-04-08 20:10:58 +00:00
m_displayMode = DisplayMixed;
}
Handle source-less asm lines selection.
2020-04-08 21:59:21 +00:00
else
{
SelectAsmLines( srcidx.Idx(), srcline, worker, false );
}
Make source location display optional.
2020-04-01 23:37:56 +00:00
}
Highlight source line corresponding to hovered asm line.
2020-04-09 20:02:06 +00:00
else
{
m_hoveredLine = srcline;
m_hoveredSource = srcidx.Idx();
}
Make source location display optional.
2020-04-01 23:37:56 +00:00
}
ImGui::SameLine( 0, 0 );
ImGui::ItemSize( ImVec2( stw * ( 32 - bufsz ), ty ), 0 );
Display source locations in assembly view.
2020-04-01 23:32:23 +00:00
}
else
{
Make source location display optional.
2020-04-01 23:37:56 +00:00
SmallColorBox( 0 );
Fix display of unknown source locations in asm view.
2020-06-04 17:39:43 +00:00
ImGui::SameLine();
TextDisabledUnformatted( "[unknown]" );
Make source location display optional.
2020-04-01 23:37:56 +00:00
ImGui::SameLine( 0, 0 );
Fix display of unknown source locations in asm view.
2020-06-04 17:39:43 +00:00
ImGui::ItemSize( ImVec2( stw * 23, ty ), 0 );
Add source file location tooltip for assembly instructions. This has bad UX, better solution is needed.
2020-04-01 22:39:17 +00:00
}
}
Allow displaying machine code bytes in disassembly.
2020-04-19 14:06:45 +00:00
if( m_asmBytes )
{
Use proper symbol address.
2020-04-24 14:16:53 +00:00
auto code = (const uint8_t*)worker.GetSymbolCode( m_baseAddr, m_codeLen );
Allow displaying machine code bytes in disassembly.
2020-04-19 14:06:45 +00:00
assert( code );
char tmp[64];
Use proper symbol address.
2020-04-24 14:16:53 +00:00
const auto len = PrintHexBytes( tmp, code + line.addr - m_baseAddr, line.len );
Allow displaying machine code bytes in disassembly.
2020-04-19 14:06:45 +00:00
ImGui::SameLine();
TextColoredUnformatted( ImVec4( 0.5, 0.5, 1, 1 ), tmp );
ImGui::SameLine( 0, 0 );
ImGui::ItemSize( ImVec2( stw * ( m_maxAsmBytes*3 - len ), ty ), 0 );
}
Draw jumps in assembly view.
2020-04-04 01:34:54 +00:00
if( m_showJumps )
{
Fix typo.
2020-04-27 14:10:43 +00:00
const auto JumpArrow = JumpArrowBase * ty / 15;
Draw jumps in assembly view.
2020-04-04 01:34:54 +00:00
ImGui::SameLine( 0, 2*ty + JumpArrow + m_maxJumpLevel * JumpSeparation );
Draw jump outs from symbols.
2020-04-04 12:29:07 +00:00
auto jit = m_jumpOut.find( line.addr );
if( jit != m_jumpOut.end() )
{
const auto ts = ImGui::CalcTextSize( " " );
const auto th2 = floor( ts.y / 2 );
const auto th4 = floor( ts.y / 4 );
const auto& mjl = m_maxJumpLevel;
const auto col = GetHsvColor( line.jumpAddr, 6 );
Allow displaying machine code bytes in disassembly.
2020-04-19 14:06:45 +00:00
const auto xoff = ( iptotal == 0 ? 0 : ( 7 * ts.x + ts.y ) ) + (3+maxAddrLen) * ts.x + ( ( m_asmShowSourceLocation && !m_sourceFiles.empty() ) ? 36 * ts.x : 0 ) + ( m_asmBytes ? m_maxAsmBytes*3 * ts.x : 0 );
Draw jump outs from symbols.
2020-04-04 12:29:07 +00:00
draw->AddLine( wpos + ImVec2( xoff + JumpSeparation * mjl + th2, th2 ), wpos + ImVec2( xoff + JumpSeparation * mjl + th2 + JumpArrow / 2, th2 ), col );
draw->AddLine( wpos + ImVec2( xoff + JumpSeparation * mjl + th2, th2 ), wpos + ImVec2( xoff + JumpSeparation * mjl + th2 + th4, th2 - th4 ), col );
draw->AddLine( wpos + ImVec2( xoff + JumpSeparation * mjl + th2, th2 ), wpos + ImVec2( xoff + JumpSeparation * mjl + th2 + th4, th2 + th4 ), col );
}
Draw jumps in assembly view.
2020-04-04 01:34:54 +00:00
}
else
{
ImGui::SameLine( 0, ty );
}
Display disassembly.
2020-03-25 21:53:05 +00:00
Separate uarch data retrieval from tooltip display.
2020-04-27 13:31:32 +00:00
const AsmVar* asmVar = nullptr;
Skip processing uarch data if AT&T mode is enabled.
2020-06-04 17:30:44 +00:00
if( !m_atnt && ( m_cpuArch == CpuArchX64 || m_cpuArch == CpuArchX86 ) )
Add micro architecture tooltips.
2020-04-26 20:26:17 +00:00
{
auto uarch = MicroArchitectureData[m_idxMicroArch];
char tmp[32];
for( size_t i=0; i<line.mnemonic.size(); i++ )
{
auto c = line.mnemonic[i];
if( c >= 'a' && c <= 'z' ) c = c - 'a' + 'A';
tmp[i] = c;
}
tmp[line.mnemonic.size()] = '\0';
Hackish support for LEA variants.
2020-04-26 22:49:37 +00:00
const char* mnemonic = tmp;
if( strcmp( mnemonic, "LEA" ) == 0 )
{
static constexpr const char* LeaTable[] = { "LEA", "LEA_B", "LEA_BD", "LEA_BI", "LEA_BID", "LEA_D", "LEA_I", "LEA_ID", "LEA_R", "LEA_RD" };
mnemonic = LeaTable[(int)line.leaData];
}
auto it = m_microArchOpMap.find( mnemonic );
Add micro architecture tooltips.
2020-04-26 20:26:17 +00:00
if( it != m_microArchOpMap.end() )
{
const auto opid = it->second;
auto oit = std::lower_bound( uarch->ops, uarch->ops + uarch->numOps, opid, []( const auto& l, const auto& r ) { return l->id < r; } );
if( oit != uarch->ops + uarch->numOps && (*oit)->id == opid )
{
const auto& op = *oit;
Workaround issues with operand width mismatch.
2020-04-26 21:32:03 +00:00
std::vector<std::pair<int, int>> res;
res.reserve( op->numVariants );
Add micro architecture tooltips.
2020-04-26 20:26:17 +00:00
for( int i=0; i<op->numVariants; i++ )
{
const auto& var = *op->variant[i];
if( var.descNum == line.params.size() )
{
Workaround issues with operand width mismatch.
2020-04-26 21:32:03 +00:00
int penalty = 0;
Add micro architecture tooltips.
2020-04-26 20:26:17 +00:00
bool match = true;
for( int j=0; j<var.descNum; j++ )
{
Workaround issues with operand width mismatch.
2020-04-26 21:32:03 +00:00
if( var.desc[j].type != line.params[j].type )
Add micro architecture tooltips.
2020-04-26 20:26:17 +00:00
{
match = false;
break;
}
Workaround issues with operand width mismatch.
2020-04-26 21:32:03 +00:00
if( var.desc[j].width != line.params[j].width ) penalty++;
Add micro architecture tooltips.
2020-04-26 20:26:17 +00:00
}
if( match )
{
Workaround issues with operand width mismatch.
2020-04-26 21:32:03 +00:00
res.emplace_back( i, penalty );
Add micro architecture tooltips.
2020-04-26 20:26:17 +00:00
}
}
}
Workaround issues with operand width mismatch.
2020-04-26 21:32:03 +00:00
if( !res.empty() )
Add micro architecture tooltips.
2020-04-26 20:26:17 +00:00
{
Workaround issues with operand width mismatch.
2020-04-26 21:32:03 +00:00
pdqsort_branchless( res.begin(), res.end(), []( const auto& l, const auto& r ) { return l.second < r.second; } );
Separate uarch data retrieval from tooltip display.
2020-04-27 13:31:32 +00:00
asmVar = op->variant[res[0].first];
}
}
}
}
Optional visualization of uarch latency.
2020-04-27 14:10:47 +00:00
if( m_showLatency && asmVar && asmVar->minlat >= 0 )
{
const auto pos = ImVec2( (int)ImGui::GetCursorScreenPos().x, (int)ImGui::GetCursorScreenPos().y );
const auto ty = ImGui::GetFontSize();
if( asmVar->minlat == 0 )
{
draw->AddLine( pos + ImVec2( 0, -1 ), pos + ImVec2( 0, ty ), 0x660000FF );
}
else
{
draw->AddRectFilled( pos, pos + ImVec2( ty * asmVar->minlat + 1, ty + 1 ), 0x660000FF );
}
if( asmVar->minlat != asmVar->maxlat )
{
draw->AddRectFilled( pos + ImVec2( ty * asmVar->minlat + 1, 0 ), pos + ImVec2( ty * asmVar->maxlat + 1, ty + 1 ), 0x5500FFFF );
}
}
Separate uarch data retrieval from tooltip display.
2020-04-27 13:31:32 +00:00
const auto msz = line.mnemonic.size();
memcpy( buf, line.mnemonic.c_str(), msz );
memset( buf+msz, ' ', m_maxMnemonicLen-msz );
Display jump labels in the UI.
2020-05-09 13:14:33 +00:00
bool hasJump = false;
if( line.jumpAddr != 0 )
{
auto lit = m_locMap.find( line.jumpAddr );
if( lit != m_locMap.end() )
{
char tmp[64];
sprintf( tmp, ".L%" PRIu32, lit->second );
strcpy( buf+m_maxMnemonicLen, tmp );
hasJump = true;
}
}
if( !hasJump )
{
memcpy( buf+m_maxMnemonicLen, line.operands.c_str(), line.operands.size() + 1 );
}
Register line selection.
2020-05-01 14:33:24 +00:00
if( asmIdx == m_asmSelected )
{
TextColoredUnformatted( ImVec4( 1, 0.25f, 0.25f, 1 ), buf );
}
Print register data in asm lines.
2020-05-01 17:15:46 +00:00
else if( line.regData[0] != 0 )
{
Don't highlight lines with no dependencies.
2020-05-01 22:39:10 +00:00
bool hasDepencency = false;
int idx = 0;
for(;;)
{
if( line.regData[idx] == 0 ) break;
if( line.regData[idx] & ( WriteBit | ReadBit ) )
{
hasDepencency = true;
break;
}
idx++;
}
if( hasDepencency )
{
TextColoredUnformatted( ImVec4( 1, 0.5f, 1, 1 ), buf );
}
else
{
ImGui::TextUnformatted( buf );
}
Print register data in asm lines.
2020-05-01 17:15:46 +00:00
}
Register line selection.
2020-05-01 14:33:24 +00:00
else
{
ImGui::TextUnformatted( buf );
}
Separate uarch data retrieval from tooltip display.
2020-04-27 13:31:32 +00:00
Display list of read and write registers.
2020-05-01 11:20:19 +00:00
if( ImGui::IsItemHovered() )
Separate uarch data retrieval from tooltip display.
2020-04-27 13:31:32 +00:00
{
Display list of read and write registers.
2020-05-01 11:20:19 +00:00
if( asmVar )
Separate uarch data retrieval from tooltip display.
2020-04-27 13:31:32 +00:00
{
Display list of read and write registers.
2020-05-01 11:20:19 +00:00
const auto& var = *asmVar;
if( m_font ) ImGui::PopFont();
ImGui::BeginTooltip();
TextFocused( "Throughput:", RealToString( var.tp ) );
Separate uarch data retrieval from tooltip display.
2020-04-27 13:31:32 +00:00
ImGui::SameLine();
Display list of read and write registers.
2020-05-01 11:20:19 +00:00
TextDisabledUnformatted( "(cycles per instruction, lower is better)" );
if( var.maxlat >= 0 )
Separate uarch data retrieval from tooltip display.
2020-04-27 13:31:32 +00:00
{
Display list of read and write registers.
2020-05-01 11:20:19 +00:00
TextDisabledUnformatted( "Latency:" );
ImGui::SameLine();
if( var.minlat == var.maxlat && var.minbound == var.maxbound )
Separate uarch data retrieval from tooltip display.
2020-04-27 13:31:32 +00:00
{
Display list of read and write registers.
2020-05-01 11:20:19 +00:00
if( var.minbound )
{
ImGui::Text( "\xe2\x89\xa4%s", RealToString( var.minlat ) );
}
else
{
ImGui::TextUnformatted( RealToString( var.minlat ) );
}
Separate uarch data retrieval from tooltip display.
2020-04-27 13:31:32 +00:00
}
else
{
Display list of read and write registers.
2020-05-01 11:20:19 +00:00
if( var.minbound )
{
ImGui::Text( "[\xe2\x89\xa4%s", RealToString( var.minlat ) );
}
else
{
ImGui::Text( "[%s", RealToString( var.minlat ) );
}
ImGui::SameLine( 0, 0 );
if( var.maxbound )
{
ImGui::Text( " \xE2\x80\x93 \xe2\x89\xa4%s]", RealToString( var.maxlat ) );
}
else
{
ImGui::Text( " \xE2\x80\x93 %s]", RealToString( var.maxlat ) );
}
Separate uarch data retrieval from tooltip display.
2020-04-27 13:31:32 +00:00
}
Display list of read and write registers.
2020-05-01 11:20:19 +00:00
ImGui::SameLine();
TextDisabledUnformatted( "(cycles in execution, may vary by used output)" );
Separate uarch data retrieval from tooltip display.
2020-04-27 13:31:32 +00:00
}
Display list of read and write registers.
2020-05-01 11:20:19 +00:00
TextFocused( "\xce\xbcops:", RealToString( var.uops ) );
if( var.port != -1 ) TextFocused( "Ports:", PortList[var.port] );
ImGui::Separator();
TextFocused( "ISA set:", IsaList[var.isaSet] );
Don't display operands, if none.
2020-05-01 14:15:33 +00:00
if( var.descNum > 0 )
Separate uarch data retrieval from tooltip display.
2020-04-27 13:31:32 +00:00
{
Don't display operands, if none.
2020-05-01 14:15:33 +00:00
TextDisabledUnformatted( "Operands:" );
ImGui::SameLine();
bool first = true;
for( int i=0; i<var.descNum; i++ )
Separate uarch data retrieval from tooltip display.
2020-04-27 13:31:32 +00:00
{
Don't display operands, if none.
2020-05-01 14:15:33 +00:00
const char* t = "?";
switch( var.desc[i].type )
Display list of read and write registers.
2020-05-01 11:20:19 +00:00
{
Don't display operands, if none.
2020-05-01 14:15:33 +00:00
case 0:
t = "Imm";
break;
case 1:
t = "Reg";
break;
case 2:
t = var.desc[i].width == 0 ? "AGen" : "Mem";
break;
default:
assert( false );
break;
Display list of read and write registers.
2020-05-01 11:20:19 +00:00
}
Don't display operands, if none.
2020-05-01 14:15:33 +00:00
if( first )
Display list of read and write registers.
2020-05-01 11:20:19 +00:00
{
Don't display operands, if none.
2020-05-01 14:15:33 +00:00
first = false;
if( var.desc[i].width == 0 )
{
ImGui::TextUnformatted( t );
}
else
{
ImGui::Text( "%s%i", t, var.desc[i].width );
}
Display list of read and write registers.
2020-05-01 11:20:19 +00:00
}
else
{
Don't display operands, if none.
2020-05-01 14:15:33 +00:00
ImGui::SameLine( 0, 0 );
if( var.desc[i].width == 0 )
{
ImGui::Text( ", %s", t );
}
else
{
ImGui::Text( ", %s%i", t, var.desc[i].width );
}
Display list of read and write registers.
2020-05-01 11:20:19 +00:00
}
Separate uarch data retrieval from tooltip display.
2020-04-27 13:31:32 +00:00
}
}
Display list of read and write registers.
2020-05-01 11:20:19 +00:00
ImGui::EndTooltip();
if( m_font ) ImGui::PushFont( m_font );
Separate uarch data retrieval from tooltip display.
2020-04-27 13:31:32 +00:00
}
Display list of read and write registers.
2020-05-01 11:20:19 +00:00
if( m_cpuArch == CpuArchX86 || m_cpuArch == CpuArchX64 )
Separate uarch data retrieval from tooltip display.
2020-04-27 13:31:32 +00:00
{
Display list of read and write registers.
2020-05-01 11:20:19 +00:00
if( line.readX86[0] != RegsX86::invalid || line.writeX86[0] != RegsX86::invalid )
Separate uarch data retrieval from tooltip display.
2020-04-27 13:31:32 +00:00
{
Display list of read and write registers.
2020-05-01 11:20:19 +00:00
if( m_font ) ImGui::PopFont();
ImGui::BeginTooltip();
if( asmVar ) ImGui::Separator();
if( line.readX86[0] != RegsX86::invalid )
Separate uarch data retrieval from tooltip display.
2020-04-27 13:31:32 +00:00
{
Display list of read and write registers.
2020-05-01 11:20:19 +00:00
TextDisabledUnformatted( "Read:" );
ImGui::SameLine();
int idx = 0;
for(;;)
{
if( line.readX86[idx] == RegsX86::invalid ) break;
if( idx == 0 )
{
ImGui::TextUnformatted( s_regNameX86[(int)line.readX86[idx++]] );
}
else
{
ImGui::SameLine( 0, 0 );
ImGui::Text( ", %s", s_regNameX86[(int)line.readX86[idx++]] );
}
}
Separate uarch data retrieval from tooltip display.
2020-04-27 13:31:32 +00:00
}
Display list of read and write registers.
2020-05-01 11:20:19 +00:00
if( line.writeX86[0] != RegsX86::invalid )
Separate uarch data retrieval from tooltip display.
2020-04-27 13:31:32 +00:00
{
Display list of read and write registers.
2020-05-01 11:20:19 +00:00
TextDisabledUnformatted( "Write:" );
ImGui::SameLine();
int idx = 0;
for(;;)
{
if( line.writeX86[idx] == RegsX86::invalid ) break;
if( idx == 0 )
{
ImGui::TextUnformatted( s_regNameX86[(int)line.writeX86[idx++]] );
}
else
{
ImGui::SameLine( 0, 0 );
ImGui::Text( ", %s", s_regNameX86[(int)line.writeX86[idx++]] );
}
}
Add micro architecture tooltips.
2020-04-26 20:26:17 +00:00
}
Display list of read and write registers.
2020-05-01 11:20:19 +00:00
ImGui::EndTooltip();
if( m_font ) ImGui::PushFont( m_font );
Add micro architecture tooltips.
2020-04-26 20:26:17 +00:00
}
}
Register line selection.
2020-05-01 14:33:24 +00:00
if( ImGui::IsMouseClicked( 0 ) )
{
m_asmSelected = asmIdx;
Calculate register dependency data.
2020-05-01 20:39:37 +00:00
ResetAsm();
int idx = 0;
for(;;)
{
if( line.readX86[idx] == RegsX86::invalid ) break;
line.regData[idx] = ReadBit | (int)line.readX86[idx];
Reduce search range.
2020-05-01 22:05:48 +00:00
FollowWrite( asmIdx, line.readX86[idx++], 64 );
Calculate register dependency data.
2020-05-01 20:39:37 +00:00
}
idx = 0;
for(;;)
{
if( line.writeX86[idx] == RegsX86::invalid ) break;
int ridx = 0;
for(;;)
{
if( line.regData[ridx] == 0 )
{
line.regData[ridx] = WriteBit | (int)line.writeX86[idx];
break;
}
else if( ( line.regData[ridx] & RegMask ) == (int)line.writeX86[idx] )
{
line.regData[ridx] |= WriteBit;
break;
}
ridx++;
}
Reduce search range.
2020-05-01 22:05:48 +00:00
FollowRead( asmIdx, line.writeX86[idx++], 64 );
Calculate register dependency data.
2020-05-01 20:39:37 +00:00
}
Register line selection.
2020-05-01 14:33:24 +00:00
}
else if( ImGui::IsMouseClicked( 1 ) )
{
m_asmSelected = -1;
Calculate register dependency data.
2020-05-01 20:39:37 +00:00
ResetAsm();
Register line selection.
2020-05-01 14:33:24 +00:00
}
Add micro architecture tooltips.
2020-04-26 20:26:17 +00:00
}
Display disassembly.
2020-03-25 21:53:05 +00:00
Display jump labels in the UI.
2020-05-09 13:14:33 +00:00
auto lit = m_locMap.find( line.addr );
if( lit != m_locMap.end() )
{
ImGui::SameLine();
ImGui::TextDisabled( "; .L%" PRIu32, lit->second );
}
Print register data in asm lines.
2020-05-01 17:15:46 +00:00
if( line.regData[0] != 0 )
{
Fix wrong indent.
2020-05-01 22:42:05 +00:00
if( !line.params.empty() )
{
ImGui::SameLine();
ImGui::Spacing();
ImGui::SameLine();
}
else
{
ImGui::SameLine( 0, 0 );
}
Print register data in asm lines.
2020-05-01 17:15:46 +00:00
TextColoredUnformatted( ImVec4( 0.5f, 0.5, 1, 1 ), "{" );
ImGui::SameLine( 0, 0 );
int idx = 0;
for(;;)
{
ImVec4 col;
if( line.regData[idx] == 0 ) break;
if( ( line.regData[idx] & ( WriteBit | ReadBit ) ) == ( WriteBit | ReadBit ) ) col = ImVec4( 1, 1, 0.5f, 1 );
else if( line.regData[idx] & WriteBit ) col = ImVec4( 1, 0.5f, 0.5f, 1 );
else if( line.regData[idx] & ReadBit ) col = ImVec4( 0.5f, 1, 0.5f, 1 );
else col = ImVec4( 0.5f, 0.5f, 0.5f, 1 );
if( idx > 0 )
{
ImGui::SameLine( 0, 0 );
TextColoredUnformatted( ImVec4( 0.5f, 0.5, 1, 1 ), ", " );
ImGui::SameLine( 0, 0 );
}
TextColoredUnformatted( col, s_regNameX86[line.regData[idx++] & RegMask] );
}
ImGui::SameLine( 0, 0 );
TextColoredUnformatted( ImVec4( 0.5f, 0.5, 1, 1 ), "}" );
}
Display jump/call target address.
2020-03-28 00:22:27 +00:00
if( line.jumpAddr != 0 )
{
uint32_t offset = 0;
const auto base = worker.GetSymbolForAddress( line.jumpAddr, offset );
auto sym = base == 0 ? worker.GetSymbolData( line.jumpAddr ) : worker.GetSymbolData( base );
if( sym )
{
ImGui::SameLine();
ImGui::Spacing();
ImGui::SameLine();
if( base == m_baseAddr )
{
ImGui::TextDisabled( "-> [%s+%" PRIu32"]", worker.GetString( sym->name ), offset );
if( ImGui::IsItemHovered() )
{
m_highlightAddr = line.jumpAddr;
if( ImGui::IsItemClicked() )
{
m_targetAddr = line.jumpAddr;
Match source and assembly selection.
2020-04-08 20:57:42 +00:00
m_selectedAddresses.clear();
m_selectedAddresses.emplace( line.jumpAddr );
Display jump/call target address.
2020-03-28 00:22:27 +00:00
}
}
}
else
{
ImGui::TextDisabled( "[%s+%" PRIu32"]", worker.GetString( sym->name ), offset );
Implement cross-symbol jumping.
2020-03-28 13:27:29 +00:00
if( ImGui::IsItemClicked() ) jumpOut = line.jumpAddr;
Display jump/call target address.
2020-03-28 00:22:27 +00:00
}
}
}
Match source and assembly selection.
2020-04-08 20:57:42 +00:00
if( lineHovered )
{
draw->AddRectFilled( wpos, wpos + ImVec2( w, ty+1 ), 0x11FFFFFF );
}
Display disassembly.
2020-03-25 21:53:05 +00:00
draw->AddLine( wpos + ImVec2( 0, ty+2 ), wpos + ImVec2( w, ty+2 ), 0x08FFFFFF );
}
Only change assembly target line when necessary.
2020-04-08 21:30:42 +00:00
void SourceView::SelectLine( uint32_t line, const Worker* worker, bool changeAsmLine, uint64_t targetAddr )
Match source and assembly selection.
2020-04-08 20:57:42 +00:00
{
m_selectedLine = line;
if( m_symAddr == 0 ) return;
assert( worker );
Separate asm lines selection.
2020-04-08 21:59:10 +00:00
SelectAsmLines( m_fileStringIdx, line, *worker, changeAsmLine, targetAddr );
}
void SourceView::SelectAsmLines( uint32_t file, uint32_t line, const Worker& worker, bool changeAsmLine, uint64_t targetAddr )
{
m_selectedAddresses.clear();
auto addresses = worker.GetAddressesForLocation( file, line );
Match source and assembly selection.
2020-04-08 20:57:42 +00:00
if( addresses )
{
const auto& addr = *addresses;
Use left and right mouse buttons for asm navigation. Left click on source line just selects the line and the corresponding asm lines. Right click does the above and focuses asm view on the first selected line.
2020-04-09 21:12:17 +00:00
if( changeAsmLine )
Only change assembly target line when necessary.
2020-04-08 21:30:42 +00:00
{
Search for address within current symbol.
2020-04-09 00:12:49 +00:00
if( targetAddr != 0 )
{
Fix typo.
2020-04-14 00:01:50 +00:00
m_targetAddr = targetAddr;
Search for address within current symbol.
2020-04-09 00:12:49 +00:00
}
else
{
for( auto& v : addr )
{
if( v >= m_baseAddr && v < m_baseAddr + m_codeLen )
{
m_targetAddr = v;
break;
}
}
}
Only change assembly target line when necessary.
2020-04-08 21:30:42 +00:00
}
Match source and assembly selection.
2020-04-08 20:57:42 +00:00
for( auto& v : addr )
{
Don't select addresses outside symbol.
2020-04-09 12:10:07 +00:00
if( v >= m_baseAddr && v < m_baseAddr + m_codeLen )
{
m_selectedAddresses.emplace( v );
}
Match source and assembly selection.
2020-04-08 20:57:42 +00:00
}
}
}
Display disassembly.
2020-03-25 21:53:05 +00:00
Highlight asm lines for hovered source line.
2020-04-09 19:57:28 +00:00
void SourceView::SelectAsmLinesHover( uint32_t file, uint32_t line, const Worker& worker )
{
assert( m_selectedAddressesHover.empty() );
auto addresses = worker.GetAddressesForLocation( file, line );
if( addresses )
{
for( auto& v : *addresses )
{
if( v >= m_baseAddr && v < m_baseAddr + m_codeLen )
{
m_selectedAddressesHover.emplace( v );
}
}
}
}
Calculate max sample counts during ip map creation.
2020-04-10 23:34:44 +00:00
void SourceView::GatherIpStats( uint64_t addr, uint32_t& iptotalSrc, uint32_t& iptotalAsm, unordered_flat_map<uint64_t, uint32_t>& ipcountSrc, unordered_flat_map<uint64_t, uint32_t>& ipcountAsm, uint32_t& ipmaxSrc, uint32_t& ipmaxAsm, const Worker& worker )
Allow showing sample data for whole symbol.
2020-04-09 20:23:57 +00:00
{
auto ipmap = worker.GetSymbolInstructionPointers( addr );
if( !ipmap ) return;
for( auto& ip : *ipmap )
{
if( m_file )
{
auto frame = worker.GetCallstackFrame( ip.first );
if( frame )
{
auto ffn = worker.GetString( frame->data[0].file );
if( strcmp( ffn, m_file ) == 0 )
{
const auto line = frame->data[0].line;
auto it = ipcountSrc.find( line );
if( it == ipcountSrc.end() )
{
ipcountSrc.emplace( line, ip.second );
Calculate max sample counts during ip map creation.
2020-04-10 23:34:44 +00:00
if( ipmaxSrc < ip.second ) ipmaxSrc = ip.second;
Allow showing sample data for whole symbol.
2020-04-09 20:23:57 +00:00
}
else
{
Calculate max sample counts during ip map creation.
2020-04-10 23:34:44 +00:00
const auto sum = it->second + ip.second;
it->second = sum;
if( ipmaxSrc < sum ) ipmaxSrc = sum;
Allow showing sample data for whole symbol.
2020-04-09 20:23:57 +00:00
}
iptotalSrc += ip.second;
}
}
}
auto addr = worker.GetCanonicalPointer( ip.first );
assert( ipcountAsm.find( addr ) == ipcountAsm.end() );
ipcountAsm.emplace( addr, ip.second );
iptotalAsm += ip.second;
Calculate max sample counts during ip map creation.
2020-04-10 23:34:44 +00:00
if( ipmaxAsm < ip.second ) ipmaxAsm = ip.second;
Allow showing sample data for whole symbol.
2020-04-09 20:23:57 +00:00
}
}
Add C++ tokenizer.
2020-04-24 21:48:18 +00:00
namespace {
static unordered_flat_set<const char*, charutil::Hasher, charutil::Comparator> GetKeywords()
{
unordered_flat_set<const char*, charutil::Hasher, charutil::Comparator> ret;
for( auto& v : {
"alignas", "alignof", "and", "and_eq", "asm", "atomic_cancel", "atomic_commit", "atomic_noexcept",
Separate coloring for types and special values.
2020-04-24 22:49:51 +00:00
"bitand", "bitor", "break", "case", "catch", "class", "compl", "concept", "const", "consteval",
"constexpr", "constinit", "const_cast", "continue", "co_await", "co_return", "co_yield", "decltype",
"default", "delete", "do", "dynamic_cast", "else", "enum", "explicit", "export", "extern", "for",
"friend", "if", "inline", "mutable", "namespace", "new", "noexcept", "not", "not_eq", "operator",
"or", "or_eq", "private", "protected", "public", "reflexpr", "register", "reinterpret_cast",
"return", "requires", "sizeof", "static", "static_assert", "static_cast", "struct", "switch",
"synchronized", "template", "thread_local", "throw", "try", "typedef", "typeid", "typename",
"union", "using", "virtual", "volatile", "while", "xor", "xor_eq", "override", "final", "import",
"module", "transaction_safe", "transaction_safe_dynamic" } )
{
ret.insert( v );
}
return ret;
}
static unordered_flat_set<const char*, charutil::Hasher, charutil::Comparator> GetTypes()
{
unordered_flat_set<const char*, charutil::Hasher, charutil::Comparator> ret;
for( auto& v : {
"bool", "char", "char8_t", "char16_t", "char32_t", "double", "float", "int", "long", "short", "signed",
"unsigned", "void", "wchar_t", "size_t", "int8_t", "int16_t", "int32_t", "int64_t", "int_fast8_t",
"int_fast16_t", "int_fast32_t", "int_fast64_t", "int_least8_t", "int_least16_t", "int_least32_t",
"int_least64_t", "intmax_t", "intptr_t", "uint8_t", "uint16_t", "uint32_t", "uint64_t", "uint_fast8_t",
"uint_fast16_t", "uint_fast32_t", "uint_fast64_t", "uint_least8_t", "uint_least16_t", "uint_least32_t",
"uint_least64_t", "uintmax_t", "uintptr_t", "type_info", "bad_typeid", "bad_cast", "type_index",
"clock_t", "time_t", "tm", "timespec", "ptrdiff_t", "nullptr_t", "max_align_t", "auto",
"__m64", "__m128", "__m128i", "__m128d", "__m256", "__m256i", "__m256d", "__m512", "__m512i",
"__m512d", "__mmask8", "__mmask16", "__mmask32", "__mmask64",
"int8x8_t", "int16x4_t", "int32x2_t", "int64x1_t", "uint8x8_t", "uint16x4_t", "uint32x2_t",
"uint64x1_t", "float32x2_t", "poly8x8_t", "poly16x4_t", "int8x16_t", "int16x8_t", "int32x4_t",
"int64x2_t", "uint8x16_t", "uint16x8_t", "uint32x4_t", "uint64x2_t", "float32x4_t", "poly8x16_t",
"poly16x8_t",
"int8x8x2_t", "int16x4x2_t", "int32x2x2_t", "int64x1x2_t", "uint8x8x2_t", "uint16x4x2_t",
"uint32x2x2_t", "uint64x1x2_t", "float32x2x2_t", "poly8x8x2_t", "poly16x4x2_t", "int8x16x2_t",
"int16x8x2_t", "int32x4x2_t", "int64x2x2_t", "uint8x16x2_t", "uint16x8x2_t", "uint32x4x2_t",
"uint64x2x2_t", "float32x4x2_t", "poly8x16x2_t", "poly16x8x2_t",
"int8x8x3_t", "int16x4x3_t", "int32x2x3_t", "int64x1x3_t", "uint8x8x3_t", "uint16x4x3_t",
"uint32x2x3_t", "uint64x1x3_t", "float32x2x3_t", "poly8x8x3_t", "poly16x4x3_t", "int8x16x3_t",
"int16x8x3_t", "int32x4x3_t", "int64x2x3_t", "uint8x16x3_t", "uint16x8x3_t", "uint32x4x3_t",
"uint64x2x3_t", "float32x4x3_t", "poly8x16x3_t", "poly16x8x3_t",
"int8x8x4_t", "int16x4x4_t", "int32x2x4_t", "int64x1x4_t", "uint8x8x4_t", "uint16x4x4_t",
"uint32x2x4_t", "uint64x1x4_t", "float32x2x4_t", "poly8x8x4_t", "poly16x4x4_t", "int8x16x4_t",
"int16x8x4_t", "int32x4x4_t", "int64x2x4_t", "uint8x16x4_t", "uint16x8x4_t", "uint32x4x4_t",
"uint64x2x4_t", "float32x4x4_t", "poly8x16x4_t", "poly16x8x4_t" } )
{
ret.insert( v );
}
return ret;
}
static unordered_flat_set<const char*, charutil::Hasher, charutil::Comparator> GetSpecial()
{
unordered_flat_set<const char*, charutil::Hasher, charutil::Comparator> ret;
for( auto& v : { "this", "nullptr", "true", "false", "goto", "NULL" } )
Add C++ tokenizer.
2020-04-24 21:48:18 +00:00
{
ret.insert( v );
}
return ret;
}
}
static bool TokenizeNumber( const char*& begin, const char* end )
{
const bool startNum = *begin >= '0' && *begin <= '9';
if( *begin != '+' && *begin != '-' && !startNum ) return false;
begin++;
bool hasNum = startNum;
while( begin < end && ( ( *begin >= '0' && *begin <= '9' ) || *begin == '\'' ) )
{
hasNum = true;
begin++;
}
if( !hasNum ) return false;
bool isFloat = false, isHex = false, isBinary = false;
if( begin < end )
{
if( *begin == '.' )
{
isFloat = true;
begin++;
while( begin < end && ( ( *begin >= '0' && *begin <= '9' ) || *begin == '\'' ) ) begin++;
}
else if( *begin == 'x' || *begin == 'X' )
{
isHex = true;
begin++;
while( begin < end && ( ( *begin >= '0' && *begin <= '9' ) || ( *begin >= 'a' && *begin <= 'f' ) || ( *begin >= 'A' && *begin <= 'F' ) || *begin == '\'' ) ) begin++;
}
else if( *begin == 'b' || *begin == 'B' )
{
isBinary = true;
begin++;
while( begin < end && ( *begin == '0' || *begin == '1' ) || *begin == '\'' ) begin++;
}
}
if( !isBinary )
{
if( begin < end && ( *begin == 'e' || *begin == 'E' || *begin == 'p' || *begin == 'P' ) )
{
isFloat = true;
begin++;
if( begin < end && ( *begin == '+' || *begin == '-' ) ) begin++;
bool hasDigits = false;
while( begin < end && ( ( *begin >= '0' && *begin <= '9' ) || ( *begin >= 'a' && *begin <= 'f' ) || ( *begin >= 'A' && *begin <= 'F' ) || *begin == '\'' ) )
{
hasDigits = true;
begin++;
}
if( !hasDigits ) return false;
}
if( begin < end && ( *begin == 'f' || *begin == 'F' || *begin == 'l' || *begin == 'L' ) ) begin++;
}
if( !isFloat )
{
while( begin < end && ( *begin == 'u' || *begin == 'U' || *begin == 'l' || *begin == 'L' ) ) begin++;
}
return true;
}
SourceView::TokenColor SourceView::IdentifyToken( const char*& begin, const char* end )
{
Postpone initialization of hashmaps.
2020-06-12 09:26:44 +00:00
static const auto s_keywords = GetKeywords();
static const auto s_types = GetTypes();
static const auto s_special = GetSpecial();
Add C++ tokenizer.
2020-04-24 21:48:18 +00:00
if( *begin == '"' )
{
begin++;
while( begin < end )
{
if( *begin == '"' )
{
begin++;
break;
}
begin += 1 + ( *begin == '\\' && end - begin > 1 && *(begin+1) == '"' );
}
return TokenColor::String;
}
if( *begin == '\'' )
{
begin++;
if( begin < end && *begin == '\\' ) begin++;
if( begin < end ) begin++;
if( begin < end && *begin == '\'' ) begin++;
return TokenColor::CharacterLiteral;
}
if( ( *begin >= 'a' && *begin <= 'z' ) || ( *begin >= 'A' && *begin <= 'Z' ) || *begin == '_' )
{
const char* tmp = begin;
begin++;
while( begin < end && ( *begin >= 'a' && *begin <= 'z' ) || ( *begin >= 'A' && *begin <= 'Z' ) || ( *begin >= '0' && *begin <= '9' ) || *begin == '_' ) begin++;
if( begin - tmp <= 24 )
{
char buf[25];
memcpy( buf, tmp, begin-tmp );
buf[begin-tmp] = '\0';
if( s_keywords.find( buf ) != s_keywords.end() ) return TokenColor::Keyword;
Separate coloring for types and special values.
2020-04-24 22:49:51 +00:00
if( s_types.find( buf ) != s_types.end() ) return TokenColor::Type;
if( s_special.find( buf ) != s_special.end() ) return TokenColor::Special;
Add C++ tokenizer.
2020-04-24 21:48:18 +00:00
}
return TokenColor::Default;
}
const char* tmp = begin;
if( TokenizeNumber( begin, end ) ) return TokenColor::Number;
begin = tmp;
if( *begin == '/' && end - begin > 1 )
{
if( *(begin+1) == '/' )
{
begin = end;
return TokenColor::Comment;
}
if( *(begin+1) == '*' )
{
begin += 2;
for(;;)
{
while( begin < end && *begin != '*' ) begin++;
if( begin == end )
{
m_tokenizer.isInComment = true;
return TokenColor::Comment;
}
begin++;
if( begin < end && *begin == '/' )
{
begin++;
return TokenColor::Comment;
}
}
}
}
while( begin < end )
{
switch( *begin )
{
case '[':
case ']':
case '{':
case '}':
case '!':
case '%':
case '^':
case '&':
case '*':
case '(':
case ')':
case '-':
case '+':
case '=':
case '~':
case '|':
case '<':
case '>':
case '?':
case ':':
case '/':
case ';':
case ',':
case '.':
begin++;
break;
default:
goto out;
}
}
out:
if( begin != tmp ) return TokenColor::Punctuation;
begin = end;
return TokenColor::Default;
}
std::vector<SourceView::Token> SourceView::Tokenize( const char* begin, const char* end )
{
std::vector<Token> ret;
if( m_tokenizer.isInPreprocessor )
{
if( begin == end )
{
m_tokenizer.isInPreprocessor = false;
return ret;
}
if( *(end-1) != '\\' ) m_tokenizer.isInPreprocessor = false;
ret.emplace_back( Token { begin, end, TokenColor::Preprocessor } );
return ret;
}
const bool first = !m_tokenizer.isInComment;
while( begin != end )
{
if( m_tokenizer.isInComment )
{
const auto pos = begin;
for(;;)
{
while( begin != end && *begin != '*' ) begin++;
begin++;
if( begin < end )
{
if( *begin == '/' )
{
begin++;
ret.emplace_back( Token { pos, begin, TokenColor::Comment } );
m_tokenizer.isInComment = false;
break;
}
}
else
{
ret.emplace_back( Token { pos, end, TokenColor::Comment } );
return ret;
}
}
}
else
{
while( begin != end && isspace( *begin ) ) begin++;
if( first && begin < end && *begin == '#' )
{
if( *(end-1) == '\\' ) m_tokenizer.isInPreprocessor = true;
ret.emplace_back( Token { begin, end, TokenColor::Preprocessor } );
return ret;
}
const auto pos = begin;
const auto col = IdentifyToken( begin, end );
ret.emplace_back( Token { pos, begin, col } );
}
}
return ret;
}
Add micro architecture tooltips.
2020-04-26 20:26:17 +00:00
void SourceView::SelectMicroArchitecture( const char* moniker )
{
int idx = 0;
for( auto& v : s_uArchUx )
{
if( strcmp( v.moniker, moniker ) == 0 )
{
m_selMicroArch = idx;
break;
}
idx++;
}
for( idx=0; idx<MicroArchitectureNum; idx++ )
{
if( strcmp( MicroArchitectureList[idx], moniker ) == 0 )
{
m_idxMicroArch = idx;
break;
}
}
assert( idx != MicroArchitectureNum );
}
Add space for register data in each asm line.
2020-05-01 14:33:09 +00:00
void SourceView::ResetAsm()
{
for( auto& line : m_asm ) memset( line.regData, 0, sizeof( line.regData ) );
}
Calculate register dependency data.
2020-05-01 20:39:37 +00:00
void SourceView::FollowRead( int line, RegsX86 reg, int limit )
{
if( limit == 0 ) return;
const auto& data = m_asm[line];
if( m_jumpOut.find( data.addr ) != m_jumpOut.end() && !data.jumpConditional ) return;
if( data.jumpAddr != 0 )
{
auto fit = std::lower_bound( m_asm.begin(), m_asm.end(), data.jumpAddr, []( const auto& l, const auto& r ) { return l.addr < r; } );
if( fit != m_asm.end() && fit->addr == data.jumpAddr )
{
CheckRead( fit - m_asm.begin(), reg, limit );
}
if( !data.jumpConditional ) return;
}
if( line+1 < m_asm.size() )
{
CheckRead( line+1, reg, limit );
}
}
void SourceView::FollowWrite( int line, RegsX86 reg, int limit )
{
if( limit == 0 ) return;
const auto& data = m_asm[line];
if( m_jumpOut.find( data.addr ) != m_jumpOut.end() && !data.jumpConditional ) return;
auto it = m_jumpTable.find( data.addr );
if( it != m_jumpTable.end() )
{
for( auto& v : it->second.source )
{
auto fit = std::lower_bound( m_asm.begin(), m_asm.end(), v, []( const auto& l, const auto& r ) { return l.addr < r; } );
assert( fit != m_asm.end() && fit->addr == v );
CheckWrite( fit - m_asm.begin(), reg, limit );
}
}
if( line-1 >= 0 )
{
CheckWrite( line-1, reg, limit );
}
}
void SourceView::CheckRead( int line, RegsX86 reg, int limit )
{
auto& data = m_asm[line];
int idx = 0;
for(;;)
{
if( data.readX86[idx] == RegsX86::invalid )
{
idx = 0;
for(;;)
{
if( data.writeX86[idx] == RegsX86::invalid )
{
FollowRead( line, reg, limit - 1 );
return;
}
if( data.writeX86[idx] == reg )
{
idx = 0;
for(;;)
{
if( data.regData[idx] == 0 )
{
data.regData[idx] = ReuseBit | (int)reg;
return;
}
if( ( data.regData[idx] & RegMask ) == (int)reg )
{
data.regData[idx] |= ReuseBit;
return;
}
idx++;
}
}
idx++;
}
}
if( data.readX86[idx] == reg )
{
idx = 0;
for(;;)
{
if( data.regData[idx] == 0 )
{
data.regData[idx] = ReadBit | (int)reg;
return;
}
if( ( data.regData[idx] & RegMask ) == (int)reg )
{
data.regData[idx] |= ReadBit;
return;
}
idx++;
}
}
idx++;
}
}
void SourceView::CheckWrite( int line, RegsX86 reg, int limit )
{
auto& data = m_asm[line];
int idx = 0;
for(;;)
{
if( data.writeX86[idx] == RegsX86::invalid )
{
idx = 0;
for(;;)
{
if( data.readX86[idx] == RegsX86::invalid )
{
FollowWrite( line, reg, limit - 1 );
return;
}
if( data.readX86[idx] == reg )
{
idx = 0;
for(;;)
{
if( data.regData[idx] == 0 )
{
data.regData[idx] = ReuseBit | (int)reg;
return;
}
if( ( data.regData[idx] & RegMask ) == (int)reg )
{
data.regData[idx] |= ReuseBit;
return;
}
idx++;
}
}
idx++;
}
}
if( data.writeX86[idx] == reg )
{
idx = 0;
for(;;)
{
if( data.regData[idx] == 0 )
{
data.regData[idx] = WriteBit | (int)reg;
return;
}
else if( ( data.regData[idx] & RegMask ) == (int)reg )
{
data.regData[idx] |= WriteBit;
return;
}
idx++;
}
}
idx++;
}
}
Support saving asm range.
2020-05-11 19:12:43 +00:00
void SourceView::Save( const Worker& worker, size_t start, size_t stop )
Extract asm saving to a separate function.
2020-05-11 19:08:50 +00:00
{
Support saving asm range.
2020-05-11 19:12:43 +00:00
assert( start < m_asm.size() );
assert( start < stop );
Extract asm saving to a separate function.
2020-05-11 19:08:50 +00:00
nfdchar_t* fn;
Set owner of file dialogs on windows.
2020-06-09 23:52:17 +00:00
auto res = NFD_SaveDialog( "asm", nullptr, &fn, m_gwcb ? m_gwcb() : nullptr );
Extract asm saving to a separate function.
2020-05-11 19:08:50 +00:00
if( res == NFD_OKAY )
{
FILE* f = nullptr;
const auto sz = strlen( fn );
if( sz < 5 || memcmp( fn + sz - 4, ".asm", 4 ) != 0 )
{
char tmp[1024];
sprintf( tmp, "%s.asm", fn );
f = fopen( tmp, "wb" );
}
else
{
f = fopen( fn, "wb" );
}
if( f )
{
char tmp[16];
auto sym = worker.GetSymbolData( m_symAddr );
assert( sym );
const char* symName;
if( sym->isInline )
{
auto parent = worker.GetSymbolData( m_baseAddr );
if( parent )
{
symName = worker.GetString( parent->name );
}
else
{
sprintf( tmp, "0x%" PRIx64, m_baseAddr );
symName = tmp;
}
}
else
{
symName = worker.GetString( sym->name );
}
fprintf( f, "; Tracy Profiler disassembly of symbol %s [%s]\n\n", symName, worker.GetCaptureProgram().c_str() );
if( !m_atnt ) fprintf( f, ".intel_syntax\n\n" );
Support saving asm range.
2020-05-11 19:12:43 +00:00
const auto end = m_asm.size() < stop ? m_asm.size() : stop;
for( size_t i=start; i<end; i++ )
Extract asm saving to a separate function.
2020-05-11 19:08:50 +00:00
{
Support saving asm range.
2020-05-11 19:12:43 +00:00
const auto& v = m_asm[i];
Extract asm saving to a separate function.
2020-05-11 19:08:50 +00:00
auto it = m_locMap.find( v.addr );
if( it != m_locMap.end() )
{
fprintf( f, ".L%" PRIu32 ":\n", it->second );
}
bool hasJump = false;
if( v.jumpAddr != 0 )
{
auto lit = m_locMap.find( v.jumpAddr );
if( lit != m_locMap.end() )
{
fprintf( f, "\t%-*s.L%" PRIu32 "\n", m_maxMnemonicLen, v.mnemonic.c_str(), lit->second );
hasJump = true;
}
}
if( !hasJump )
{
if( v.operands.empty() )
{
fprintf( f, "\t%s\n", v.mnemonic.c_str() );
}
else
{
fprintf( f, "\t%-*s%s\n", m_maxMnemonicLen, v.mnemonic.c_str(), v.operands.c_str() );
}
}
}
fclose( f );
}
}
}
Replace source file viewer with one that actually works. This is much simpler, custom implementation of a text file viewer. It is able to perform these two tasks as intended: - center source view on the selected line, - highlight that line.
2020-03-22 19:53:59 +00:00
}
Reference in New Issue Copy Permalink