[Lldb-commits] [lldb] r240663 - Submitting patch from Abhishek for:
Vince Harron
vince at nethacker.com
Fri Jun 26 17:05:24 PDT 2015
Hi Abhishek,
I don't see any XFAILs removed. What tests does this fix?
On Thu, Jun 25, 2015 at 10:50 AM, Greg Clayton <gclayton at apple.com> wrote:
> Author: gclayton
> Date: Thu Jun 25 12:50:15 2015
> New Revision: 240663
>
> URL: http://llvm.org/viewvc/llvm-project?rev=240663&view=rev
> Log:
> Submitting patch from Abhishek for:
>
> http://reviews.llvm.org/D10309
>
>
> Added:
> lldb/trunk/source/Plugins/ABI/SysV-i386/
> lldb/trunk/source/Plugins/ABI/SysV-i386/ABISysV_i386.cpp
> lldb/trunk/source/Plugins/ABI/SysV-i386/ABISysV_i386.h
> lldb/trunk/source/Plugins/ABI/SysV-i386/CMakeLists.txt
> lldb/trunk/source/Plugins/ABI/SysV-i386/Makefile
> Modified:
> lldb/trunk/cmake/LLDBDependencies.cmake
> lldb/trunk/lib/Makefile
> lldb/trunk/lldb.xcodeproj/project.pbxproj
> lldb/trunk/source/API/SystemInitializerFull.cpp
> lldb/trunk/source/Plugins/ABI/CMakeLists.txt
> lldb/trunk/source/Plugins/Makefile
>
> Modified: lldb/trunk/cmake/LLDBDependencies.cmake
> URL:
> http://llvm.org/viewvc/llvm-project/lldb/trunk/cmake/LLDBDependencies.cmake?rev=240663&r1=240662&r2=240663&view=diff
>
> ==============================================================================
> --- lldb/trunk/cmake/LLDBDependencies.cmake (original)
> +++ lldb/trunk/cmake/LLDBDependencies.cmake Thu Jun 25 12:50:15 2015
> @@ -48,6 +48,7 @@ set( LLDB_USED_LIBS
> lldbPluginABIMacOSX_i386
> lldbPluginABISysV_arm
> lldbPluginABISysV_arm64
> + lldbPluginABISysV_i386
> lldbPluginABISysV_x86_64
> lldbPluginABISysV_hexagon
> lldbPluginABISysV_ppc
>
> Modified: lldb/trunk/lib/Makefile
> URL:
> http://llvm.org/viewvc/llvm-project/lldb/trunk/lib/Makefile?rev=240663&r1=240662&r2=240663&view=diff
>
> ==============================================================================
> --- lldb/trunk/lib/Makefile (original)
> +++ lldb/trunk/lib/Makefile Thu Jun 25 12:50:15 2015
> @@ -41,6 +41,7 @@ USEDLIBS = lldbAPI.a \
> lldbPluginABISysV_ppc64.a \
> lldbPluginABISysV_mips.a \
> lldbPluginABISysV_mips64.a \
> + lldbPluginABISysV_i386.a \
> lldbPluginABISysV_x86_64.a \
> lldbPluginABISysV_hexagon.a \
> lldbPluginDisassemblerLLVM.a \
> @@ -50,8 +51,8 @@ USEDLIBS = lldbAPI.a \
> lldbPluginDynamicLoaderMacOSX.a \
> lldbPluginEmulateInstructionARM.a \
> lldbPluginEmulateInstructionARM64.a \
> - lldbPluginEmulateInstructionMIPS.a \
> - lldbPluginEmulateInstructionMIPS64.a \
> + lldbPluginEmulateInstructionMIPS.a \
> + lldbPluginEmulateInstructionMIPS64.a \
> lldbPluginInstrumentationRuntimeAddressSanitizer.a \
> lldbPluginLanguageRuntimeCPlusPlusItaniumABI.a \
> lldbPluginLanguageRuntimeObjCAppleObjCRuntime.a \
>
> Modified: lldb/trunk/lldb.xcodeproj/project.pbxproj
> URL:
> http://llvm.org/viewvc/llvm-project/lldb/trunk/lldb.xcodeproj/project.pbxproj?rev=240663&r1=240662&r2=240663&view=diff
>
> ==============================================================================
> --- lldb/trunk/lldb.xcodeproj/project.pbxproj (original)
> +++ lldb/trunk/lldb.xcodeproj/project.pbxproj Thu Jun 25 12:50:15 2015
> @@ -638,6 +638,10 @@
> 26BC17B218C7F4CB00D2196D /* ThreadElfCore.h in Headers */
> = {isa = PBXBuildFile; fileRef = 26BC17A918C7F4CB00D2196D /*
> ThreadElfCore.h */; };
> 26BCFC521368AE38006DC050 /* OptionGroupFormat.cpp in
> Sources */ = {isa = PBXBuildFile; fileRef = 26BCFC511368AE38006DC050 /*
> OptionGroupFormat.cpp */; };
> 26BD407F135D2AE000237D80 /* FileLineResolver.cpp in
> Sources */ = {isa = PBXBuildFile; fileRef = 26BD407E135D2ADF00237D80 /*
> FileLineResolver.cpp */; };
> + 26BF51F31B3C754400016294 /* ABISysV_hexagon.cpp in Sources
> */ = {isa = PBXBuildFile; fileRef = 26BF51EA1B3C754400016294 /*
> ABISysV_hexagon.cpp */; };
> + 26BF51F41B3C754400016294 /* ABISysV_hexagon.h in Headers
> */ = {isa = PBXBuildFile; fileRef = 26BF51EB1B3C754400016294 /*
> ABISysV_hexagon.h */; };
> + 26BF51F61B3C754400016294 /* ABISysV_i386.cpp in Sources */
> = {isa = PBXBuildFile; fileRef = 26BF51EF1B3C754400016294 /*
> ABISysV_i386.cpp */; };
> + 26BF51F71B3C754400016294 /* ABISysV_i386.h in Headers */ =
> {isa = PBXBuildFile; fileRef = 26BF51F01B3C754400016294 /* ABISysV_i386.h
> */; };
> 26C72C94124322890068DC16 /* SBStream.h in Headers */ =
> {isa = PBXBuildFile; fileRef = 26C72C93124322890068DC16 /* SBStream.h */;
> settings = {ATTRIBUTES = (Public, ); }; };
> 26C72C961243229A0068DC16 /* SBStream.cpp in Sources */ =
> {isa = PBXBuildFile; fileRef = 26C72C951243229A0068DC16 /* SBStream.cpp */;
> };
> 26CA97A1172B1FD5005DC71B /*
> RegisterContextThreadMemory.cpp in Sources */ = {isa = PBXBuildFile;
> fileRef = 26CA979F172B1FD5005DC71B /* RegisterContextThreadMemory.cpp */; };
> @@ -2111,6 +2115,10 @@
> 26BCFC541368B4B8006DC050 /* OptionGroupOutputFile.h */ =
> {isa = PBXFileReference; lastKnownFileType = sourcecode.c.h; name =
> OptionGroupOutputFile.h; path =
> include/lldb/Interpreter/OptionGroupOutputFile.h; sourceTree = "<group>"; };
> 26BD407D135D2AC400237D80 /* FileLineResolver.h */ = {isa =
> PBXFileReference; lastKnownFileType = sourcecode.c.h; name =
> FileLineResolver.h; path = include/lldb/Core/FileLineResolver.h; sourceTree
> = "<group>"; };
> 26BD407E135D2ADF00237D80 /* FileLineResolver.cpp */ = {isa
> = PBXFileReference; fileEncoding = 4; lastKnownFileType =
> sourcecode.cpp.cpp; name = FileLineResolver.cpp; path =
> source/Core/FileLineResolver.cpp; sourceTree = "<group>"; };
> + 26BF51EA1B3C754400016294 /* ABISysV_hexagon.cpp */ = {isa
> = PBXFileReference; fileEncoding = 4; lastKnownFileType =
> sourcecode.cpp.cpp; path = ABISysV_hexagon.cpp; sourceTree = "<group>"; };
> + 26BF51EB1B3C754400016294 /* ABISysV_hexagon.h */ = {isa =
> PBXFileReference; fileEncoding = 4; lastKnownFileType = sourcecode.c.h;
> path = ABISysV_hexagon.h; sourceTree = "<group>"; };
> + 26BF51EF1B3C754400016294 /* ABISysV_i386.cpp */ = {isa =
> PBXFileReference; fileEncoding = 4; lastKnownFileType = sourcecode.cpp.cpp;
> path = ABISysV_i386.cpp; sourceTree = "<group>"; };
> + 26BF51F01B3C754400016294 /* ABISysV_i386.h */ = {isa =
> PBXFileReference; fileEncoding = 4; lastKnownFileType = sourcecode.c.h;
> path = ABISysV_i386.h; sourceTree = "<group>"; };
> 26C5577B132575AD008FD8FE /* PlatformMacOSX.cpp */ = {isa =
> PBXFileReference; fileEncoding = 4; lastKnownFileType = sourcecode.cpp.cpp;
> path = PlatformMacOSX.cpp; sourceTree = "<group>"; };
> 26C5577C132575AD008FD8FE /* PlatformMacOSX.h */ = {isa =
> PBXFileReference; fileEncoding = 4; lastKnownFileType = sourcecode.c.h;
> path = PlatformMacOSX.h; sourceTree = "<group>"; };
> 26C6886D137880B900407EDF /* RegisterValue.h */ = {isa =
> PBXFileReference; lastKnownFileType = sourcecode.c.h; name =
> RegisterValue.h; path = include/lldb/Core/RegisterValue.h; sourceTree =
> "<group>"; };
> @@ -4751,6 +4759,24 @@
> name = MacOSX;
> sourceTree = "<group>";
> };
> + 26BF51E91B3C754400016294 /* SysV-hexagon */ = {
> + isa = PBXGroup;
> + children = (
> + 26BF51EA1B3C754400016294 /*
> ABISysV_hexagon.cpp */,
> + 26BF51EB1B3C754400016294 /*
> ABISysV_hexagon.h */,
> + );
> + path = "SysV-hexagon";
> + sourceTree = "<group>";
> + };
> + 26BF51EE1B3C754400016294 /* SysV-i386 */ = {
> + isa = PBXGroup;
> + children = (
> + 26BF51EF1B3C754400016294 /*
> ABISysV_i386.cpp */,
> + 26BF51F01B3C754400016294 /* ABISysV_i386.h
> */,
> + );
> + path = "SysV-i386";
> + sourceTree = "<group>";
> + };
> 26C5577E132575B6008FD8FE /* Platform */ = {
> isa = PBXGroup;
> children = (
> @@ -4813,6 +4839,8 @@
> 26DB3E0E1379E7AD0080DC73 /* MacOSX-i386 */,
> AF20F7621AF18F5E00751A6E /* SysV-arm */,
> AF20F7631AF18F6800751A6E /* SysV-arm64 */,
> + 26BF51E91B3C754400016294 /* SysV-hexagon
> */,
> + 26BF51EE1B3C754400016294 /* SysV-i386 */,
> 9694FA6E1B32AA35005EBB16 /* SysV-mips */,
> 263641141B34AEE200145B2F /* SysV-mips64 */,
> AF77E08B1A033C3E0096C0EA /* SysV-ppc */,
> @@ -5538,6 +5566,7 @@
> 26474CCC18D0CB5B0073DEBA /*
> RegisterContextPOSIX_mips64.h in Headers */,
> 26474CBD18D0CB2D0073DEBA /*
> RegisterContextMach_arm.h in Headers */,
> 260CC63415D04377002BF2E0 /*
> OptionValueFileSpec.h in Headers */,
> + 26BF51F41B3C754400016294 /*
> ABISysV_hexagon.h in Headers */,
> 26CFDCA11861638D000E63E5 /* Editline.h in
> Headers */,
> 26BC17B018C7F4CB00D2196D /*
> RegisterContextPOSIXCore_x86_64.h in Headers */,
> 6D55BAF01A8CD0BD00A70529 /*
> PlatformAndroidRemoteGDBServer.h in Headers */,
> @@ -5564,6 +5593,7 @@
> 256CBDBD1ADD107200BC6CDC /*
> RegisterContextLinux_mips64.h in Headers */,
> AF061F8C182C980000B6A19C /*
> HistoryUnwind.h in Headers */,
> 264A58EC1A7DBC8C00A6B1B0 /*
> OptionValueFormatEntity.h in Headers */,
> + 26BF51F71B3C754400016294 /* ABISysV_i386.h
> in Headers */,
> 260CC63815D04377002BF2E0 /*
> OptionValueString.h in Headers */,
> 260CC63915D04377002BF2E0 /*
> OptionValueUInt64.h in Headers */,
> 256CBDC11ADD11C000BC6CDC /*
> RegisterContextPOSIX_arm.h in Headers */,
> @@ -6300,6 +6330,7 @@
> AF9B8F33182DB52900DA866F /*
> SystemRuntimeMacOSX.cpp in Sources */,
> 2689008113353E2200698AC0 /*
> CommandObject.cpp in Sources */,
> 3F8160A61AB9F7DD001DA9DF /* Logging.cpp in
> Sources */,
> + 26BF51F61B3C754400016294 /*
> ABISysV_i386.cpp in Sources */,
> 2689008313353E2200698AC0 /*
> CommandObjectMultiword.cpp in Sources */,
> 2689008413353E2200698AC0 /*
> CommandObjectRegexCommand.cpp in Sources */,
> 2689008513353E2200698AC0 /*
> CommandReturnObject.cpp in Sources */,
> @@ -6425,6 +6456,7 @@
> 268900FA13353E6F00698AC0 /* ThreadList.cpp
> in Sources */,
> 268900FB13353E6F00698AC0 /* ThreadPlan.cpp
> in Sources */,
> 256CBDBC1ADD107200BC6CDC /*
> RegisterContextLinux_mips64.cpp in Sources */,
> + 26BF51F31B3C754400016294 /*
> ABISysV_hexagon.cpp in Sources */,
> 232CB619191E00CD00EF39FC /*
> NativeProcessProtocol.cpp in Sources */,
> 8CF02AEF19DD16B100B14BE0 /*
> InstrumentationRuntimeStopInfo.cpp in Sources */,
> 268900FC13353E6F00698AC0 /*
> ThreadPlanBase.cpp in Sources */,
>
> Modified: lldb/trunk/source/API/SystemInitializerFull.cpp
> URL:
> http://llvm.org/viewvc/llvm-project/lldb/trunk/source/API/SystemInitializerFull.cpp?rev=240663&r1=240662&r2=240663&view=diff
>
> ==============================================================================
> --- lldb/trunk/source/API/SystemInitializerFull.cpp (original)
> +++ lldb/trunk/source/API/SystemInitializerFull.cpp Thu Jun 25 12:50:15
> 2015
> @@ -19,6 +19,7 @@
> #include "Plugins/ABI/MacOSX-arm64/ABIMacOSX_arm64.h"
> #include "Plugins/ABI/SysV-arm/ABISysV_arm.h"
> #include "Plugins/ABI/SysV-arm64/ABISysV_arm64.h"
> +#include "Plugins/ABI/SysV-i386/ABISysV_i386.h"
> #include "Plugins/ABI/SysV-x86_64/ABISysV_x86_64.h"
> #include "Plugins/ABI/SysV-ppc/ABISysV_ppc.h"
> #include "Plugins/ABI/SysV-ppc64/ABISysV_ppc64.h"
> @@ -236,6 +237,7 @@ SystemInitializerFull::Initialize()
> ABIMacOSX_arm64::Initialize();
> ABISysV_arm::Initialize();
> ABISysV_arm64::Initialize();
> + ABISysV_i386::Initialize();
> ABISysV_x86_64::Initialize();
> ABISysV_ppc::Initialize();
> ABISysV_ppc64::Initialize();
> @@ -337,6 +339,7 @@ SystemInitializerFull::Terminate()
> ABIMacOSX_arm64::Terminate();
> ABISysV_arm::Terminate();
> ABISysV_arm64::Terminate();
> + ABISysV_i386::Terminate();
> ABISysV_x86_64::Terminate();
> ABISysV_ppc::Terminate();
> ABISysV_ppc64::Terminate();
>
> Modified: lldb/trunk/source/Plugins/ABI/CMakeLists.txt
> URL:
> http://llvm.org/viewvc/llvm-project/lldb/trunk/source/Plugins/ABI/CMakeLists.txt?rev=240663&r1=240662&r2=240663&view=diff
>
> ==============================================================================
> --- lldb/trunk/source/Plugins/ABI/CMakeLists.txt (original)
> +++ lldb/trunk/source/Plugins/ABI/CMakeLists.txt Thu Jun 25 12:50:15 2015
> @@ -5,6 +5,7 @@ add_subdirectory(SysV-ppc)
> add_subdirectory(SysV-ppc64)
> add_subdirectory(SysV-mips)
> add_subdirectory(SysV-mips64)
> +add_subdirectory(SysV-i386)
> add_subdirectory(SysV-x86_64)
> add_subdirectory(MacOSX-i386)
> add_subdirectory(MacOSX-arm)
>
> Added: lldb/trunk/source/Plugins/ABI/SysV-i386/ABISysV_i386.cpp
> URL:
> http://llvm.org/viewvc/llvm-project/lldb/trunk/source/Plugins/ABI/SysV-i386/ABISysV_i386.cpp?rev=240663&view=auto
>
> ==============================================================================
> --- lldb/trunk/source/Plugins/ABI/SysV-i386/ABISysV_i386.cpp (added)
> +++ lldb/trunk/source/Plugins/ABI/SysV-i386/ABISysV_i386.cpp Thu Jun 25
> 12:50:15 2015
> @@ -0,0 +1,815 @@
> +//===----------------------- ABISysV_i386.cpp -------------------*- C++
> -*-===//
> +//
> +// The LLVM Compiler Infrastructure
> +//
> +// This file is distributed under the University of Illinois Open Source
> License.
> +// See LICENSE.TXT for details.
>
> +//===----------------------------------------------------------------------===//
> +
> +#include "ABISysV_i386.h"
> +
> +#include "lldb/Core/ConstString.h"
> +#include "lldb/Core/DataExtractor.h"
> +#include "lldb/Core/Error.h"
> +#include "lldb/Core/Log.h"
> +#include "lldb/Core/Module.h"
> +#include "lldb/Core/PluginManager.h"
> +#include "lldb/Core/RegisterValue.h"
> +#include "lldb/Core/Value.h"
> +#include "lldb/Core/ValueObjectConstResult.h"
> +#include "lldb/Core/ValueObjectRegister.h"
> +#include "lldb/Core/ValueObjectMemory.h"
> +#include "lldb/Symbol/ClangASTContext.h"
> +#include "lldb/Symbol/UnwindPlan.h"
> +#include "lldb/Target/Target.h"
> +#include "lldb/Target/Process.h"
> +#include "lldb/Target/RegisterContext.h"
> +#include "lldb/Target/StackFrame.h"
> +#include "lldb/Target/Thread.h"
> +
> +#include "llvm/ADT/STLExtras.h"
> +#include "llvm/ADT/Triple.h"
> +
> +using namespace lldb;
> +using namespace lldb_private;
> +
> +
> +
> +// This source file uses the following document as a reference:
> +//====================================================================
> +// System V Application Binary Interface
> +// Intel386 Architecture Processor Supplement, Version 1.0
> +// Edited by
> +// H.J. Lu, David L Kreitzer, Milind Girkar, Zia Ansari
> +//
> +// (Based on
> +// System V Application Binary Interface,
> +// AMD64 Architecture Processor Supplement,
> +// Edited by
> +// H.J. Lu, Michael Matz, Milind Girkar, Jan Hubicka,
> +// Andreas Jaeger, Mark Mitchell)
> +//
> +// February 3, 2015
> +//====================================================================
> +
> +
> +
> +// DWARF Register Number Mapping
> +// See Table 2.14 of the reference document (specified on top of this
> file)
> +// Comment: Table 2.14 is followed till 'mm' entries.
> +// After that, all entries are ignored here.
> +
> +enum gcc_dwarf_regnums
> +{
> + gcc_dwarf_eax = 0,
> + gcc_dwarf_ecx,
> + gcc_dwarf_edx,
> + gcc_dwarf_ebx,
> + gcc_dwarf_esp,
> + gcc_dwarf_ebp,
> + gcc_dwarf_esi,
> + gcc_dwarf_edi,
> + gcc_dwarf_eip,
> + gcc_dwarf_eflags,
> +
> + gcc_dwarf_st0 = 11,
> + gcc_dwarf_st1,
> + gcc_dwarf_st2,
> + gcc_dwarf_st3,
> + gcc_dwarf_st4,
> + gcc_dwarf_st5,
> + gcc_dwarf_st6,
> + gcc_dwarf_st7,
> +
> + gcc_dwarf_xmm0 = 21,
> + gcc_dwarf_xmm1,
> + gcc_dwarf_xmm2,
> + gcc_dwarf_xmm3,
> + gcc_dwarf_xmm4,
> + gcc_dwarf_xmm5,
> + gcc_dwarf_xmm6,
> + gcc_dwarf_xmm7,
> + gcc_dwarf_ymm0 = gcc_dwarf_xmm0,
> + gcc_dwarf_ymm1 = gcc_dwarf_xmm1,
> + gcc_dwarf_ymm2 = gcc_dwarf_xmm2,
> + gcc_dwarf_ymm3 = gcc_dwarf_xmm3,
> + gcc_dwarf_ymm4 = gcc_dwarf_xmm4,
> + gcc_dwarf_ymm5 = gcc_dwarf_xmm5,
> + gcc_dwarf_ymm6 = gcc_dwarf_xmm6,
> + gcc_dwarf_ymm7 = gcc_dwarf_xmm7,
> +
> + gcc_dwarf_mm0 = 29,
> + gcc_dwarf_mm1,
> + gcc_dwarf_mm2,
> + gcc_dwarf_mm3,
> + gcc_dwarf_mm4,
> + gcc_dwarf_mm5,
> + gcc_dwarf_mm6,
> + gcc_dwarf_mm7
> +};
> +
> +
> +enum gdb_regnums
> +{
> + gdb_eax = 0,
> + gdb_ecx = 1,
> + gdb_edx = 2,
> + gdb_ebx = 3,
> + gdb_esp = 4,
> + gdb_ebp = 5,
> + gdb_esi = 6,
> + gdb_edi = 7,
> + gdb_eip = 8,
> + gdb_eflags = 9,
> + gdb_cs = 10,
> + gdb_ss = 11,
> + gdb_ds = 12,
> + gdb_es = 13,
> + gdb_fs = 14,
> + gdb_gs = 15,
> + gdb_st0 = 16,
> + gdb_st1 = 17,
> + gdb_st2 = 18,
> + gdb_st3 = 19,
> + gdb_st4 = 20,
> + gdb_st5 = 21,
> + gdb_st6 = 22,
> + gdb_st7 = 23,
> + gdb_fctrl = 24, gdb_fcw = gdb_fctrl,
> + gdb_fstat = 25, gdb_fsw = gdb_fstat,
> + gdb_ftag = 26, gdb_ftw = gdb_ftag,
> + gdb_fiseg = 27, gdb_fpu_cs = gdb_fiseg,
> + gdb_fioff = 28, gdb_ip = gdb_fioff,
> + gdb_foseg = 29, gdb_fpu_ds = gdb_foseg,
> + gdb_fooff = 30, gdb_dp = gdb_fooff,
> + gdb_fop = 31,
> + gdb_xmm0 = 32,
> + gdb_xmm1 = 33,
> + gdb_xmm2 = 34,
> + gdb_xmm3 = 35,
> + gdb_xmm4 = 36,
> + gdb_xmm5 = 37,
> + gdb_xmm6 = 38,
> + gdb_xmm7 = 39,
> + gdb_mxcsr = 40,
> + gdb_mm0 = 41,
> + gdb_mm1 = 42,
> + gdb_mm2 = 43,
> + gdb_mm3 = 44,
> + gdb_mm4 = 45,
> + gdb_mm5 = 46,
> + gdb_mm6 = 47,
> + gdb_mm7 = 48,
> + gdb_ymm0 = gdb_xmm0,
> + gdb_ymm1 = gdb_xmm1,
> + gdb_ymm2 = gdb_xmm2,
> + gdb_ymm3 = gdb_xmm3,
> + gdb_ymm4 = gdb_xmm4,
> + gdb_ymm5 = gdb_xmm5,
> + gdb_ymm6 = gdb_xmm6,
> + gdb_ymm7 = gdb_xmm7
> +};
> +
> +
> +static RegisterInfo g_register_infos[] =
> +{
> + // NAME ALT SZ OFF ENCODING FORMAT
> COMPILER DWARF GENERIC
> GDB LLDB NATIVE VALUE REGS INVALIDATE
> REGS
> + // ====== ======= == === ============= ============
> ===================== ===================== ============================
> ==================== ====================== ==========
> ===============
> + { "eax", nullptr, 4, 0, eEncodingUint , eFormatHex ,
> { gcc_dwarf_eax , gcc_dwarf_eax , LLDB_INVALID_REGNUM
> , gdb_eax , LLDB_INVALID_REGNUM }, nullptr,
> nullptr},
> + { "ebx" , nullptr, 4, 0, eEncodingUint , eFormatHex ,
> { gcc_dwarf_ebx , gcc_dwarf_ebx , LLDB_INVALID_REGNUM
> , gdb_ebx , LLDB_INVALID_REGNUM }, nullptr,
> nullptr},
> + { "ecx" , nullptr, 4, 0, eEncodingUint , eFormatHex ,
> { gcc_dwarf_ecx , gcc_dwarf_ecx , LLDB_REGNUM_GENERIC_ARG4
> , gdb_ecx , LLDB_INVALID_REGNUM }, nullptr, nullptr},
> + { "edx" , nullptr, 4, 0, eEncodingUint , eFormatHex ,
> { gcc_dwarf_edx , gcc_dwarf_edx , LLDB_REGNUM_GENERIC_ARG3
> , gdb_edx , LLDB_INVALID_REGNUM }, nullptr, nullptr},
> + { "esi" , nullptr, 4, 0, eEncodingUint , eFormatHex ,
> { gcc_dwarf_esi , gcc_dwarf_esi , LLDB_REGNUM_GENERIC_ARG2
> , gdb_esi , LLDB_INVALID_REGNUM }, nullptr, nullptr},
> + { "edi" , nullptr, 4, 0, eEncodingUint , eFormatHex ,
> { gcc_dwarf_edi , gcc_dwarf_edi , LLDB_REGNUM_GENERIC_ARG1
> , gdb_edi , LLDB_INVALID_REGNUM }, nullptr, nullptr},
> + { "ebp" , "fp", 4, 0, eEncodingUint , eFormatHex ,
> { gcc_dwarf_ebp , gcc_dwarf_ebp , LLDB_REGNUM_GENERIC_FP
> , gdb_ebp , LLDB_INVALID_REGNUM }, nullptr, nullptr},
> + { "esp" , "sp", 4, 0, eEncodingUint , eFormatHex ,
> { gcc_dwarf_esp , gcc_dwarf_esp , LLDB_REGNUM_GENERIC_SP
> , gdb_esp , LLDB_INVALID_REGNUM }, nullptr, nullptr},
> + { "eip" , "pc", 4, 0, eEncodingUint , eFormatHex ,
> { gcc_dwarf_eip , gcc_dwarf_eip , LLDB_REGNUM_GENERIC_PC
> , gdb_eip , LLDB_INVALID_REGNUM }, nullptr, nullptr},
> + { "eflags", nullptr, 4, 0, eEncodingUint , eFormatHex ,
> { LLDB_INVALID_REGNUM , LLDB_INVALID_REGNUM , LLDB_REGNUM_GENERIC_FLAGS
> , gdb_eflags , LLDB_INVALID_REGNUM }, nullptr, nullptr},
> + { "cs" , nullptr, 4, 0, eEncodingUint , eFormatHex ,
> { LLDB_INVALID_REGNUM , LLDB_INVALID_REGNUM , LLDB_INVALID_REGNUM
> , gdb_cs , LLDB_INVALID_REGNUM }, nullptr,
> nullptr},
> + { "ss" , nullptr, 4, 0, eEncodingUint , eFormatHex ,
> { LLDB_INVALID_REGNUM , LLDB_INVALID_REGNUM , LLDB_INVALID_REGNUM
> , gdb_ss , LLDB_INVALID_REGNUM }, nullptr,
> nullptr},
> + { "ds" , nullptr, 4, 0, eEncodingUint , eFormatHex ,
> { LLDB_INVALID_REGNUM , LLDB_INVALID_REGNUM , LLDB_INVALID_REGNUM
> , gdb_ds , LLDB_INVALID_REGNUM }, nullptr,
> nullptr},
> + { "es" , nullptr, 4, 0, eEncodingUint , eFormatHex ,
> { LLDB_INVALID_REGNUM , LLDB_INVALID_REGNUM , LLDB_INVALID_REGNUM
> , gdb_es , LLDB_INVALID_REGNUM }, nullptr,
> nullptr},
> + { "fs" , nullptr, 4, 0, eEncodingUint , eFormatHex ,
> { LLDB_INVALID_REGNUM , LLDB_INVALID_REGNUM , LLDB_INVALID_REGNUM
> , gdb_fs , LLDB_INVALID_REGNUM }, nullptr,
> nullptr},
> + { "gs" , nullptr, 4, 0, eEncodingUint , eFormatHex ,
> { LLDB_INVALID_REGNUM , LLDB_INVALID_REGNUM , LLDB_INVALID_REGNUM
> , gdb_gs , LLDB_INVALID_REGNUM }, nullptr,
> nullptr},
> + { "st0" , nullptr, 10, 0, eEncodingVector, eFormatVectorOfUInt8,
> { LLDB_INVALID_REGNUM , gcc_dwarf_st0 , LLDB_INVALID_REGNUM
> , gdb_st0 , LLDB_INVALID_REGNUM }, nullptr,
> nullptr},
> + { "st1" , nullptr, 10, 0, eEncodingVector, eFormatVectorOfUInt8,
> { LLDB_INVALID_REGNUM , gcc_dwarf_st1 , LLDB_INVALID_REGNUM
> , gdb_st1 , LLDB_INVALID_REGNUM }, nullptr,
> nullptr},
> + { "st2" , nullptr, 10, 0, eEncodingVector, eFormatVectorOfUInt8,
> { LLDB_INVALID_REGNUM , gcc_dwarf_st2 , LLDB_INVALID_REGNUM
> , gdb_st2 , LLDB_INVALID_REGNUM }, nullptr,
> nullptr},
> + { "st3" , nullptr, 10, 0, eEncodingVector, eFormatVectorOfUInt8,
> { LLDB_INVALID_REGNUM , gcc_dwarf_st3 , LLDB_INVALID_REGNUM
> , gdb_st3 , LLDB_INVALID_REGNUM }, nullptr,
> nullptr},
> + { "st4" , nullptr, 10, 0, eEncodingVector, eFormatVectorOfUInt8,
> { LLDB_INVALID_REGNUM , gcc_dwarf_st4 , LLDB_INVALID_REGNUM
> , gdb_st4 , LLDB_INVALID_REGNUM }, nullptr,
> nullptr},
> + { "st5" , nullptr, 10, 0, eEncodingVector, eFormatVectorOfUInt8,
> { LLDB_INVALID_REGNUM , gcc_dwarf_st5 , LLDB_INVALID_REGNUM
> , gdb_st5 , LLDB_INVALID_REGNUM }, nullptr,
> nullptr},
> + { "st6" , nullptr, 10, 0, eEncodingVector, eFormatVectorOfUInt8,
> { LLDB_INVALID_REGNUM , gcc_dwarf_st6 , LLDB_INVALID_REGNUM
> , gdb_st6 , LLDB_INVALID_REGNUM }, nullptr,
> nullptr},
> + { "st7" , nullptr, 10, 0, eEncodingVector, eFormatVectorOfUInt8,
> { LLDB_INVALID_REGNUM , gcc_dwarf_st7 , LLDB_INVALID_REGNUM
> , gdb_st7 , LLDB_INVALID_REGNUM }, nullptr,
> nullptr},
> + { "fctrl" , nullptr, 4, 0, eEncodingUint , eFormatHex ,
> { LLDB_INVALID_REGNUM , LLDB_INVALID_REGNUM , LLDB_INVALID_REGNUM
> , gdb_fctrl , LLDB_INVALID_REGNUM }, nullptr,
> nullptr},
> + { "fstat" , nullptr, 4, 0, eEncodingUint , eFormatHex ,
> { LLDB_INVALID_REGNUM , LLDB_INVALID_REGNUM , LLDB_INVALID_REGNUM
> , gdb_fstat , LLDB_INVALID_REGNUM }, nullptr,
> nullptr},
> + { "ftag" , nullptr, 4, 0, eEncodingUint , eFormatHex ,
> { LLDB_INVALID_REGNUM , LLDB_INVALID_REGNUM , LLDB_INVALID_REGNUM
> , gdb_ftag , LLDB_INVALID_REGNUM }, nullptr,
> nullptr},
> + { "fiseg" , nullptr, 4, 0, eEncodingUint , eFormatHex ,
> { LLDB_INVALID_REGNUM , LLDB_INVALID_REGNUM , LLDB_INVALID_REGNUM
> , gdb_fiseg , LLDB_INVALID_REGNUM }, nullptr,
> nullptr},
> + { "fioff" , nullptr, 4, 0, eEncodingUint , eFormatHex ,
> { LLDB_INVALID_REGNUM , LLDB_INVALID_REGNUM , LLDB_INVALID_REGNUM
> , gdb_fioff , LLDB_INVALID_REGNUM }, nullptr,
> nullptr},
> + { "foseg" , nullptr, 4, 0, eEncodingUint , eFormatHex ,
> { LLDB_INVALID_REGNUM , LLDB_INVALID_REGNUM , LLDB_INVALID_REGNUM
> , gdb_foseg , LLDB_INVALID_REGNUM }, nullptr,
> nullptr},
> + { "fooff" , nullptr, 4, 0, eEncodingUint , eFormatHex ,
> { LLDB_INVALID_REGNUM , LLDB_INVALID_REGNUM , LLDB_INVALID_REGNUM
> , gdb_fooff , LLDB_INVALID_REGNUM }, nullptr,
> nullptr},
> + { "fop" , nullptr, 4, 0, eEncodingUint , eFormatHex ,
> { LLDB_INVALID_REGNUM , LLDB_INVALID_REGNUM , LLDB_INVALID_REGNUM
> , gdb_fop , LLDB_INVALID_REGNUM }, nullptr,
> nullptr},
> + { "xmm0" , nullptr, 16, 0, eEncodingVector, eFormatVectorOfUInt8,
> { LLDB_INVALID_REGNUM , gcc_dwarf_xmm0 , LLDB_INVALID_REGNUM
> , gdb_xmm0 , LLDB_INVALID_REGNUM }, nullptr,
> nullptr},
> + { "xmm1" , nullptr, 16, 0, eEncodingVector, eFormatVectorOfUInt8,
> { LLDB_INVALID_REGNUM , gcc_dwarf_xmm1 , LLDB_INVALID_REGNUM
> , gdb_xmm1 , LLDB_INVALID_REGNUM }, nullptr,
> nullptr},
> + { "xmm2" , nullptr, 16, 0, eEncodingVector, eFormatVectorOfUInt8,
> { LLDB_INVALID_REGNUM , gcc_dwarf_xmm2 , LLDB_INVALID_REGNUM
> , gdb_xmm2 , LLDB_INVALID_REGNUM }, nullptr,
> nullptr},
> + { "xmm3" , nullptr, 16, 0, eEncodingVector, eFormatVectorOfUInt8,
> { LLDB_INVALID_REGNUM , gcc_dwarf_xmm3 , LLDB_INVALID_REGNUM
> , gdb_xmm3 , LLDB_INVALID_REGNUM }, nullptr,
> nullptr},
> + { "xmm4" , nullptr, 16, 0, eEncodingVector, eFormatVectorOfUInt8,
> { LLDB_INVALID_REGNUM , gcc_dwarf_xmm4 , LLDB_INVALID_REGNUM
> , gdb_xmm4 , LLDB_INVALID_REGNUM }, nullptr,
> nullptr},
> + { "xmm5" , nullptr, 16, 0, eEncodingVector, eFormatVectorOfUInt8,
> { LLDB_INVALID_REGNUM , gcc_dwarf_xmm5 , LLDB_INVALID_REGNUM
> , gdb_xmm5 , LLDB_INVALID_REGNUM }, nullptr,
> nullptr},
> + { "xmm6" , nullptr, 16, 0, eEncodingVector, eFormatVectorOfUInt8,
> { LLDB_INVALID_REGNUM , gcc_dwarf_xmm6 , LLDB_INVALID_REGNUM
> , gdb_xmm6 , LLDB_INVALID_REGNUM }, nullptr,
> nullptr},
> + { "xmm7" , nullptr, 16, 0, eEncodingVector, eFormatVectorOfUInt8,
> { LLDB_INVALID_REGNUM , gcc_dwarf_xmm7 , LLDB_INVALID_REGNUM
> , gdb_xmm7 , LLDB_INVALID_REGNUM }, nullptr,
> nullptr},
> + { "mxcsr" , nullptr, 4, 0, eEncodingUint , eFormatHex ,
> { LLDB_INVALID_REGNUM , LLDB_INVALID_REGNUM , LLDB_INVALID_REGNUM
> , gdb_mxcsr , LLDB_INVALID_REGNUM }, nullptr,
> nullptr},
> + { "ymm0" , nullptr, 32, 0, eEncodingVector, eFormatVectorOfUInt8,
> { LLDB_INVALID_REGNUM , gcc_dwarf_ymm0 , LLDB_INVALID_REGNUM
> , gdb_ymm0 , LLDB_INVALID_REGNUM }, nullptr,
> nullptr},
> + { "ymm1" , nullptr, 32, 0, eEncodingVector, eFormatVectorOfUInt8,
> { LLDB_INVALID_REGNUM , gcc_dwarf_ymm1 , LLDB_INVALID_REGNUM
> , gdb_ymm1 , LLDB_INVALID_REGNUM }, nullptr,
> nullptr},
> + { "ymm2" , nullptr, 32, 0, eEncodingVector, eFormatVectorOfUInt8,
> { LLDB_INVALID_REGNUM , gcc_dwarf_ymm2 , LLDB_INVALID_REGNUM
> , gdb_ymm2 , LLDB_INVALID_REGNUM }, nullptr,
> nullptr},
> + { "ymm3" , nullptr, 32, 0, eEncodingVector, eFormatVectorOfUInt8,
> { LLDB_INVALID_REGNUM , gcc_dwarf_ymm3 , LLDB_INVALID_REGNUM
> , gdb_ymm3 , LLDB_INVALID_REGNUM }, nullptr,
> nullptr},
> + { "ymm4" , nullptr, 32, 0, eEncodingVector, eFormatVectorOfUInt8,
> { LLDB_INVALID_REGNUM , gcc_dwarf_ymm4 , LLDB_INVALID_REGNUM
> , gdb_ymm4 , LLDB_INVALID_REGNUM }, nullptr,
> nullptr},
> + { "ymm5" , nullptr, 32, 0, eEncodingVector, eFormatVectorOfUInt8,
> { LLDB_INVALID_REGNUM , gcc_dwarf_ymm5 , LLDB_INVALID_REGNUM
> , gdb_ymm5 , LLDB_INVALID_REGNUM }, nullptr,
> nullptr},
> + { "ymm6" , nullptr, 32, 0, eEncodingVector, eFormatVectorOfUInt8,
> { LLDB_INVALID_REGNUM , gcc_dwarf_ymm6 , LLDB_INVALID_REGNUM
> , gdb_ymm6 , LLDB_INVALID_REGNUM }, nullptr,
> nullptr},
> + { "ymm7" , nullptr, 32, 0, eEncodingVector, eFormatVectorOfUInt8,
> { LLDB_INVALID_REGNUM , gcc_dwarf_ymm7 , LLDB_INVALID_REGNUM
> , gdb_ymm7 , LLDB_INVALID_REGNUM }, nullptr, nullptr}
> +};
> +
> +static const uint32_t k_num_register_infos =
> llvm::array_lengthof(g_register_infos);
> +static bool g_register_info_names_constified = false;
> +
> +const lldb_private::RegisterInfo *
> +ABISysV_i386::GetRegisterInfoArray (uint32_t &count)
> +{
> + // Make the C-string names and alt_names for the register infos into
> const
> + // C-string values by having the ConstString unique the names in the
> global
> + // constant C-string pool.
> + if (!g_register_info_names_constified)
> + {
> + g_register_info_names_constified = true;
> + for (uint32_t i=0; i<k_num_register_infos; ++i)
> + {
> + if (g_register_infos[i].name)
> + g_register_infos[i].name =
> ConstString(g_register_infos[i].name).GetCString();
> + if (g_register_infos[i].alt_name)
> + g_register_infos[i].alt_name =
> ConstString(g_register_infos[i].alt_name).GetCString();
> + }
> + }
> + count = k_num_register_infos;
> + return g_register_infos;
> +}
> +
> +
> +//------------------------------------------------------------------
> +// Static Functions
> +//------------------------------------------------------------------
> +ABISP
> +ABISysV_i386::CreateInstance (const ArchSpec &arch)
> +{
> + static ABISP g_abi_sp;
> + if ((arch.GetTriple().getArch() == llvm::Triple::x86) &&
> + arch.GetTriple().isOSLinux())
> + {
> + if (!g_abi_sp)
> + g_abi_sp.reset (new ABISysV_i386);
> + return g_abi_sp;
> + }
> + return ABISP();
> +}
> +
> +bool
> +ABISysV_i386::PrepareTrivialCall (Thread &thread,
> + addr_t sp,
> + addr_t func_addr,
> + addr_t return_addr,
> + llvm::ArrayRef<addr_t> args) const
> +{
> + RegisterContext *reg_ctx = thread.GetRegisterContext().get();
> +
> + if (!reg_ctx)
> + return false;
> +
> + uint32_t pc_reg_num = reg_ctx->ConvertRegisterKindToRegisterNumber
> (eRegisterKindGeneric, LLDB_REGNUM_GENERIC_PC);
> + uint32_t sp_reg_num = reg_ctx->ConvertRegisterKindToRegisterNumber
> (eRegisterKindGeneric, LLDB_REGNUM_GENERIC_SP);
> +
> + // While using register info to write a register value to memory, the
> register info
> + // just needs to have the correct size of a 32 bit register, the
> actual register it
> + // pertains to is not important, just the size needs to be correct.
> + // "eax" is used here for this purpose.
> + const RegisterInfo *reg_info_32 =
> reg_ctx->GetRegisterInfoByName("eax");
> + if (!reg_info_32)
> + return false; // TODO this should actually never happen
> +
> + Error error;
> + RegisterValue reg_value;
> +
> + // Make room for the argument(s) on the stack
> + sp -= 4 * args.size();
> +
> + // SP Alignment
> + sp &= ~(16ull-1ull); // 16-byte alignment
> +
> + // Write arguments onto the stack
> + addr_t arg_pos = sp;
> + for (addr_t arg : args)
> + {
> + reg_value.SetUInt32(arg);
> + error = reg_ctx->WriteRegisterValueToMemory (reg_info_32,
> + arg_pos,
> +
> reg_info_32->byte_size,
> + reg_value);
> + if (error.Fail())
> + return false;
> + arg_pos += 4;
> + }
> +
> + // The return address is pushed onto the stack
> + sp -= 4;
> + reg_value.SetUInt32(return_addr);
> + error = reg_ctx->WriteRegisterValueToMemory (reg_info_32,
> + sp,
> + reg_info_32->byte_size,
> + reg_value);
> + if (error.Fail())
> + return false;
> +
> + // Setting %esp to the actual stack value.
> + if (!reg_ctx->WriteRegisterFromUnsigned (sp_reg_num, sp))
> + return false;
> +
> + // Setting %eip to the address of the called function.
> + if (!reg_ctx->WriteRegisterFromUnsigned (pc_reg_num, func_addr))
> + return false;
> +
> + return true;
> +}
> +
> +
> +static bool
> +ReadIntegerArgument (Scalar &scalar,
> + unsigned int bit_width,
> + bool is_signed,
> + Process *process,
> + addr_t ¤t_stack_argument)
> +{
> + uint32_t byte_size = (bit_width + (8-1))/8;
> + Error error;
> +
> + if (!process)
> + return false;
> +
> + if (process->ReadScalarIntegerFromMemory(current_stack_argument,
> byte_size, is_signed, scalar, error))
> + {
> + current_stack_argument += byte_size;
> + return true;
> + }
> + return false;
> +}
> +
> +
> +bool
> +ABISysV_i386::GetArgumentValues (Thread &thread,
> + ValueList &values) const
> +{
> + unsigned int num_values = values.GetSize();
> + unsigned int value_index;
> +
> + RegisterContext *reg_ctx = thread.GetRegisterContext().get();
> +
> + if (!reg_ctx)
> + return false;
> +
> + // Get pointer to the first stack argument
> + addr_t sp = reg_ctx->GetSP(0);
> + if (!sp)
> + return false;
> +
> + addr_t current_stack_argument = sp + 4; // jump over return address
> +
> + for (value_index = 0;
> + value_index < num_values;
> + ++value_index)
> + {
> + Value *value = values.GetValueAtIndex(value_index);
> +
> + if (!value)
> + return false;
> +
> + // Currently: Support for extracting values with Clang QualTypes
> only.
> + ClangASTType clang_type (value->GetClangType());
> + if (clang_type)
> + {
> + bool is_signed;
> + if (clang_type.IsIntegerType (is_signed))
> + {
> + ReadIntegerArgument(value->GetScalar(),
> + clang_type.GetBitSize(&thread),
> + is_signed,
> + thread.GetProcess().get(),
> + current_stack_argument);
> + }
> + else if (clang_type.IsPointerType())
> + {
> + ReadIntegerArgument(value->GetScalar(),
> + clang_type.GetBitSize(&thread),
> + false,
> + thread.GetProcess().get(),
> + current_stack_argument);
> + }
> + }
> + }
> + return true;
> +}
> +
> +
> +
> +Error
> +ABISysV_i386::SetReturnValueObject(lldb::StackFrameSP &frame_sp,
> lldb::ValueObjectSP &new_value_sp)
> +{
> + Error error;
> + //ToDo: Yet to be implemented
> + error.SetErrorString("ABISysV_i386::SetReturnValueObject(): Not
> implemented yet");
> + return error;
> +}
> +
> +
> +ValueObjectSP
> +ABISysV_i386::GetReturnValueObjectSimple (Thread &thread,
> + ClangASTType
> &return_clang_type) const
> +{
> + ValueObjectSP return_valobj_sp;
> + Value value;
> +
> + if (!return_clang_type)
> + return return_valobj_sp;
> +
> + value.SetClangType (return_clang_type);
> +
> + RegisterContext *reg_ctx = thread.GetRegisterContext().get();
> + if (!reg_ctx)
> + return return_valobj_sp;
> +
> + const uint32_t type_flags = return_clang_type.GetTypeInfo ();
> +
> + unsigned eax_id = reg_ctx->GetRegisterInfoByName("eax",
> 0)->kinds[eRegisterKindLLDB];
> + unsigned edx_id = reg_ctx->GetRegisterInfoByName("edx",
> 0)->kinds[eRegisterKindLLDB];
> +
> +
> + // Following "IF ELSE" block categorizes various 'Fundamental Data
> Types'.
> + // The terminology 'Fundamental Data Types' used here is adopted from
> + // Table 2.1 of the reference document (specified on top of this file)
> +
> + if (type_flags & eTypeIsPointer) // 'Pointer'
> + {
> + uint32_t ptr =
> thread.GetRegisterContext()->ReadRegisterAsUnsigned(eax_id, 0) & 0xffffffff
> ;
> + value.SetValueType(Value::eValueTypeScalar);
> + value.GetScalar() = ptr;
> + return_valobj_sp = ValueObjectConstResult::Create
> (thread.GetStackFrameAtIndex(0).get(),
> + value,
> +
> ConstString(""));
> + }
> +
> + else if ((type_flags & eTypeIsScalar) || (type_flags &
> eTypeIsEnumeration)) //'Integral' + 'Floating Point'
> + {
> + value.SetValueType(Value::eValueTypeScalar);
> + const size_t byte_size = return_clang_type.GetByteSize(nullptr);
> + bool success = false;
> +
> + if (type_flags & eTypeIsInteger) // 'Integral' except enum
> + {
> + const bool is_signed = ((type_flags & eTypeIsSigned) != 0);
> + uint64_t raw_value =
> thread.GetRegisterContext()->ReadRegisterAsUnsigned(eax_id, 0) & 0xffffffff
> ;
> + raw_value |=
> (thread.GetRegisterContext()->ReadRegisterAsUnsigned(edx_id, 0) &
> 0xffffffff) << 32;
> +
> + switch (byte_size)
> + {
> + default:
> + break;
> +
> + case 16:
> + // For clang::BuiltinType::UInt128 & Int128
> + // ToDo: Need to decide how to handle it
> + break ;
> +
> + case 8:
> + if (is_signed)
> + value.GetScalar() = (int64_t)(raw_value);
> + else
> + value.GetScalar() = (uint64_t)(raw_value);
> + success = true;
> + break;
> +
> + case 4:
> + if (is_signed)
> + value.GetScalar() = (int32_t)(raw_value &
> UINT32_MAX);
> + else
> + value.GetScalar() = (uint32_t)(raw_value &
> UINT32_MAX);
> + success = true;
> + break;
> +
> + case 2:
> + if (is_signed)
> + value.GetScalar() = (int16_t)(raw_value &
> UINT16_MAX);
> + else
> + value.GetScalar() = (uint16_t)(raw_value &
> UINT16_MAX);
> + success = true;
> + break;
> +
> + case 1:
> + if (is_signed)
> + value.GetScalar() = (int8_t)(raw_value &
> UINT8_MAX);
> + else
> + value.GetScalar() = (uint8_t)(raw_value &
> UINT8_MAX);
> + success = true;
> + break;
> + }
> +
> + if (success)
> + return_valobj_sp = ValueObjectConstResult::Create
> (thread.GetStackFrameAtIndex(0).get(),
> + value,
> +
> ConstString(""));
> + }
> +
> + else if (type_flags & eTypeIsEnumeration) // handles enum
> + {
> + uint32_t enm =
> thread.GetRegisterContext()->ReadRegisterAsUnsigned(eax_id, 0) & 0xffffffff
> ;
> + value.SetValueType(Value::eValueTypeScalar);
> + value.GetScalar() = enm;
> + return_valobj_sp = ValueObjectConstResult::Create
> (thread.GetStackFrameAtIndex(0).get(),
> + value,
> +
> ConstString(""));
> + }
> +
> + else if (type_flags & eTypeIsFloat) // 'Floating Point'
> + {
> + if (byte_size <= 12) // handles float, double, long
> double, __float80
> + {
> + const RegisterInfo *st0_info =
> reg_ctx->GetRegisterInfoByName("st0", 0);
> + RegisterValue st0_value;
> +
> + if (reg_ctx->ReadRegister (st0_info, st0_value))
> + {
> + DataExtractor data;
> + if (st0_value.GetData(data))
> + {
> + lldb::offset_t offset = 0;
> + long double value_long_double =
> data.GetLongDouble(&offset);
> +
> + if (byte_size == 4) // float is 4 bytes
> + {
> + float value_float = (float)value_long_double;
> + value.GetScalar() = value_float;
> + success = true;
> + }
> + else if (byte_size == 8) // double is 8 bytes
> + {
> + // On Android Platform: long double is also 8
> bytes
> + // It will be handled here only.
> + double value_double =
> (double)value_long_double;
> + value.GetScalar() = value_double;
> + success = true;
> + }
> + else if (byte_size == 12) // long double and
> __float80 are 12 bytes on i386
> + {
> + value.GetScalar() = value_long_double;
> + success = true;
> + }
> + }
> + }
> +
> + if (success)
> + return_valobj_sp = ValueObjectConstResult::Create
> (thread.GetStackFrameAtIndex(0).get(),
> +
> value,
> +
> ConstString(""));
> + }
> + else if(byte_size == 16) // handles __float128
> + {
> + lldb::addr_t storage_addr =
> (uint32_t)(thread.GetRegisterContext()->ReadRegisterAsUnsigned(eax_id, 0) &
> 0xffffffff);
> + return_valobj_sp = ValueObjectMemory::Create (&thread,
> + "",
> + Address
> (storage_addr, nullptr),
> +
> return_clang_type);
> + }
> + }
> +
> + else // Neither 'Integral' nor 'Floating Point'
> + {
> + // If flow reaches here then check type_flags
> + // This type_flags is unhandled
> + }
> + }
> +
> + else if (type_flags & eTypeIsComplex) // 'Complex Floating Point'
> + {
> + // ToDo: Yet to be implemented
> + }
> +
> + else if (type_flags & eTypeIsVector) // 'Packed'
> + {
> + const size_t byte_size = return_clang_type.GetByteSize(nullptr);
> + if (byte_size > 0)
> + {
> + const RegisterInfo *vec_reg =
> reg_ctx->GetRegisterInfoByName("ymm0", 0);
> + if (vec_reg == nullptr)
> + {
> + vec_reg = reg_ctx->GetRegisterInfoByName("xmm0", 0);
> + if (vec_reg == nullptr)
> + vec_reg = reg_ctx->GetRegisterInfoByName("mm0", 0);
> + }
> +
> + if (vec_reg)
> + {
> + if (byte_size <= vec_reg->byte_size)
> + {
> + ProcessSP process_sp (thread.GetProcess());
> + if (process_sp)
> + {
> + std::unique_ptr<DataBufferHeap> heap_data_ap (new
> DataBufferHeap(byte_size, 0));
> + const ByteOrder byte_order =
> process_sp->GetByteOrder();
> + RegisterValue reg_value;
> + if (reg_ctx->ReadRegister(vec_reg, reg_value))
> + {
> + Error error;
> + if (reg_value.GetAsMemoryData (vec_reg,
> +
> heap_data_ap->GetBytes(),
> +
> heap_data_ap->GetByteSize(),
> + byte_order,
> + error))
> + {
> + DataExtractor data (DataBufferSP
> (heap_data_ap.release()),
> + byte_order,
> +
> process_sp->GetTarget().GetArchitecture().GetAddressByteSize());
> + return_valobj_sp =
> ValueObjectConstResult::Create (&thread,
> +
> return_clang_type,
> +
> ConstString(""),
> +
> data);
> + }
> + }
> + }
> + }
> + }
> + }
> + }
> +
> + else // 'Decimal Floating Point'
> + {
> + //ToDo: Yet to be implemented
> + }
> + return return_valobj_sp;
> +}
> +
> +
> +ValueObjectSP
> +ABISysV_i386::GetReturnValueObjectImpl (Thread &thread, ClangASTType
> &return_clang_type) const
> +{
> + ValueObjectSP return_valobj_sp;
> +
> + if (!return_clang_type)
> + return return_valobj_sp;
> +
> + ExecutionContext exe_ctx (thread.shared_from_this());
> + return_valobj_sp = GetReturnValueObjectSimple(thread,
> return_clang_type);
> + if (return_valobj_sp)
> + return return_valobj_sp;
> +
> + RegisterContextSP reg_ctx_sp = thread.GetRegisterContext();
> + if (!reg_ctx_sp)
> + return return_valobj_sp;
> +
> + if (return_clang_type.IsAggregateType())
> + {
> + unsigned eax_id = reg_ctx_sp->GetRegisterInfoByName("eax",
> 0)->kinds[eRegisterKindLLDB];
> + lldb::addr_t storage_addr =
> (uint32_t)(thread.GetRegisterContext()->ReadRegisterAsUnsigned(eax_id, 0) &
> 0xffffffff);
> + return_valobj_sp = ValueObjectMemory::Create (&thread,
> + "",
> + Address
> (storage_addr, nullptr),
> + return_clang_type);
> + }
> +
> + return return_valobj_sp;
> +}
> +
> +// This defines CFA as esp+4
> +// The saved pc is at CFA-4 (i.e. esp+0)
> +// The saved esp is CFA+0
> +
> +bool
> +ABISysV_i386::CreateFunctionEntryUnwindPlan (UnwindPlan &unwind_plan)
> +{
> + unwind_plan.Clear();
> + unwind_plan.SetRegisterKind (eRegisterKindDWARF);
> +
> + uint32_t sp_reg_num = gcc_dwarf_esp;
> + uint32_t pc_reg_num = gcc_dwarf_eip;
> +
> + UnwindPlan::RowSP row(new UnwindPlan::Row);
> + row->GetCFAValue().SetIsRegisterPlusOffset(sp_reg_num, 4);
> + row->SetRegisterLocationToAtCFAPlusOffset(pc_reg_num, -4, false);
> + row->SetRegisterLocationToIsCFAPlusOffset(sp_reg_num, 0, true);
> + unwind_plan.AppendRow (row);
> + unwind_plan.SetSourceName ("i386 at-func-entry default");
> + unwind_plan.SetSourcedFromCompiler (eLazyBoolNo);
> + return true;
> +}
> +
> +// This defines CFA as ebp+8
> +// The saved pc is at CFA-4 (i.e. ebp+4)
> +// The saved ebp is at CFA-8 (i.e. ebp+0)
> +// The saved esp is CFA+0
> +
> +bool
> +ABISysV_i386::CreateDefaultUnwindPlan (UnwindPlan &unwind_plan)
> +{
> + unwind_plan.Clear();
> + unwind_plan.SetRegisterKind (eRegisterKindDWARF);
> +
> + uint32_t fp_reg_num = gcc_dwarf_ebp;
> + uint32_t sp_reg_num = gcc_dwarf_esp;
> + uint32_t pc_reg_num = gcc_dwarf_eip;
> +
> + UnwindPlan::RowSP row(new UnwindPlan::Row);
> + const int32_t ptr_size = 4;
> +
> + row->GetCFAValue().SetIsRegisterPlusOffset(fp_reg_num, 2 * ptr_size);
> + row->SetOffset (0);
> +
> + row->SetRegisterLocationToAtCFAPlusOffset(fp_reg_num, ptr_size * -2,
> true);
> + row->SetRegisterLocationToAtCFAPlusOffset(pc_reg_num, ptr_size * -1,
> true);
> + row->SetRegisterLocationToIsCFAPlusOffset(sp_reg_num, 0, true);
> +
> + unwind_plan.AppendRow (row);
> + unwind_plan.SetSourceName ("i386 default unwind plan");
> + unwind_plan.SetSourcedFromCompiler (eLazyBoolNo);
> + unwind_plan.SetUnwindPlanValidAtAllInstructions (eLazyBoolNo);
> + return true;
> +}
> +
> +
> +// According to "Register Usage" in reference document (specified on top
> +// of this source file) ebx, ebp, esi, edi and esp registers are preserved
> +// i.e. non-volatile i.e. callee-saved on i386
> +bool
> +ABISysV_i386::RegisterIsCalleeSaved (const RegisterInfo *reg_info)
> +{
> + if (!reg_info)
> + return false;
> +
> + // Saved registers are ebx, ebp, esi, edi, esp, eip
> + const char *name = reg_info->name;
> + if (name[0] == 'e')
> + {
> + switch (name[1])
> + {
> + case 'b':
> + if (name[2] == 'x' || name[2] == 'p')
> + return name[3] == '\0';
> + break;
> + case 'd':
> + if (name[2] == 'i')
> + return name[3] == '\0';
> + break;
> + case 'i':
> + if (name[2] == 'p')
> + return name[3] == '\0';
> + break;
> + case 's':
> + if (name[2] == 'i' || name[2] == 'p')
> + return name[3] == '\0';
> + break;
> + }
> + }
> +
> + if (name[0] == 's' && name[1] == 'p' && name[2] == '\0') // sp
> + return true;
> + if (name[0] == 'f' && name[1] == 'p' && name[2] == '\0') // fp
> + return true;
> + if (name[0] == 'p' && name[1] == 'c' && name[2] == '\0') // pc
> + return true;
> +
> + return false;
> +}
> +
> +
> +void
> +ABISysV_i386::Initialize()
> +{
> + PluginManager::RegisterPlugin (GetPluginNameStatic(),
> + "System V ABI for i386 targets",
> + CreateInstance);
> +}
> +
> +
> +void
> +ABISysV_i386::Terminate()
> +{
> + PluginManager::UnregisterPlugin (CreateInstance);
> +}
> +
> +
> +//------------------------------------------------------------------
> +// PluginInterface protocol
> +//------------------------------------------------------------------
> +lldb_private::ConstString
> +ABISysV_i386::GetPluginNameStatic()
> +{
> + static ConstString g_name("sysv-i386");
> + return g_name;
> +}
> +
> +
> +lldb_private::ConstString
> +ABISysV_i386::GetPluginName()
> +{
> + return GetPluginNameStatic();
> +}
>
> Added: lldb/trunk/source/Plugins/ABI/SysV-i386/ABISysV_i386.h
> URL:
> http://llvm.org/viewvc/llvm-project/lldb/trunk/source/Plugins/ABI/SysV-i386/ABISysV_i386.h?rev=240663&view=auto
>
> ==============================================================================
> --- lldb/trunk/source/Plugins/ABI/SysV-i386/ABISysV_i386.h (added)
> +++ lldb/trunk/source/Plugins/ABI/SysV-i386/ABISysV_i386.h Thu Jun 25
> 12:50:15 2015
> @@ -0,0 +1,138 @@
> +//===------------------- ABISysV_i386.h -------------------------*- C++
> -*-===//
> +//
> +// The LLVM Compiler Infrastructure
> +//
> +// This file is distributed under the University of Illinois Open Source
> +// License. See LICENSE.TXT for details.
> +//
>
> +//===----------------------------------------------------------------------===//
> +
> +#ifndef liblldb_ABISysV_i386_h_
> +#define liblldb_ABISysV_i386_h_
> +
> +// C Includes
> +// C++ Includes
> +// Other libraries and framework includes
> +// Project includes
> +#include "lldb/lldb-private.h"
> +#include "lldb/Target/ABI.h"
> +
> +class ABISysV_i386 :
> + public lldb_private::ABI
> +{
> +public:
> +
> + ~ABISysV_i386()
> + {
> + }
> +
> + size_t
> + GetRedZoneSize () const override
> + {
> + return 0; // There is no red zone for i386 Architecture
> + }
> +
> + bool
> + PrepareTrivialCall (lldb_private::Thread &thread,
> + lldb::addr_t sp,
> + lldb::addr_t functionAddress,
> + lldb::addr_t returnAddress,
> + llvm::ArrayRef<lldb::addr_t> args) const override;
> +
> + bool
> + GetArgumentValues (lldb_private::Thread &thread,
> + lldb_private::ValueList &values) const override;
> +
> + lldb_private::Error
> + SetReturnValueObject(lldb::StackFrameSP &frame_sp,
> lldb::ValueObjectSP &new_value) override;
> +
> +protected:
> + lldb::ValueObjectSP
> + GetReturnValueObjectSimple (lldb_private::Thread &thread,
> + lldb_private::ClangASTType &ast_type)
> const;
> +
> + bool
> + RegisterIsCalleeSaved (const lldb_private::RegisterInfo *reg_info);
> +
> +public:
> + lldb::ValueObjectSP
> + GetReturnValueObjectImpl (lldb_private::Thread &thread,
> + lldb_private::ClangASTType &type) const
> override;
> +
> + bool
> + CreateFunctionEntryUnwindPlan (lldb_private::UnwindPlan &unwind_plan)
> override;
> +
> + bool
> + CreateDefaultUnwindPlan (lldb_private::UnwindPlan &unwind_plan)
> override;
> +
> + bool
> + RegisterIsVolatile (const lldb_private::RegisterInfo *reg_info)
> override
> + {
> + return !RegisterIsCalleeSaved (reg_info);
> + }
> +
> + // The SysV i386 ABI requires that stack frames be 16 byte aligned.
> + // When there is a trap handler on the stack, e.g. _sigtramp in
> userland
> + // code, we've seen that the stack pointer is often not aligned
> properly
> + // before the handler is invoked. This means that lldb will stop the
> unwind
> + // early -- before the function which caused the trap.
> + //
> + // To work around this, we relax that alignment to be just word-size
> (4-bytes).
> + // Whitelisting the trap handlers for user space would be easy
> (_sigtramp) but
> + // in other environments there can be a large number of different
> functions
> + // involved in async traps.
> +
> + // ToDo: When __m256 arguments are passed then stack frames should be
> + // 32 byte aligned. Decide what to do for 32 byte alignment checking
> + bool
> + CallFrameAddressIsValid (lldb::addr_t cfa) override
> + {
> + // Make sure the stack call frame addresses are 4 byte aligned
> + if (cfa & (4ull - 1ull))
> + return false; // Not 4 byte aligned
> + if (cfa == 0)
> + return false; // Zero is not a valid stack address
> + return true;
> + }
> +
> + bool
> + CodeAddressIsValid (lldb::addr_t pc) override
> + {
> + // Check whether the address is a valid 32 bit address
> + return (pc <= UINT32_MAX);
> + }
> +
> + const lldb_private::RegisterInfo *
> + GetRegisterInfoArray (uint32_t &count) override;
> + //------------------------------------------------------------------
> + // Static Functions
> + //------------------------------------------------------------------
> + static void
> + Initialize();
> +
> + static void
> + Terminate();
> +
> + static lldb::ABISP
> + CreateInstance (const lldb_private::ArchSpec &arch);
> +
> + //------------------------------------------------------------------
> + // PluginInterface protocol
> + //------------------------------------------------------------------
> + static lldb_private::ConstString
> + GetPluginNameStatic();
> +
> + virtual lldb_private::ConstString
> + GetPluginName();
> +
> + virtual uint32_t
> + GetPluginVersion()
> + {
> + return 1;
> + }
> +
> +private:
> + ABISysV_i386() : lldb_private::ABI() { } // Call CreateInstance
> instead.
> +};
> +
> +#endif // liblldb_ABI_h
>
> Added: lldb/trunk/source/Plugins/ABI/SysV-i386/CMakeLists.txt
> URL:
> http://llvm.org/viewvc/llvm-project/lldb/trunk/source/Plugins/ABI/SysV-i386/CMakeLists.txt?rev=240663&view=auto
>
> ==============================================================================
> --- lldb/trunk/source/Plugins/ABI/SysV-i386/CMakeLists.txt (added)
> +++ lldb/trunk/source/Plugins/ABI/SysV-i386/CMakeLists.txt Thu Jun 25
> 12:50:15 2015
> @@ -0,0 +1,5 @@
> +set(LLVM_NO_RTTI 1)
> +
> +add_lldb_library(lldbPluginABISysV_i386
> + ABISysV_i386.cpp
> + )
>
> Added: lldb/trunk/source/Plugins/ABI/SysV-i386/Makefile
> URL:
> http://llvm.org/viewvc/llvm-project/lldb/trunk/source/Plugins/ABI/SysV-i386/Makefile?rev=240663&view=auto
>
> ==============================================================================
> --- lldb/trunk/source/Plugins/ABI/SysV-i386/Makefile (added)
> +++ lldb/trunk/source/Plugins/ABI/SysV-i386/Makefile Thu Jun 25 12:50:15
> 2015
> @@ -0,0 +1,14 @@
> +##===- source/Plugins/ABI/SysV-i386/Makefile -------------*- Makefile
> -*-===##
> +#
> +# The LLVM Compiler Infrastructure
> +#
> +# This file is distributed under the University of Illinois Open Source
> +# License. See LICENSE.TXT for details.
> +#
>
> +##===----------------------------------------------------------------------===##
> +
> +LLDB_LEVEL := ../../../..
> +LIBRARYNAME := lldbPluginABISysV_i386
> +BUILD_ARCHIVE = 1
> +
> +include $(LLDB_LEVEL)/Makefile
>
> Modified: lldb/trunk/source/Plugins/Makefile
> URL:
> http://llvm.org/viewvc/llvm-project/lldb/trunk/source/Plugins/Makefile?rev=240663&r1=240662&r2=240663&view=diff
>
> ==============================================================================
> --- lldb/trunk/source/Plugins/Makefile (original)
> +++ lldb/trunk/source/Plugins/Makefile Thu Jun 25 12:50:15 2015
> @@ -12,7 +12,7 @@ LLDB_LEVEL := ../..
> include $(LLDB_LEVEL)/../../Makefile.config
>
>
> -PARALLEL_DIRS := ABI/MacOSX-arm ABI/MacOSX-arm64 ABI/MacOSX-i386
> ABI/SysV-x86_64 \
> +PARALLEL_DIRS := ABI/MacOSX-arm ABI/MacOSX-arm64 ABI/MacOSX-i386
> ABI/SysV-i386 ABI/SysV-x86_64 \
> ABI/SysV-arm ABI/SysV-arm64 ABI/SysV-hexagon ABI/SysV-ppc
> ABI/SysV-ppc64 \
> Disassembler/llvm \
> ObjectContainer/BSD-Archive ObjectFile/ELF ObjectFile/PECOFF \
>
>
> _______________________________________________
> lldb-commits mailing list
> lldb-commits at cs.uiuc.edu
> http://lists.cs.uiuc.edu/mailman/listinfo/lldb-commits
>
-------------- next part --------------
An HTML attachment was scrubbed...
URL: <http://lists.llvm.org/pipermail/lldb-commits/attachments/20150626/d3d15508/attachment.html>
More information about the lldb-commits
mailing list