freebsd-dev/utils/TableGen/TableGen.cpp

404 lines
14 KiB
C++
Raw Normal View History

2009-06-02 17:52:33 +00:00
//===- 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.
//
//===----------------------------------------------------------------------===//
2009-11-19 08:59:28 +00:00
#include "AsmMatcherEmitter.h"
#include "AsmWriterEmitter.h"
2009-06-02 17:52:33 +00:00
#include "CallingConvEmitter.h"
2010-05-27 15:15:58 +00:00
#include "ClangASTNodesEmitter.h"
2010-07-13 17:19:57 +00:00
#include "ClangAttrEmitter.h"
2009-11-19 08:59:28 +00:00
#include "ClangDiagnosticsEmitter.h"
#include "ClangSACheckersEmitter.h"
2009-06-02 17:52:33 +00:00
#include "CodeEmitterGen.h"
#include "DAGISelEmitter.h"
2009-12-01 11:07:05 +00:00
#include "DisassemblerEmitter.h"
2010-02-16 09:30:23 +00:00
#include "EDEmitter.h"
#include "Error.h"
2009-06-02 17:52:33 +00:00
#include "FastISelEmitter.h"
2009-11-19 08:59:28 +00:00
#include "InstrInfoEmitter.h"
2009-06-02 17:52:33 +00:00
#include "IntrinsicEmitter.h"
#include "LLVMCConfigurationEmitter.h"
2010-07-13 17:19:57 +00:00
#include "NeonEmitter.h"
2009-11-19 08:59:28 +00:00
#include "OptParserEmitter.h"
#include "PseudoLoweringEmitter.h"
2009-11-19 08:59:28 +00:00
#include "Record.h"
#include "RegisterInfoEmitter.h"
2010-04-03 07:51:10 +00:00
#include "ARMDecoderEmitter.h"
2009-11-19 08:59:28 +00:00
#include "SubtargetEmitter.h"
#include "SetTheory.h"
2009-11-19 08:59:28 +00:00
#include "TGParser.h"
#include "llvm/ADT/OwningPtr.h"
2009-10-14 17:57:32 +00:00
#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"
2009-06-02 17:52:33 +00:00
#include <algorithm>
#include <cstdio>
using namespace llvm;
enum ActionType {
PrintRecords,
GenEmitter,
GenRegisterInfo,
GenInstrInfo,
GenAsmWriter,
GenAsmMatcher,
2010-04-03 07:51:10 +00:00
GenARMDecoder,
2009-12-01 11:07:05 +00:00
GenDisassembler,
GenPseudoLowering,
2009-06-02 17:52:33 +00:00
GenCallingConv,
2010-07-13 17:19:57 +00:00
GenClangAttrClasses,
GenClangAttrImpl,
2010-07-13 17:19:57 +00:00
GenClangAttrList,
GenClangAttrPCHRead,
GenClangAttrPCHWrite,
GenClangAttrSpellingList,
2009-06-02 17:52:33 +00:00
GenClangDiagsDefs,
GenClangDiagGroups,
GenClangDiagsIndexName,
2010-07-13 17:19:57 +00:00
GenClangDeclNodes,
2010-05-27 15:15:58 +00:00
GenClangStmtNodes,
GenClangSACheckers,
2009-06-02 17:52:33 +00:00
GenDAGISel,
GenFastISel,
2009-11-19 08:59:28 +00:00
GenOptParserDefs, GenOptParserImpl,
2009-06-02 17:52:33 +00:00
GenSubtarget,
GenIntrinsic,
GenTgtIntrinsic,
GenLLVMCConf,
GenEDInfo,
2010-07-13 17:19:57 +00:00
GenArmNeon,
GenArmNeonSema,
GenArmNeonTest,
PrintEnums,
PrintSets
2009-06-02 17:52:33 +00:00
};
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",
2009-06-02 17:52:33 +00:00
"Generate instruction descriptions"),
clEnumValN(GenCallingConv, "gen-callingconv",
"Generate calling convention descriptions"),
clEnumValN(GenAsmWriter, "gen-asm-writer",
"Generate assembly writer"),
2010-04-03 07:51:10 +00:00
clEnumValN(GenARMDecoder, "gen-arm-decoder",
"Generate decoders for ARM/Thumb"),
2009-12-01 11:07:05 +00:00
clEnumValN(GenDisassembler, "gen-disassembler",
"Generate disassembler"),
clEnumValN(GenPseudoLowering, "gen-pseudo-lowering",
"Generate pseudo instruction lowering"),
2009-10-14 17:57:32 +00:00
clEnumValN(GenAsmMatcher, "gen-asm-matcher",
"Generate assembly instruction matcher"),
2009-06-02 17:52:33 +00:00
clEnumValN(GenDAGISel, "gen-dag-isel",
"Generate a DAG instruction selector"),
clEnumValN(GenFastISel, "gen-fast-isel",
"Generate a \"fast\" instruction selector"),
2009-11-19 08:59:28 +00:00
clEnumValN(GenOptParserDefs, "gen-opt-parser-defs",
"Generate option definitions"),
clEnumValN(GenOptParserImpl, "gen-opt-parser-impl",
"Generate option parser implementation"),
2009-06-02 17:52:33 +00:00
clEnumValN(GenSubtarget, "gen-subtarget",
"Generate subtarget enumerations"),
clEnumValN(GenIntrinsic, "gen-intrinsic",
"Generate intrinsic information"),
clEnumValN(GenTgtIntrinsic, "gen-tgt-intrinsic",
"Generate target intrinsic information"),
2010-07-13 17:19:57 +00:00
clEnumValN(GenClangAttrClasses, "gen-clang-attr-classes",
"Generate clang attribute clases"),
clEnumValN(GenClangAttrImpl, "gen-clang-attr-impl",
"Generate clang attribute implementations"),
2010-07-13 17:19:57 +00:00
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"),
2009-06-02 17:52:33 +00:00
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"),
2010-07-13 17:19:57 +00:00
clEnumValN(GenClangDeclNodes, "gen-clang-decl-nodes",
"Generate Clang AST declaration nodes"),
2010-05-27 15:15:58 +00:00
clEnumValN(GenClangStmtNodes, "gen-clang-stmt-nodes",
"Generate Clang AST statement nodes"),
clEnumValN(GenClangSACheckers, "gen-clang-sa-checkers",
"Generate Clang Static Analyzer checkers"),
2009-06-02 17:52:33 +00:00
clEnumValN(GenLLVMCConf, "gen-llvmc",
"Generate LLVMC configuration library"),
2010-02-16 09:30:23 +00:00
clEnumValN(GenEDInfo, "gen-enhanced-disassembly-info",
"Generate enhanced disassembly info"),
2010-07-13 17:19:57 +00:00
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"),
2009-06-02 17:52:33 +00:00
clEnumValN(PrintEnums, "print-enums",
"Print enum values for a class"),
clEnumValN(PrintSets, "print-sets",
"Print expanded sets for testing DAG exprs"),
2009-06-02 17:52:33 +00:00
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(""));
2009-06-02 17:52:33 +00:00
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);
2010-05-27 15:15:58 +00:00
2009-06-02 17:52:33 +00:00
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;
2009-06-02 17:52:33 +00:00
sys::PrintStackTraceOnErrorSignal();
PrettyStackTraceProgram X(argc, argv);
cl::ParseCommandLineOptions(argc, argv);
2010-05-27 15:15:58 +00:00
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();
2009-06-02 17:52:33 +00:00
// 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() << DependFilename << ":";
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();
}
2009-06-02 17:52:33 +00:00
switch (Action) {
case PrintRecords:
Out.os() << Records; // No argument, dump all contents
2009-06-02 17:52:33 +00:00
break;
case GenEmitter:
CodeEmitterGen(Records).run(Out.os());
2009-06-02 17:52:33 +00:00
break;
case GenRegisterInfo:
RegisterInfoEmitter(Records).run(Out.os());
2009-06-02 17:52:33 +00:00
break;
case GenInstrInfo:
InstrInfoEmitter(Records).run(Out.os());
2009-06-02 17:52:33 +00:00
break;
case GenCallingConv:
CallingConvEmitter(Records).run(Out.os());
2009-06-02 17:52:33 +00:00
break;
case GenAsmWriter:
AsmWriterEmitter(Records).run(Out.os());
2009-06-02 17:52:33 +00:00
break;
2010-04-03 07:51:10 +00:00
case GenARMDecoder:
ARMDecoderEmitter(Records).run(Out.os());
2010-04-03 07:51:10 +00:00
break;
2009-10-14 17:57:32 +00:00
case GenAsmMatcher:
AsmMatcherEmitter(Records).run(Out.os());
2010-07-13 17:19:57 +00:00
break;
case GenClangAttrClasses:
ClangAttrClassEmitter(Records).run(Out.os());
break;
case GenClangAttrImpl:
ClangAttrImplEmitter(Records).run(Out.os());
2010-07-13 17:19:57 +00:00
break;
case GenClangAttrList:
ClangAttrListEmitter(Records).run(Out.os());
break;
case GenClangAttrPCHRead:
ClangAttrPCHReadEmitter(Records).run(Out.os());
break;
case GenClangAttrPCHWrite:
ClangAttrPCHWriteEmitter(Records).run(Out.os());
2009-10-14 17:57:32 +00:00
break;
case GenClangAttrSpellingList:
ClangAttrSpellingListEmitter(Records).run(Out.os());
break;
2009-06-02 17:52:33 +00:00
case GenClangDiagsDefs:
ClangDiagsDefsEmitter(Records, ClangComponent).run(Out.os());
2009-06-02 17:52:33 +00:00
break;
case GenClangDiagGroups:
ClangDiagGroupsEmitter(Records).run(Out.os());
2010-07-13 17:19:57 +00:00
break;
case GenClangDiagsIndexName:
ClangDiagsIndexNameEmitter(Records).run(Out.os());
break;
2010-07-13 17:19:57 +00:00
case GenClangDeclNodes:
ClangASTNodesEmitter(Records, "Decl", "Decl").run(Out.os());
ClangDeclContextEmitter(Records).run(Out.os());
2009-11-19 08:59:28 +00:00
break;
2010-05-27 15:15:58 +00:00
case GenClangStmtNodes:
ClangASTNodesEmitter(Records, "Stmt", "").run(Out.os());
2010-05-27 15:15:58 +00:00
break;
case GenClangSACheckers:
ClangSACheckersEmitter(Records).run(Out.os());
break;
2009-12-01 11:07:05 +00:00
case GenDisassembler:
DisassemblerEmitter(Records).run(Out.os());
2009-12-01 11:07:05 +00:00
break;
case GenPseudoLowering:
PseudoLoweringEmitter(Records).run(Out.os());
break;
2009-11-19 08:59:28 +00:00
case GenOptParserDefs:
OptParserEmitter(Records, true).run(Out.os());
2009-11-19 08:59:28 +00:00
break;
case GenOptParserImpl:
OptParserEmitter(Records, false).run(Out.os());
2009-11-19 08:59:28 +00:00
break;
2009-06-02 17:52:33 +00:00
case GenDAGISel:
DAGISelEmitter(Records).run(Out.os());
2009-06-02 17:52:33 +00:00
break;
case GenFastISel:
FastISelEmitter(Records).run(Out.os());
2009-06-02 17:52:33 +00:00
break;
case GenSubtarget:
SubtargetEmitter(Records).run(Out.os());
2009-06-02 17:52:33 +00:00
break;
case GenIntrinsic:
IntrinsicEmitter(Records).run(Out.os());
2009-06-02 17:52:33 +00:00
break;
case GenTgtIntrinsic:
IntrinsicEmitter(Records, true).run(Out.os());
2009-06-02 17:52:33 +00:00
break;
case GenLLVMCConf:
LLVMCConfigurationEmitter(Records).run(Out.os());
2010-02-16 09:30:23 +00:00
break;
case GenEDInfo:
EDEmitter(Records).run(Out.os());
2010-07-13 17:19:57 +00:00
break;
case GenArmNeon:
NeonEmitter(Records).run(Out.os());
2010-07-13 17:19:57 +00:00
break;
case GenArmNeonSema:
NeonEmitter(Records).runHeader(Out.os());
2009-06-02 17:52:33 +00:00
break;
case GenArmNeonTest:
NeonEmitter(Records).runTests(Out.os());
break;
2009-06-02 17:52:33 +00:00
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";
2009-06-02 17:52:33 +00:00
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;
}
2009-06-02 17:52:33 +00:00
default:
assert(1 && "Invalid Action");
return 1;
}
2010-05-27 15:15:58 +00:00
// Declare success.
Out.keep();
2009-06-02 17:52:33 +00:00
return 0;
2010-05-27 15:15:58 +00:00
2009-06-02 17:52:33 +00:00
} catch (const TGError &Error) {
PrintError(Error);
2009-06-02 17:52:33 +00:00
} catch (const std::string &Error) {
PrintError(Error);
2009-06-02 17:52:33 +00:00
} catch (const char *Error) {
PrintError(Error);
2009-06-02 17:52:33 +00:00
} catch (...) {
2009-07-04 13:58:26 +00:00
errs() << argv[0] << ": Unknown unexpected exception occurred.\n";
2009-06-02 17:52:33 +00:00
}
2010-05-27 15:15:58 +00:00
2009-06-02 17:52:33 +00:00
return 1;
}