mirror of
https://github.com/RPCS3/llvm.git
synced 2024-12-02 16:56:39 +00:00
eae5a13078
git-svn-id: https://llvm.org/svn/llvm-project/llvm/trunk@140121 91177308-0d34-0410-b5e6-96231b3b80d8
404 lines
14 KiB
C++
404 lines
14 KiB
C++
//===- TableGen.cpp - Top-Level TableGen implementation -------------------===//
|
|
//
|
|
// The LLVM Compiler Infrastructure
|
|
//
|
|
// This file is distributed under the University of Illinois Open Source
|
|
// License. See LICENSE.TXT for details.
|
|
//
|
|
//===----------------------------------------------------------------------===//
|
|
//
|
|
// TableGen is a tool which can be used to build up a description of something,
|
|
// then invoke one or more "tablegen backends" to emit information about the
|
|
// description in some predefined format. In practice, this is used by the LLVM
|
|
// code generators to automate generation of a code generator through a
|
|
// high-level description of the target.
|
|
//
|
|
//===----------------------------------------------------------------------===//
|
|
|
|
#include "AsmMatcherEmitter.h"
|
|
#include "AsmWriterEmitter.h"
|
|
#include "CallingConvEmitter.h"
|
|
#include "ClangASTNodesEmitter.h"
|
|
#include "ClangAttrEmitter.h"
|
|
#include "ClangDiagnosticsEmitter.h"
|
|
#include "ClangSACheckersEmitter.h"
|
|
#include "CodeEmitterGen.h"
|
|
#include "DAGISelEmitter.h"
|
|
#include "DisassemblerEmitter.h"
|
|
#include "EDEmitter.h"
|
|
#include "Error.h"
|
|
#include "FastISelEmitter.h"
|
|
#include "InstrInfoEmitter.h"
|
|
#include "IntrinsicEmitter.h"
|
|
#include "NeonEmitter.h"
|
|
#include "OptParserEmitter.h"
|
|
#include "PseudoLoweringEmitter.h"
|
|
#include "Record.h"
|
|
#include "RegisterInfoEmitter.h"
|
|
#include "ARMDecoderEmitter.h"
|
|
#include "SubtargetEmitter.h"
|
|
#include "SetTheory.h"
|
|
#include "TGParser.h"
|
|
#include "llvm/ADT/OwningPtr.h"
|
|
#include "llvm/Support/CommandLine.h"
|
|
#include "llvm/Support/MemoryBuffer.h"
|
|
#include "llvm/Support/PrettyStackTrace.h"
|
|
#include "llvm/Support/ToolOutputFile.h"
|
|
#include "llvm/Support/Signals.h"
|
|
#include "llvm/Support/system_error.h"
|
|
#include <algorithm>
|
|
#include <cstdio>
|
|
using namespace llvm;
|
|
|
|
enum ActionType {
|
|
PrintRecords,
|
|
GenEmitter,
|
|
GenRegisterInfo,
|
|
GenInstrInfo,
|
|
GenAsmWriter,
|
|
GenAsmMatcher,
|
|
GenARMDecoder,
|
|
GenDisassembler,
|
|
GenPseudoLowering,
|
|
GenCallingConv,
|
|
GenClangAttrClasses,
|
|
GenClangAttrImpl,
|
|
GenClangAttrList,
|
|
GenClangAttrPCHRead,
|
|
GenClangAttrPCHWrite,
|
|
GenClangAttrSpellingList,
|
|
GenClangAttrLateParsedList,
|
|
GenClangDiagsDefs,
|
|
GenClangDiagGroups,
|
|
GenClangDiagsIndexName,
|
|
GenClangDeclNodes,
|
|
GenClangStmtNodes,
|
|
GenClangSACheckers,
|
|
GenDAGISel,
|
|
GenFastISel,
|
|
GenOptParserDefs, GenOptParserImpl,
|
|
GenSubtarget,
|
|
GenIntrinsic,
|
|
GenTgtIntrinsic,
|
|
GenEDInfo,
|
|
GenArmNeon,
|
|
GenArmNeonSema,
|
|
GenArmNeonTest,
|
|
PrintEnums,
|
|
PrintSets
|
|
};
|
|
|
|
namespace {
|
|
cl::opt<ActionType>
|
|
Action(cl::desc("Action to perform:"),
|
|
cl::values(clEnumValN(PrintRecords, "print-records",
|
|
"Print all records to stdout (default)"),
|
|
clEnumValN(GenEmitter, "gen-emitter",
|
|
"Generate machine code emitter"),
|
|
clEnumValN(GenRegisterInfo, "gen-register-info",
|
|
"Generate registers and register classes info"),
|
|
clEnumValN(GenInstrInfo, "gen-instr-info",
|
|
"Generate instruction descriptions"),
|
|
clEnumValN(GenCallingConv, "gen-callingconv",
|
|
"Generate calling convention descriptions"),
|
|
clEnumValN(GenAsmWriter, "gen-asm-writer",
|
|
"Generate assembly writer"),
|
|
clEnumValN(GenARMDecoder, "gen-arm-decoder",
|
|
"Generate decoders for ARM/Thumb"),
|
|
clEnumValN(GenDisassembler, "gen-disassembler",
|
|
"Generate disassembler"),
|
|
clEnumValN(GenPseudoLowering, "gen-pseudo-lowering",
|
|
"Generate pseudo instruction lowering"),
|
|
clEnumValN(GenAsmMatcher, "gen-asm-matcher",
|
|
"Generate assembly instruction matcher"),
|
|
clEnumValN(GenDAGISel, "gen-dag-isel",
|
|
"Generate a DAG instruction selector"),
|
|
clEnumValN(GenFastISel, "gen-fast-isel",
|
|
"Generate a \"fast\" instruction selector"),
|
|
clEnumValN(GenOptParserDefs, "gen-opt-parser-defs",
|
|
"Generate option definitions"),
|
|
clEnumValN(GenOptParserImpl, "gen-opt-parser-impl",
|
|
"Generate option parser implementation"),
|
|
clEnumValN(GenSubtarget, "gen-subtarget",
|
|
"Generate subtarget enumerations"),
|
|
clEnumValN(GenIntrinsic, "gen-intrinsic",
|
|
"Generate intrinsic information"),
|
|
clEnumValN(GenTgtIntrinsic, "gen-tgt-intrinsic",
|
|
"Generate target intrinsic information"),
|
|
clEnumValN(GenClangAttrClasses, "gen-clang-attr-classes",
|
|
"Generate clang attribute clases"),
|
|
clEnumValN(GenClangAttrImpl, "gen-clang-attr-impl",
|
|
"Generate clang attribute implementations"),
|
|
clEnumValN(GenClangAttrList, "gen-clang-attr-list",
|
|
"Generate a clang attribute list"),
|
|
clEnumValN(GenClangAttrPCHRead, "gen-clang-attr-pch-read",
|
|
"Generate clang PCH attribute reader"),
|
|
clEnumValN(GenClangAttrPCHWrite, "gen-clang-attr-pch-write",
|
|
"Generate clang PCH attribute writer"),
|
|
clEnumValN(GenClangAttrSpellingList,
|
|
"gen-clang-attr-spelling-list",
|
|
"Generate a clang attribute spelling list"),
|
|
clEnumValN(GenClangAttrLateParsedList,
|
|
"gen-clang-attr-late-parsed-list",
|
|
"Generate a clang attribute LateParsed list"),
|
|
clEnumValN(GenClangDiagsDefs, "gen-clang-diags-defs",
|
|
"Generate Clang diagnostics definitions"),
|
|
clEnumValN(GenClangDiagGroups, "gen-clang-diag-groups",
|
|
"Generate Clang diagnostic groups"),
|
|
clEnumValN(GenClangDiagsIndexName,
|
|
"gen-clang-diags-index-name",
|
|
"Generate Clang diagnostic name index"),
|
|
clEnumValN(GenClangDeclNodes, "gen-clang-decl-nodes",
|
|
"Generate Clang AST declaration nodes"),
|
|
clEnumValN(GenClangStmtNodes, "gen-clang-stmt-nodes",
|
|
"Generate Clang AST statement nodes"),
|
|
clEnumValN(GenClangSACheckers, "gen-clang-sa-checkers",
|
|
"Generate Clang Static Analyzer checkers"),
|
|
clEnumValN(GenEDInfo, "gen-enhanced-disassembly-info",
|
|
"Generate enhanced disassembly info"),
|
|
clEnumValN(GenArmNeon, "gen-arm-neon",
|
|
"Generate arm_neon.h for clang"),
|
|
clEnumValN(GenArmNeonSema, "gen-arm-neon-sema",
|
|
"Generate ARM NEON sema support for clang"),
|
|
clEnumValN(GenArmNeonTest, "gen-arm-neon-test",
|
|
"Generate ARM NEON tests for clang"),
|
|
clEnumValN(PrintEnums, "print-enums",
|
|
"Print enum values for a class"),
|
|
clEnumValN(PrintSets, "print-sets",
|
|
"Print expanded sets for testing DAG exprs"),
|
|
clEnumValEnd));
|
|
|
|
cl::opt<std::string>
|
|
Class("class", cl::desc("Print Enum list for this class"),
|
|
cl::value_desc("class name"));
|
|
|
|
cl::opt<std::string>
|
|
OutputFilename("o", cl::desc("Output filename"), cl::value_desc("filename"),
|
|
cl::init("-"));
|
|
|
|
cl::opt<std::string>
|
|
DependFilename("d", cl::desc("Dependency filename"), cl::value_desc("filename"),
|
|
cl::init(""));
|
|
|
|
cl::opt<std::string>
|
|
InputFilename(cl::Positional, cl::desc("<input file>"), cl::init("-"));
|
|
|
|
cl::list<std::string>
|
|
IncludeDirs("I", cl::desc("Directory of include files"),
|
|
cl::value_desc("directory"), cl::Prefix);
|
|
|
|
cl::opt<std::string>
|
|
ClangComponent("clang-component",
|
|
cl::desc("Only use warnings from specified component"),
|
|
cl::value_desc("component"), cl::Hidden);
|
|
}
|
|
|
|
|
|
int main(int argc, char **argv) {
|
|
RecordKeeper Records;
|
|
|
|
sys::PrintStackTraceOnErrorSignal();
|
|
PrettyStackTraceProgram X(argc, argv);
|
|
cl::ParseCommandLineOptions(argc, argv);
|
|
|
|
|
|
try {
|
|
// Parse the input file.
|
|
OwningPtr<MemoryBuffer> File;
|
|
if (error_code ec = MemoryBuffer::getFileOrSTDIN(InputFilename.c_str(), File)) {
|
|
errs() << "Could not open input file '" << InputFilename << "': "
|
|
<< ec.message() <<"\n";
|
|
return 1;
|
|
}
|
|
MemoryBuffer *F = File.take();
|
|
|
|
// Tell SrcMgr about this buffer, which is what TGParser will pick up.
|
|
SrcMgr.AddNewSourceBuffer(F, SMLoc());
|
|
|
|
// Record the location of the include directory so that the lexer can find
|
|
// it later.
|
|
SrcMgr.setIncludeDirs(IncludeDirs);
|
|
|
|
TGParser Parser(SrcMgr, Records);
|
|
|
|
if (Parser.ParseFile())
|
|
return 1;
|
|
|
|
std::string Error;
|
|
tool_output_file Out(OutputFilename.c_str(), Error);
|
|
if (!Error.empty()) {
|
|
errs() << argv[0] << ": error opening " << OutputFilename
|
|
<< ":" << Error << "\n";
|
|
return 1;
|
|
}
|
|
if (!DependFilename.empty()) {
|
|
if (OutputFilename == "-") {
|
|
errs() << argv[0] << ": the option -d must be used together with -o\n";
|
|
return 1;
|
|
}
|
|
tool_output_file DepOut(DependFilename.c_str(), Error);
|
|
if (!Error.empty()) {
|
|
errs() << argv[0] << ": error opening " << DependFilename
|
|
<< ":" << Error << "\n";
|
|
return 1;
|
|
}
|
|
DepOut.os() << OutputFilename << ":";
|
|
const std::vector<std::string> &Dependencies = Parser.getDependencies();
|
|
for (std::vector<std::string>::const_iterator I = Dependencies.begin(),
|
|
E = Dependencies.end();
|
|
I != E; ++I) {
|
|
DepOut.os() << " " << (*I);
|
|
}
|
|
DepOut.os() << "\n";
|
|
DepOut.keep();
|
|
}
|
|
|
|
switch (Action) {
|
|
case PrintRecords:
|
|
Out.os() << Records; // No argument, dump all contents
|
|
break;
|
|
case GenEmitter:
|
|
CodeEmitterGen(Records).run(Out.os());
|
|
break;
|
|
case GenRegisterInfo:
|
|
RegisterInfoEmitter(Records).run(Out.os());
|
|
break;
|
|
case GenInstrInfo:
|
|
InstrInfoEmitter(Records).run(Out.os());
|
|
break;
|
|
case GenCallingConv:
|
|
CallingConvEmitter(Records).run(Out.os());
|
|
break;
|
|
case GenAsmWriter:
|
|
AsmWriterEmitter(Records).run(Out.os());
|
|
break;
|
|
case GenARMDecoder:
|
|
ARMDecoderEmitter(Records).run(Out.os());
|
|
break;
|
|
case GenAsmMatcher:
|
|
AsmMatcherEmitter(Records).run(Out.os());
|
|
break;
|
|
case GenClangAttrClasses:
|
|
ClangAttrClassEmitter(Records).run(Out.os());
|
|
break;
|
|
case GenClangAttrImpl:
|
|
ClangAttrImplEmitter(Records).run(Out.os());
|
|
break;
|
|
case GenClangAttrList:
|
|
ClangAttrListEmitter(Records).run(Out.os());
|
|
break;
|
|
case GenClangAttrPCHRead:
|
|
ClangAttrPCHReadEmitter(Records).run(Out.os());
|
|
break;
|
|
case GenClangAttrPCHWrite:
|
|
ClangAttrPCHWriteEmitter(Records).run(Out.os());
|
|
break;
|
|
case GenClangAttrSpellingList:
|
|
ClangAttrSpellingListEmitter(Records).run(Out.os());
|
|
break;
|
|
case GenClangAttrLateParsedList:
|
|
ClangAttrLateParsedListEmitter(Records).run(Out.os());
|
|
break;
|
|
case GenClangDiagsDefs:
|
|
ClangDiagsDefsEmitter(Records, ClangComponent).run(Out.os());
|
|
break;
|
|
case GenClangDiagGroups:
|
|
ClangDiagGroupsEmitter(Records).run(Out.os());
|
|
break;
|
|
case GenClangDiagsIndexName:
|
|
ClangDiagsIndexNameEmitter(Records).run(Out.os());
|
|
break;
|
|
case GenClangDeclNodes:
|
|
ClangASTNodesEmitter(Records, "Decl", "Decl").run(Out.os());
|
|
ClangDeclContextEmitter(Records).run(Out.os());
|
|
break;
|
|
case GenClangStmtNodes:
|
|
ClangASTNodesEmitter(Records, "Stmt", "").run(Out.os());
|
|
break;
|
|
case GenClangSACheckers:
|
|
ClangSACheckersEmitter(Records).run(Out.os());
|
|
break;
|
|
case GenDisassembler:
|
|
DisassemblerEmitter(Records).run(Out.os());
|
|
break;
|
|
case GenPseudoLowering:
|
|
PseudoLoweringEmitter(Records).run(Out.os());
|
|
break;
|
|
case GenOptParserDefs:
|
|
OptParserEmitter(Records, true).run(Out.os());
|
|
break;
|
|
case GenOptParserImpl:
|
|
OptParserEmitter(Records, false).run(Out.os());
|
|
break;
|
|
case GenDAGISel:
|
|
DAGISelEmitter(Records).run(Out.os());
|
|
break;
|
|
case GenFastISel:
|
|
FastISelEmitter(Records).run(Out.os());
|
|
break;
|
|
case GenSubtarget:
|
|
SubtargetEmitter(Records).run(Out.os());
|
|
break;
|
|
case GenIntrinsic:
|
|
IntrinsicEmitter(Records).run(Out.os());
|
|
break;
|
|
case GenTgtIntrinsic:
|
|
IntrinsicEmitter(Records, true).run(Out.os());
|
|
break;
|
|
case GenEDInfo:
|
|
EDEmitter(Records).run(Out.os());
|
|
break;
|
|
case GenArmNeon:
|
|
NeonEmitter(Records).run(Out.os());
|
|
break;
|
|
case GenArmNeonSema:
|
|
NeonEmitter(Records).runHeader(Out.os());
|
|
break;
|
|
case GenArmNeonTest:
|
|
NeonEmitter(Records).runTests(Out.os());
|
|
break;
|
|
case PrintEnums:
|
|
{
|
|
std::vector<Record*> Recs = Records.getAllDerivedDefinitions(Class);
|
|
for (unsigned i = 0, e = Recs.size(); i != e; ++i)
|
|
Out.os() << Recs[i]->getName() << ", ";
|
|
Out.os() << "\n";
|
|
break;
|
|
}
|
|
case PrintSets:
|
|
{
|
|
SetTheory Sets;
|
|
Sets.addFieldExpander("Set", "Elements");
|
|
std::vector<Record*> Recs = Records.getAllDerivedDefinitions("Set");
|
|
for (unsigned i = 0, e = Recs.size(); i != e; ++i) {
|
|
Out.os() << Recs[i]->getName() << " = [";
|
|
const std::vector<Record*> *Elts = Sets.expand(Recs[i]);
|
|
assert(Elts && "Couldn't expand Set instance");
|
|
for (unsigned ei = 0, ee = Elts->size(); ei != ee; ++ei)
|
|
Out.os() << ' ' << (*Elts)[ei]->getName();
|
|
Out.os() << " ]\n";
|
|
}
|
|
break;
|
|
}
|
|
default:
|
|
assert(1 && "Invalid Action");
|
|
return 1;
|
|
}
|
|
|
|
// Declare success.
|
|
Out.keep();
|
|
return 0;
|
|
|
|
} catch (const TGError &Error) {
|
|
PrintError(Error);
|
|
} catch (const std::string &Error) {
|
|
PrintError(Error);
|
|
} catch (const char *Error) {
|
|
PrintError(Error);
|
|
} catch (...) {
|
|
errs() << argv[0] << ": Unknown unexpected exception occurred.\n";
|
|
}
|
|
|
|
return 1;
|
|
}
|