diff options
author | Nate Begeman <natebegeman@mac.com> | 2010-05-28 01:08:32 +0000 |
---|---|---|
committer | Nate Begeman <natebegeman@mac.com> | 2010-05-28 01:08:32 +0000 |
commit | f0767ba1940a38f530ee4b78aaae30d0f4513b3b (patch) | |
tree | 318c709b3d77821a6e08284bdf10b8ca30a4cd5a /utils | |
parent | 91a0905536ad0c5ee542b19726aea8244835b247 (diff) | |
download | external_llvm-f0767ba1940a38f530ee4b78aaae30d0f4513b3b.zip external_llvm-f0767ba1940a38f530ee4b78aaae30d0f4513b3b.tar.gz external_llvm-f0767ba1940a38f530ee4b78aaae30d0f4513b3b.tar.bz2 |
Add support to tablegen for auto-generating arm_neon.h from a tablegen description
of the intrinsics. The goal is to auto-generate both support for GCC-style (vector)
and ARM-style (struct of vector) intrinsics.
This is work in progress, but will be completed soon.
git-svn-id: https://llvm.org/svn/llvm-project/llvm/trunk@104910 91177308-0d34-0410-b5e6-96231b3b80d8
Diffstat (limited to 'utils')
-rw-r--r-- | utils/TableGen/CMakeLists.txt | 1 | ||||
-rw-r--r-- | utils/TableGen/NeonEmitter.cpp | 62 | ||||
-rw-r--r-- | utils/TableGen/NeonEmitter.h | 34 | ||||
-rw-r--r-- | utils/TableGen/TableGen.cpp | 7 |
4 files changed, 104 insertions, 0 deletions
diff --git a/utils/TableGen/CMakeLists.txt b/utils/TableGen/CMakeLists.txt index 731cde92..05520c1 100644 --- a/utils/TableGen/CMakeLists.txt +++ b/utils/TableGen/CMakeLists.txt @@ -22,6 +22,7 @@ add_executable(tblgen InstrInfoEmitter.cpp IntrinsicEmitter.cpp LLVMCConfigurationEmitter.cpp + NeonEmitter.cpp OptParserEmitter.cpp Record.cpp RegisterInfoEmitter.cpp diff --git a/utils/TableGen/NeonEmitter.cpp b/utils/TableGen/NeonEmitter.cpp new file mode 100644 index 0000000..dcbcf75 --- /dev/null +++ b/utils/TableGen/NeonEmitter.cpp @@ -0,0 +1,62 @@ +//===- NeonEmitter.cpp - Generate arm_neon.h for use with clang -*- C++ -*-===// +// +// The LLVM Compiler Infrastructure +// +// This file is distributed under the University of Illinois Open Source +// License. See LICENSE.TXT for details. +// +//===----------------------------------------------------------------------===// +// +// This tablegen backend is responsible for emitting arm_neon.h, which includes +// a declaration and definition of each function specified by the ARM NEON +// compiler interface. See ARM document DUI0348B. +// +//===----------------------------------------------------------------------===// + +#include "NeonEmitter.h" +#include "Record.h" +#include "llvm/ADT/StringExtras.h" +#include "llvm/ADT/StringMap.h" +#include <string> + +using namespace llvm; + +void NeonEmitter::run(raw_ostream &OS) { + EmitSourceFileHeader("ARM NEON Header", OS); + + // FIXME: emit license into file? + + OS << "#ifndef __ARM_NEON_H\n"; + OS << "#define __ARM_NEON_H\n\n"; + + OS << "#ifndef __ARM_NEON__\n"; + OS << "#error \"NEON support not enabled\"\n"; + OS << "#endif\n\n"; + + OS << "#include <stdint.h>\n\n"; + + // EmitTypedefs(OS); + + // Process Records + + std::vector<Record*> RV = Records.getAllDerivedDefinitions("Inst"); + + // Unique the pattern types, and assign them + + // emit #define directives for uniq'd prototypes + + // emit record directives + + for (unsigned i = 0, e = RV.size(); i != e; ++i) { + Record *R = RV[i]; + + OS << LowercaseString(R->getName()) << "\n"; + + std::string Types = R->getValueAsString("Types"); + std::string Pattern = R->getValueAsString("Pattern"); + + OS << Types << "\n" << Pattern << "\n\n"; + } + + OS << "#endif /* __ARM_NEON_H */\n"; +} diff --git a/utils/TableGen/NeonEmitter.h b/utils/TableGen/NeonEmitter.h new file mode 100644 index 0000000..dc20794 --- /dev/null +++ b/utils/TableGen/NeonEmitter.h @@ -0,0 +1,34 @@ +//===- NeonEmitter.h - Generate arm_neon.h for use with clang ---*- C++ -*-===// +// +// The LLVM Compiler Infrastructure +// +// This file is distributed under the University of Illinois Open Source +// License. See LICENSE.TXT for details. +// +//===----------------------------------------------------------------------===// +// +// This tablegen backend is responsible for emitting arm_neon.h, which includes +// a declaration and definition of each function specified by the ARM NEON +// compiler interface. See ARM document DUI0348B. +// +//===----------------------------------------------------------------------===// + +#ifndef NEON_EMITTER_H +#define NEON_EMITTER_H + +#include "TableGenBackend.h" + +namespace llvm { + + class NeonEmitter : public TableGenBackend { + RecordKeeper &Records; + public: + NeonEmitter(RecordKeeper &R) : Records(R) {} + + // runHeader - Emit a header file that allows use of the instruction table. + void run(raw_ostream &o); + }; + +} // End llvm namespace + +#endif diff --git a/utils/TableGen/TableGen.cpp b/utils/TableGen/TableGen.cpp index 0fbfec3..9485864 100644 --- a/utils/TableGen/TableGen.cpp +++ b/utils/TableGen/TableGen.cpp @@ -29,6 +29,7 @@ #include "InstrInfoEmitter.h" #include "IntrinsicEmitter.h" #include "LLVMCConfigurationEmitter.h" +#include "NeonEmitter.h" #include "OptParserEmitter.h" #include "Record.h" #include "RegisterInfoEmitter.h" @@ -63,6 +64,7 @@ enum ActionType { GenTgtIntrinsic, GenLLVMCConf, GenEDHeader, GenEDInfo, + GenNeonHeader, PrintEnums }; @@ -119,6 +121,8 @@ namespace { "Generate enhanced disassembly info header"), clEnumValN(GenEDInfo, "gen-enhanced-disassembly-info", "Generate enhanced disassembly info"), + clEnumValN(GenNeonHeader, "gen-arm-neon-header", + "Generate arm_neon.h for clang"), clEnumValN(PrintEnums, "print-enums", "Print enum values for a class"), clEnumValEnd)); @@ -280,6 +284,9 @@ int main(int argc, char **argv) { case GenEDInfo: EDEmitter(Records).run(Out); break; + case GenNeonHeader: + NeonEmitter(Records).run(*Out); + break; case PrintEnums: { std::vector<Record*> Recs = Records.getAllDerivedDefinitions(Class); |