Compare commits
| Author | SHA1 | Date | |
|---|---|---|---|
|
|
55d62ff354 | ||
|
|
e311b1098a | ||
|
|
aea633ac8d | ||
|
|
9f9902c613 | ||
|
|
eb4e0f4529 | ||
|
|
821ead0c7a | ||
|
|
351d809306 | ||
|
|
840b816804 | ||
|
|
b17ab2d148 |
No files matched your search
+7
-5
@@ -1,10 +1,12 @@
|
||||
**/__pycache__
|
||||
**/.ipynb_checkpoints
|
||||
**/.pytest_cache
|
||||
**/.DS_Store
|
||||
**/*.pyc
|
||||
__pycache__
|
||||
.ipynb_checkpoints
|
||||
.pytest_cache
|
||||
.DS_Store
|
||||
*.pyc
|
||||
docs/_build
|
||||
build
|
||||
dist
|
||||
.idea
|
||||
.vscode
|
||||
src/kyupy.egg-info
|
||||
*nogit*
|
||||
@@ -0,0 +1,20 @@
|
||||
version: 2
|
||||
|
||||
build:
|
||||
os: "ubuntu-20.04"
|
||||
tools:
|
||||
python: "3.8"
|
||||
jobs:
|
||||
post_create_environment:
|
||||
- python -m pip install sphinx_rtd_theme
|
||||
|
||||
sphinx:
|
||||
fail_on_warning: true
|
||||
configuration: docs/conf.py
|
||||
|
||||
python:
|
||||
# Install our python package before building the docs
|
||||
install:
|
||||
- method: pip
|
||||
path: .
|
||||
|
||||
-1344
File diff suppressed because it is too large.
Load diff
+1
-1
@@ -1,6 +1,6 @@
|
||||
MIT License
|
||||
|
||||
Copyright (c) 2020-2021 Stefan Holst
|
||||
Copyright (c) 2020-2023 Stefan Holst
|
||||
|
||||
Permission is hereby granted, free of charge, to any person obtaining a copy
|
||||
of this software and associated documentation files (the "Software"), to deal
|
||||
|
||||
+1
-1
@@ -1,5 +1,5 @@
|
||||
include *.ipynb
|
||||
include *.txt
|
||||
recursive-include examples *.ipynb
|
||||
recursive-include tests *.bench
|
||||
recursive-include tests *.gz
|
||||
recursive-include tests *.py
|
||||
|
||||
+9
-5
@@ -6,7 +6,7 @@ It contains fundamental building blocks for research software in the fields of V
|
||||
|
||||
* Efficient data structures for gate-level circuits and related design data.
|
||||
* Partial `lark <https://github.com/lark-parser/lark>`_ parsers for common design files like
|
||||
bench, gate-level verilog, standard delay format (SDF), standard test interface language (STIL).
|
||||
bench, gate-level Verilog, standard delay format (SDF), standard test interface language (STIL), design exchange format (DEF).
|
||||
* Bit-parallel gate-level 2-, 4-, and 8-valued logic simulation.
|
||||
* GPU-accelerated high-throughput gate-level timing simulation.
|
||||
* High-performance through the use of `numpy <https://numpy.org>`_ and `numba <https://numba.pydata.org>`_.
|
||||
@@ -16,13 +16,17 @@ Getting Started
|
||||
---------------
|
||||
|
||||
KyuPy is available in `PyPI <https://pypi.org/project/kyupy>`_.
|
||||
It requires Python 3.6 or newer, `lark-parser <https://pypi.org/project/lark-parser>`_, and `numpy`_.
|
||||
It requires Python 3.8 or newer, `lark-parser <https://pypi.org/project/lark-parser>`_, and `numpy`_.
|
||||
Although optional, `numba`_ should be installed for best performance.
|
||||
GPU/CUDA support in numba may `require some additional setup <https://numba.pydata.org/numba-doc/latest/cuda/index.html>`_.
|
||||
GPU/CUDA support in numba may `require some additional setup <https://numba.readthedocs.io/en/stable/cuda/index.html>`_.
|
||||
If numba is not available, KyuPy will automatically fall back to slow, pure Python execution.
|
||||
|
||||
The Jupyter Notebook `Demo.ipynb <https://github.com/s-holst/kyupy/blob/main/Demo.ipynb>`_ contains some useful examples to get familiar with the API.
|
||||
The Jupyter Notebook `Introduction.ipynb <https://github.com/s-holst/kyupy/blob/main/examples/Introduction.ipynb>`_ contains some useful examples to get familiar with the API.
|
||||
|
||||
|
||||
Development
|
||||
-----------
|
||||
|
||||
To work with the latest pre-release source code, clone the `KyuPy GitHub repository <https://github.com/s-holst/kyupy>`_.
|
||||
Run ``pip3 install --user -e .`` within your local checkout to make the package available in your Python environment.
|
||||
Run ``pip install -e .`` within your local checkout to make the package available in your Python environment.
|
||||
The source code comes with tests that can be run with ``pytest``.
|
||||
@@ -1,3 +1,5 @@
|
||||
# pip install sphinx sphinx-rtd-theme
|
||||
#
|
||||
# Minimal makefile for Sphinx documentation
|
||||
#
|
||||
|
||||
|
||||
@@ -0,0 +1,13 @@
|
||||
Circuit Graph - :mod:`kyupy.circuit`
|
||||
====================================
|
||||
|
||||
.. automodule:: kyupy.circuit
|
||||
|
||||
.. autoclass:: kyupy.circuit.Node
|
||||
:members:
|
||||
|
||||
.. autoclass:: kyupy.circuit.Line
|
||||
:members:
|
||||
|
||||
.. autoclass:: kyupy.circuit.Circuit
|
||||
:members:
|
||||
+3
-3
@@ -20,11 +20,11 @@ sys.path.insert(0, os.path.abspath('../src'))
|
||||
# -- Project information -----------------------------------------------------
|
||||
|
||||
project = 'KyuPy'
|
||||
copyright = '2020-2021, Stefan Holst'
|
||||
copyright = '2020-2023, Stefan Holst'
|
||||
author = 'Stefan Holst'
|
||||
|
||||
# The full version, including alpha/beta/rc tags
|
||||
release = '0.0.3'
|
||||
release = '0.0.5'
|
||||
|
||||
|
||||
# -- General configuration ---------------------------------------------------
|
||||
@@ -57,7 +57,7 @@ html_theme = 'sphinx_rtd_theme'
|
||||
# Add any paths that contain custom static files (such as style sheets) here,
|
||||
# relative to this directory. They are copied after the builtin static files,
|
||||
# so a file named "default.css" will overwrite the builtin "default.css".
|
||||
html_static_path = ['_static']
|
||||
#html_static_path = ['_static']
|
||||
|
||||
autodoc_default_options = {
|
||||
'member-order': 'bysource',
|
||||
|
||||
@@ -1,29 +0,0 @@
|
||||
Data Structures
|
||||
===============
|
||||
|
||||
KyuPy provides two types of core data structures, one for gate-level circuits, and a few others for representing and storing logic data and signal values.
|
||||
The data structures are designed to work together nicely with numpy arrays.
|
||||
For example, all the nodes and connections in the circuit graph have consecutive integer indices that can be used to access ndarrays with associated data.
|
||||
Circuit graphs also define an ordering of inputs, outputs and other nodes to easily process test vector data and alike.
|
||||
|
||||
Circuit Graph - :mod:`kyupy.circuit`
|
||||
------------------------------------
|
||||
|
||||
.. automodule:: kyupy.circuit
|
||||
|
||||
.. autoclass:: kyupy.circuit.Node
|
||||
:members:
|
||||
|
||||
.. autoclass:: kyupy.circuit.Line
|
||||
:members:
|
||||
|
||||
.. autoclass:: kyupy.circuit.Circuit
|
||||
:members:
|
||||
|
||||
Multi-Valued Logic - :mod:`kyupy.logic`
|
||||
---------------------------------------
|
||||
|
||||
.. automodule:: kyupy.logic
|
||||
:members:
|
||||
|
||||
|
||||
+4
-2
@@ -4,9 +4,11 @@ API Reference
|
||||
-------------
|
||||
|
||||
.. toctree::
|
||||
:maxdepth: 2
|
||||
:maxdepth: 1
|
||||
|
||||
datastructures
|
||||
circuit
|
||||
logic
|
||||
techlib
|
||||
parsers
|
||||
simulators
|
||||
miscellaneous
|
||||
|
||||
@@ -0,0 +1,7 @@
|
||||
Multi-Valued Logic - :mod:`kyupy.logic`
|
||||
=======================================
|
||||
|
||||
.. automodule:: kyupy.logic
|
||||
:members:
|
||||
|
||||
|
||||
@@ -4,7 +4,3 @@ Miscellaneous
|
||||
.. automodule:: kyupy
|
||||
:members:
|
||||
|
||||
.. automodule:: kyupy.techlib
|
||||
:members:
|
||||
|
||||
|
||||
@@ -40,3 +40,12 @@ Standard Delay Format - :mod:`kyupy.sdf`
|
||||
|
||||
.. autoclass:: kyupy.sdf.DelayFile
|
||||
:members:
|
||||
|
||||
Design Exchange Format - :mod:`kyupy.def_file`
|
||||
----------------------------------------------
|
||||
|
||||
.. automodule:: kyupy.def_file
|
||||
:members: parse, load
|
||||
|
||||
.. autoclass:: kyupy.def_file.DefFile
|
||||
:members:
|
||||
@@ -1,6 +1,11 @@
|
||||
Simulators
|
||||
==========
|
||||
|
||||
KyuPy's simulators are optimized for cells with at most 4 inputs and 1 output.
|
||||
|
||||
More complex cells must be mapped to simulation primitives first.
|
||||
|
||||
|
||||
Logic Simulation - :mod:`kyupy.logic_sim`
|
||||
-----------------------------------------
|
||||
|
||||
|
||||
@@ -0,0 +1,7 @@
|
||||
Technology Libraries
|
||||
====================
|
||||
|
||||
.. automodule:: kyupy.techlib
|
||||
:members:
|
||||
|
||||
|
||||
File diff suppressed because it is too large.
Load diff
@@ -0,0 +1,32 @@
|
||||
[project]
|
||||
name = "kyupy"
|
||||
version = "0.0.5"
|
||||
authors = [
|
||||
{ name="Stefan Holst", email="mail@s-holst.de" },
|
||||
]
|
||||
description = 'High-performance processing and analysis of non-hierarchical VLSI designs'
|
||||
readme = "README.rst"
|
||||
requires_python = ">=3.8"
|
||||
dependencies = [
|
||||
"numpy>=1.17.0",
|
||||
"lark-parser>=0.8.0",
|
||||
]
|
||||
classifiers = [
|
||||
"Development Status :: 3 - Alpha",
|
||||
"Environment :: GPU :: NVIDIA CUDA",
|
||||
"Intended Audience :: Science/Research",
|
||||
"Topic :: Scientific/Engineering :: Electronic Design Automation (EDA)",
|
||||
"License :: OSI Approved :: MIT License",
|
||||
"Operating System :: OS Independent",
|
||||
"Programming Language :: Python :: 3",
|
||||
]
|
||||
license = "MIT"
|
||||
license-files = ["LICENSE.txt"]
|
||||
|
||||
[project.urls]
|
||||
homepage = "https://github.com/s-holst/kyupy"
|
||||
|
||||
[build-system]
|
||||
requires = ["hatchling"]
|
||||
build-backend = "hatchling.build"
|
||||
|
||||
@@ -1,41 +0,0 @@
|
||||
from setuptools import setup, find_packages
|
||||
|
||||
with open('README.rst', 'r') as f:
|
||||
long_description = f.read()
|
||||
|
||||
setup(
|
||||
name='kyupy',
|
||||
version='0.0.3',
|
||||
description='High-performance processing and analysis of non-hierarchical VLSI designs',
|
||||
long_description=long_description,
|
||||
long_description_content_type='text/x-rst',
|
||||
packages=find_packages(where='src'),
|
||||
package_dir={'': 'src'},
|
||||
url='https://github.com/s-holst/kyupy',
|
||||
author='Stefan Holst',
|
||||
author_email='mail@s-holst.de',
|
||||
python_requires='>=3.6',
|
||||
install_requires=[
|
||||
'numpy>=1.17.0',
|
||||
'lark-parser>=0.8.0'
|
||||
],
|
||||
extras_requires={
|
||||
'dev': [
|
||||
'pytest>=6.1',
|
||||
],
|
||||
},
|
||||
classifiers=[
|
||||
'Development Status :: 3 - Alpha',
|
||||
'Environment :: GPU :: NVIDIA CUDA',
|
||||
'Intended Audience :: Science/Research',
|
||||
'Topic :: Scientific/Engineering :: Electronic Design Automation (EDA)',
|
||||
'License :: OSI Approved :: MIT License',
|
||||
'Operating System :: OS Independent',
|
||||
'Programming Language :: Python :: 3',
|
||||
'Programming Language :: Python :: 3 :: Only',
|
||||
'Programming Language :: Python :: 3.6',
|
||||
'Programming Language :: Python :: 3.7',
|
||||
'Programming Language :: Python :: 3.8',
|
||||
'Programming Language :: Python :: 3.9',
|
||||
],
|
||||
)
|
||||
+114
-16
@@ -1,11 +1,12 @@
|
||||
"""A package for processing and analysis of non-hierarchical gate-level VLSI designs.
|
||||
"""The kyupy package itself contains a miscellaneous utility functions.
|
||||
|
||||
The kyupy package itself contains a logger and other simple utility functions.
|
||||
In addition, it defines a ``numba`` and a ``cuda`` objects that point to the actual packages
|
||||
if they are available and otherwise point to mocks.
|
||||
"""
|
||||
|
||||
import time
|
||||
import sys
|
||||
from collections import defaultdict
|
||||
import importlib.util
|
||||
import gzip
|
||||
|
||||
@@ -15,15 +16,19 @@ import numpy as np
|
||||
_pop_count_lut = np.asarray([bin(x).count('1') for x in range(256)])
|
||||
|
||||
|
||||
def cdiv(x, y):
|
||||
return -(x // -y)
|
||||
|
||||
|
||||
def popcount(a):
|
||||
"""Returns the number of 1-bits in a given packed numpy array."""
|
||||
"""Returns the number of 1-bits in a given packed numpy array of type ``uint8``."""
|
||||
return np.sum(_pop_count_lut[a])
|
||||
|
||||
|
||||
def readtext(file):
|
||||
"""Reads and returns the text in a given file. Transparently decompresses \\*.gz files."""
|
||||
if hasattr(file, 'read'):
|
||||
return file.read()
|
||||
return file.read().decode()
|
||||
if str(file).endswith('.gz'):
|
||||
with gzip.open(file, 'rt') as f:
|
||||
return f.read()
|
||||
@@ -52,6 +57,18 @@ def hr_bytes(nbytes):
|
||||
multiplier += 1
|
||||
return f'{nbytes:.1f}{["", "ki", "Mi", "Gi", "Ti", "Pi"][multiplier]}B'
|
||||
|
||||
def eng(number):
|
||||
"""Formats a given number using engineering notation."""
|
||||
exponent = 0
|
||||
if abs(number) < 1:
|
||||
while abs(number) >= 1000:
|
||||
number *= 1000
|
||||
exponent -= 3
|
||||
else:
|
||||
while abs(number) >= 1000:
|
||||
number /= 1000
|
||||
exponent += 3
|
||||
return f'{number:.0f}' + (f'e{exponent}' if exponent != 0 else '')
|
||||
|
||||
def hr_time(seconds):
|
||||
"""Formats a given time interval for human readability."""
|
||||
@@ -74,24 +91,100 @@ def hr_time(seconds):
|
||||
return s
|
||||
|
||||
|
||||
def batchrange(nitems, maxsize):
|
||||
"""A simple generator that produces offsets and sizes for batch-loops."""
|
||||
for offset in range(0, nitems, maxsize):
|
||||
yield offset, min(nitems-offset, maxsize)
|
||||
|
||||
|
||||
class Timer:
|
||||
def __init__(self, s=0): self.s = s
|
||||
def __enter__(self): self.start_time = time.perf_counter(); return self
|
||||
def __exit__(self, *args): self.s += time.perf_counter() - self.start_time
|
||||
@property
|
||||
def ms(self): return self.s*1e3
|
||||
@property
|
||||
def us(self): return self.s*1e6
|
||||
def __repr__(self): return f'{self.s:.3f}'
|
||||
def __add__(self, t):
|
||||
return Timer(self.s + t.s)
|
||||
|
||||
|
||||
class Timers:
|
||||
def __init__(self, t={}): self.timers = defaultdict(Timer) | t
|
||||
def __getitem__(self, name): return self.timers[name]
|
||||
def __repr__(self): return '{' + ', '.join([f'{k}: {v}' for k, v in self.timers.items()]) + '}'
|
||||
def __add__(self, t):
|
||||
tmr = Timers(self.timers)
|
||||
for k, v in t.timers.items(): tmr.timers[k] += v
|
||||
return tmr
|
||||
def sum(self):
|
||||
return sum([v.s for v in self.timers.values()])
|
||||
def dict(self):
|
||||
return dict([(k, v.s) for k, v in self.timers.items()])
|
||||
|
||||
|
||||
class Log:
|
||||
"""A very simple logger that formats the messages with the number of seconds since
|
||||
program start.
|
||||
"""
|
||||
|
||||
def __init__(self):
|
||||
self.start = time.perf_counter()
|
||||
self.logfile = None
|
||||
self.logfile = sys.stdout
|
||||
"""When set to a file handle, log messages are written to it instead to standard output.
|
||||
After each write, ``flush()`` is called as well.
|
||||
"""
|
||||
self.indent = 0
|
||||
self._limit = -1
|
||||
self.filtered = 0
|
||||
|
||||
def limit(self, log_limit):
|
||||
class Limiter:
|
||||
def __init__(self, l): self.l = l
|
||||
def __enter__(self): self.l.start_limit(log_limit); return self
|
||||
def __exit__(self, *args): self.l.stop_limit()
|
||||
return Limiter(self)
|
||||
|
||||
def start_limit(self, limit):
|
||||
self.filtered = 0
|
||||
self._limit = limit
|
||||
|
||||
def stop_limit(self):
|
||||
self._limit = -1
|
||||
if self.filtered > 0:
|
||||
self.info(f'{self.filtered} more messages (filtered).')
|
||||
self.filtered = 0
|
||||
|
||||
def __getstate__(self):
|
||||
return {'elapsed': time.perf_counter() - self.start}
|
||||
|
||||
def __setstate__(self, state):
|
||||
self.logfile = sys.stdout
|
||||
self.indent = 0
|
||||
self._limit = -1
|
||||
self.filtered = 0
|
||||
self.start = time.perf_counter() - state['elapsed']
|
||||
|
||||
def write(self, s, indent=0):
|
||||
self.logfile.write(' '*indent + s + '\n')
|
||||
self.logfile.flush()
|
||||
|
||||
def li(self, item): self.write('- ' + str(item).replace('\n', '\n'+' '*(self.indent+1)), self.indent)
|
||||
def lib(self): self.write('-', self.indent); self.indent += 1
|
||||
def lin(self): self.write('-', self.indent-1)
|
||||
def di(self, key, value): self.write(str(key) + ': ' + str(value).replace('\n', '\n'+' '*(self.indent+1)), self.indent)
|
||||
def dib(self, key): self.write(str(key) + ':', self.indent); self.indent += 1
|
||||
def din(self, key): self.write(str(key) + ':', self.indent-1)
|
||||
def ie(self, n=1): self.indent -= n
|
||||
|
||||
def log(self, level, message):
|
||||
if self._limit == 0:
|
||||
self.filtered += 1
|
||||
return
|
||||
t = time.perf_counter() - self.start
|
||||
if self.logfile is None:
|
||||
print(f'{t:011.3f} {level} {message}')
|
||||
else:
|
||||
self.logfile.write(f'{t:011.3f} {level} {message}\n')
|
||||
self.logfile.flush()
|
||||
self.logfile.write(f'# {t:011.3f} {level} {message}\n')
|
||||
#self.logfile.flush()
|
||||
self._limit -= 1
|
||||
|
||||
def info(self, message):
|
||||
"""Log an informational message."""
|
||||
@@ -120,7 +213,8 @@ class Log:
|
||||
elapsed_time = current_time - start_time
|
||||
total_time = elapsed_time / done
|
||||
rem_time = total_time - elapsed_time
|
||||
self.log(':', f'{done*100:.0f}% done {hr_time(elapsed_time)} elapsed {hr_time(rem_time)} remaining')
|
||||
self.log(
|
||||
':', f'{done*100:.0f}% done {hr_time(elapsed_time)} elapsed {hr_time(rem_time)} remaining')
|
||||
log_interval = min(600, int(log_interval*1.5))
|
||||
lastlog_time = current_time
|
||||
|
||||
@@ -147,7 +241,7 @@ class MockCuda:
|
||||
self.x = 0
|
||||
self.y = 0
|
||||
|
||||
def jit(self, device=False):
|
||||
def jit(self, func=None, device=False):
|
||||
_ = device # silence "not used" warning
|
||||
outer = self
|
||||
|
||||
@@ -167,13 +261,15 @@ class MockCuda:
|
||||
for grid_y in range(grid_dim[1]):
|
||||
for block_x in range(block_dim[0]):
|
||||
for block_y in range(block_dim[1]):
|
||||
outer.x = grid_x * block_dim[0] + block_x
|
||||
outer.y = grid_y * block_dim[1] + block_y
|
||||
outer.x = grid_x * \
|
||||
block_dim[0] + block_x
|
||||
outer.y = grid_y * \
|
||||
block_dim[1] + block_y
|
||||
self.func(*args, **kwargs)
|
||||
return inner
|
||||
return Launcher(func)
|
||||
|
||||
return make_launcher
|
||||
return make_launcher(func) if func else make_launcher
|
||||
|
||||
@staticmethod
|
||||
def to_device(array, to=None):
|
||||
@@ -197,6 +293,8 @@ if importlib.util.find_spec('numba') is not None:
|
||||
try:
|
||||
list(numba.cuda.gpus)
|
||||
from numba import cuda
|
||||
from numba.core import config
|
||||
config.CUDA_LOW_OCCUPANCY_WARNINGS = False
|
||||
except CudaSupportError:
|
||||
log.warn('Cuda unavailable. Falling back to pure Python.')
|
||||
cuda = MockCuda()
|
||||
|
||||
+4
-4
@@ -21,9 +21,9 @@ class BenchTransformer(Transformer):
|
||||
|
||||
def start(self, _): return self.c
|
||||
|
||||
def parameters(self, args): return [self.c.get_or_add_fork(name) for name in args]
|
||||
def parameters(self, args): return [self.c.get_or_add_fork(str(name)) for name in args]
|
||||
|
||||
def interface(self, args): self.c.interface.extend(args[0])
|
||||
def interface(self, args): self.c.io_nodes.extend(args[0])
|
||||
|
||||
def assignment(self, args):
|
||||
name, cell_type, drivers = args
|
||||
@@ -57,8 +57,8 @@ def parse(text, name=None):
|
||||
def load(file, name=None):
|
||||
"""Parses the contents of ``file`` as ISCAS89 bench code.
|
||||
|
||||
:param file: The file to be loaded.
|
||||
:param name: The name of the circuit. If none given, the file name is used as circuit name.
|
||||
:param file: The file to be loaded. Files with `.gz`-suffix are decompressed on-the-fly.
|
||||
:param name: The name of the circuit. If None, the file name is used as circuit name.
|
||||
:return: A :class:`Circuit` object.
|
||||
"""
|
||||
return parse(readtext(file), name=name or str(file))
|
||||
+404
-52
@@ -1,21 +1,49 @@
|
||||
"""Data structures for representing non-hierarchical gate-level circuits.
|
||||
"""Core module for handling non-hierarchical gate-level circuits.
|
||||
|
||||
The class :class:`Circuit` is a container of nodes connected by lines.
|
||||
A node is an instance of class :class:`Node`,
|
||||
and a line is an instance of class :class:`Line`.
|
||||
|
||||
The data structures are designed to work together nicely with numpy arrays.
|
||||
For example, all the nodes and connections in the circuit graph have consecutive integer indices that can be used to access ndarrays with associated data.
|
||||
Circuit graphs also define an ordering of inputs, outputs and other nodes to easily process test vector data and alike.
|
||||
|
||||
"""
|
||||
|
||||
from collections import deque
|
||||
from __future__ import annotations
|
||||
|
||||
from collections import deque, defaultdict
|
||||
import re
|
||||
from typing import Union
|
||||
|
||||
import numpy as np
|
||||
|
||||
|
||||
class GrowingList(list):
|
||||
def __setitem__(self, index, value):
|
||||
if index >= len(self):
|
||||
self.extend([None] * (index + 1 - len(self)))
|
||||
if value is None: self.has_nones = True
|
||||
if index == len(self): return super().append(value)
|
||||
if index > len(self):
|
||||
super().extend([None] * (index + 1 - len(self)))
|
||||
self.has_nones = True
|
||||
super().__setitem__(index, value)
|
||||
|
||||
def free_index(self):
|
||||
return next((i for i, x in enumerate(self) if x is None), len(self))
|
||||
def __getitem__(self, index):
|
||||
if isinstance(index, slice): return super().__getitem__(index)
|
||||
return super().__getitem__(index) if index < len(self) else None
|
||||
|
||||
@property
|
||||
def free_idx(self):
|
||||
fi = len(self)
|
||||
if hasattr(self, 'has_nones') and self.has_nones:
|
||||
fi = next((i for i, x in enumerate(self) if x is None), len(self))
|
||||
self.has_nones = fi < len(self)
|
||||
return fi
|
||||
|
||||
def without_nones(self):
|
||||
for item in self:
|
||||
if item is not None:
|
||||
yield item
|
||||
|
||||
|
||||
class IndexList(list):
|
||||
@@ -64,14 +92,14 @@ class Node:
|
||||
self.index = len(circuit.nodes) - 1
|
||||
"""A unique and consecutive integer index of the node within the circuit.
|
||||
|
||||
It can be used to store additional data about the node :code:`n`
|
||||
It can be used to associate additional data to a node :code:`n`
|
||||
by allocating an array or list :code:`my_data` of length :code:`len(n.circuit.nodes)` and
|
||||
accessing it by :code:`my_data[n.index]`.
|
||||
accessing it by :code:`my_data[n.index]` or simply by :code:`my_data[n]`.
|
||||
"""
|
||||
self.ins = GrowingList()
|
||||
self.ins: GrowingList[Line] = GrowingList()
|
||||
"""A list of input connections (:class:`Line` objects).
|
||||
"""
|
||||
self.outs = GrowingList()
|
||||
self.outs: GrowingList[Line] = GrowingList()
|
||||
"""A list of output connections (:class:`Line` objects).
|
||||
"""
|
||||
|
||||
@@ -81,7 +109,9 @@ class Node:
|
||||
def __repr__(self):
|
||||
ins = ' '.join([f'<{line.index}' if line is not None else '<None' for line in self.ins])
|
||||
outs = ' '.join([f'>{line.index}' if line is not None else '>None' for line in self.outs])
|
||||
return f'{self.index}:{self.kind}"{self.name}" {ins} {outs}'
|
||||
ins = ' ' + ins if len(ins) else ''
|
||||
outs = ' ' + outs if len(outs) else ''
|
||||
return f'{self.index}:{self.kind}"{self.name}"{ins}{outs}'
|
||||
|
||||
def remove(self):
|
||||
"""Removes the node from its circuit.
|
||||
@@ -99,6 +129,16 @@ class Node:
|
||||
del self.circuit.cells[self.name]
|
||||
self.circuit = None
|
||||
|
||||
def __eq__(self, other):
|
||||
"""Checks equality of node name and kind. Does not check pin connections.
|
||||
|
||||
This is ok, because (name, kind) is unique within a circuit.
|
||||
"""
|
||||
return self.name == other.name and self.kind == other.kind
|
||||
|
||||
def __hash__(self):
|
||||
return hash((self.name, self.kind))
|
||||
|
||||
|
||||
class Line:
|
||||
"""A line is a directional 1:1 connection between two nodes.
|
||||
@@ -115,7 +155,7 @@ class Line:
|
||||
Use the explicit case only if connections to specific pins are required.
|
||||
It may overwrite any previous line references in the connection list of the nodes.
|
||||
"""
|
||||
def __init__(self, circuit, driver, reader):
|
||||
def __init__(self, circuit: Circuit, driver: Union[Node, tuple[Node, int]], reader: Union[Node, tuple[Node, int]]):
|
||||
self.circuit = circuit
|
||||
"""The :class:`Circuit` object the line is part of.
|
||||
"""
|
||||
@@ -125,26 +165,26 @@ class Line:
|
||||
|
||||
It can be used to store additional data about the line :code:`l`
|
||||
by allocating an array or list :code:`my_data` of length :code:`len(l.circuit.lines)` and
|
||||
accessing it by :code:`my_data[l.index]`.
|
||||
accessing it by :code:`my_data[l.index]` or simply by :code:`my_data[l]`.
|
||||
"""
|
||||
if not isinstance(driver, tuple): driver = (driver, driver.outs.free_index())
|
||||
if not isinstance(driver, tuple): driver = (driver, driver.outs.free_idx)
|
||||
self.driver = driver[0]
|
||||
"""The :class:`Node` object that drives this line.
|
||||
"""
|
||||
self.driver_pin = driver[1]
|
||||
"""The output pin position of the driver node this line is connected to.
|
||||
|
||||
This is the position in the outs-list of the driving node this line referenced from:
|
||||
This is the position in the list :py:attr:`Node.outs` of the driving node this line referenced from:
|
||||
:code:`self.driver.outs[self.driver_pin] == self`.
|
||||
"""
|
||||
if not isinstance(reader, tuple): reader = (reader, reader.ins.free_index())
|
||||
if not isinstance(reader, tuple): reader = (reader, reader.ins.free_idx)
|
||||
self.reader = reader[0]
|
||||
"""The :class:`Node` object that reads this line.
|
||||
"""
|
||||
self.reader_pin = reader[1]
|
||||
"""The input pin position of the reader node this line is connected to.
|
||||
|
||||
This is the position in the ins-list of the reader node this line referenced from:
|
||||
This is the position in the list :py:attr:`Node.ins` of the reader node this line referenced from:
|
||||
:code:`self.reader.ins[self.reader_pin] == self`.
|
||||
"""
|
||||
self.driver.outs[self.driver_pin] = self
|
||||
@@ -156,7 +196,11 @@ class Line:
|
||||
To keep the indices consecutive, the line with the highest index within the circuit
|
||||
will be assigned the index of the removed line.
|
||||
"""
|
||||
if self.driver is not None: self.driver.outs[self.driver_pin] = None
|
||||
if self.driver is not None:
|
||||
self.driver.outs[self.driver_pin] = None
|
||||
if self.driver.kind == '__fork__': # squeeze outputs
|
||||
del self.driver.outs[self.driver_pin]
|
||||
for i, l in enumerate(self.driver.outs): l.driver_pin = i
|
||||
if self.reader is not None: self.reader.ins[self.reader_pin] = None
|
||||
if self.circuit is not None: del self.circuit.lines[self.index]
|
||||
self.driver = None
|
||||
@@ -172,6 +216,13 @@ class Line:
|
||||
def __lt__(self, other):
|
||||
return self.index < other.index
|
||||
|
||||
def __eq__(self, other):
|
||||
return self.driver == other.driver and self.driver_pin == other.driver_pin and \
|
||||
self.reader == other.reader and self.reader_pin == other.reader_pin
|
||||
|
||||
def __hash__(self):
|
||||
return hash((self.driver, self.driver_pin, self.reader, self.reader_pin))
|
||||
|
||||
|
||||
class Circuit:
|
||||
"""A Circuit is a container for interconnected nodes and lines.
|
||||
@@ -185,41 +236,268 @@ class Circuit:
|
||||
to enforce consecutiveness.
|
||||
|
||||
A subset of nodes can be designated as primary input- or output-ports of the circuit.
|
||||
This is done by adding them to the :py:attr:`interface` list.
|
||||
This is done by adding them to the :py:attr:`io_nodes` list.
|
||||
"""
|
||||
def __init__(self, name=None):
|
||||
self.name = name
|
||||
"""The name of the circuit.
|
||||
"""
|
||||
self.nodes = IndexList()
|
||||
self.nodes : list[Node] = IndexList()
|
||||
"""A list of all :class:`Node` objects contained in the circuit.
|
||||
|
||||
The position of a node in this list equals its index :code:`self.nodes[42].index == 42`.
|
||||
This list must not be changed directly.
|
||||
Use the :class:`Node` constructor and :py:attr:`Node.remove()` to add and remove nodes.
|
||||
"""
|
||||
self.lines = IndexList()
|
||||
self.lines : list[Line] = IndexList()
|
||||
"""A list of all :class:`Line` objects contained in the circuit.
|
||||
|
||||
The position of a line in this list equals its index :code:`self.lines[42].index == 42`.
|
||||
This list must not be changed directly.
|
||||
Use the :class:`Line` constructor and :py:attr:`Line.remove()` to add and remove lines.
|
||||
"""
|
||||
self.interface = GrowingList()
|
||||
self.io_nodes : list[Node] = GrowingList()
|
||||
"""A list of nodes that are designated as primary input- or output-ports.
|
||||
|
||||
Port-nodes are contained in :py:attr:`nodes` as well as :py:attr:`interface`.
|
||||
The position of a node in the interface list corresponds to positions of logic values in test vectors.
|
||||
Port-nodes are contained in :py:attr:`nodes` as well as :py:attr:`io_nodes`.
|
||||
The position of a node in the io_nodes list corresponds to positions of logic values in test vectors.
|
||||
The port direction is not stored explicitly.
|
||||
Usually, nodes in the interface list without any lines in their :py:attr:`Node.ins` list are primary inputs,
|
||||
and nodes without any lines in their :py:attr:`Node.outs` list are regarded as primary outputs.
|
||||
Usually, nodes in the io_nodes list without any lines in their :py:attr:`Node.ins` list are primary inputs,
|
||||
and all other nodes in the io_nodes list are regarded as primary outputs.
|
||||
"""
|
||||
self.cells = {}
|
||||
self.cells : dict[str, Node] = {}
|
||||
"""A dictionary to access cells by name.
|
||||
|
||||
This dictionary must not be changed directly.
|
||||
Use the :class:`Node` constructor and :py:attr:`Node.remove()` to add and remove nodes.
|
||||
"""
|
||||
self.forks = {}
|
||||
self.forks : dict[str, Node] = {}
|
||||
"""A dictionary to access forks by name.
|
||||
|
||||
This dictionary must not be changed directly.
|
||||
Use the :class:`Node` constructor and :py:attr:`Node.remove()` to add and remove nodes.
|
||||
"""
|
||||
|
||||
@property
|
||||
def s_nodes(self):
|
||||
"""A list of all primary I/Os as well as all flip-flops and latches in the circuit (in that order).
|
||||
|
||||
The s_nodes list defines the order of all ports and all sequential elements in the circuit.
|
||||
This list is constructed on-the-fly. If used in some inner toop, consider caching the list for better performance.
|
||||
"""
|
||||
return list(self.io_nodes) + [n for n in self.nodes if 'dff' in n.kind.lower()] + [n for n in self.nodes if 'latch' in n.kind.lower()]
|
||||
|
||||
def io_locs(self, prefix):
|
||||
"""Returns the indices of primary I/Os that start with given name prefix.
|
||||
|
||||
The returned values are used to index into the :py:attr:`io_nodes` array.
|
||||
If only one I/O cell matches the given prefix, a single integer is returned.
|
||||
If a bus matches the given prefix, a sorted list of indices is returned.
|
||||
Busses are identified by integers in the cell names following the given prefix.
|
||||
Lists for bus indices are sorted from LSB (e.g. :code:`data[0]`) to MSB (e.g. :code:`data[31]`).
|
||||
If a prefix matches multiple different signals or busses, alphanumerically sorted
|
||||
lists of lists are returned. Therefore, higher-dimensional busses
|
||||
(e.g. :code:`data0[0], data0[1], ...`, :code:`data1[0], data1[1], ...`) are supported as well.
|
||||
"""
|
||||
return self._locs(prefix, list(self.io_nodes))
|
||||
|
||||
def s_locs(self, prefix):
|
||||
"""Returns the indices of I/Os and sequential elements that start with given name prefix.
|
||||
|
||||
The returned values are used to index into the :py:attr:`s_nodes` list.
|
||||
It works the same as :py:attr:`io_locs`. See there for more details.
|
||||
"""
|
||||
return self._locs(prefix, self.s_nodes)
|
||||
|
||||
def _locs(self, prefix, nodes):
|
||||
d_top = dict()
|
||||
for i, n in enumerate(nodes):
|
||||
if m := re.match(fr'({re.escape(prefix)}.*?)((?:[\d_\[\]])*$)', n.name):
|
||||
path = [m[1]] + [int(v) for v in re.split(r'[_\[\]]+', m[2]) if len(v) > 0]
|
||||
d = d_top
|
||||
for j in path[:-1]:
|
||||
d[j] = d.get(j, dict())
|
||||
d = d[j]
|
||||
d[path[-1]] = i
|
||||
|
||||
# sort recursively for multi-dimensional lists.
|
||||
def sorted_values(d): return [sorted_values(v) for k, v in sorted(d.items())] if isinstance(d, dict) else d
|
||||
l = sorted_values(d_top)
|
||||
while isinstance(l, list) and len(l) == 1: l = l[0]
|
||||
return None if isinstance(l, list) and len(l) == 0 else l
|
||||
|
||||
@property
|
||||
def stats(self):
|
||||
"""A dictionary with the counts of all different elements in the circuit.
|
||||
|
||||
The dictionary contains the number of all different kinds of nodes, the number
|
||||
of lines, as well various sums like number of combinational gates, number of
|
||||
primary I/Os, number of sequential elements, and so on.
|
||||
|
||||
The count of regular cells use their :py:attr:`Node.kind` as key, other statistics use
|
||||
dunder-keys like: `__comb__`, `__io__`, `__seq__`, and so on.
|
||||
"""
|
||||
stats = defaultdict(int)
|
||||
stats['__node__'] = len(self.nodes)
|
||||
stats['__cell__'] = len(self.cells)
|
||||
stats['__fork__'] = len(self.forks)
|
||||
stats['__io__'] = len(self.io_nodes)
|
||||
stats['__line__'] = len(self.lines)
|
||||
for n in self.cells.values():
|
||||
stats[n.kind] += 1
|
||||
if 'dff' in n.kind.lower(): stats['__dff__'] += 1
|
||||
elif 'latch' in n.kind.lower(): stats['__latch__'] += 1
|
||||
elif 'put' not in n.kind.lower(): stats['__comb__'] += 1 # no input or output
|
||||
stats['__seq__'] = stats['__dff__'] + stats['__latch__']
|
||||
return dict(stats)
|
||||
|
||||
def get_or_add_fork(self, name):
|
||||
return self.forks[name] if name in self.forks else Node(self, name)
|
||||
|
||||
def remove_dangling_nodes(self, root_node:Node, keep=[]):
|
||||
if len([l for l in root_node.outs if l is not None]) > 0: return
|
||||
lines = [l for l in root_node.ins if l is not None]
|
||||
drivers = [l.driver for l in lines]
|
||||
if root_node in keep: return
|
||||
root_node.remove()
|
||||
for l in lines:
|
||||
l.remove()
|
||||
for d in drivers:
|
||||
self.remove_dangling_nodes(d, keep=keep)
|
||||
|
||||
def eliminate_1to1_forks(self):
|
||||
"""Removes all forks that drive only one node.
|
||||
|
||||
Such forks are inserted by parsers to annotate signal names. If this
|
||||
information is not needed, such forks can be removed and the two neighbors
|
||||
can be connected directly using one line. Forks that drive more than one node
|
||||
are not removed by this function.
|
||||
|
||||
This function may remove some nodes and some lines from the circuit.
|
||||
Therefore that indices of other nodes and lines may change to keep the indices consecutive.
|
||||
It may therefore invalidate external data for nodes and lines.
|
||||
"""
|
||||
ios = set(self.io_nodes)
|
||||
for n in list(self.forks.values()):
|
||||
if n in ios: continue
|
||||
if len(n.outs) != 1: continue
|
||||
in_line = n.ins[0]
|
||||
out_line = n.outs[0]
|
||||
out_reader = out_line.reader
|
||||
out_reader_pin = out_line.reader_pin
|
||||
n.remove()
|
||||
out_line.remove()
|
||||
in_line.reader = out_reader
|
||||
in_line.reader_pin = out_reader_pin
|
||||
in_line.reader.ins[in_line.reader_pin] = in_line
|
||||
|
||||
def remove_forks(self):
|
||||
ios = set(self.io_nodes)
|
||||
for n in list(self.forks.values()):
|
||||
if n in ios: continue
|
||||
d = None
|
||||
if (l := n.ins[0]) is not None:
|
||||
d = l.driver
|
||||
l.remove()
|
||||
for l in list(n.outs):
|
||||
if l is None: continue
|
||||
r, rp = l.reader, l.reader_pin
|
||||
l.remove()
|
||||
if d is not None: Line(self, d, (r, rp))
|
||||
n.remove()
|
||||
|
||||
def substitute(self, node, impl):
|
||||
"""Replaces a given node with the given implementation circuit.
|
||||
|
||||
The given node will be removed, the implementation is copied in and
|
||||
the signal lines are connected appropriately. The number and arrangement
|
||||
of the input and output ports must match the pins of the replaced node.
|
||||
|
||||
This function tries to preserve node and line indices as much as possible.
|
||||
Usually, it only adds additional nodes and lines, preserving the order of
|
||||
all existing nodes and lines. If an implementation is empty, however, nodes
|
||||
and lines may get removed, changing indices and invalidating external data.
|
||||
"""
|
||||
ios = set(impl.io_nodes)
|
||||
impl_in_nodes = [n for n in impl.io_nodes if len(n.ins) == 0]
|
||||
impl_out_lines = [n.ins[0] for n in impl.io_nodes if len(n.ins) > 0]
|
||||
designated_cell = None
|
||||
if len(impl_out_lines) > 0:
|
||||
n = impl_out_lines[0].driver
|
||||
while n.kind == '__fork__' and n not in ios:
|
||||
n = n.ins[0].driver
|
||||
designated_cell = n
|
||||
node_in_lines = list(node.ins) + [None] * (len(impl_in_nodes)-len(node.ins))
|
||||
node_out_lines = list(node.outs) + [None] * (len(impl_out_lines)-len(node.outs))
|
||||
assert len(node_in_lines) == len(impl_in_nodes)
|
||||
assert len(node_out_lines) == len(impl_out_lines)
|
||||
node_map = dict()
|
||||
if designated_cell is not None:
|
||||
node.kind = designated_cell.kind
|
||||
node_map[designated_cell] = node
|
||||
node.ins = GrowingList()
|
||||
node.outs = GrowingList()
|
||||
else:
|
||||
node.remove()
|
||||
ios = set(impl.io_nodes)
|
||||
for n in impl.nodes: # add all nodes to main circuit
|
||||
if n not in ios:
|
||||
if n != designated_cell:
|
||||
node_map[n] = Node(self, f'{node.name}~{n.name}', n.kind)
|
||||
elif len(n.outs) > 0 and len(n.ins) > 0: # output is also read by impl. circuit, need to add a fork.
|
||||
node_map[n] = Node(self, f'{node.name}~{n.name}')
|
||||
elif len(n.ins) == 0 and len(n.outs) > 1: # input is read by multiple nodes, need to add fork.
|
||||
node_map[n] = Node(self, f'{node.name}~{n.name}')
|
||||
for l in impl.lines: # add all internal lines to main circuit
|
||||
if l.reader in node_map and l.driver in node_map:
|
||||
Line(self, (node_map[l.driver], l.driver_pin), (node_map[l.reader], l.reader_pin))
|
||||
for inn, ll in zip(impl_in_nodes, node_in_lines): # connect inputs
|
||||
if ll is None: continue
|
||||
if len(inn.outs) == 1:
|
||||
l = inn.outs[0]
|
||||
ll.reader = node_map[l.reader]
|
||||
ll.reader_pin = l.reader_pin
|
||||
else:
|
||||
ll.reader = node_map[inn] # connect to existing fork
|
||||
ll.reader_pin = 0
|
||||
ll.reader.ins[ll.reader_pin] = ll
|
||||
for l, ll in zip(impl_out_lines, node_out_lines): # connect outputs
|
||||
if ll is None:
|
||||
if l.driver in node_map:
|
||||
self.remove_dangling_nodes(node_map[l.driver], keep=ios)
|
||||
continue
|
||||
if len(l.reader.outs) > 0: # output is also read by impl. circuit, connect to fork.
|
||||
ll.driver = node_map[l.reader]
|
||||
ll.driver_pin = len(l.reader.outs)
|
||||
else:
|
||||
ll.driver = node_map[l.driver]
|
||||
ll.driver_pin = l.driver_pin
|
||||
ll.driver.outs[ll.driver_pin] = ll
|
||||
|
||||
def resolve_tlib_cells(self, tlib):
|
||||
"""Substitute all technology library cells with kyupy native simulation primitives.
|
||||
|
||||
See :py:attr:`substitute()` for more detail.
|
||||
"""
|
||||
for n in list(self.nodes):
|
||||
if n.kind in tlib.cells:
|
||||
self.substitute(n, tlib.cells[n.kind][0])
|
||||
|
||||
def remove_constants(self):
|
||||
c1gen = None
|
||||
for n in self.nodes:
|
||||
if n.kind == '__const0__': # just remove, unconnected inputs are defined 0.
|
||||
for l in n.outs:
|
||||
l.remove()
|
||||
n.remove()
|
||||
elif n.kind == '__const1__':
|
||||
if c1gen is None: c1gen = Node(self, '__const1gen__', 'INV1') # one unique const 1 generator
|
||||
for l in n.outs:
|
||||
r, rp = l.reader, l.reader_pin
|
||||
l.remove()
|
||||
Line(self, c1gen, (r, rp))
|
||||
n.remove()
|
||||
|
||||
def copy(self):
|
||||
"""Returns a deep copy of the circuit.
|
||||
"""
|
||||
@@ -230,43 +508,72 @@ class Circuit:
|
||||
d = c.forks[line.driver.name] if line.driver.kind == '__fork__' else c.cells[line.driver.name]
|
||||
r = c.forks[line.reader.name] if line.reader.kind == '__fork__' else c.cells[line.reader.name]
|
||||
Line(c, (d, line.driver_pin), (r, line.reader_pin))
|
||||
for node in self.interface:
|
||||
for node in self.io_nodes:
|
||||
if node.kind == '__fork__':
|
||||
n = c.forks[node.name]
|
||||
else:
|
||||
n = c.cells[node.name]
|
||||
c.interface.append(n)
|
||||
c.io_nodes.append(n)
|
||||
return c
|
||||
|
||||
def dump(self):
|
||||
"""Returns a string representation of the circuit and all its nodes.
|
||||
"""
|
||||
header = f'{self.name}({",".join([str(n.index) for n in self.interface])})\n'
|
||||
return header + '\n'.join([str(n) for n in self.nodes])
|
||||
def __getstate__(self):
|
||||
nodes = [(node.name, node.kind) for node in self.nodes]
|
||||
lines = [(line.driver.index, line.driver_pin, line.reader.index, line.reader_pin) for line in self.lines]
|
||||
io_nodes = [n.index for n in self.io_nodes]
|
||||
return {'name': self.name,
|
||||
'nodes': nodes,
|
||||
'lines': lines,
|
||||
'io_nodes': io_nodes }
|
||||
|
||||
def __setstate__(self, state):
|
||||
self.name = state['name']
|
||||
self.nodes = IndexList()
|
||||
self.lines = IndexList()
|
||||
self.io_nodes = GrowingList()
|
||||
self.cells = {}
|
||||
self.forks = {}
|
||||
for s in state['nodes']:
|
||||
Node(self, *s)
|
||||
for driver, driver_pin, reader, reader_pin in state['lines']:
|
||||
Line(self, (self.nodes[driver], driver_pin), (self.nodes[reader], reader_pin))
|
||||
for n in state['io_nodes']:
|
||||
self.io_nodes.append(self.nodes[n])
|
||||
|
||||
def __eq__(self, other):
|
||||
return self.nodes == other.nodes and self.lines == other.lines and self.io_nodes == other.io_nodes
|
||||
|
||||
def __repr__(self):
|
||||
name = f' {self.name}' if self.name else ''
|
||||
return f'<Circuit{name} cells={len(self.cells)} forks={len(self.forks)} ' + \
|
||||
f'lines={len(self.lines)} ports={len(self.interface)}>'
|
||||
return f'{{name: "{self.name}", cells: {len(self.cells)}, forks: {len(self.forks)}, lines: {len(self.lines)}, io_nodes: {len(self.io_nodes)}}}'
|
||||
|
||||
def topological_order(self):
|
||||
"""Generator function to iterate over all nodes in topological order.
|
||||
|
||||
Nodes without input lines and nodes whose :py:attr:`Node.kind` contains the substring 'DFF' are
|
||||
yielded first.
|
||||
Nodes without input lines and nodes whose :py:attr:`Node.kind` contains the
|
||||
substrings 'dff' or 'latch' are yielded first.
|
||||
"""
|
||||
visit_count = [0] * len(self.nodes)
|
||||
queue = deque(n for n in self.nodes if len(n.ins) == 0 or 'DFF' in n.kind)
|
||||
visit_count = np.zeros(len(self.nodes), dtype=np.uint32)
|
||||
start = set(n for n in self.nodes if len(n.ins) == 0 or 'dff' in n.kind.lower() or 'latch' in n.kind.lower())
|
||||
queue = deque(start)
|
||||
while len(queue) > 0:
|
||||
n = queue.popleft()
|
||||
for line in n.outs:
|
||||
if line is None: continue
|
||||
succ = line.reader
|
||||
visit_count[succ] += 1
|
||||
if visit_count[succ] == len(succ.ins) and 'DFF' not in succ.kind:
|
||||
if visit_count[succ] == len(succ.ins) and succ not in start:
|
||||
queue.append(succ)
|
||||
yield n
|
||||
|
||||
def topological_order_with_level(self):
|
||||
level = np.zeros(len(self.nodes), dtype=np.int32) - 1
|
||||
for n in self.topological_order():
|
||||
if len(n.ins) == 0 or 'dff' in n.kind.lower() or 'latch' in n.kind.lower():
|
||||
l = 0
|
||||
else:
|
||||
l = level[[l.driver.index for l in n.ins if l is not None]].max() + 1
|
||||
level[n] = l
|
||||
yield n, l
|
||||
|
||||
def topological_line_order(self):
|
||||
"""Generator function to iterate over all lines in topological order.
|
||||
"""
|
||||
@@ -278,17 +585,17 @@ class Circuit:
|
||||
def reversed_topological_order(self):
|
||||
"""Generator function to iterate over all nodes in reversed topological order.
|
||||
|
||||
Nodes without output lines and nodes whose :py:attr:`Node.kind` contains the substring 'DFF' are
|
||||
yielded first.
|
||||
Nodes without output lines and nodes whose :py:attr:`Node.kind` contains the
|
||||
substrings 'dff' or 'latch' are yielded first.
|
||||
"""
|
||||
visit_count = [0] * len(self.nodes)
|
||||
queue = deque(n for n in self.nodes if len(n.outs) == 0 or 'DFF' in n.kind)
|
||||
queue = deque(n for n in self.nodes if len(n.outs) == 0 or 'dff' in n.kind.lower() or 'latch' in n.kind.lower())
|
||||
while len(queue) > 0:
|
||||
n = queue.popleft()
|
||||
for line in n.ins:
|
||||
pred = line.driver
|
||||
visit_count[pred] += 1
|
||||
if visit_count[pred] == len(pred.outs) and 'DFF' not in pred.kind:
|
||||
if visit_count[pred] == len(pred.outs) and 'dff' not in pred.kind.lower() and 'latch' not in pred.kind.lower():
|
||||
queue.append(pred)
|
||||
yield n
|
||||
|
||||
@@ -308,23 +615,68 @@ class Circuit:
|
||||
if marks[n]:
|
||||
yield n
|
||||
|
||||
def fanout(self, origin_nodes):
|
||||
"""Generator function to iterate over the fan-out cone of a given list of origin nodes.
|
||||
|
||||
Nodes are yielded in topological order.
|
||||
"""
|
||||
marks = [False] * len(self.nodes)
|
||||
for n in origin_nodes:
|
||||
marks[n] = True
|
||||
for n in self.topological_order():
|
||||
if not marks[n]:
|
||||
for line in n.ins.without_nones():
|
||||
marks[n] |= marks[line.driver]
|
||||
if marks[n]:
|
||||
yield n
|
||||
|
||||
def fanout_free_regions(self):
|
||||
for stem in self.reversed_topological_order():
|
||||
if len(stem.outs) == 1 and 'DFF' not in stem.kind: continue
|
||||
if len(stem.outs) == 1 and 'dff' not in stem.kind.lower(): continue
|
||||
region = []
|
||||
if 'DFF' in stem.kind:
|
||||
if 'dff' in stem.kind.lower():
|
||||
n = stem.ins[0]
|
||||
if len(n.driver.outs) == 1 and 'DFF' not in n.driver.kind:
|
||||
if len(n.driver.outs) == 1 and 'dff' not in n.driver.kind.lower():
|
||||
queue = deque([n.driver])
|
||||
else:
|
||||
queue = deque()
|
||||
else:
|
||||
queue = deque(n.driver for n in stem.ins
|
||||
if len(n.driver.outs) == 1 and 'DFF' not in n.driver.kind)
|
||||
if len(n.driver.outs) == 1 and 'dff' not in n.driver.kind.lower())
|
||||
while len(queue) > 0:
|
||||
n = queue.popleft()
|
||||
preds = [pred.driver for pred in n.ins
|
||||
if len(pred.driver.outs) == 1 and 'DFF' not in pred.driver.kind]
|
||||
if len(pred.driver.outs) == 1 and 'dff' not in pred.driver.kind.lower()]
|
||||
queue.extend(preds)
|
||||
region.append(n)
|
||||
yield stem, region
|
||||
|
||||
def dot(self, format='svg'):
|
||||
from graphviz import Digraph
|
||||
dot = Digraph(format=format, graph_attr={'rankdir': 'LR', 'splines': 'true'})
|
||||
|
||||
s_dict = dict((n, i) for i, n in enumerate(self.s_nodes))
|
||||
node_level = np.zeros(len(self.nodes), dtype=np.uint32)
|
||||
level_nodes = defaultdict(list)
|
||||
for n, lv in self.topological_order_with_level():
|
||||
level_nodes[lv].append(n)
|
||||
node_level[n] = lv
|
||||
|
||||
for lv in level_nodes:
|
||||
with dot.subgraph() as s:
|
||||
s.attr(rank='same')
|
||||
for n in level_nodes[lv]:
|
||||
ins = '|'.join([f'<i{i}>{i}' for i in range(len(n.ins))])
|
||||
outs = '|'.join([f'<o{i}>{i}' for i in range(len(n.outs))])
|
||||
io = f' [{s_dict[n]}]' if n in s_dict else ''
|
||||
s.node(name=str(n.index), label = f'{{{{{ins}}}|{n.index}{io}\n{n.kind}\n{n.name}|{{{outs}}}}}', shape='record')
|
||||
|
||||
for l in self.lines:
|
||||
driver, reader = f'{l.driver.index}:o{l.driver_pin}', f'{l.reader.index}:i{l.reader_pin}'
|
||||
if node_level[l.driver] >= node_level[l.reader]:
|
||||
dot.edge(driver, reader, style='dotted', label=str(l.index))
|
||||
pass
|
||||
else:
|
||||
dot.edge(driver, reader, label=str(l.index))
|
||||
|
||||
return dot
|
||||
@@ -0,0 +1,297 @@
|
||||
"""A simple and incomplete parser for the Design Exchange Format (DEF).
|
||||
|
||||
This parser extracts information on components and nets from DEF files and make them available
|
||||
as an intermediate representation (:class:`DefFile` object).
|
||||
"""
|
||||
|
||||
from collections import defaultdict
|
||||
|
||||
from lark import Lark, Transformer, Tree
|
||||
|
||||
from kyupy import readtext
|
||||
|
||||
|
||||
class DefNet:
|
||||
def __init__(self, name):
|
||||
self.name = name
|
||||
self.pins = []
|
||||
|
||||
@property
|
||||
def wires(self):
|
||||
ww = defaultdict(list)
|
||||
[ww[dw.layer].append((int(dw.width), dw.wire_points)) for dw in self.routed if len(dw.wire_points) > 0]
|
||||
return ww
|
||||
|
||||
@property
|
||||
def vias(self):
|
||||
vv = defaultdict(list)
|
||||
[vv[vtype].extend(locs) for dw in self.routed for vtype, locs in dw.vias.items()]
|
||||
return vv
|
||||
|
||||
|
||||
class DefWire:
|
||||
def __init__(self):
|
||||
self.layer = None
|
||||
self.width = None
|
||||
self.points = []
|
||||
|
||||
@property
|
||||
def wire_points(self):
|
||||
start = [self.points[0]]
|
||||
rest = [p for p in self.points[1:] if not isinstance(p[0], str)] # skip over vias
|
||||
return start + rest if len(rest) > 0 else []
|
||||
|
||||
@property
|
||||
def vias(self):
|
||||
vv = defaultdict(list)
|
||||
loc = self.points[0]
|
||||
for p in self.points[1:]:
|
||||
if not isinstance(p[0], str): # new location
|
||||
loc = (loc[0] if p[0] is None else p[0], loc[1] if p[1] is None else p[1]) # if None, keep previous value
|
||||
continue
|
||||
vtype, param = p
|
||||
if isinstance(param, tuple): # expand "DO x BY y STEP xs ys"
|
||||
x_cnt, y_cnt, x_sp, y_sp = param
|
||||
[vv[vtype].append((loc[0] + x*x_sp, loc[1] + y*y_sp, 'N')) for x in range(x_cnt) for y in range(y_cnt)]
|
||||
else:
|
||||
vv[vtype].append((loc[0], loc[1], param or 'N'))
|
||||
return vv
|
||||
|
||||
def __repr__(self):
|
||||
return f'<DefWire {self.layer} {self.width} {self.points}>'
|
||||
|
||||
|
||||
class DefVia:
|
||||
def __init__(self, name):
|
||||
self.name = name
|
||||
self.rowcol = [1, 1]
|
||||
self.cutspacing = [0, 0]
|
||||
|
||||
|
||||
class DefPin:
|
||||
def __init__(self, name):
|
||||
self.name = name
|
||||
self.points = []
|
||||
|
||||
|
||||
class DefFile:
|
||||
"""Intermediate representation of a DEF file."""
|
||||
def __init__(self):
|
||||
self.rows = []
|
||||
self.tracks = []
|
||||
self.units = []
|
||||
self.vias = {}
|
||||
self.components = {}
|
||||
self.pins = {}
|
||||
self.specialnets = {}
|
||||
self.nets = {}
|
||||
|
||||
|
||||
class DefTransformer(Transformer):
|
||||
def __init__(self): self.def_file = DefFile()
|
||||
def start(self, args): return self.def_file
|
||||
def design(self, args): self.def_file.design = args[0].value
|
||||
def point(self, args): return tuple(int(arg.value) if arg != '*' else None for arg in args)
|
||||
def do_step(self, args): return tuple(map(int, args))
|
||||
def spnet_wires(self, args): return args[0].lower(), args[1:]
|
||||
def net_wires(self, args): return args[0].lower(), args[1:]
|
||||
def sppoints(self, args): return args
|
||||
def points(self, args): return args
|
||||
def net_pin(self, args): return '__pin__', (args[0].value, args[1].value)
|
||||
def net_opt(self, args): return args[0].lower(), args[1].value
|
||||
|
||||
def file_stmt(self, args):
|
||||
value = args[1].value
|
||||
value = value[1:-1] if value[0] == '"' else value
|
||||
setattr(self.def_file, args[0].lower(), value)
|
||||
|
||||
def design_stmt(self, args):
|
||||
stmt = args[0].lower()
|
||||
if stmt == 'units': self.def_file.units.append((args[1].value, args[2].value, int(args[3])))
|
||||
elif stmt == 'diearea': self.def_file.diearea = args[1:]
|
||||
elif stmt == 'row':
|
||||
self.def_file.rows.append((args[1].value, # rowName
|
||||
args[2].value, # siteName
|
||||
(int(args[3]), int(args[4])), # origin x/y
|
||||
args[5].value, # orientation
|
||||
max(args[6][0], args[6][1]), # number of sites
|
||||
max(args[6][2], args[6][3]) # site width
|
||||
))
|
||||
elif stmt == 'tracks':
|
||||
self.def_file.tracks.append((args[1].value, # orientation
|
||||
int(args[2]), # start
|
||||
int(args[3]), # number of tracks
|
||||
int(args[4]), # spacing
|
||||
args[5].value # layer
|
||||
))
|
||||
|
||||
def vias_stmt(self, args):
|
||||
via = DefVia(args[0].value)
|
||||
[setattr(via, opt, val) for opt, val in args[1:]]
|
||||
self.def_file.vias[via.name] = via
|
||||
|
||||
def vias_opt(self, args):
|
||||
opt = args[0].lower()
|
||||
if opt in ['viarule', 'pattern']: val = args[1].value
|
||||
elif opt in ['layers']: val = [arg.value for arg in args[1:]]
|
||||
else: val = [int(arg) for arg in args[1:]]
|
||||
return opt, val
|
||||
|
||||
def comp_stmt(self, args):
|
||||
name = args[0].value
|
||||
kind = args[1].value
|
||||
point = args[2]
|
||||
orientation = args[3].value
|
||||
self.def_file.components[name] = (kind, point, orientation)
|
||||
|
||||
def pins_stmt(self, args):
|
||||
pin = DefPin(args[0].value)
|
||||
[pin.points.append(val) if opt == 'placed' else setattr(pin, opt, val) for opt, val in args[1:]]
|
||||
self.def_file.pins[pin.name] = pin
|
||||
|
||||
def pins_opt(self, args):
|
||||
opt = args[0].lower()
|
||||
if opt in ['net', 'direction', 'use']: val = args[1].value
|
||||
elif opt in ['layer']: val = [args[1].value] + args[2:]
|
||||
elif opt in ['placed']: val = (args[1][0], args[1][1], args[2].value)
|
||||
else: val = []
|
||||
return opt, val
|
||||
|
||||
def spnets_stmt(self, args):
|
||||
dnet = DefNet(args[0].value)
|
||||
for arg in args[1:]:
|
||||
if arg[0] == '__pin__': dnet.pins.append(arg[1])
|
||||
else: setattr(dnet, arg[0], arg[1])
|
||||
self.def_file.specialnets[dnet.name] = dnet
|
||||
|
||||
def nets_stmt(self, args):
|
||||
dnet = DefNet(args[0].value)
|
||||
for arg in args[1:]:
|
||||
if arg[0] == '__pin__': dnet.pins.append(arg[1])
|
||||
else: setattr(dnet, arg[0], arg[1])
|
||||
self.def_file.nets[dnet.name] = dnet
|
||||
|
||||
def spwire(self, args):
|
||||
wire = DefWire()
|
||||
wire.layer = args[0].value
|
||||
wire.width = args[1].value
|
||||
wire.points = args[-1]
|
||||
return wire
|
||||
|
||||
def wire(self, args):
|
||||
wire = DefWire()
|
||||
wire.layer = args[0].value
|
||||
wire.points = args[-1]
|
||||
return wire
|
||||
|
||||
def sppoints_via(self, args):
|
||||
if len(args) == 1: return args[0].value, None
|
||||
else: return args[0].value, args[1]
|
||||
|
||||
def points_via(self, args):
|
||||
if len(args) == 1: return args[0].value, 'N'
|
||||
else: return args[0].value, args[1].value.strip()
|
||||
|
||||
|
||||
GRAMMAR = r"""
|
||||
start: /#[^\n]*/? file_stmt*
|
||||
|
||||
?file_stmt: /VERSION/ ID ";"
|
||||
| /DIVIDERCHAR/ STRING ";"
|
||||
| /BUSBITCHARS/ STRING ";"
|
||||
| design
|
||||
|
||||
design: "DESIGN" ID ";" design_stmt* "END" "DESIGN"
|
||||
|
||||
?design_stmt: /UNITS/ ID ID NUMBER ";"
|
||||
| /DIEAREA/ point+ ";"
|
||||
| /ROW/ ID ID NUMBER NUMBER ID do_step ";"
|
||||
| /TRACKS/ /[XY]/ NUMBER "DO" NUMBER "STEP" NUMBER "LAYER" ID ";"
|
||||
| propdef | vias | nondef | comp | pins | pinprop | spnets | nets
|
||||
|
||||
propdef: "PROPERTYDEFINITIONS" propdef_stmt* "END" "PROPERTYDEFINITIONS"
|
||||
propdef_stmt: /COMPONENTPIN/ ID ID ";"
|
||||
|
||||
vias: "VIAS" NUMBER ";" vias_stmt* "END" "VIAS"
|
||||
vias_stmt: "-" ID vias_opt* ";"
|
||||
vias_opt: "+" /VIARULE/ ID
|
||||
| "+" /CUTSIZE/ NUMBER NUMBER
|
||||
| "+" /LAYERS/ ID ID ID
|
||||
| "+" /CUTSPACING/ NUMBER NUMBER
|
||||
| "+" /ENCLOSURE/ NUMBER NUMBER NUMBER NUMBER
|
||||
| "+" /ROWCOL/ NUMBER NUMBER
|
||||
| "+" /PATTERN/ ID
|
||||
|
||||
nondef: "NONDEFAULTRULES" NUMBER ";" nondef_stmt+ "END" "NONDEFAULTRULES"
|
||||
nondef_stmt: "-" ID ( "+" /HARDSPACING/
|
||||
| "+" /LAYER/ ID "WIDTH" NUMBER "SPACING" NUMBER
|
||||
| "+" /VIA/ ID )* ";"
|
||||
|
||||
comp: "COMPONENTS" NUMBER ";" comp_stmt* "END" "COMPONENTS"
|
||||
comp_stmt: "-" ID ID "+" "PLACED" point ID ";"
|
||||
|
||||
pins: "PINS" NUMBER ";" pins_stmt* "END" "PINS"
|
||||
pins_stmt: "-" ID pins_opt* ";"
|
||||
pins_opt: "+" /NET/ ID
|
||||
| "+" /SPECIAL/
|
||||
| "+" /DIRECTION/ ID
|
||||
| "+" /USE/ ID
|
||||
| "+" /PORT/
|
||||
| "+" /LAYER/ ID point point
|
||||
| "+" /PLACED/ point ID
|
||||
|
||||
pinprop: "PINPROPERTIES" NUMBER ";" pinprop_stmt* "END" "PINPROPERTIES"
|
||||
pinprop_stmt: "-" "PIN" ID "+" "PROPERTY" ID STRING ";"
|
||||
|
||||
spnets: "SPECIALNETS" NUMBER ";" spnets_stmt* "END" "SPECIALNETS"
|
||||
spnets_stmt: "-" ID ( net_pin | net_opt | spnet_wires )* ";"
|
||||
|
||||
spnet_wires: "+" ( /COVER/ | /FIXED/ | /ROUTED/ ) spwire ( "NEW" spwire )*
|
||||
|
||||
spwire: ID NUMBER spwire_opt* sppoints
|
||||
spwire_opt: "+" /SHAPE/ ID
|
||||
| "+" /STYLE/ ID
|
||||
|
||||
sppoints: point ( point | sppoints_via )+
|
||||
sppoints_via: ID do_step?
|
||||
|
||||
nets: "NETS" NUMBER ";" nets_stmt* "END" "NETS"
|
||||
nets_stmt: "-" ID ( net_pin | net_opt | net_wires )* ";"
|
||||
|
||||
net_pin: "(" ID ID ")"
|
||||
net_opt: "+" /USE/ ID
|
||||
| "+" /NONDEFAULTRULE/ ID
|
||||
net_wires: "+" ( /COVER/ | /FIXED/ | /ROUTED/ | /NOSHIELD/ ) wire ( "NEW" wire )*
|
||||
|
||||
wire: ID wire_opt points
|
||||
wire_opt: ( "TAPER" | "TAPERRULE" ID )? ("STYLE" ID)?
|
||||
|
||||
points: point ( point | points_via )+
|
||||
points_via: ID ORIENTATION?
|
||||
|
||||
point: "(" (NUMBER|/\*/) (NUMBER|/\*/) NUMBER? ")"
|
||||
|
||||
do_step: "DO" NUMBER "BY" NUMBER "STEP" (NUMBER|SIGNED_NUMBER) (NUMBER|SIGNED_NUMBER)
|
||||
|
||||
ORIENTATION.2: /F?[NWES]/ WS
|
||||
ID: /[^ \t\f\r\n+][^ \t\f\r\n]*/
|
||||
STRING : "\"" /.*?/s /(?<!\\)(\\\\)*?/ "\""
|
||||
WS: /[ \t\f\r\n]/
|
||||
|
||||
%import common.NUMBER
|
||||
%import common.SIGNED_NUMBER
|
||||
%ignore WS (/#[^\n]*/)?
|
||||
"""
|
||||
|
||||
|
||||
def parse(text):
|
||||
"""Parses the given ``text`` and returns a :class:`DefFile` object."""
|
||||
return Lark(GRAMMAR, parser="lalr", transformer=DefTransformer()).parse(text)
|
||||
|
||||
|
||||
def load(file):
|
||||
"""Parses the contents of ``file`` and returns a :class:`DefFile` object.
|
||||
|
||||
Files with `.gz`-suffix are decompressed on-the-fly.
|
||||
"""
|
||||
return parse(readtext(file))
|
||||
+241
-254
@@ -1,4 +1,9 @@
|
||||
"""This module contains definitions and data structures for 2-, 4-, and 8-valued logic operations.
|
||||
"""Core module for handling 2-, 4-, and 8-valued logic data and signal values.
|
||||
|
||||
Logic values are stored in numpy arrays with data type ``np.uint8``.
|
||||
There are no explicit data structures in KyuPy for holding patterns, pattern sets or vectors.
|
||||
However, there are conventions on logic value encoding and on the order of axes.
|
||||
Utility functions defined here follow these conventions.
|
||||
|
||||
8 logic values are defined as integer constants.
|
||||
|
||||
@@ -6,21 +11,39 @@
|
||||
* 4-valued logic adds: ``UNASSIGNED`` and ``UNKNOWN``
|
||||
* 8-valued logic adds: ``RISE``, ``FALL``, ``PPULSE``, and ``NPULSE``.
|
||||
|
||||
The bits in these constants have the following meaning:
|
||||
In general, the bits in these constants have the following meaning:
|
||||
|
||||
* bit 0: Final/settled binary value of a signal
|
||||
* bit 1: Initial binary value of a signal
|
||||
* bit 2: Activity or transitions are present on a signal
|
||||
* bit0: Final/settled binary value of a signal
|
||||
* bit1: Initial binary value of a signal
|
||||
* bit2: Activity or transitions are present on a signal
|
||||
|
||||
Special meaning is given to values where bits 0 and 1 differ, but bit 2 (activity) is 0.
|
||||
These values are interpreted as ``UNKNOWN`` or ``UNASSIGNED`` in 4-valued and 8-valued logic.
|
||||
Except when bit0 differs from bit1, but bit2 (activity) is 0:
|
||||
|
||||
* bit0 = 1, bit1 = 0, bit2 = 0 means ``UNKNOWN`` in 4-valued and 8-valued logic.
|
||||
* bit0 = 0, bit1 = 1, bit2 = 0 means ``UNASSIGNED`` in 4-valued and 8-valued logic.
|
||||
|
||||
2-valued logic only considers bit0, but should store logic one as ``ONE=0b011`` for interoperability.
|
||||
4-valued logic only considers bit0 and bit1.
|
||||
8-valued logic considers all 3 bits.
|
||||
|
||||
Logic values are stored in numpy arrays of data type ``np.uint8``.
|
||||
The axis convention is as follows:
|
||||
|
||||
* The **last** axis goes along patterns/vectors. I.e. ``values[...,0]`` is pattern 0, ``values[...,1]`` is pattern 1, etc.
|
||||
* The **second-to-last** axis goes along the I/O and flip-flops of circuits. For a circuit ``c``, this axis is usually
|
||||
``len(c.s_nodes)`` long. The values of all inputs, outputs and flip-flops are stored within the same array and the location
|
||||
along the second-to-last axis is determined by the order in :py:attr:`~kyupy.circuit.Circuit.s_nodes`.
|
||||
|
||||
Two storage formats are used in KyuPy:
|
||||
|
||||
* ``mv...`` (for "multi-valued"): Each logic value is stored in the least significant 3 bits of ``np.uint8``.
|
||||
* ``bp...`` (for "bit-parallel"): Groups of 8 logic values are stored as three ``np.uint8``. This format is used
|
||||
for bit-parallel logic simulations. It is also more memory-efficient.
|
||||
|
||||
The functions in this module use the ``mv...`` and ``bp...`` prefixes to signify the storage format they operate on.
|
||||
|
||||
In general, 2-valued logic only considers bit 0, 4-valued logic considers bits 0 and 1, and 8-valued logic
|
||||
considers all 3 bits.
|
||||
The only exception is constant ``ONE=0b11`` which has two bits set for all logics including 2-valued logic.
|
||||
"""
|
||||
|
||||
import math
|
||||
from collections.abc import Iterable
|
||||
|
||||
import numpy as np
|
||||
@@ -66,135 +89,55 @@ def interpret(value):
|
||||
"""
|
||||
if isinstance(value, Iterable) and not (isinstance(value, str) and len(value) == 1):
|
||||
return list(map(interpret, value))
|
||||
if value in [0, '0', False, 'L', 'l']:
|
||||
return ZERO
|
||||
if value in [1, '1', True, 'H', 'h']:
|
||||
return ONE
|
||||
if value in [None, '-', 'Z', 'z']:
|
||||
return UNASSIGNED
|
||||
if value in ['R', 'r', '/']:
|
||||
return RISE
|
||||
if value in ['F', 'f', '\\']:
|
||||
return FALL
|
||||
if value in ['P', 'p', '^']:
|
||||
return PPULSE
|
||||
if value in ['N', 'n', 'v']:
|
||||
return NPULSE
|
||||
if value in [0, '0', False, 'L', 'l']: return ZERO
|
||||
if value in [1, '1', True, 'H', 'h']: return ONE
|
||||
if value in [None, '-', 'Z', 'z']: return UNASSIGNED
|
||||
if value in ['R', 'r', '/']: return RISE
|
||||
if value in ['F', 'f', '\\']: return FALL
|
||||
if value in ['P', 'p', '^']: return PPULSE
|
||||
if value in ['N', 'n', 'v']: return NPULSE
|
||||
return UNKNOWN
|
||||
|
||||
|
||||
_bit_in_lut = np.array([2 ** x for x in range(7, -1, -1)], dtype='uint8')
|
||||
def mvarray(*a):
|
||||
"""Converts (lists of) Boolean values or strings into a multi-valued array.
|
||||
|
||||
|
||||
@numba.njit
|
||||
def bit_in(a, pos):
|
||||
return a[pos >> 3] & _bit_in_lut[pos & 7]
|
||||
|
||||
|
||||
class MVArray:
|
||||
"""An n-dimensional array of m-valued logic values.
|
||||
|
||||
This class wraps a numpy.ndarray of type uint8 and adds support for encoding and
|
||||
interpreting 2-valued, 4-valued, and 8-valued logic values.
|
||||
Each logic value is stored as an uint8, manipulations of individual values are cheaper than in
|
||||
:py:class:`BPArray`.
|
||||
|
||||
:param a: If a tuple is given, it is interpreted as desired shape. To make an array of ``n`` vectors
|
||||
compatible with a simulator ``sim``, use ``(len(sim.interface), n)``. If a :py:class:`BPArray` or
|
||||
:py:class:`MVArray` is given, a deep copy is made. If a string, a list of strings, a list of characters,
|
||||
or a list of lists of characters are given, the data is interpreted best-effort and the array is
|
||||
initialized accordingly.
|
||||
:param m: The arity of the logic. Can be set to 2, 4, or 8. If None is given, the arity of a given
|
||||
:py:class:`BPArray` or :py:class:`MVArray` is used, or, if the array is initialized differently, 8 is used.
|
||||
The given values are interpreted and the axes are arranged as per KyuPy's convention.
|
||||
Use this function to convert strings into multi-valued arrays.
|
||||
"""
|
||||
mva = np.array(interpret(a), dtype=np.uint8)
|
||||
if mva.ndim < 2: return mva
|
||||
if mva.shape[-2] > 1: return mva.swapaxes(-1, -2)
|
||||
return mva[..., 0, :]
|
||||
|
||||
def __init__(self, a, m=None):
|
||||
self.m = m or 8
|
||||
assert self.m in [2, 4, 8]
|
||||
|
||||
# Try our best to interpret given a.
|
||||
if isinstance(a, MVArray):
|
||||
self.data = a.data.copy()
|
||||
"""The wrapped 2-dimensional ndarray of logic values.
|
||||
|
||||
* Axis 0 is PI/PO/FF position, the length of this axis is called "width".
|
||||
* Axis 1 is vector/pattern, the length of this axis is called "length".
|
||||
def mv_str(mva, delim='\n'):
|
||||
"""Renders a given multi-valued array into a string.
|
||||
"""
|
||||
self.m = m or a.m
|
||||
elif hasattr(a, 'data'): # assume it is a BPArray. Can't use isinstance() because BPArray isn't declared yet.
|
||||
self.data = np.zeros((a.width, a.length), dtype=np.uint8)
|
||||
self.m = m or a.m
|
||||
for i in range(a.data.shape[-2]):
|
||||
self.data[...] <<= 1
|
||||
self.data[...] |= np.unpackbits(a.data[..., -i-1, :], axis=1)[:, :a.length]
|
||||
if a.data.shape[-2] == 1:
|
||||
self.data *= 3
|
||||
elif isinstance(a, int):
|
||||
self.data = np.full((a, 1), UNASSIGNED, dtype=np.uint8)
|
||||
elif isinstance(a, tuple):
|
||||
self.data = np.full(a, UNASSIGNED, dtype=np.uint8)
|
||||
else:
|
||||
if isinstance(a, str): a = [a]
|
||||
self.data = np.asarray(interpret(a), dtype=np.uint8)
|
||||
self.data = self.data[:, np.newaxis] if self.data.ndim == 1 else np.moveaxis(self.data, -2, -1)
|
||||
|
||||
# Cast data to m-valued logic.
|
||||
if self.m == 2:
|
||||
self.data[...] = ((self.data & 0b001) & ((self.data >> 1) & 0b001) | (self.data == RISE)) * ONE
|
||||
elif self.m == 4:
|
||||
self.data[...] = (self.data & 0b011) & ((self.data != FALL) * ONE) | ((self.data == RISE) * ONE)
|
||||
elif self.m == 8:
|
||||
self.data[...] = self.data & 0b111
|
||||
|
||||
self.length = self.data.shape[-1]
|
||||
self.width = self.data.shape[-2]
|
||||
|
||||
def __repr__(self):
|
||||
return f'<MVArray length={self.length} width={self.width} m={self.m} mem={hr_bytes(self.data.nbytes)}>'
|
||||
|
||||
def __str__(self):
|
||||
return str([self[idx] for idx in range(self.length)])
|
||||
|
||||
def __getitem__(self, vector_idx):
|
||||
"""Returns a string representing the desired vector."""
|
||||
chars = ["0", "X", "-", "1", "P", "R", "F", "N"]
|
||||
return ''.join(chars[v] for v in self.data[:, vector_idx])
|
||||
|
||||
def __len__(self):
|
||||
return self.length
|
||||
sa = np.choose(mva, np.array([*'0X-1PRFN'], dtype=np.unicode_))
|
||||
if not hasattr(mva, 'ndim') or mva.ndim == 0: return sa
|
||||
if mva.ndim == 1: return ''.join(sa)
|
||||
return delim.join([''.join(c) for c in sa.swapaxes(-1,-2)])
|
||||
|
||||
|
||||
def mv_cast(*args, m=8):
|
||||
return [a if isinstance(a, MVArray) else MVArray(a, m=m) for a in args]
|
||||
|
||||
|
||||
def mv_getm(*args):
|
||||
return max([a.m for a in args if isinstance(a, MVArray)] + [0]) or 8
|
||||
|
||||
|
||||
def _mv_not(m, out, inp):
|
||||
def _mv_not(out, inp):
|
||||
np.bitwise_xor(inp, 0b11, out=out) # this also exchanges UNASSIGNED <-> UNKNOWN
|
||||
if m > 2:
|
||||
np.putmask(out, (inp == UNKNOWN), UNKNOWN) # restore UNKNOWN
|
||||
|
||||
|
||||
def mv_not(x1, out=None):
|
||||
def mv_not(x1 : np.ndarray, out=None):
|
||||
"""A multi-valued NOT operator.
|
||||
|
||||
:param x1: An :py:class:`MVArray` or data the :py:class:`MVArray` constructor accepts.
|
||||
:param out: Optionally an :py:class:`MVArray` as storage destination. If None, a new :py:class:`MVArray`
|
||||
is returned.
|
||||
:return: An :py:class:`MVArray` with the result.
|
||||
:param x1: A multi-valued array.
|
||||
:param out: An optional storage destination. If None, a new multi-valued array is returned.
|
||||
:return: A multi-valued array with the result.
|
||||
"""
|
||||
m = mv_getm(x1)
|
||||
x1 = mv_cast(x1, m=m)[0]
|
||||
out = out or MVArray(x1.data.shape, m=m)
|
||||
_mv_not(m, out.data, x1.data)
|
||||
out = out or np.empty(x1.shape, dtype=np.uint8)
|
||||
_mv_not(out, x1)
|
||||
return out
|
||||
|
||||
|
||||
def _mv_or(m, out, *ins):
|
||||
if m > 2:
|
||||
def _mv_or(out, *ins):
|
||||
any_unknown = (ins[0] == UNKNOWN) | (ins[0] == UNASSIGNED)
|
||||
for inp in ins[1:]: any_unknown |= (inp == UNKNOWN) | (inp == UNASSIGNED)
|
||||
any_one = (ins[0] == ONE)
|
||||
@@ -205,29 +148,22 @@ def _mv_or(m, out, *ins):
|
||||
for inp in ins:
|
||||
np.bitwise_or(out, inp, out=out, where=~any_one)
|
||||
np.putmask(out, (any_unknown & ~any_one), UNKNOWN)
|
||||
else:
|
||||
out[...] = ZERO
|
||||
for inp in ins: np.bitwise_or(out, inp, out=out)
|
||||
|
||||
|
||||
def mv_or(x1, x2, out=None):
|
||||
"""A multi-valued OR operator.
|
||||
|
||||
:param x1: An :py:class:`MVArray` or data the :py:class:`MVArray` constructor accepts.
|
||||
:param x2: An :py:class:`MVArray` or data the :py:class:`MVArray` constructor accepts.
|
||||
:param out: Optionally an :py:class:`MVArray` as storage destination. If None, a new :py:class:`MVArray`
|
||||
is returned.
|
||||
:return: An :py:class:`MVArray` with the result.
|
||||
:param x1: A multi-valued array.
|
||||
:param x2: A multi-valued array.
|
||||
:param out: An optional storage destination. If None, a new multi-valued array is returned.
|
||||
:return: A multi-valued array with the result.
|
||||
"""
|
||||
m = mv_getm(x1, x2)
|
||||
x1, x2 = mv_cast(x1, x2, m=m)
|
||||
out = out or MVArray(np.broadcast(x1.data, x2.data).shape, m=m)
|
||||
_mv_or(m, out.data, x1.data, x2.data)
|
||||
out = out or np.empty(np.broadcast(x1, x2).shape, dtype=np.uint8)
|
||||
_mv_or(out, x1, x2)
|
||||
return out
|
||||
|
||||
|
||||
def _mv_and(m, out, *ins):
|
||||
if m > 2:
|
||||
def _mv_and(out, *ins):
|
||||
any_unknown = (ins[0] == UNKNOWN) | (ins[0] == UNASSIGNED)
|
||||
for inp in ins[1:]: any_unknown |= (inp == UNKNOWN) | (inp == UNASSIGNED)
|
||||
any_zero = (ins[0] == ZERO)
|
||||
@@ -237,163 +173,161 @@ def _mv_and(m, out, *ins):
|
||||
np.putmask(out, any_zero, ZERO)
|
||||
for inp in ins:
|
||||
np.bitwise_and(out, inp | 0b100, out=out, where=~any_zero)
|
||||
if m > 4: np.bitwise_or(out, inp & 0b100, out=out, where=~any_zero)
|
||||
np.bitwise_or(out, inp & 0b100, out=out, where=~any_zero)
|
||||
np.putmask(out, (any_unknown & ~any_zero), UNKNOWN)
|
||||
else:
|
||||
out[...] = ONE
|
||||
for inp in ins: np.bitwise_and(out, inp, out=out)
|
||||
|
||||
|
||||
def mv_and(x1, x2, out=None):
|
||||
"""A multi-valued AND operator.
|
||||
|
||||
:param x1: An :py:class:`MVArray` or data the :py:class:`MVArray` constructor accepts.
|
||||
:param x2: An :py:class:`MVArray` or data the :py:class:`MVArray` constructor accepts.
|
||||
:param out: Optionally an :py:class:`MVArray` as storage destination. If None, a new :py:class:`MVArray`
|
||||
is returned.
|
||||
:return: An :py:class:`MVArray` with the result.
|
||||
:param x1: A multi-valued array.
|
||||
:param x2: A multi-valued array.
|
||||
:param out: An optional storage destination. If None, a new multi-valued array is returned.
|
||||
:return: A multi-valued array with the result.
|
||||
"""
|
||||
m = mv_getm(x1, x2)
|
||||
x1, x2 = mv_cast(x1, x2, m=m)
|
||||
out = out or MVArray(np.broadcast(x1.data, x2.data).shape, m=m)
|
||||
_mv_and(m, out.data, x1.data, x2.data)
|
||||
out = out or np.empty(np.broadcast(x1, x2).shape, dtype=np.uint8)
|
||||
_mv_and(out, x1, x2)
|
||||
return out
|
||||
|
||||
|
||||
def _mv_xor(m, out, *ins):
|
||||
if m > 2:
|
||||
def _mv_xor(out, *ins):
|
||||
any_unknown = (ins[0] == UNKNOWN) | (ins[0] == UNASSIGNED)
|
||||
for inp in ins[1:]: any_unknown |= (inp == UNKNOWN) | (inp == UNASSIGNED)
|
||||
|
||||
out[...] = ZERO
|
||||
for inp in ins:
|
||||
np.bitwise_xor(out, inp & 0b011, out=out)
|
||||
if m > 4: np.bitwise_or(out, inp & 0b100, out=out)
|
||||
np.bitwise_or(out, inp & 0b100, out=out)
|
||||
np.putmask(out, any_unknown, UNKNOWN)
|
||||
else:
|
||||
out[...] = ZERO
|
||||
for inp in ins: np.bitwise_xor(out, inp, out=out)
|
||||
|
||||
|
||||
def mv_xor(x1, x2, out=None):
|
||||
"""A multi-valued XOR operator.
|
||||
|
||||
:param x1: An :py:class:`MVArray` or data the :py:class:`MVArray` constructor accepts.
|
||||
:param x2: An :py:class:`MVArray` or data the :py:class:`MVArray` constructor accepts.
|
||||
:param out: Optionally an :py:class:`MVArray` as storage destination. If None, a new :py:class:`MVArray`
|
||||
is returned.
|
||||
:return: An :py:class:`MVArray` with the result.
|
||||
:param x1: A multi-valued array.
|
||||
:param x2: A multi-valued array.
|
||||
:param out: An optional storage destination. If None, a new multi-valued array is returned.
|
||||
:return: A multi-valued array with the result.
|
||||
"""
|
||||
m = mv_getm(x1, x2)
|
||||
x1, x2 = mv_cast(x1, x2, m=m)
|
||||
out = out or MVArray(np.broadcast(x1.data, x2.data).shape, m=m)
|
||||
_mv_xor(m, out.data, x1.data, x2.data)
|
||||
out = out or np.empty(np.broadcast(x1, x2).shape, dtype=np.uint8)
|
||||
_mv_xor(out, x1, x2)
|
||||
return out
|
||||
|
||||
|
||||
def mv_latch(d, t, q_prev, out=None):
|
||||
"""A multi-valued latch operator.
|
||||
|
||||
A latch outputs ``d`` when transparent (``t`` is high).
|
||||
It outputs ``q_prev`` when in latched state (``t`` is low).
|
||||
|
||||
:param d: A multi-valued array for the data input.
|
||||
:param t: A multi-valued array for the control input.
|
||||
:param q_prev: A multi-valued array with the output value of this latch from the previous clock cycle.
|
||||
:param out: An optional storage destination. If None, a new multi-valued array is returned.
|
||||
:return: A multi-valued array for the latch output ``q``.
|
||||
"""
|
||||
out = out or np.empty(np.broadcast(d, t, q_prev).shape, dtype=np.uint8)
|
||||
out[...] = t & d & 0b011
|
||||
out[...] |= ~t & 0b010 & (q_prev << 1)
|
||||
out[...] |= ~t & 0b001 & (out >> 1)
|
||||
out[...] |= ((out << 1) ^ (out << 2)) & 0b100
|
||||
unknown = (t == UNKNOWN) \
|
||||
| (t == UNASSIGNED) \
|
||||
| (((d == UNKNOWN) | (d == UNASSIGNED)) & (t != ZERO))
|
||||
np.putmask(out, unknown, UNKNOWN)
|
||||
return out
|
||||
|
||||
|
||||
def mv_transition(init, final, out=None):
|
||||
"""Computes the logic transitions from the initial values of ``init`` to the final values of ``final``.
|
||||
Pulses in the input data are ignored. If any of the inputs are ``UNKNOWN``, the result is ``UNKNOWN``.
|
||||
If init is ``UNASSIGNED``, the result is the final value of ``final``.
|
||||
If final is ``UNASSIGNED``, the result is the initial value of ``init``.
|
||||
If both inputs are ``UNASSIGNED``, the result is ``UNASSIGNED``.
|
||||
|
||||
:param init: An :py:class:`MVArray` or data the :py:class:`MVArray` constructor accepts.
|
||||
:param final: An :py:class:`MVArray` or data the :py:class:`MVArray` constructor accepts.
|
||||
:param out: Optionally an :py:class:`MVArray` as storage destination. If None, a new :py:class:`MVArray`
|
||||
is returned.
|
||||
:return: An :py:class:`MVArray` with the result.
|
||||
:param init: A multi-valued array.
|
||||
:param final: A multi-valued array.
|
||||
:param out: An optional storage destination. If None, a new multi-valued array is returned.
|
||||
:return: A multi-valued array with the result.
|
||||
"""
|
||||
m = mv_getm(init, final)
|
||||
init, final = mv_cast(init, final, m=m)
|
||||
init = init.data
|
||||
final = final.data
|
||||
out = out or MVArray(np.broadcast(init, final).shape, m=8)
|
||||
out.data[...] = (init & 0b010) | (final & 0b001)
|
||||
out.data[...] |= ((out.data << 1) ^ (out.data << 2)) & 0b100
|
||||
unknown = (init == UNKNOWN) | (init == UNASSIGNED) | (final == UNKNOWN) | (final == UNASSIGNED)
|
||||
out = out or np.empty(np.broadcast(init, final).shape, dtype=np.uint8)
|
||||
out[...] = (init & 0b010) | (final & 0b001)
|
||||
out[...] |= ((out << 1) ^ (out << 2)) & 0b100
|
||||
out[...] = np.choose(init == UNASSIGNED, [out, (final & 0b001) * ONE])
|
||||
out[...] = np.choose(final == UNASSIGNED, [out, ((init & 0b010) >> 1) * ONE])
|
||||
unknown = (init == UNKNOWN) | (final == UNKNOWN)
|
||||
unassigned = (init == UNASSIGNED) & (final == UNASSIGNED)
|
||||
np.putmask(out.data, unknown, UNKNOWN)
|
||||
np.putmask(out.data, unassigned, UNASSIGNED)
|
||||
np.putmask(out, unknown, UNKNOWN)
|
||||
np.putmask(out, unassigned, UNASSIGNED)
|
||||
return out
|
||||
|
||||
|
||||
class BPArray:
|
||||
"""An n-dimensional array of m-valued logic values that uses bit-parallel storage.
|
||||
|
||||
The primary use of this format is in aiding efficient bit-parallel logic simulation.
|
||||
The secondary benefit over :py:class:`MVArray` is its memory efficiency.
|
||||
Accessing individual values is more expensive than with :py:class:`MVArray`.
|
||||
Therefore it may be more efficient to unpack the data into an :py:class:`MVArray` and pack it again into a
|
||||
:py:class:`BPArray` for simulation.
|
||||
|
||||
See :py:class:`MVArray` for constructor parameters.
|
||||
def mv_to_bp(mva):
|
||||
"""Converts a multi-valued array into a bit-parallel array.
|
||||
"""
|
||||
if mva.ndim == 1: mva = mva[..., np.newaxis]
|
||||
return np.packbits(unpackbits(mva)[...,:3], axis=-2, bitorder='little').swapaxes(-1,-2)
|
||||
|
||||
def __init__(self, a, m=None):
|
||||
if not isinstance(a, MVArray) and not isinstance(a, BPArray):
|
||||
a = MVArray(a, m)
|
||||
self.m = a.m
|
||||
if isinstance(a, MVArray):
|
||||
if m is not None and m != a.m:
|
||||
a = MVArray(a, m) # cast data
|
||||
self.m = a.m
|
||||
assert self.m in [2, 4, 8]
|
||||
nwords = math.ceil(math.log2(self.m))
|
||||
nbytes = (a.data.shape[-1] - 1) // 8 + 1
|
||||
self.data = np.zeros(a.data.shape[:-1] + (nwords, nbytes), dtype=np.uint8)
|
||||
"""The wrapped 3-dimensional ndarray.
|
||||
|
||||
* Axis 0 is PI/PO/FF position, the length of this axis is called "width".
|
||||
* Axis 1 has length ``ceil(log2(m))`` for storing all bits.
|
||||
* Axis 2 are the vectors/patterns packed into uint8 words.
|
||||
def mv_init(mva):
|
||||
"""Returns the initial binary values for mva.
|
||||
"""
|
||||
for i in range(self.data.shape[-2]):
|
||||
self.data[..., i, :] = np.packbits((a.data >> i) & 1, axis=-1)
|
||||
else: # we have a BPArray
|
||||
self.data = a.data.copy() # TODO: support conversion to different m
|
||||
self.m = a.m
|
||||
self.length = a.length
|
||||
self.width = a.width
|
||||
|
||||
def __repr__(self):
|
||||
return f'<BPArray length={self.length} width={self.width} m={self.m} mem={hr_bytes(self.data.nbytes)}>'
|
||||
|
||||
def __len__(self):
|
||||
return self.length
|
||||
return (mva>>1) & ((mva>>2)|mva) & 1
|
||||
|
||||
|
||||
def bp_buf(out, inp):
|
||||
md = out.shape[-2]
|
||||
assert md == inp.shape[-2]
|
||||
if md > 1:
|
||||
def mv_final(mva):
|
||||
"""Returns the final binary value of mva.
|
||||
"""
|
||||
return mva & ((mva>>2)|(mva>>1)) & 1
|
||||
|
||||
|
||||
def bparray(*a):
|
||||
"""Converts (lists of) Boolean values or strings into a bit-parallel array.
|
||||
|
||||
The given values are interpreted and the axes are arranged as per KyuPy's convention.
|
||||
Use this function to convert strings into bit-parallel arrays.
|
||||
"""
|
||||
return mv_to_bp(mvarray(*a))
|
||||
|
||||
|
||||
def bp_to_mv(bpa):
|
||||
"""Converts a bit-parallel array into a multi-valued array.
|
||||
"""
|
||||
return packbits(np.unpackbits(bpa, axis=-1, bitorder='little').swapaxes(-1,-2))
|
||||
|
||||
|
||||
def bp4v_buf(out, inp):
|
||||
unknown = inp[..., 0, :] ^ inp[..., 1, :]
|
||||
if md > 2: unknown &= ~inp[..., 2, :]
|
||||
out[..., 0, :] = inp[..., 0, :] | unknown
|
||||
out[..., 1, :] = inp[..., 1, :] & ~unknown
|
||||
if md > 2: out[..., 2, :] = inp[..., 2, :] & ~unknown
|
||||
else:
|
||||
out[..., 0, :] = inp[..., 0, :]
|
||||
return out
|
||||
|
||||
|
||||
def bp_not(out, inp):
|
||||
md = out.shape[-2]
|
||||
assert md == inp.shape[-2]
|
||||
if md > 1:
|
||||
def bp8v_buf(out, inp):
|
||||
unknown = (inp[..., 0, :] ^ inp[..., 1, :]) & ~inp[..., 2, :]
|
||||
out[..., 0, :] = inp[..., 0, :] | unknown
|
||||
out[..., 1, :] = inp[..., 1, :] & ~unknown
|
||||
out[..., 2, :] = inp[..., 2, :] & ~unknown
|
||||
return out
|
||||
|
||||
|
||||
def bp4v_not(out, inp):
|
||||
unknown = inp[..., 0, :] ^ inp[..., 1, :]
|
||||
if md > 2: unknown &= ~inp[..., 2, :]
|
||||
out[..., 0, :] = ~inp[..., 0, :] | unknown
|
||||
out[..., 1, :] = ~inp[..., 1, :] & ~unknown
|
||||
if md > 2: out[..., 2, :] = inp[..., 2, :] & ~unknown
|
||||
else:
|
||||
out[..., 0, :] = ~inp[..., 0, :]
|
||||
return out
|
||||
|
||||
|
||||
def bp_or(out, *ins):
|
||||
md = out.shape[-2]
|
||||
for inp in ins: assert md == inp.shape[-2]
|
||||
def bp8v_not(out, inp):
|
||||
unknown = (inp[..., 0, :] ^ inp[..., 1, :]) & ~inp[..., 2, :]
|
||||
out[..., 0, :] = ~inp[..., 0, :] | unknown
|
||||
out[..., 1, :] = ~inp[..., 1, :] & ~unknown
|
||||
out[..., 2, :] = inp[..., 2, :] & ~unknown
|
||||
return out
|
||||
|
||||
|
||||
def bp4v_or(out, *ins):
|
||||
out[...] = 0
|
||||
if md == 1:
|
||||
for inp in ins: out[..., 0, :] |= inp[..., 0, :]
|
||||
elif md == 2:
|
||||
any_unknown = ins[0][..., 0, :] ^ ins[0][..., 1, :]
|
||||
for inp in ins[1:]: any_unknown |= inp[..., 0, :] ^ inp[..., 1, :]
|
||||
any_one = ins[0][..., 0, :] & ins[0][..., 1, :]
|
||||
@@ -401,7 +335,11 @@ def bp_or(out, *ins):
|
||||
for inp in ins:
|
||||
out[..., 0, :] |= inp[..., 0, :] | any_unknown
|
||||
out[..., 1, :] |= inp[..., 1, :] & (~any_unknown | any_one)
|
||||
else:
|
||||
return out
|
||||
|
||||
|
||||
def bp8v_or(out, *ins):
|
||||
out[...] = 0
|
||||
any_unknown = (ins[0][..., 0, :] ^ ins[0][..., 1, :]) & ~ins[0][..., 2, :]
|
||||
for inp in ins[1:]: any_unknown |= (inp[..., 0, :] ^ inp[..., 1, :]) & ~inp[..., 2, :]
|
||||
any_one = ins[0][..., 0, :] & ins[0][..., 1, :] & ~ins[0][..., 2, :]
|
||||
@@ -410,15 +348,11 @@ def bp_or(out, *ins):
|
||||
out[..., 0, :] |= inp[..., 0, :] | any_unknown
|
||||
out[..., 1, :] |= inp[..., 1, :] & (~any_unknown | any_one)
|
||||
out[..., 2, :] |= inp[..., 2, :] & (~any_unknown | any_one) & ~any_one
|
||||
return out
|
||||
|
||||
|
||||
def bp_and(out, *ins):
|
||||
md = out.shape[-2]
|
||||
for inp in ins: assert md == inp.shape[-2]
|
||||
def bp4v_and(out, *ins):
|
||||
out[...] = 0xff
|
||||
if md == 1:
|
||||
for inp in ins: out[..., 0, :] &= inp[..., 0, :]
|
||||
elif md == 2:
|
||||
any_unknown = ins[0][..., 0, :] ^ ins[0][..., 1, :]
|
||||
for inp in ins[1:]: any_unknown |= inp[..., 0, :] ^ inp[..., 1, :]
|
||||
any_zero = ~ins[0][..., 0, :] & ~ins[0][..., 1, :]
|
||||
@@ -426,7 +360,11 @@ def bp_and(out, *ins):
|
||||
for inp in ins:
|
||||
out[..., 0, :] &= inp[..., 0, :] | (any_unknown & ~any_zero)
|
||||
out[..., 1, :] &= inp[..., 1, :] & ~any_unknown
|
||||
else:
|
||||
return out
|
||||
|
||||
|
||||
def bp8v_and(out, *ins):
|
||||
out[...] = 0xff
|
||||
any_unknown = (ins[0][..., 0, :] ^ ins[0][..., 1, :]) & ~ins[0][..., 2, :]
|
||||
for inp in ins[1:]: any_unknown |= (inp[..., 0, :] ^ inp[..., 1, :]) & ~inp[..., 2, :]
|
||||
any_zero = ~ins[0][..., 0, :] & ~ins[0][..., 1, :] & ~ins[0][..., 2, :]
|
||||
@@ -436,21 +374,23 @@ def bp_and(out, *ins):
|
||||
out[..., 0, :] &= inp[..., 0, :] | (any_unknown & ~any_zero)
|
||||
out[..., 1, :] &= inp[..., 1, :] & ~any_unknown
|
||||
out[..., 2, :] |= inp[..., 2, :] & (~any_unknown | any_zero) & ~any_zero
|
||||
return out
|
||||
|
||||
|
||||
def bp_xor(out, *ins):
|
||||
md = out.shape[-2]
|
||||
for inp in ins: assert md == inp.shape[-2]
|
||||
def bp4v_xor(out, *ins):
|
||||
out[...] = 0
|
||||
if md == 1:
|
||||
for inp in ins: out[..., 0, :] ^= inp[..., 0, :]
|
||||
elif md == 2:
|
||||
any_unknown = ins[0][..., 0, :] ^ ins[0][..., 1, :]
|
||||
for inp in ins[1:]: any_unknown |= inp[..., 0, :] ^ inp[..., 1, :]
|
||||
for inp in ins: out[...] ^= inp
|
||||
for inp in ins:
|
||||
out[..., 0, :] ^= inp[..., 0, :]
|
||||
out[..., 1, :] ^= inp[..., 1, :]
|
||||
out[..., 0, :] |= any_unknown
|
||||
out[..., 1, :] &= ~any_unknown
|
||||
else:
|
||||
return out
|
||||
|
||||
|
||||
def bp8v_xor(out, *ins):
|
||||
out[...] = 0
|
||||
any_unknown = (ins[0][..., 0, :] ^ ins[0][..., 1, :]) & ~ins[0][..., 2, :]
|
||||
for inp in ins[1:]: any_unknown |= (inp[..., 0, :] ^ inp[..., 1, :]) & ~inp[..., 2, :]
|
||||
for inp in ins:
|
||||
@@ -460,3 +400,50 @@ def bp_xor(out, *ins):
|
||||
out[..., 0, :] |= any_unknown
|
||||
out[..., 1, :] &= ~any_unknown
|
||||
out[..., 2, :] &= ~any_unknown
|
||||
return out
|
||||
|
||||
|
||||
def bp8v_latch(out, d, t, q_prev):
|
||||
any_unknown = (t[..., 0, :] ^ t[..., 1, :]) & ~t[..., 2, :]
|
||||
any_unknown |= ((d[..., 0, :] ^ d[..., 1, :]) & ~d[..., 2, :]) & (t[..., 0, :] | t[..., 1, :] | t[..., 2, :])
|
||||
out[..., 1, :] = (d[..., 1, :] & t[..., 1, :]) | (q_prev[..., 0, :] & ~t[..., 1, :])
|
||||
out[..., 0, :] = (d[..., 0, :] & t[..., 0, :]) | (out[..., 1, :] & ~t[..., 0, :])
|
||||
out[..., 2, :] = out[..., 1, :] ^ out[..., 0, :]
|
||||
out[..., 0, :] |= any_unknown
|
||||
out[..., 1, :] &= ~any_unknown
|
||||
out[..., 2, :] &= ~any_unknown
|
||||
return out
|
||||
|
||||
|
||||
_bit_in_lut = np.array([2 ** x for x in range(7, -1, -1)], dtype='uint8')
|
||||
|
||||
|
||||
@numba.njit
|
||||
def bit_in(a, pos):
|
||||
return a[pos >> 3] & _bit_in_lut[pos & 7]
|
||||
|
||||
|
||||
def unpackbits(a : np.ndarray):
|
||||
"""Unpacks the bits of given ndarray ``a``.
|
||||
|
||||
Similar to ``np.unpackbits``, but accepts any dtype, preserves the shape of ``a`` and
|
||||
adds a new last axis with the bits of each item. Bits are in 'little'-order, i.e.,
|
||||
a[...,0] is the least significant bit of each item.
|
||||
"""
|
||||
return np.unpackbits(a.view(np.uint8), bitorder='little').reshape(*a.shape, 8*a.itemsize)
|
||||
|
||||
|
||||
def packbits(a, dtype=np.uint8):
|
||||
"""Packs the values of a boolean-valued array ``a`` along its last axis into bits.
|
||||
|
||||
Similar to ``np.packbits``, but returns an array of given dtype and the shape of ``a`` with the last axis removed.
|
||||
The last axis of `a` is truncated or padded according to the bit-width of the given dtype.
|
||||
Signed integer datatypes are padded with the most significant bit, all others are padded with `0`.
|
||||
"""
|
||||
dtype = np.dtype(dtype)
|
||||
bits = 8 * dtype.itemsize
|
||||
a = a[...,:bits]
|
||||
if a.shape[-1] < bits:
|
||||
p = [(0,0)]*(len(a.shape)-1) + [(0, bits-a.shape[-1])]
|
||||
a = np.pad(a, p, 'edge') if dtype.name[0] == 'i' else np.pad(a, p, 'constant', constant_values=0)
|
||||
return np.packbits(a, bitorder='little').view(dtype).reshape(a.shape[:-1])
|
||||
+420
-145
@@ -1,7 +1,7 @@
|
||||
"""A high-throughput combinational logic simulator.
|
||||
|
||||
The class :py:class:`~kyupy.logic_sim.LogicSim` performs parallel simulations of the combinational part of a circuit.
|
||||
The logic operations are performed bit-parallel on packed numpy arrays.
|
||||
The logic operations are performed bit-parallel on packed numpy arrays (see bit-parallel (bp) array description in :py:mod:`~kyupy.logic`).
|
||||
Simple sequential circuits can be simulated by repeated assignments and propagations.
|
||||
However, this simulator ignores the clock network and simply assumes that all state-elements are clocked all the time.
|
||||
"""
|
||||
@@ -10,186 +10,461 @@ import math
|
||||
|
||||
import numpy as np
|
||||
|
||||
from . import logic, hr_bytes
|
||||
from . import numba, logic, hr_bytes, sim, eng, cdiv
|
||||
from .circuit import Circuit
|
||||
|
||||
|
||||
class LogicSim:
|
||||
class LogicSim(sim.SimOps):
|
||||
"""A bit-parallel naïve combinational simulator for 2-, 4-, or 8-valued logic.
|
||||
|
||||
:param circuit: The circuit to simulate.
|
||||
:type circuit: :py:class:`~kyupy.circuit.Circuit`
|
||||
:param sims: The number of parallel logic simulations to perform.
|
||||
:type sims: int
|
||||
:param m: The arity of the logic, must be 2, 4, or 8.
|
||||
:type m: int
|
||||
:param c_reuse: If True, intermediate signal values may get overwritten when not needed anymore to save memory.
|
||||
:param strip_forks: If True, forks are not included in the simulation model to save memory and simulation time.
|
||||
"""
|
||||
def __init__(self, circuit, sims=8, m=8):
|
||||
def __init__(self, circuit: Circuit, sims: int = 8, m: int = 8, c_reuse: bool = False, strip_forks: bool = False):
|
||||
assert m in [2, 4, 8]
|
||||
super().__init__(circuit, c_reuse=c_reuse, strip_forks=strip_forks)
|
||||
self.m = m
|
||||
mdim = math.ceil(math.log2(m))
|
||||
self.circuit = circuit
|
||||
self.mdim = math.ceil(math.log2(m))
|
||||
self.sims = sims
|
||||
nbytes = (sims - 1) // 8 + 1
|
||||
self.interface = list(circuit.interface) + [n for n in circuit.nodes if 'dff' in n.kind.lower()]
|
||||
self.width = len(self.interface)
|
||||
"""The number of bits in the circuit state (number of ports + number of state-elements)."""
|
||||
self.state = np.zeros((len(circuit.lines), mdim, nbytes), dtype='uint8')
|
||||
self.state_epoch = np.zeros(len(circuit.nodes), dtype='int8') - 1
|
||||
self.tmp = np.zeros((5, mdim, nbytes), dtype='uint8')
|
||||
self.zero = np.zeros((mdim, nbytes), dtype='uint8')
|
||||
self.epoch = 0
|
||||
nbytes = cdiv(sims, 8)
|
||||
|
||||
known_fct = [(f[:-4], getattr(self, f)) for f in dir(self) if f.endswith('_fct')]
|
||||
self.node_fct = []
|
||||
for n in circuit.nodes:
|
||||
t = n.kind.lower().replace('__fork__', 'fork')
|
||||
t = t.replace('nbuff', 'fork')
|
||||
t = t.replace('input', 'fork')
|
||||
t = t.replace('output', 'fork')
|
||||
t = t.replace('__const0__', 'const0')
|
||||
t = t.replace('__const1__', 'const1')
|
||||
t = t.replace('tieh', 'const1')
|
||||
t = t.replace('ibuff', 'not')
|
||||
t = t.replace('inv', 'not')
|
||||
self.c = np.zeros((self.c_len, self.mdim, nbytes), dtype=np.uint8)
|
||||
self.s = np.zeros((2, self.s_len, 3, nbytes), dtype=np.uint8)
|
||||
"""Logic values of the sequential elements (flip-flops) and ports.
|
||||
|
||||
fcts = [f for n, f in known_fct if t.startswith(n)]
|
||||
if len(fcts) < 1:
|
||||
raise ValueError(f'Unknown node kind {n.kind}')
|
||||
self.node_fct.append(fcts[0])
|
||||
It is a pair of arrays in bit-parallel (bp) storage format:
|
||||
|
||||
* ``s[0]`` Assigned values. Simulator will read (P)PI value from here.
|
||||
* ``s[1]`` Result values. Simulator will write (P)PO values here.
|
||||
|
||||
Access this array to assign new values to the (P)PIs or read values from the (P)POs.
|
||||
"""
|
||||
self.s[:,:,1,:] = 255 # unassigned
|
||||
|
||||
def __repr__(self):
|
||||
return f'<LogicSim {self.circuit.name} sims={self.sims} m={self.m} state_mem={hr_bytes(self.state.nbytes)}>'
|
||||
return f'{{name: "{self.circuit.name}", sims: {self.sims}, m: {self.m}, c_bytes: {eng(self.c.nbytes)}}}'
|
||||
|
||||
def assign(self, stimuli):
|
||||
"""Assign stimuli to the primary inputs and state-elements (flip-flops).
|
||||
|
||||
:param stimuli: The input data to assign. Must be in bit-parallel storage format and in a compatible shape.
|
||||
:type stimuli: :py:class:`~kyupy.logic.BPArray`
|
||||
:returns: The given stimuli object.
|
||||
def s_to_c(self):
|
||||
"""Copies the values from ``s[0]`` the inputs of the combinational portion.
|
||||
"""
|
||||
for node, stim in zip(self.interface, stimuli.data if hasattr(stimuli, 'data') else stimuli):
|
||||
if len(node.outs) == 0: continue
|
||||
outputs = [self.state[line] if line else self.tmp[3] for line in node.outs]
|
||||
self.node_fct[node]([stim], outputs)
|
||||
for line in node.outs:
|
||||
if line is not None: self.state_epoch[line.reader] = self.epoch
|
||||
for n in self.circuit.nodes:
|
||||
if n.kind in ('__const1__', '__const0__'):
|
||||
outputs = [self.state[line] if line else self.tmp[3] for line in n.outs]
|
||||
self.node_fct[n]([], outputs)
|
||||
for line in n.outs:
|
||||
if line is not None: self.state_epoch[line.reader] = self.epoch
|
||||
return stimuli
|
||||
self.c[self.pippi_c_locs] = self.s[0, self.pippi_s_locs, :self.mdim]
|
||||
|
||||
def capture(self, responses):
|
||||
"""Capture the current values at the primary outputs and in the state-elements (flip-flops).
|
||||
|
||||
:param responses: A bit-parallel storage target for the responses in a compatible shape.
|
||||
:type responses: :py:class:`~kyupy.logic.BPArray`
|
||||
:returns: The given responses object.
|
||||
"""
|
||||
for node, resp in zip(self.interface, responses.data if hasattr(responses, 'data') else responses):
|
||||
if len(node.ins) > 0: resp[...] = self.state[node.ins[0]]
|
||||
return responses
|
||||
|
||||
def propagate(self, inject_cb=None):
|
||||
"""Propagate the input values towards the outputs (Perform all logic operations in topological order).
|
||||
def c_prop(self, sims=None, inject_cb=None, fault_line=-1, fault_mask=None, fault_model=2):
|
||||
"""Propagate the input values through the combinational circuit towards the outputs.
|
||||
|
||||
Performs all logic operations in topological order.
|
||||
If the circuit is sequential (it contains flip-flops), one call simulates one clock cycle.
|
||||
Multiple clock cycles are simulated by a assign-propagate-capture loop:
|
||||
|
||||
.. code-block:: python
|
||||
|
||||
# initial state in state_bp
|
||||
for cycle in range(10): # simulate 10 clock cycles
|
||||
sim.assign(state_bp)
|
||||
sim.propagate()
|
||||
sim.capture(state_bp)
|
||||
|
||||
:param inject_cb: A callback function for manipulating intermediate signal values.
|
||||
This function is called with a line index and its new logic values (in bit-parallel format) after
|
||||
This function is called with a line and its new logic values (in bit-parallel format) after
|
||||
evaluation of a node. The callback may manipulate the given values in-place, the simulation
|
||||
resumes with the manipulated values after the callback returns.
|
||||
:type inject_cb: ``f(int, ndarray)``
|
||||
:type inject_cb: ``f(Line, ndarray)``
|
||||
"""
|
||||
for node in self.circuit.topological_order():
|
||||
if self.state_epoch[node] != self.epoch: continue
|
||||
inputs = [self.state[line] if line else self.zero for line in node.ins]
|
||||
outputs = [self.state[line] if line else self.tmp[3] for line in node.outs]
|
||||
# print('sim', node)
|
||||
self.node_fct[node](inputs, outputs)
|
||||
for line in node.outs:
|
||||
if inject_cb is not None: inject_cb(line, self.state[line])
|
||||
self.state_epoch[line.reader] = self.epoch
|
||||
self.epoch = (self.epoch + 1) % 128
|
||||
t0 = self.c_locs[self.tmp_idx]
|
||||
t1 = self.c_locs[self.tmp2_idx]
|
||||
if self.m == 2:
|
||||
if inject_cb is None:
|
||||
if fault_mask is None:
|
||||
fault_mask = np.full(self.c.shape[-1], 255, dtype=np.uint8)
|
||||
else:
|
||||
if len(fault_mask) < self.c.shape[-1]:
|
||||
fault_mask2 = np.full(self.c.shape[-1], 0, dtype=np.uint8)
|
||||
fault_mask2[:len(fault_mask)] = fault_mask
|
||||
fault_mask = fault_mask2
|
||||
_prop_cpu(self.ops, self.c_locs, self.c, int(fault_line), fault_mask, int(fault_model))
|
||||
else:
|
||||
for op, o0l, i0l, i1l, i2l, i3l in self.ops[:,:6]:
|
||||
o0, i0, i1, i2, i3 = [self.c_locs[x] for x in (o0l, i0l, i1l, i2l, i3l)]
|
||||
if op == sim.BUF1: self.c[o0]=self.c[i0]
|
||||
elif op == sim.INV1: self.c[o0] = ~self.c[i0]
|
||||
elif op == sim.AND2: self.c[o0] = self.c[i0] & self.c[i1]
|
||||
elif op == sim.AND3: self.c[o0] = self.c[i0] & self.c[i1] & self.c[i2]
|
||||
elif op == sim.AND4: self.c[o0] = self.c[i0] & self.c[i1] & self.c[i2] & self.c[i3]
|
||||
elif op == sim.NAND2: self.c[o0] = ~(self.c[i0] & self.c[i1])
|
||||
elif op == sim.NAND3: self.c[o0] = ~(self.c[i0] & self.c[i1] & self.c[i2])
|
||||
elif op == sim.NAND4: self.c[o0] = ~(self.c[i0] & self.c[i1] & self.c[i2] & self.c[i3])
|
||||
elif op == sim.OR2: self.c[o0] = self.c[i0] | self.c[i1]
|
||||
elif op == sim.OR3: self.c[o0] = self.c[i0] | self.c[i1] | self.c[i2]
|
||||
elif op == sim.OR4: self.c[o0] = self.c[i0] | self.c[i1] | self.c[i2] | self.c[i3]
|
||||
elif op == sim.NOR2: self.c[o0] = ~(self.c[i0] | self.c[i1])
|
||||
elif op == sim.NOR3: self.c[o0] = ~(self.c[i0] | self.c[i1] | self.c[i2])
|
||||
elif op == sim.NOR4: self.c[o0] = ~(self.c[i0] | self.c[i1] | self.c[i2] | self.c[i3])
|
||||
elif op == sim.XOR2: self.c[o0] = self.c[i0] ^ self.c[i1]
|
||||
elif op == sim.XOR3: self.c[o0] = self.c[i0] ^ self.c[i1] ^ self.c[i2]
|
||||
elif op == sim.XOR4: self.c[o0] = self.c[i0] ^ self.c[i1] ^ self.c[i2] ^ self.c[i3]
|
||||
elif op == sim.XNOR2: self.c[o0] = ~(self.c[i0] ^ self.c[i1])
|
||||
elif op == sim.XNOR3: self.c[o0] = ~(self.c[i0] ^ self.c[i1] ^ self.c[i2])
|
||||
elif op == sim.XNOR4: self.c[o0] = ~(self.c[i0] ^ self.c[i1] ^ self.c[i2] ^ self.c[i3])
|
||||
elif op == sim.AO21: self.c[o0] = (self.c[i0] & self.c[i1]) | self.c[i2]
|
||||
elif op == sim.AOI21: self.c[o0] = ~((self.c[i0] & self.c[i1]) | self.c[i2])
|
||||
elif op == sim.OA21: self.c[o0] = (self.c[i0] | self.c[i1]) & self.c[i2]
|
||||
elif op == sim.OAI21: self.c[o0] = ~((self.c[i0] | self.c[i1]) & self.c[i2])
|
||||
elif op == sim.AO22: self.c[o0] = (self.c[i0] & self.c[i1]) | (self.c[i2] & self.c[i3])
|
||||
elif op == sim.AOI22: self.c[o0] = ~((self.c[i0] & self.c[i1]) | (self.c[i2] & self.c[i3]))
|
||||
elif op == sim.OA22: self.c[o0] = (self.c[i0] | self.c[i1]) & (self.c[i2] | self.c[i3])
|
||||
elif op == sim.OAI22: self.c[o0] = ~((self.c[i0] | self.c[i1]) & (self.c[i2] | self.c[i3]))
|
||||
elif op == sim.AO211: self.c[o0] = (self.c[i0] & self.c[i1]) | self.c[i2] | self.c[i3]
|
||||
elif op == sim.AOI211:self.c[o0] = ~((self.c[i0] & self.c[i1]) | self.c[i2] | self.c[i3])
|
||||
elif op == sim.OA211: self.c[o0] = (self.c[i0] | self.c[i1]) & self.c[i2] & self.c[i3]
|
||||
elif op == sim.OAI211:self.c[o0] = ~((self.c[i0] | self.c[i1]) & self.c[i2] & self.c[i3])
|
||||
elif op == sim.MUX21: self.c[o0] = (self.c[i0] & ~self.c[i2]) | (self.c[i1] & self.c[i2])
|
||||
else: print(f'unknown op {op}')
|
||||
inject_cb(o0l, self.c[o0])
|
||||
elif self.m == 4:
|
||||
for op, o0l, i0l, i1l, i2l, i3l in self.ops[:,:6]:
|
||||
o0, i0, i1, i2, i3 = [self.c_locs[x] for x in (o0l, i0l, i1l, i2l, i3l)]
|
||||
if op == sim.BUF1: self.c[o0]=self.c[i0]
|
||||
elif op == sim.INV1: logic.bp4v_not(self.c[o0], self.c[i0])
|
||||
elif op == sim.AND2: logic.bp4v_and(self.c[o0], self.c[i0], self.c[i1])
|
||||
elif op == sim.AND3: logic.bp4v_and(self.c[o0], self.c[i0], self.c[i1], self.c[i2])
|
||||
elif op == sim.AND4: logic.bp4v_and(self.c[o0], self.c[i0], self.c[i1], self.c[i2], self.c[i3])
|
||||
elif op == sim.NAND2: logic.bp4v_and(self.c[o0], self.c[i0], self.c[i1]); logic.bp4v_not(self.c[o0], self.c[o0])
|
||||
elif op == sim.NAND3: logic.bp4v_and(self.c[o0], self.c[i0], self.c[i1], self.c[i2]); logic.bp4v_not(self.c[o0], self.c[o0])
|
||||
elif op == sim.NAND4: logic.bp4v_and(self.c[o0], self.c[i0], self.c[i1], self.c[i2], self.c[i3]); logic.bp4v_not(self.c[o0], self.c[o0])
|
||||
elif op == sim.OR2: logic.bp4v_or(self.c[o0], self.c[i0], self.c[i1])
|
||||
elif op == sim.OR3: logic.bp4v_or(self.c[o0], self.c[i0], self.c[i1], self.c[i2])
|
||||
elif op == sim.OR4: logic.bp4v_or(self.c[o0], self.c[i0], self.c[i1], self.c[i2], self.c[i3])
|
||||
elif op == sim.NOR2: logic.bp4v_or(self.c[o0], self.c[i0], self.c[i1]); logic.bp4v_not(self.c[o0], self.c[o0])
|
||||
elif op == sim.NOR3: logic.bp4v_or(self.c[o0], self.c[i0], self.c[i1], self.c[i2]); logic.bp4v_not(self.c[o0], self.c[o0])
|
||||
elif op == sim.NOR4: logic.bp4v_or(self.c[o0], self.c[i0], self.c[i1], self.c[i2], self.c[i3]); logic.bp4v_not(self.c[o0], self.c[o0])
|
||||
elif op == sim.XOR2: logic.bp4v_xor(self.c[o0], self.c[i0], self.c[i1])
|
||||
elif op == sim.XOR3: logic.bp4v_xor(self.c[o0], self.c[i0], self.c[i1], self.c[i2])
|
||||
elif op == sim.XOR4: logic.bp4v_xor(self.c[o0], self.c[i0], self.c[i1], self.c[i2], self.c[i3])
|
||||
elif op == sim.XNOR2: logic.bp4v_xor(self.c[o0], self.c[i0], self.c[i1]); logic.bp4v_not(self.c[o0], self.c[o0])
|
||||
elif op == sim.XNOR3: logic.bp4v_xor(self.c[o0], self.c[i0], self.c[i1], self.c[i2]); logic.bp4v_not(self.c[o0], self.c[o0])
|
||||
elif op == sim.XNOR4: logic.bp4v_xor(self.c[o0], self.c[i0], self.c[i1], self.c[i2], self.c[i3]); logic.bp4v_not(self.c[o0], self.c[o0])
|
||||
elif op == sim.AO21:
|
||||
logic.bp4v_and(self.c[t0], self.c[i0], self.c[i1])
|
||||
logic.bp4v_or(self.c[o0], self.c[t0], self.c[i2])
|
||||
elif op == sim.AOI21:
|
||||
logic.bp4v_and(self.c[t0], self.c[i0], self.c[i1])
|
||||
logic.bp4v_or(self.c[o0], self.c[t0], self.c[i2])
|
||||
logic.bp4v_not(self.c[o0], self.c[o0])
|
||||
elif op == sim.OA21:
|
||||
logic.bp4v_or(self.c[t0], self.c[i0], self.c[i1])
|
||||
logic.bp4v_and(self.c[o0], self.c[t0], self.c[i2])
|
||||
elif op == sim.OAI21:
|
||||
logic.bp4v_or(self.c[t0], self.c[i0], self.c[i1])
|
||||
logic.bp4v_and(self.c[o0], self.c[t0], self.c[i2])
|
||||
logic.bp4v_not(self.c[o0], self.c[o0])
|
||||
elif op == sim.AO22:
|
||||
logic.bp4v_and(self.c[t0], self.c[i0], self.c[i1])
|
||||
logic.bp4v_and(self.c[t1], self.c[i2], self.c[i3])
|
||||
logic.bp4v_or(self.c[o0], self.c[t0], self.c[t1])
|
||||
elif op == sim.AOI22:
|
||||
logic.bp4v_and(self.c[t0], self.c[i0], self.c[i1])
|
||||
logic.bp4v_and(self.c[t1], self.c[i2], self.c[i3])
|
||||
logic.bp4v_or(self.c[o0], self.c[t0], self.c[t1])
|
||||
logic.bp4v_not(self.c[o0], self.c[o0])
|
||||
elif op == sim.OA22:
|
||||
logic.bp4v_or(self.c[t0], self.c[i0], self.c[i1])
|
||||
logic.bp4v_or(self.c[t1], self.c[i2], self.c[i3])
|
||||
logic.bp4v_and(self.c[o0], self.c[t0], self.c[t1])
|
||||
elif op == sim.OAI22:
|
||||
logic.bp4v_or(self.c[t0], self.c[i0], self.c[i1])
|
||||
logic.bp4v_or(self.c[t1], self.c[i2], self.c[i3])
|
||||
logic.bp4v_and(self.c[o0], self.c[t0], self.c[t1])
|
||||
logic.bp4v_not(self.c[o0], self.c[o0])
|
||||
elif op == sim.AO211:
|
||||
logic.bp4v_and(self.c[t0], self.c[i0], self.c[i1])
|
||||
logic.bp4v_or(self.c[o0], self.c[t0], self.c[i2], self.c[i3])
|
||||
elif op == sim.AOI211:
|
||||
logic.bp4v_and(self.c[t0], self.c[i0], self.c[i1])
|
||||
logic.bp4v_or(self.c[o0], self.c[t0], self.c[i2], self.c[i3])
|
||||
logic.bp4v_not(self.c[o0], self.c[o0])
|
||||
elif op == sim.OA211:
|
||||
logic.bp4v_or(self.c[t0], self.c[i0], self.c[i1])
|
||||
logic.bp4v_and(self.c[o0], self.c[t0], self.c[i2], self.c[i3])
|
||||
elif op == sim.OAI211:
|
||||
logic.bp4v_or(self.c[t0], self.c[i0], self.c[i1])
|
||||
logic.bp4v_and(self.c[o0], self.c[t0], self.c[i2], self.c[i3])
|
||||
logic.bp4v_not(self.c[o0], self.c[o0])
|
||||
elif op == sim.MUX21:
|
||||
logic.bp4v_not(self.c[t1], self.c[i2])
|
||||
logic.bp4v_and(self.c[t0], self.c[i0], self.c[t1])
|
||||
logic.bp4v_and(self.c[t1], self.c[i1], self.c[i2])
|
||||
logic.bp4v_or(self.c[o0], self.c[t0], self.c[t1])
|
||||
else: print(f'unknown op {op}')
|
||||
if inject_cb is not None: inject_cb(o0l, self.c[o0])
|
||||
else:
|
||||
for op, o0l, i0l, i1l, i2l, i3l in self.ops[:,:6]:
|
||||
o0, i0, i1, i2, i3 = [self.c_locs[x] for x in (o0l, i0l, i1l, i2l, i3l)]
|
||||
if op == sim.BUF1: self.c[o0]=self.c[i0]
|
||||
elif op == sim.INV1: logic.bp8v_not(self.c[o0], self.c[i0])
|
||||
elif op == sim.AND2: logic.bp8v_and(self.c[o0], self.c[i0], self.c[i1])
|
||||
elif op == sim.AND3: logic.bp8v_and(self.c[o0], self.c[i0], self.c[i1], self.c[i2])
|
||||
elif op == sim.AND4: logic.bp8v_and(self.c[o0], self.c[i0], self.c[i1], self.c[i2], self.c[i3])
|
||||
elif op == sim.NAND2: logic.bp8v_and(self.c[o0], self.c[i0], self.c[i1]); logic.bp8v_not(self.c[o0], self.c[o0])
|
||||
elif op == sim.NAND3: logic.bp8v_and(self.c[o0], self.c[i0], self.c[i1], self.c[i2]); logic.bp8v_not(self.c[o0], self.c[o0])
|
||||
elif op == sim.NAND4: logic.bp8v_and(self.c[o0], self.c[i0], self.c[i1], self.c[i2], self.c[i3]); logic.bp8v_not(self.c[o0], self.c[o0])
|
||||
elif op == sim.OR2: logic.bp8v_or(self.c[o0], self.c[i0], self.c[i1])
|
||||
elif op == sim.OR3: logic.bp8v_or(self.c[o0], self.c[i0], self.c[i1], self.c[i2])
|
||||
elif op == sim.OR4: logic.bp8v_or(self.c[o0], self.c[i0], self.c[i1], self.c[i2], self.c[i3])
|
||||
elif op == sim.NOR2: logic.bp8v_or(self.c[o0], self.c[i0], self.c[i1]); logic.bp8v_not(self.c[o0], self.c[o0])
|
||||
elif op == sim.NOR3: logic.bp8v_or(self.c[o0], self.c[i0], self.c[i1], self.c[i2]); logic.bp8v_not(self.c[o0], self.c[o0])
|
||||
elif op == sim.NOR4: logic.bp8v_or(self.c[o0], self.c[i0], self.c[i1], self.c[i2], self.c[i3]); logic.bp8v_not(self.c[o0], self.c[o0])
|
||||
elif op == sim.XOR2: logic.bp8v_xor(self.c[o0], self.c[i0], self.c[i1])
|
||||
elif op == sim.XOR3: logic.bp8v_xor(self.c[o0], self.c[i0], self.c[i1], self.c[i2])
|
||||
elif op == sim.XOR4: logic.bp8v_xor(self.c[o0], self.c[i0], self.c[i1], self.c[i2], self.c[i3])
|
||||
elif op == sim.XNOR2: logic.bp8v_xor(self.c[o0], self.c[i0], self.c[i1]); logic.bp8v_not(self.c[o0], self.c[o0])
|
||||
elif op == sim.XNOR3: logic.bp8v_xor(self.c[o0], self.c[i0], self.c[i1], self.c[i2]); logic.bp8v_not(self.c[o0], self.c[o0])
|
||||
elif op == sim.XNOR4: logic.bp8v_xor(self.c[o0], self.c[i0], self.c[i1], self.c[i2], self.c[i3]); logic.bp8v_not(self.c[o0], self.c[o0])
|
||||
elif op == sim.AO21:
|
||||
logic.bp8v_and(self.c[t0], self.c[i0], self.c[i1])
|
||||
logic.bp8v_or(self.c[o0], self.c[t0], self.c[i2])
|
||||
elif op == sim.AOI21:
|
||||
logic.bp8v_and(self.c[t0], self.c[i0], self.c[i1])
|
||||
logic.bp8v_or(self.c[o0], self.c[t0], self.c[i2])
|
||||
logic.bp8v_not(self.c[o0], self.c[o0])
|
||||
elif op == sim.OA21:
|
||||
logic.bp8v_or(self.c[t0], self.c[i0], self.c[i1])
|
||||
logic.bp8v_and(self.c[o0], self.c[t0], self.c[i2])
|
||||
elif op == sim.OAI21:
|
||||
logic.bp8v_or(self.c[t0], self.c[i0], self.c[i1])
|
||||
logic.bp8v_and(self.c[o0], self.c[t0], self.c[i2])
|
||||
logic.bp8v_not(self.c[o0], self.c[o0])
|
||||
elif op == sim.AO22:
|
||||
logic.bp8v_and(self.c[t0], self.c[i0], self.c[i1])
|
||||
logic.bp8v_and(self.c[t1], self.c[i2], self.c[i3])
|
||||
logic.bp8v_or(self.c[o0], self.c[t0], self.c[t1])
|
||||
elif op == sim.AOI22:
|
||||
logic.bp8v_and(self.c[t0], self.c[i0], self.c[i1])
|
||||
logic.bp8v_and(self.c[t1], self.c[i2], self.c[i3])
|
||||
logic.bp8v_or(self.c[o0], self.c[t0], self.c[t1])
|
||||
logic.bp8v_not(self.c[o0], self.c[o0])
|
||||
elif op == sim.OA22:
|
||||
logic.bp8v_or(self.c[t0], self.c[i0], self.c[i1])
|
||||
logic.bp8v_or(self.c[t1], self.c[i2], self.c[i3])
|
||||
logic.bp8v_and(self.c[o0], self.c[t0], self.c[t1])
|
||||
elif op == sim.OAI22:
|
||||
logic.bp8v_or(self.c[t0], self.c[i0], self.c[i1])
|
||||
logic.bp8v_or(self.c[t1], self.c[i2], self.c[i3])
|
||||
logic.bp8v_and(self.c[o0], self.c[t0], self.c[t1])
|
||||
logic.bp8v_not(self.c[o0], self.c[o0])
|
||||
elif op == sim.AO211:
|
||||
logic.bp8v_and(self.c[t0], self.c[i0], self.c[i1])
|
||||
logic.bp8v_or(self.c[o0], self.c[t0], self.c[i2], self.c[i3])
|
||||
elif op == sim.AOI211:
|
||||
logic.bp8v_and(self.c[t0], self.c[i0], self.c[i1])
|
||||
logic.bp8v_or(self.c[o0], self.c[t0], self.c[i2], self.c[i3])
|
||||
logic.bp8v_not(self.c[o0], self.c[o0])
|
||||
elif op == sim.OA211:
|
||||
logic.bp8v_or(self.c[t0], self.c[i0], self.c[i1])
|
||||
logic.bp8v_and(self.c[o0], self.c[t0], self.c[i2], self.c[i3])
|
||||
elif op == sim.OAI211:
|
||||
logic.bp8v_or(self.c[t0], self.c[i0], self.c[i1])
|
||||
logic.bp8v_and(self.c[o0], self.c[t0], self.c[i2], self.c[i3])
|
||||
logic.bp8v_not(self.c[o0], self.c[o0])
|
||||
elif op == sim.MUX21:
|
||||
logic.bp8v_not(self.c[t1], self.c[i2])
|
||||
logic.bp8v_and(self.c[t0], self.c[i0], self.c[t1])
|
||||
logic.bp8v_and(self.c[t1], self.c[i1], self.c[i2])
|
||||
logic.bp8v_or(self.c[o0], self.c[t0], self.c[t1])
|
||||
else: print(f'unknown op {op}')
|
||||
if inject_cb is not None: inject_cb(o0l, self.c[o0])
|
||||
|
||||
def cycle(self, state, inject_cb=None):
|
||||
"""Assigns the given state, propagates it and captures the new state.
|
||||
|
||||
:param state: A bit-parallel array in a compatible shape holding the current circuit state.
|
||||
The contained data is assigned to the PI and PPI and overwritten by data at the PO and PPO after
|
||||
propagation.
|
||||
:type state: :py:class:`~kyupy.logic.BPArray`
|
||||
:param inject_cb: A callback function for manipulating intermediate signal values. See :py:func:`propagate`.
|
||||
:returns: The given state object.
|
||||
def c_to_s(self):
|
||||
"""Copies (captures) the results of the combinational portion to ``s[1]``.
|
||||
"""
|
||||
self.assign(state)
|
||||
self.propagate(inject_cb)
|
||||
return self.capture(state)
|
||||
self.s[1, self.poppo_s_locs, :self.mdim] = self.c[self.poppo_c_locs]
|
||||
if self.mdim == 1:
|
||||
self.s[1, self.poppo_s_locs, 1:2] = self.c[self.poppo_c_locs]
|
||||
|
||||
@staticmethod
|
||||
def fork_fct(inputs, outputs):
|
||||
for o in outputs: o[...] = inputs[0]
|
||||
def s_ppo_to_ppi(self):
|
||||
"""Constructs a new assignment based on the current data in ``s``.
|
||||
|
||||
@staticmethod
|
||||
def const0_fct(_, outputs):
|
||||
for o in outputs: o[...] = 0
|
||||
Use this function for simulating consecutive clock cycles.
|
||||
|
||||
@staticmethod
|
||||
def const1_fct(_, outputs):
|
||||
for o in outputs:
|
||||
o[...] = 0
|
||||
logic.bp_not(o, o)
|
||||
For 2-valued or 4-valued simulations, all valued from PPOs (in ``s[1]``) and copied to the PPIs (in ``s[0]``).
|
||||
For 8-valued simulations, PPI transitions are constructed from the final values of the assignment (in ``s[0]``) and the
|
||||
final values of the results (in ``s[1]``).
|
||||
"""
|
||||
# TODO: handle latches correctly
|
||||
if self.mdim < 3:
|
||||
self.s[0, self.ppio_s_locs] = self.s[1, self.ppio_s_locs]
|
||||
else:
|
||||
self.s[0, self.ppio_s_locs, 1] = self.s[0, self.ppio_s_locs, 0] # initial value is previously assigned final value
|
||||
self.s[0, self.ppio_s_locs, 0] = self.s[1, self.ppio_s_locs, 0] # final value is newly captured final value
|
||||
self.s[0, self.ppio_s_locs, 2] = self.s[0, self.ppio_s_locs, 0] ^ self.s[0, self.ppio_s_locs, 1] # TODO: not correct for X, -
|
||||
|
||||
@staticmethod
|
||||
def not_fct(inputs, outputs):
|
||||
logic.bp_not(outputs[0], inputs[0])
|
||||
def cycle(self, cycles: int = 1, inject_cb=None):
|
||||
"""Repeatedly assigns a state, propagates it, captures the new state, and transfers PPOs to PPIs.
|
||||
|
||||
@staticmethod
|
||||
def and_fct(inputs, outputs):
|
||||
logic.bp_and(outputs[0], *inputs)
|
||||
:param cycles: The number of cycles to simulate.
|
||||
:param inject_cb: A callback function for manipulating intermediate signal values. See :py:func:`c_prop`.
|
||||
"""
|
||||
for _ in range(cycles):
|
||||
self.s_to_c()
|
||||
self.c_prop(inject_cb)
|
||||
self.c_to_s()
|
||||
self.s_ppo_to_ppi()
|
||||
|
||||
@staticmethod
|
||||
def or_fct(inputs, outputs):
|
||||
logic.bp_or(outputs[0], *inputs)
|
||||
|
||||
@staticmethod
|
||||
def xor_fct(inputs, outputs):
|
||||
logic.bp_xor(outputs[0], *inputs)
|
||||
@numba.njit
|
||||
def _prop_cpu(ops, c_locs, c, fault_line, fault_mask, fault_model):
|
||||
for op, o0l, i0l, i1l, i2l, i3l in ops[:,:6]:
|
||||
o0, i0, i1, i2, i3 = [c_locs[x] for x in (o0l, i0l, i1l, i2l, i3l)]
|
||||
if op == sim.BUF1: c[o0]=c[i0]
|
||||
elif op == sim.INV1: c[o0] = ~c[i0]
|
||||
elif op == sim.AND2: c[o0] = c[i0] & c[i1]
|
||||
elif op == sim.AND3: c[o0] = c[i0] & c[i1] & c[i2]
|
||||
elif op == sim.AND4: c[o0] = c[i0] & c[i1] & c[i2] & c[i3]
|
||||
elif op == sim.NAND2: c[o0] = ~(c[i0] & c[i1])
|
||||
elif op == sim.NAND3: c[o0] = ~(c[i0] & c[i1] & c[i2])
|
||||
elif op == sim.NAND4: c[o0] = ~(c[i0] & c[i1] & c[i2] & c[i3])
|
||||
elif op == sim.OR2: c[o0] = c[i0] | c[i1]
|
||||
elif op == sim.OR3: c[o0] = c[i0] | c[i1] | c[i2]
|
||||
elif op == sim.OR4: c[o0] = c[i0] | c[i1] | c[i2] | c[i3]
|
||||
elif op == sim.NOR2: c[o0] = ~(c[i0] | c[i1])
|
||||
elif op == sim.NOR3: c[o0] = ~(c[i0] | c[i1] | c[i2])
|
||||
elif op == sim.NOR4: c[o0] = ~(c[i0] | c[i1] | c[i2] | c[i3])
|
||||
elif op == sim.XOR2: c[o0] = c[i0] ^ c[i1]
|
||||
elif op == sim.XOR3: c[o0] = c[i0] ^ c[i1] ^ c[i2]
|
||||
elif op == sim.XOR4: c[o0] = c[i0] ^ c[i1] ^ c[i2] ^ c[i3]
|
||||
elif op == sim.XNOR2: c[o0] = ~(c[i0] ^ c[i1])
|
||||
elif op == sim.XNOR3: c[o0] = ~(c[i0] ^ c[i1] ^ c[i2])
|
||||
elif op == sim.XNOR4: c[o0] = ~(c[i0] ^ c[i1] ^ c[i2] ^ c[i3])
|
||||
elif op == sim.AO21: c[o0] = (c[i0] & c[i1]) | c[i2]
|
||||
elif op == sim.OA21: c[o0] = (c[i0] | c[i1]) & c[i2]
|
||||
elif op == sim.AO22: c[o0] = (c[i0] & c[i1]) | (c[i2] & c[i3])
|
||||
elif op == sim.OA22: c[o0] = (c[i0] | c[i1]) & (c[i2] | c[i3])
|
||||
elif op == sim.AOI21: c[o0] = ~((c[i0] & c[i1]) | c[i2])
|
||||
elif op == sim.OAI21: c[o0] = ~((c[i0] | c[i1]) & c[i2])
|
||||
elif op == sim.AOI22: c[o0] = ~((c[i0] & c[i1]) | (c[i2] & c[i3]))
|
||||
elif op == sim.OAI22: c[o0] = ~((c[i0] | c[i1]) & (c[i2] | c[i3]))
|
||||
elif op == sim.AO211: c[o0] = (c[i0] & c[i1]) | c[i2] | c[i3]
|
||||
elif op == sim.OA211: c[o0] = (c[i0] | c[i1]) & c[i2] & c[i3]
|
||||
elif op == sim.AOI211: c[o0] = ~((c[i0] & c[i1]) | c[i2] | c[i3])
|
||||
elif op == sim.OAI211: c[o0] = ~((c[i0] | c[i1]) & c[i2] & c[i3])
|
||||
elif op == sim.MUX21: c[o0] = (c[i0] & ~c[i2]) | (c[i1] & c[i2])
|
||||
else: print(f'unknown op {op}')
|
||||
if fault_line >= 0 and o0l == fault_line:
|
||||
#n = len(fault_mask)
|
||||
if fault_model == 0:
|
||||
c[o0] = c[o0] & ~fault_mask
|
||||
elif fault_model == 1:
|
||||
c[o0] = c[o0] | fault_mask
|
||||
else:
|
||||
c[o0] = c[o0] ^ fault_mask
|
||||
|
||||
@staticmethod
|
||||
def sdff_fct(inputs, outputs):
|
||||
logic.bp_buf(outputs[0], inputs[0])
|
||||
if len(outputs) > 1:
|
||||
logic.bp_not(outputs[1], inputs[0])
|
||||
|
||||
@staticmethod
|
||||
def dff_fct(inputs, outputs):
|
||||
logic.bp_buf(outputs[0], inputs[0])
|
||||
if len(outputs) > 1:
|
||||
logic.bp_not(outputs[1], inputs[0])
|
||||
class LogicSim6V(sim.SimOps):
|
||||
"""A bit-parallel naïve combinational simulator for 6-valued logic.
|
||||
|
||||
@staticmethod
|
||||
def nand_fct(inputs, outputs):
|
||||
logic.bp_and(outputs[0], *inputs)
|
||||
logic.bp_not(outputs[0], outputs[0])
|
||||
:param circuit: The circuit to simulate.
|
||||
:param sims: The number of parallel logic simulations to perform.
|
||||
:param c_reuse: If True, intermediate signal values may get overwritten when not needed anymore to save memory.
|
||||
:param strip_forks: If True, forks are not included in the simulation model to save memory and simulation time.
|
||||
"""
|
||||
def __init__(self, circuit: Circuit, sims: int = 8, c_reuse: bool = False, strip_forks: bool = False):
|
||||
super().__init__(circuit, c_reuse=c_reuse, strip_forks=strip_forks)
|
||||
self.sims = sims
|
||||
nbytes = cdiv(sims, 8)
|
||||
|
||||
@staticmethod
|
||||
def nor_fct(inputs, outputs):
|
||||
logic.bp_or(outputs[0], *inputs)
|
||||
logic.bp_not(outputs[0], outputs[0])
|
||||
self.c = np.zeros((self.c_len, 3, nbytes), dtype=np.uint8)
|
||||
self.s = np.zeros((2, self.s_len, self.sims), dtype=np.uint8)
|
||||
"""Logic values of the sequential elements (flip-flops) and ports.
|
||||
|
||||
@staticmethod
|
||||
def xnor_fct(inputs, outputs):
|
||||
logic.bp_xor(outputs[0], *inputs)
|
||||
logic.bp_not(outputs[0], outputs[0])
|
||||
It is a pair of arrays in mv storage format:
|
||||
|
||||
* ``s[0]`` Assigned values. Simulator will read (P)PI value from here.
|
||||
* ``s[1]`` Result values. Simulator will write (P)PO values here.
|
||||
|
||||
Access this array to assign new values to the (P)PIs or read values from the (P)POs.
|
||||
"""
|
||||
|
||||
def __repr__(self):
|
||||
return f'{{name: "{self.circuit.name}", sims: {self.sims}, c_bytes: {eng(self.c.nbytes)}}}'
|
||||
|
||||
def s_to_c(self):
|
||||
"""Assigns the values from ``s[0]`` to the inputs of the combinational portion.
|
||||
"""
|
||||
self.c[self.pippi_c_locs] = logic.mv_to_bp(self.s[0, self.pippi_s_locs])
|
||||
|
||||
def c_prop(self):
|
||||
c_prop_cpu(self.ops, self.c, self.c_locs, self.tmp_idx, self.tmp2_idx)
|
||||
|
||||
def c_to_s(self):
|
||||
"""Captures the results of the combinational portion into ``s[1]``.
|
||||
"""
|
||||
self.s[1, self.poppo_s_locs] = logic.bp_to_mv(self.c[self.poppo_c_locs])[:,:self.sims]
|
||||
|
||||
|
||||
@numba.njit
|
||||
def c_prop_cpu(ops, c, c_locs, tmp_idx, tmp2_idx):
|
||||
t0 = c[c_locs[tmp_idx]]
|
||||
t1 = c[c_locs[tmp2_idx]]
|
||||
inv_op = np.array([255, 255, 0], dtype=np.uint8)[np.newaxis, :, np.newaxis]
|
||||
for op, o0l, i0l, i1l, i2l, i3l in ops[:,:6]:
|
||||
o0, i0, i1, i2, i3 = [c[c_locs[x]] for x in (o0l, i0l, i1l, i2l, i3l)]
|
||||
if op == sim.BUF1 or op == sim.INV1:
|
||||
o0[...] = i0
|
||||
elif op == sim.AND2 or op == sim.NAND2:
|
||||
o0[0] = i0[0] & i1[0]
|
||||
o0[1] = i0[1] & i1[1]
|
||||
o0[2] = (i0[2]&(i1[0]|i1[1]|i1[2])|
|
||||
i1[2]&(i0[0]|i0[1]|i0[2]))
|
||||
elif op == sim.AND3 or op == sim.NAND3:
|
||||
o0[0] = i0[0] & i1[0] & i2[0]
|
||||
o0[1] = i0[1] & i1[1] & i2[1]
|
||||
o0[2] = (i0[2]&(i1[0]|i1[1]|i1[2])&(i2[0]|i2[1]|i2[2])|
|
||||
i1[2]&(i0[0]|i0[1]|i0[2])&(i2[0]|i2[1]|i2[2])|
|
||||
i2[2]&(i0[0]|i0[1]|i0[2])&(i1[0]|i1[1]|i1[2]))
|
||||
elif op == sim.AND4 or op == sim.NAND4:
|
||||
o0[0] = i0[0] & i1[0] & i2[0] & i3[0]
|
||||
o0[1] = i0[1] & i1[1] & i2[1] & i3[1]
|
||||
o0[2] = (i0[2]&(i1[0]|i1[1]|i1[2])&(i2[0]|i2[1]|i2[2])&(i3[0]|i3[1]|i3[2])|
|
||||
i1[2]&(i0[0]|i0[1]|i0[2])&(i2[0]|i2[1]|i2[2])&(i3[0]|i3[1]|i3[2])|
|
||||
i2[2]&(i0[0]|i0[1]|i0[2])&(i1[0]|i1[1]|i1[2])&(i3[0]|i3[1]|i3[2])|
|
||||
i3[2]&(i0[0]|i0[1]|i0[2])&(i1[0]|i1[1]|i1[2])&(i2[0]|i2[1]|i2[2]))
|
||||
elif op == sim.OR2 or op == sim.NOR2:
|
||||
o0[0] = i0[0] | i1[0]
|
||||
o0[1] = i0[1] | i1[1]
|
||||
o0[2] = (i0[2]&(~i1[0]|~i1[1]|i1[2])|
|
||||
i1[2]&(~i0[0]|~i0[1]|i0[2]))
|
||||
elif op == sim.OR3 or op == sim.NOR3:
|
||||
o0[0] = i0[0] | i1[0] | i2[0]
|
||||
o0[1] = i0[1] | i1[1] | i2[1]
|
||||
o0[2] = (i0[2]&(~i1[0]|~i1[1]|i1[2])&(~i2[0]|~i2[1]|i2[2])|
|
||||
i1[2]&(~i0[0]|~i0[1]|i0[2])&(~i2[0]|~i2[1]|i2[2])|
|
||||
i2[2]&(~i0[0]|~i0[1]|i0[2])&(~i1[0]|~i1[1]|i1[2]))
|
||||
elif op == sim.OR4 or op == sim.NOR4:
|
||||
o0[0] = i0[0] | i1[0] | i2[0] | i3[0]
|
||||
o0[1] = i0[1] | i1[1] | i2[1] | i3[1]
|
||||
o0[2] = (i0[2]&(~i1[0]|~i1[1]|i1[2])&(~i2[0]|~i2[1]|i2[2])&(~i3[0]|~i3[1]|i3[2])|
|
||||
i1[2]&(~i0[0]|~i0[1]|i0[2])&(~i2[0]|~i2[1]|i2[2])&(~i3[0]|~i3[1]|i3[2])|
|
||||
i2[2]&(~i0[0]|~i0[1]|i0[2])&(~i1[0]|~i1[1]|i1[2])&(~i3[0]|~i3[1]|i3[2])|
|
||||
i3[2]&(~i0[0]|~i0[1]|i0[2])&(~i1[0]|~i1[1]|i1[2])&(~i2[0]|~i2[1]|i2[2]))
|
||||
elif op == sim.XOR2 or op == sim.XNOR2:
|
||||
o0[0] = i0[0] ^ i1[0]
|
||||
o0[1] = i0[1] ^ i1[1]
|
||||
o0[2] = i0[2] | i1[2]
|
||||
elif op == sim.MUX21:
|
||||
# t1 = ~i2
|
||||
t1[...] = i2 ^ inv_op
|
||||
# t0 = i0 & t1
|
||||
t0[0] = i0[0] & t1[0]
|
||||
t0[1] = i0[1] & t1[1]
|
||||
t0[2] = (i0[2]&(t1[0]|t1[1]|t1[2])|
|
||||
t1[2]&(i0[0]|i0[1]|i0[2]))
|
||||
# t1 = i1 & i2
|
||||
t1[0] = i1[0] & i2[0]
|
||||
t1[1] = i1[1] & i2[1]
|
||||
t1[2] = (i1[2]&(i2[0]|i2[1]|i2[2])|
|
||||
i2[2]&(i1[0]|i1[1]|i1[2]))
|
||||
# o0 = t0 | t1
|
||||
o0[0] = t0[0] | t1[0]
|
||||
o0[1] = t0[1] | t1[1]
|
||||
o0[2] = (t0[2]&(~t1[0]|~t1[1]|t1[2])|
|
||||
t1[2]&(~t0[0]|~t0[1]|t0[2]))
|
||||
else: print(f'unknown op {op}')
|
||||
|
||||
if (op == sim.INV1 or
|
||||
op == sim.NAND2 or op == sim.NAND3 or op == sim.NAND4 or
|
||||
op == sim.NOR2 or op == sim.NOR3 or op == sim.NOR4 or
|
||||
op == sim.XNOR2):
|
||||
o0[...] = o0 ^ inv_op
|
||||
+110
-122
@@ -1,19 +1,20 @@
|
||||
"""A simple and incomplete parser for the Standard Delay Format (SDF).
|
||||
|
||||
The main purpose of this parser is to extract pin-to-pin delay and interconnect delay information from SDF files.
|
||||
Sophisticated timing specifications (timing checks, conditional delays, etc.) are currently not supported.
|
||||
|
||||
The functions :py:func:`load` and :py:func:`read` return an intermediate representation (:class:`DelayFile` object).
|
||||
Call :py:func:`DelayFile.annotation` to match the intermediate representation to a given circuit.
|
||||
This parser extracts pin-to-pin delay and interconnect delay information from SDF files.
|
||||
Sophisticated timing specifications (timing checks, conditional delays, etc.) are ignored.
|
||||
|
||||
The functions :py:func:`parse` and :py:func:`load` return an intermediate representation (:class:`DelayFile` object).
|
||||
Call :py:func:`DelayFile.iopaths` and :py:func:`DelayFile.interconnects` to generate delay information for a given circuit.
|
||||
"""
|
||||
|
||||
from collections import namedtuple
|
||||
import re
|
||||
|
||||
import numpy as np
|
||||
from lark import Lark, Transformer
|
||||
|
||||
from . import log, readtext
|
||||
from .circuit import Circuit
|
||||
from .techlib import TechLib
|
||||
|
||||
|
||||
@@ -26,142 +27,122 @@ class DelayFile:
|
||||
"""
|
||||
def __init__(self, name, cells):
|
||||
self.name = name
|
||||
if None in cells:
|
||||
self.interconnects = cells[None]
|
||||
else:
|
||||
self.interconnects = None
|
||||
self._interconnects = cells.get(None, None)
|
||||
self.cells = dict((n, l) for n, l in cells.items() if n)
|
||||
|
||||
def __repr__(self):
|
||||
return '\n'.join(f'{n}: {l}' for n, l in self.cells.items()) + '\n' + \
|
||||
'\n'.join(str(i) for i in self.interconnects)
|
||||
'\n'.join(str(i) for i in self._interconnects)
|
||||
|
||||
def annotation(self, circuit, tlib=TechLib(), dataset=1, interconnect=True, ffdelays=True):
|
||||
"""Constructs an 3-dimensional ndarray with timing data for each line in ``circuit``.
|
||||
def iopaths(self, circuit:Circuit, tlib:TechLib):
|
||||
"""Constructs an ndarray containing all IOPATH delays.
|
||||
|
||||
An IOPATH delay for a node is annotated to the line connected to the input pin specified in the IOPATH.
|
||||
All IOPATH delays for a node ``n`` are annotated to the line connected to the input pin specified in the IOPATH.
|
||||
|
||||
Currently, only ABSOLUTE IOPATH and INTERCONNECT delays are supported.
|
||||
Pulse rejection limits are derived from absolute delays, explicit declarations (PATHPULSE etc.) are ignored.
|
||||
Limited support of SDF spec:
|
||||
|
||||
* Only ABSOLUTE delay values are supported.
|
||||
* Only two delvals per delval_list is supported. First is rising/posedge, second is falling/negedge
|
||||
transition at the output of the IOPATH (SDF spec, pp. 3-17).
|
||||
* PATHPULSE declarations are ignored.
|
||||
|
||||
The axes convention of KyuPy's delay data arrays is as follows:
|
||||
|
||||
* Axis 0: dataset (usually 3 datasets per SDF-file)
|
||||
* Axis 1: line index (e.g. ``n.ins[0]``, ``n.ins[1]``)
|
||||
* Axis 2: polarity of the transition at the IOPATH-input (e.g. at ``n.ins[0]`` or ``n.ins[1]``), 0='rising/posedge', 1='falling/negedge'
|
||||
* Axis 3: polarity of the transition at the IOPATH-output (at ``n.outs[0]``), 0='rising/posedge', 1='falling/negedge'
|
||||
"""
|
||||
|
||||
def find_cell(name:str):
|
||||
if name not in circuit.cells: name = name.replace('\\', '')
|
||||
if name not in circuit.cells: name = name.replace('[', '_').replace(']', '_')
|
||||
return circuit.cells.get(name, None)
|
||||
|
||||
delays = np.zeros((len(circuit.lines), 2, 2, 3)) # dataset last during construction.
|
||||
|
||||
with log.limit(50):
|
||||
for name, iopaths in self.cells.items():
|
||||
name = name.replace('\\', '')
|
||||
if cell := circuit.cells.get(name, None):
|
||||
for i_pin_spec, o_pin_spec, *dels in iopaths:
|
||||
if i_pin_spec.startswith('(posedge '): i_pol_idxs = [0]
|
||||
elif i_pin_spec.startswith('(negedge '): i_pol_idxs = [1]
|
||||
else: i_pol_idxs = [0, 1]
|
||||
i_pin_spec = re.sub(r'\((neg|pos)edge ([^)]+)\)', r'\2', i_pin_spec)
|
||||
if line := cell.ins[tlib.pin_index(cell.kind, i_pin_spec)]:
|
||||
delays[line, i_pol_idxs] = [d if len(d) > 0 else [0, 0, 0] for d in dels]
|
||||
else:
|
||||
log.warn(f'No line to annotate in circuit: {i_pin_spec} for {cell}')
|
||||
else:
|
||||
log.warn(f'Name from SDF not found in circuit: {name}')
|
||||
|
||||
return np.moveaxis(delays, -1, 0)
|
||||
|
||||
def interconnects(self, circuit:Circuit, tlib:TechLib):
|
||||
"""Constructs an ndarray containing all INTERCONNECT delays.
|
||||
|
||||
:param circuit: The circuit to annotate. Names from the STIL file are matched to the node names.
|
||||
:type circuit: :class:`~kyupy.circuit.Circuit`
|
||||
:param tlib: A technology library object that provides pin name mappings.
|
||||
:type tlib: :py:class:`~kyupy.techlib.TechLib`
|
||||
:param dataset: SDFs store multiple values for each delay (e.g. minimum, typical, maximum).
|
||||
An integer selects the dataset to use (default is 1 for 'typical').
|
||||
If a tuple is given, the annotator will calculate the average of multiple datasets.
|
||||
:type dataset: ``int`` or ``tuple``
|
||||
:param interconnect: Whether or not to include the delays of interconnects in the annotation.
|
||||
To properly annotate interconnect delays, the circuit model has to include a '__fork__' node on
|
||||
every signal and every fanout-branch. The Verilog parser aids in this by setting the parameter
|
||||
`branchforks=True` in :py:func:`kyupy.verilog.parse`.
|
||||
:type interconnect: ``bool``
|
||||
:param ffdelays: Whether or not to include the delays of flip-flops in the annotation.
|
||||
:type ffdelays: ``bool``
|
||||
:return: A 3-dimensional ndarray with timing data.
|
||||
`branchforks=True` in :py:func:`~kyupy.verilog.parse` or :py:func:`~kyupy.verilog.load`.
|
||||
|
||||
* Axis 0: line index.
|
||||
* Axis 1: type of timing data: 0='delay', 1='pulse rejection limit'.
|
||||
* Axis 2: The polarity of the output transition of the reading node: 0='rising', 1='falling'.
|
||||
Limited support of SDF spec:
|
||||
|
||||
The polarity for pulse rejection is determined by the latter transition of the pulse.
|
||||
E.g., ``timing[42, 1, 0]`` is the rejection limit of a negative pulse at the output
|
||||
of the reader of line 42.
|
||||
* Only ABSOLUTE delay values are supported.
|
||||
* Only two delvals per delval_list is supported. First is rising/posedge, second is falling/negedge
|
||||
transition.
|
||||
* PATHPULSE declarations are ignored.
|
||||
|
||||
The axes convention of KyuPy's delay data arrays is as follows:
|
||||
|
||||
* Axis 0: dataset (usually 3 datasets per SDF-file)
|
||||
* Axis 1: line index. Usually input line of a __fork__.
|
||||
* Axis 2: (axis of size 2 for compatability to IOPATH results. Values are broadcast along this axis.)
|
||||
* Axis 3: polarity of the transition, 0='rising/posedge', 1='falling/negedge'
|
||||
"""
|
||||
def select_del(_delvals, idx):
|
||||
if isinstance(dataset, tuple):
|
||||
return sum(_delvals[idx][d] for d in dataset) / len(dataset)
|
||||
return _delvals[idx][dataset]
|
||||
|
||||
def find_cell(name):
|
||||
if name not in circuit.cells:
|
||||
name = name.replace('\\', '')
|
||||
if name not in circuit.cells:
|
||||
name = name.replace('[', '_').replace(']', '_')
|
||||
if name not in circuit.cells:
|
||||
return None
|
||||
return circuit.cells[name]
|
||||
delays = np.zeros((len(circuit.lines), 2, 2, 3)) # dataset last during construction.
|
||||
|
||||
timing = np.zeros((len(circuit.lines), 2, 2))
|
||||
for cn, iopaths in self.cells.items():
|
||||
for ipn, opn, *delvals in iopaths:
|
||||
nonfork_annotations = 0
|
||||
for n1, n2, *delvals in self._interconnects:
|
||||
delvals = [d if len(d) > 0 else [0, 0, 0] for d in delvals]
|
||||
if max(max(delvals)) == 0:
|
||||
if max(max(delvals)) == 0: continue
|
||||
cn1, pn1 = (n1, None) if (slash := n1.rfind('/')) < 0 else (n1[:slash], n1[slash+1:])
|
||||
cn2, pn2 = (n2, None) if (slash := n2.rfind('/')) < 0 else (n2[:slash], n2[slash+1:])
|
||||
cn1 = cn1.replace('\\','')
|
||||
cn2 = cn2.replace('\\','')
|
||||
c1, c2 = circuit.cells[cn1], circuit.cells[cn2]
|
||||
p1 = tlib.pin_index(c1.kind, pn1) if pn1 is not None else 0
|
||||
p2 = tlib.pin_index(c2.kind, pn2) if pn2 is not None else 0
|
||||
if len(c1.outs) <= p1 or c1.outs[p1] is None:
|
||||
log.warn(f'No line to annotate pin {pn1} of {c1}')
|
||||
continue
|
||||
cell = find_cell(cn)
|
||||
if cell is None:
|
||||
log.warn(f'Cell from SDF not found in circuit: {cn}')
|
||||
if len(c2.ins) <= p2 or c2.ins[p2] is None:
|
||||
log.warn(f'No line to annotate pin {pn2} of {c2}')
|
||||
continue
|
||||
ipin = tlib.pin_index(cell.kind, ipn)
|
||||
opin = tlib.pin_index(cell.kind, opn)
|
||||
kind = cell.kind.lower()
|
||||
|
||||
ipn2 = ipn.replace('(posedge A1)', 'A1').replace('(negedge A1)', 'A1')\
|
||||
.replace('(posedge A2)', 'A2').replace('(negedge A2)', 'A2')
|
||||
|
||||
def add_delays(_line):
|
||||
if _line is not None:
|
||||
timing[_line, :, 0] += select_del(delvals, 0)
|
||||
timing[_line, :, 1] += select_del(delvals, 1)
|
||||
|
||||
take_avg = False
|
||||
if kind.startswith('sdff'):
|
||||
if not ipn.startswith('(posedge CLK'):
|
||||
continue
|
||||
if ffdelays and (len(cell.outs) > opin):
|
||||
add_delays(cell.outs[opin])
|
||||
f1, f2 = c1.outs[p1].reader, c2.ins[p2].driver # find the forks between cells.
|
||||
if f1 == c2 and f2 == c1:
|
||||
nonfork_annotations += 1
|
||||
if nonfork_annotations < 10:
|
||||
log.warn(f'No fork between {c1.name}/{p1} and {c2.name}/{p2}, using {c2.name}/{p2}')
|
||||
line = c2.ins[p2]
|
||||
else:
|
||||
if kind.startswith(('xor', 'xnor')):
|
||||
ipin = tlib.pin_index(cell.kind, ipn2)
|
||||
# print(ipn, ipin, times[cell.i_lines[ipin], 0, 0])
|
||||
take_avg = timing[cell.ins[ipin]].sum() > 0
|
||||
add_delays(cell.ins[ipin])
|
||||
if take_avg:
|
||||
timing[cell.ins[ipin]] /= 2
|
||||
|
||||
if not interconnect or self.interconnects is None:
|
||||
return timing
|
||||
|
||||
for n1, n2, *delvals in self.interconnects:
|
||||
delvals = [d if len(d) > 0 else [0, 0, 0] for d in delvals]
|
||||
if max(max(delvals)) == 0:
|
||||
continue
|
||||
if '/' in n1:
|
||||
i = n1.rfind('/')
|
||||
cn1 = n1[0:i]
|
||||
pn1 = n1[i+1:]
|
||||
else:
|
||||
cn1, pn1 = (n1, 'Z')
|
||||
if '/' in n2:
|
||||
i = n2.rfind('/')
|
||||
cn2 = n2[0:i]
|
||||
pn2 = n2[i+1:]
|
||||
else:
|
||||
cn2, pn2 = (n2, 'IN')
|
||||
c1 = find_cell(cn1)
|
||||
if c1 is None:
|
||||
log.warn(f'Cell from SDF not found in circuit: {cn1}')
|
||||
continue
|
||||
c2 = find_cell(cn2)
|
||||
if c2 is None:
|
||||
log.warn(f'Cell from SDF not found in circuit: {cn2}')
|
||||
continue
|
||||
p1, p2 = tlib.pin_index(c1.kind, pn1), tlib.pin_index(c2.kind, pn2)
|
||||
line = None
|
||||
f1, f2 = c1.outs[p1].reader, c2.ins[p2].driver
|
||||
if f1 != f2: # possible branchfork
|
||||
assert len(f2.ins) == 1
|
||||
assert f1.kind == '__fork__'
|
||||
assert f2.kind == '__fork__'
|
||||
if len(f2.outs) == 1:
|
||||
assert f1 == f2 or f1.outs[f2.ins[0].driver_pin] == f2.ins[0]
|
||||
line = f2.ins[0]
|
||||
assert f1.outs[f2.ins[0].driver_pin] == line
|
||||
elif len(f2.outs) == 1: # no fanout?
|
||||
line = f2.ins[0]
|
||||
if line is not None:
|
||||
timing[line, :, 0] += select_del(delvals, 0)
|
||||
timing[line, :, 1] += select_del(delvals, 1)
|
||||
else:
|
||||
log.warn(f'No branchfork for annotating interconnect delay {c1.name}/{p1}->{c2.name}/{p2}')
|
||||
return timing
|
||||
nonfork_annotations += 1
|
||||
if nonfork_annotations < 10:
|
||||
log.warn(f'No branchfork between {c1.name}/{p1} and {c2.name}/{p2}, using {c2.name}/{p2}')
|
||||
line = c2.ins[p2]
|
||||
delays[line, :] = delvals
|
||||
|
||||
if nonfork_annotations > 0:
|
||||
log.warn(f'{nonfork_annotations} interconnect annotations were moved to gate inputs due to missing forks.')
|
||||
|
||||
return np.moveaxis(delays, -1, 0)
|
||||
|
||||
|
||||
def sanitize(args):
|
||||
@@ -185,6 +166,10 @@ class SdfTransformer(Transformer):
|
||||
entries = [e for a in args if hasattr(a, 'children') for e in a.children]
|
||||
return name, entries
|
||||
|
||||
@staticmethod
|
||||
def cond(args): # ignore conditions
|
||||
return args[1]
|
||||
|
||||
@staticmethod
|
||||
def start(args):
|
||||
name = next((a for a in args if isinstance(a, str)), None)
|
||||
@@ -209,9 +194,12 @@ GRAMMAR = r"""
|
||||
| "(INSTANCE" ID? ")"
|
||||
| "(TIMINGCHECK" _ignore* ")"
|
||||
| delay )* ")"
|
||||
delay: "(DELAY" "(ABSOLUTE" (interconnect | iopath)* ")" ")"
|
||||
delay: "(DELAY" "(ABSOLUTE" (interconnect | iopath | cond)* ")" ")"
|
||||
interconnect: "(INTERCONNECT" ID ID triple* ")"
|
||||
iopath: "(IOPATH" ID_OR_EDGE ID_OR_EDGE triple* ")"
|
||||
cond: "(" "COND" cond_port_expr iopath ")"
|
||||
?cond_port_expr: ID | "(" cond_port_expr ")" | cond_port_expr BINARY_OP cond_port_expr
|
||||
BINARY_OP: /&&/ | /==/
|
||||
NAME: /[^"]+/
|
||||
ID_OR_EDGE: ( /[^() ]+/ | "(" /[^)]+/ ")" )
|
||||
ID: ( /[^"() ]+/ | "\"" /[^"]+/ "\"" )
|
||||
@@ -232,6 +220,6 @@ def parse(text):
|
||||
def load(file):
|
||||
"""Parses the contents of ``file`` and returns a :class:`DelayFile` object.
|
||||
|
||||
The given file may be gzip compressed.
|
||||
Files with `.gz`-suffix are decompressed on-the-fly.
|
||||
"""
|
||||
return parse(readtext(file))
|
||||
@@ -0,0 +1,341 @@
|
||||
|
||||
from collections import defaultdict
|
||||
from bisect import bisect, insort_left
|
||||
|
||||
import numpy as np
|
||||
|
||||
from .circuit import Circuit
|
||||
|
||||
BUF1 = np.uint16(0b1010_1010_1010_1010)
|
||||
INV1 = ~BUF1
|
||||
|
||||
__const0__ = BUF1
|
||||
__const1__ = INV1
|
||||
|
||||
AND2 = np.uint16(0b1000_1000_1000_1000)
|
||||
AND3 = np.uint16(0b1000_0000_1000_0000)
|
||||
AND4 = np.uint16(0b1000_0000_0000_0000)
|
||||
|
||||
NAND2, NAND3, NAND4 = ~AND2, ~AND3, ~AND4
|
||||
|
||||
OR2 = np.uint16(0b1110_1110_1110_1110)
|
||||
OR3 = np.uint16(0b1111_1110_1111_1110)
|
||||
OR4 = np.uint16(0b1111_1111_1111_1110)
|
||||
|
||||
NOR2, NOR3, NOR4 = ~OR2, ~OR3, ~OR4
|
||||
|
||||
XOR2 = np.uint16(0b0110_0110_0110_0110)
|
||||
XOR3 = np.uint16(0b1001_0110_1001_0110)
|
||||
XOR4 = np.uint16(0b0110_1001_1001_0110)
|
||||
|
||||
XNOR2, XNOR3, XNOR4 = ~XOR2, ~XOR3, ~XOR4
|
||||
|
||||
AO21 = np.uint16(0b1111_1000_1111_1000) # (i0 & i1) | i2
|
||||
AO22 = np.uint16(0b1111_1000_1000_1000) # (i0 & i1) | (i2 & i3)
|
||||
OA21 = np.uint16(0b1110_0000_1110_0000) # (i0 | i1) & i2
|
||||
OA22 = np.uint16(0b1110_1110_1110_0000) # (i0 | i1) & (i2 | i3)
|
||||
|
||||
AOI21, AOI22, OAI21, OAI22 = ~AO21, ~AO22, ~OA21, ~OA22
|
||||
|
||||
AO211 = np.uint16(0b1111_1111_1111_1000) # (i0 & i1) | i2 | i3
|
||||
OA211 = np.uint16(0b1110_0000_0000_0000) # (i0 | i1) & i2 & i3
|
||||
|
||||
AOI211, OAI211 = ~AO211, ~OA211
|
||||
|
||||
MUX21 = np.uint16(0b1100_1010_1100_1010) # z = i1 if i2 else i0 (i2 is select)
|
||||
|
||||
names = dict([(v, k) for k, v in globals().items() if isinstance(v, np.uint16) and '__' not in k])
|
||||
|
||||
prim2name = dict([(v, k) for k, v in globals().items() if isinstance(v, np.uint16) and '__' not in k])
|
||||
name2prim = dict([(k, v) for k, v in globals().items() if isinstance(v, np.uint16)])
|
||||
|
||||
kind_prefixes = {
|
||||
'nand': (NAND4, NAND3, NAND2),
|
||||
'nor': (NOR4, NOR3, NOR2),
|
||||
'and': (AND4, AND3, AND2),
|
||||
'or': (OR4, OR3, OR2),
|
||||
'isolor': (OR2, OR2, OR2),
|
||||
'xor': (XOR4, XOR3, XOR2),
|
||||
'xnor': (XNOR4, XNOR3, XNOR2),
|
||||
|
||||
'not': (INV1, INV1, INV1),
|
||||
'inv': (INV1, INV1, INV1),
|
||||
'ibuf': (INV1, INV1, INV1),
|
||||
'__const1__': (INV1, INV1, INV1),
|
||||
'tieh': (INV1, INV1, INV1),
|
||||
|
||||
'buf': (BUF1, BUF1, BUF1),
|
||||
'nbuf': (BUF1, BUF1, BUF1),
|
||||
'delln': (BUF1, BUF1, BUF1),
|
||||
'__const0__': (BUF1, BUF1, BUF1),
|
||||
'tiel': (BUF1, BUF1, BUF1),
|
||||
|
||||
'ao211': (AO211, AO211, AO211),
|
||||
'oa211': (OA211, OA211, OA211),
|
||||
'aoi211': (AOI211, AOI211, AOI211),
|
||||
'oai211': (OAI211, OAI211, OAI211),
|
||||
|
||||
'ao22': (AO22, AO22, AO22),
|
||||
'aoi22': (AOI22, AOI22, AOI22),
|
||||
'ao21': (AO21, AO21, AO21),
|
||||
'aoi21': (AOI21, AOI21, AOI21),
|
||||
|
||||
'oa22': (OA22, OA22, OA22),
|
||||
'oai22': (OAI22, OAI22, OAI22),
|
||||
'oa21': (OA21, OA21, OA21),
|
||||
'oai21': (OAI21, OAI21, OAI21),
|
||||
|
||||
'mux21': (MUX21, MUX21, MUX21),
|
||||
}
|
||||
|
||||
class Heap:
|
||||
def __init__(self):
|
||||
self.chunks = dict() # map start location to chunk size
|
||||
self.released = list() # chunks that were released
|
||||
self.current_size = 0
|
||||
self.max_size = 0
|
||||
|
||||
def alloc(self, size):
|
||||
for idx, loc in enumerate(self.released):
|
||||
if self.chunks[loc] == size:
|
||||
del self.released[idx]
|
||||
return loc
|
||||
if self.chunks[loc] > size: # split chunk
|
||||
chunksize = self.chunks[loc]
|
||||
self.chunks[loc] = size
|
||||
self.chunks[loc + size] = chunksize - size
|
||||
self.released[idx] = loc + size # move released pointer: loc -> loc+size
|
||||
return loc
|
||||
# no previously released chunk; make new one
|
||||
loc = self.current_size
|
||||
self.chunks[loc] = size
|
||||
self.current_size += size
|
||||
self.max_size = max(self.max_size, self.current_size)
|
||||
return loc
|
||||
|
||||
def free(self, loc):
|
||||
size = self.chunks[loc]
|
||||
if loc + size == self.current_size: # end of managed area, remove chunk
|
||||
del self.chunks[loc]
|
||||
self.current_size -= size
|
||||
# check and remove prev chunk if free
|
||||
if len(self.released) > 0:
|
||||
prev = self.released[-1]
|
||||
if prev + self.chunks[prev] == self.current_size:
|
||||
chunksize = self.chunks[prev]
|
||||
del self.chunks[prev]
|
||||
del self.released[-1]
|
||||
self.current_size -= chunksize
|
||||
return
|
||||
released_idx = bisect(self.released, loc)
|
||||
if released_idx < len(self.released) and loc + size == self.released[released_idx]: # next chunk is free, merge
|
||||
chunksize = size + self.chunks[loc + size]
|
||||
del self.chunks[loc + size]
|
||||
self.chunks[loc] = chunksize
|
||||
size = self.chunks[loc]
|
||||
self.released[released_idx] = loc
|
||||
else:
|
||||
insort_left(self.released, loc) # put in a new release
|
||||
if released_idx > 0: # check if previous chunk is free
|
||||
prev = self.released[released_idx - 1]
|
||||
if prev + self.chunks[prev] == loc: # previous chunk is adjacent to freed one, merge
|
||||
chunksize = size + self.chunks[prev]
|
||||
del self.chunks[loc]
|
||||
self.chunks[prev] = chunksize
|
||||
del self.released[released_idx]
|
||||
|
||||
def __repr__(self):
|
||||
r = []
|
||||
for loc in sorted(self.chunks.keys()):
|
||||
size = self.chunks[loc]
|
||||
released_idx = bisect(self.released, loc)
|
||||
is_released = released_idx > 0 and len(self.released) > 0 and self.released[released_idx - 1] == loc
|
||||
r.append(f'{loc:5d}: {"free" if is_released else "used"} {size}')
|
||||
return "\n".join(r)
|
||||
|
||||
|
||||
class SimOps:
|
||||
"""A static scheduler that translates a Circuit into a topologically sorted list of basic logic operations (self.ops) and
|
||||
a memory mapping (self.c_locs, self.c_caps) for use in simulators.
|
||||
|
||||
:param circuit: The circuit to create a schedule for.
|
||||
:param strip_forks: If enabled, the scheduler will not include fork nodes to safe simulation time.
|
||||
Stripping forks will cause interconnect delay annotations of lines read by fork nodes to be ignored.
|
||||
:param c_reuse: If enabled, memory of intermediate signal waveforms will be re-used. This greatly reduces
|
||||
memory footprint, but intermediate signal waveforms become unaccessible after a propagation.
|
||||
"""
|
||||
def __init__(self, circuit: Circuit, c_caps=1, c_caps_min=1, a_ctrl=None, c_reuse=False, strip_forks=False):
|
||||
self.circuit = circuit
|
||||
self.s_len = len(circuit.s_nodes)
|
||||
|
||||
if isinstance(c_caps, int):
|
||||
c_caps = [c_caps] * (len(circuit.lines)+3)
|
||||
|
||||
if a_ctrl is None:
|
||||
a_ctrl = np.zeros((len(circuit.lines)+3, 3), dtype=np.int32) # add 3 for zero, tmp, tmp2
|
||||
a_ctrl[:,0] = -1
|
||||
|
||||
# special locations and offsets in c_locs/c_caps
|
||||
self.zero_idx = len(circuit.lines)
|
||||
self.tmp_idx = self.zero_idx + 1
|
||||
self.tmp2_idx = self.tmp_idx + 1
|
||||
self.ppi_offset = self.tmp2_idx + 1
|
||||
self.ppo_offset = self.ppi_offset + self.s_len
|
||||
self.c_locs_len = self.ppo_offset + self.s_len
|
||||
|
||||
# ALAP-toposort the circuit into self.ops
|
||||
levels = []
|
||||
|
||||
ppio2idx = dict((n, i) for i, n in enumerate(circuit.s_nodes))
|
||||
ppos = set([n for n in circuit.s_nodes if len(n.ins) > 0])
|
||||
readers = np.array([1 if l.reader in ppos else len(l.reader.outs) for l in circuit.lines], dtype=np.int32) # for ref-counting forks
|
||||
|
||||
level_lines = [n.ins[0] for n in ppos] # start from PPOs
|
||||
# FIXME: Should probably instanciate buffers for PPOs and attach DFF clocks
|
||||
|
||||
while len(level_lines) > 0: # traverse the circuit level-wise back towards (P)PIs
|
||||
level_ops = []
|
||||
prev_level_lines = []
|
||||
|
||||
for l in level_lines:
|
||||
n = l.driver
|
||||
in_idxs = [n.ins[x].index if len(n.ins) > x and n.ins[x] is not None else self.zero_idx for x in [0,1,2,3]]
|
||||
if n in ppio2idx:
|
||||
in_idxs[0] = self.ppi_offset + ppio2idx[n]
|
||||
if l.driver_pin == 1 and 'dff' in n.kind.lower(): # second output of DFF is inverted
|
||||
level_ops.append((INV1, l.index, *in_idxs, *a_ctrl[l]))
|
||||
else:
|
||||
level_ops.append((BUF1, l.index, *in_idxs, *a_ctrl[l]))
|
||||
elif n.kind == '__fork__':
|
||||
readers[n.ins[0]] -= 1
|
||||
if readers[n.ins[0]] == 0: prev_level_lines.append(n.ins[0])
|
||||
if not strip_forks: level_ops.append((BUF1, l.index, *in_idxs, *a_ctrl[l]))
|
||||
else:
|
||||
prev_level_lines += n.ins
|
||||
sp = None
|
||||
kind = n.kind.lower()
|
||||
for prefix, prims in kind_prefixes.items():
|
||||
if kind.startswith(prefix):
|
||||
sp = prims[0]
|
||||
if in_idxs[3] == self.zero_idx:
|
||||
sp = prims[1]
|
||||
if in_idxs[2] == self.zero_idx:
|
||||
sp = prims[2]
|
||||
break
|
||||
if sp is None:
|
||||
print('unknown cell type', kind)
|
||||
else:
|
||||
level_ops.append((sp, l.index, *in_idxs, *a_ctrl[l]))
|
||||
|
||||
if len(level_ops) > 0: levels.append(level_ops)
|
||||
level_lines = prev_level_lines
|
||||
|
||||
self.levels = [np.asarray(lv, dtype=np.int32) for lv in levels[::-1]]
|
||||
level_sums = np.cumsum([0]+[len(lv) for lv in self.levels], dtype=np.int32)
|
||||
self.level_starts, self.level_stops = level_sums[:-1], level_sums[1:]
|
||||
self.ops = np.vstack(self.levels)
|
||||
|
||||
# create a map from fanout lines to stem lines for fork stripping
|
||||
stems = np.full(self.c_locs_len, -1, dtype=np.int32) # default to -1: 'no fanout line'
|
||||
if strip_forks:
|
||||
for f in circuit.forks.values():
|
||||
prev_line = f.ins[0]
|
||||
while prev_line.driver.kind == '__fork__':
|
||||
prev_line = prev_line.driver.ins[0]
|
||||
for ol in f.outs:
|
||||
if ol is not None:
|
||||
stems[ol] = prev_line.index
|
||||
|
||||
ref_count = np.zeros(self.c_locs_len, dtype=np.int32)
|
||||
|
||||
for op in self.ops:
|
||||
for x in [2, 3, 4, 5]:
|
||||
ref_count[stems[op[x]] if stems[op[x]] >= 0 else op[x]] += 1
|
||||
|
||||
# combinational signal allocation table. maps line and interface indices to self.c memory locations
|
||||
self.c_locs = np.full((self.c_locs_len,), -1, dtype=np.int32)
|
||||
self.c_caps = np.zeros((self.c_locs_len,), dtype=np.int32)
|
||||
|
||||
h = Heap()
|
||||
|
||||
# allocate and keep memory for special fields
|
||||
self.c_locs[self.zero_idx], self.c_caps[self.zero_idx] = h.alloc(c_caps_min), c_caps_min
|
||||
self.c_locs[self.tmp_idx], self.c_caps[self.tmp_idx] = h.alloc(c_caps_min), c_caps_min
|
||||
self.c_locs[self.tmp2_idx], self.c_caps[self.tmp2_idx] = h.alloc(c_caps_min), c_caps_min
|
||||
ref_count[self.zero_idx] += 1
|
||||
ref_count[self.tmp_idx] += 1
|
||||
ref_count[self.tmp2_idx] += 1
|
||||
|
||||
# allocate and keep memory for PI/PPI, keep memory for PO/PPO (allocated later)
|
||||
for i, n in enumerate(circuit.s_nodes):
|
||||
if len(n.outs) > 0:
|
||||
self.c_locs[self.ppi_offset + i], self.c_caps[self.ppi_offset + i] = h.alloc(c_caps_min), c_caps_min
|
||||
ref_count[self.ppi_offset + i] += 1
|
||||
if len(n.ins) > 0:
|
||||
i0_idx = stems[n.ins[0]] if stems[n.ins[0]] >= 0 else n.ins[0]
|
||||
ref_count[i0_idx] += 1
|
||||
|
||||
# allocate memory for the rest of the circuit
|
||||
for ops in self.levels:
|
||||
free_set = set()
|
||||
for op in ops:
|
||||
# if we fork-strip, always take the stems
|
||||
i0_idx = stems[op[2]] if stems[op[2]] >= 0 else op[2]
|
||||
i1_idx = stems[op[3]] if stems[op[3]] >= 0 else op[3]
|
||||
i2_idx = stems[op[4]] if stems[op[4]] >= 0 else op[4]
|
||||
i3_idx = stems[op[5]] if stems[op[5]] >= 0 else op[5]
|
||||
ref_count[i0_idx] -= 1
|
||||
ref_count[i1_idx] -= 1
|
||||
ref_count[i2_idx] -= 1
|
||||
ref_count[i3_idx] -= 1
|
||||
if ref_count[i0_idx] <= 0: free_set.add(self.c_locs[i0_idx])
|
||||
if ref_count[i1_idx] <= 0: free_set.add(self.c_locs[i1_idx])
|
||||
if ref_count[i2_idx] <= 0: free_set.add(self.c_locs[i2_idx])
|
||||
if ref_count[i3_idx] <= 0: free_set.add(self.c_locs[i3_idx])
|
||||
o_idx = op[1]
|
||||
cap = max(c_caps_min, c_caps[o_idx])
|
||||
self.c_locs[o_idx], self.c_caps[o_idx] = h.alloc(cap), cap
|
||||
if c_reuse:
|
||||
for loc in free_set:
|
||||
if loc >= 0: # DFF clocks are not allocated. Ignore for now.
|
||||
h.free(loc)
|
||||
|
||||
# copy memory location and capacity from stems to fanout lines
|
||||
for lidx, stem in enumerate(stems):
|
||||
if stem >= 0: # if at a fanout line
|
||||
self.c_locs[lidx], self.c_caps[lidx] = self.c_locs[stem], self.c_caps[stem]
|
||||
|
||||
# copy memory location to PO/PPO area
|
||||
for i, n in enumerate(circuit.s_nodes):
|
||||
if len(n.ins) > 0:
|
||||
self.c_locs[self.ppo_offset + i], self.c_caps[self.ppo_offset + i] = self.c_locs[n.ins[0]], self.c_caps[n.ins[0]]
|
||||
|
||||
# line use information
|
||||
self.line_use_start = np.full(self.c_locs_len, -1, dtype=np.int32)
|
||||
self.line_use_stop = np.full(self.c_locs_len, len(self.levels), dtype=np.int32)
|
||||
for i, lv in enumerate(self.levels):
|
||||
for op in lv:
|
||||
self.line_use_start[op[1]] = i
|
||||
for x in [2, 3, 4, 5]:
|
||||
self.line_use_stop[op[x]] = i
|
||||
|
||||
self.c_len = h.max_size
|
||||
|
||||
d = defaultdict(int)
|
||||
for op in self.ops[:,0]: d[names[op]] += 1
|
||||
self.prim_counts = dict(d)
|
||||
|
||||
self.pi_s_locs = np.flatnonzero(self.c_locs[self.ppi_offset+np.arange(len(self.circuit.io_nodes))] >= 0)
|
||||
self.po_s_locs = np.flatnonzero(self.c_locs[self.ppo_offset+np.arange(len(self.circuit.io_nodes))] >= 0)
|
||||
self.ppio_s_locs = np.arange(len(self.circuit.io_nodes), self.s_len)
|
||||
|
||||
self.pippi_s_locs = np.concatenate([self.pi_s_locs, self.ppio_s_locs])
|
||||
self.poppo_s_locs = np.concatenate([self.po_s_locs, self.ppio_s_locs])
|
||||
|
||||
self.pi_c_locs = self.c_locs[self.ppi_offset+self.pi_s_locs]
|
||||
self.po_c_locs = self.c_locs[self.ppo_offset+self.po_s_locs]
|
||||
self.ppi_c_locs = self.c_locs[self.ppi_offset+self.ppio_s_locs]
|
||||
self.ppo_c_locs = self.c_locs[self.ppo_offset+self.ppio_s_locs]
|
||||
|
||||
self.pippi_c_locs = np.concatenate([self.pi_c_locs, self.ppi_c_locs])
|
||||
self.poppo_c_locs = np.concatenate([self.po_c_locs, self.ppo_c_locs])
|
||||
+78
-53
@@ -1,16 +1,17 @@
|
||||
"""A simple and incomplete parser for the Standard Test Interface Language (STIL).
|
||||
|
||||
The main purpose of this parser is to load scan pattern sets from STIL files.
|
||||
It supports only a very limited subset of STIL.
|
||||
It supports only a subset of STIL.
|
||||
|
||||
The functions :py:func:`load` and :py:func:`read` return an intermediate representation (:class:`StilFile` object).
|
||||
Call :py:func:`StilFile.tests`, :py:func:`StilFile.tests_loc`, or :py:func:`StilFile.responses` to
|
||||
The functions :py:func:`parse` and :py:func:`load` return an intermediate representation (:py:class:`StilFile` object).
|
||||
Call :py:func:`StilFile.tests()`, :py:func:`StilFile.tests_loc()`, or :py:func:`StilFile.responses()` to
|
||||
obtain the appropriate vector sets.
|
||||
"""
|
||||
|
||||
import re
|
||||
from collections import namedtuple
|
||||
|
||||
import numpy as np
|
||||
from lark import Lark, Transformer
|
||||
|
||||
from . import readtext, logic
|
||||
@@ -40,23 +41,20 @@ class StilFile:
|
||||
unload = {}
|
||||
for so_port in self.so_ports:
|
||||
if so_port in call.parameters:
|
||||
unload[so_port] = call.parameters[so_port].replace('\n', '')
|
||||
if len(launch) > 0:
|
||||
unload[so_port] = call.parameters[so_port]
|
||||
if len(capture) > 0:
|
||||
self.patterns.append(ScanPattern(sload, launch, capture, unload))
|
||||
capture = {}
|
||||
launch = {}
|
||||
sload = {}
|
||||
for si_port in self.si_ports:
|
||||
if si_port in call.parameters:
|
||||
sload[si_port] = call.parameters[si_port].replace('\n', '')
|
||||
if call.name.endswith('_launch') or call.name.endswith('_capture'):
|
||||
if len(launch) == 0:
|
||||
launch = dict((k, v.replace('\n', '')) for k, v in call.parameters.items())
|
||||
else:
|
||||
capture = dict((k, v.replace('\n', '')) for k, v in call.parameters.items())
|
||||
sload[si_port] = call.parameters[si_port]
|
||||
if call.name.endswith('_launch'): launch = call.parameters
|
||||
if call.name.endswith('_capture'): capture = call.parameters
|
||||
|
||||
def _maps(self, c):
|
||||
interface = list(c.interface) + [n for n in c.nodes if 'DFF' in n.kind]
|
||||
interface = list(c.io_nodes) + [n for n in c.nodes if 'DFF' in n.kind]
|
||||
intf_pos = dict((n.name, i) for i, n in enumerate(interface))
|
||||
pi_map = [intf_pos[n] for n in self.signal_groups['_pi']]
|
||||
po_map = [intf_pos[n] for n in self.signal_groups['_po']]
|
||||
@@ -82,73 +80,99 @@ class StilFile:
|
||||
scan_out_inversion.append(inversion)
|
||||
scan_maps[chain[0]] = scan_map
|
||||
scan_maps[chain[-1]] = scan_map
|
||||
scan_inversions[chain[0]] = scan_in_inversion
|
||||
scan_inversions[chain[-1]] = scan_out_inversion
|
||||
scan_inversions[chain[0]] = logic.mvarray(scan_in_inversion)[0]
|
||||
scan_inversions[chain[-1]] = logic.mvarray(scan_out_inversion)[0]
|
||||
return interface, pi_map, po_map, scan_maps, scan_inversions
|
||||
|
||||
def tests(self, circuit):
|
||||
"""Assembles and returns a scan test pattern set for given circuit.
|
||||
|
||||
This function assumes a static (stuck-at fault) test.
|
||||
|
||||
:param circuit: The circuit to assemble the patterns for. The patterns will follow the
|
||||
:py:attr:`~kyupy.circuit.Circuit.s_nodes` ordering of the this circuit.
|
||||
:return: A 4-valued multi-valued (mv) logic array (see :py:mod:`~kyupy.logic`).
|
||||
The values for primary inputs and sequential elements are filled, the primary outputs are left unassigned.
|
||||
"""
|
||||
interface, pi_map, _, scan_maps, scan_inversions = self._maps(circuit)
|
||||
tests = logic.MVArray((len(interface), len(self.patterns)))
|
||||
tests = np.full((len(interface), len(self.patterns)), logic.UNASSIGNED)
|
||||
for i, p in enumerate(self.patterns):
|
||||
for si_port in self.si_ports.keys():
|
||||
pattern = logic.mv_xor(p.load[si_port], scan_inversions[si_port])
|
||||
tests.data[scan_maps[si_port], i] = pattern.data[:, 0]
|
||||
tests.data[pi_map, i] = logic.MVArray(p.launch['_pi']).data[:, 0]
|
||||
pattern = logic.mvarray(p.load[si_port][0])
|
||||
inversions = np.choose((pattern == logic.UNASSIGNED) | (pattern == logic.UNKNOWN),
|
||||
[scan_inversions[si_port], logic.ZERO]).astype(np.uint8)
|
||||
np.bitwise_xor(pattern, inversions, out=pattern)
|
||||
tests[scan_maps[si_port], i] = pattern
|
||||
tests[pi_map, i] = logic.mvarray(p.capture['_pi'][0])
|
||||
return tests
|
||||
|
||||
def tests_loc(self, circuit):
|
||||
def tests_loc(self, circuit, init_filter=None, launch_filter=None):
|
||||
"""Assembles and returns a LoC scan test pattern set for given circuit.
|
||||
|
||||
This function assumes a launch-on-capture (LoC) delay test.
|
||||
It performs a logic simulation to obtain the first capture pattern (the one that launches the
|
||||
delay test) and assembles the test pattern set from from pairs for initialization- and launch-patterns.
|
||||
It performs a logic simulation to obtain the first capture pattern (the one that launches the delay
|
||||
test) and assembles the test pattern set from from pairs for initialization- and launch-patterns.
|
||||
|
||||
:param circuit: The circuit to assemble the patterns for. The patterns will follow the
|
||||
:py:attr:`~kyupy.circuit.Circuit.s_nodes` ordering of the this circuit.
|
||||
:param init_filter: A function for filtering the initialization patterns. This function is called
|
||||
with the initialization patterns from the STIL file as mvarray before logic simulation.
|
||||
It shall return an mvarray with the same shape. This function can be used, for example, to fill
|
||||
patterns.
|
||||
:param launch_filter: A function for filtering the launch patterns. This function is called
|
||||
with the launch patterns generated by logic simulation before they are combined with
|
||||
the initialization patterns to form the final 8-valued test patterns.
|
||||
The function shall return an mvarray with the same shape. This function can be used, for example, to fill
|
||||
patterns.
|
||||
:return: An 8-valued multi-valued (mv) logic array (see :py:mod:`~kyupy.logic`). The values for primary
|
||||
inputs and sequential elements are filled, the primary outputs are left unassigned.
|
||||
"""
|
||||
interface, pi_map, po_map, scan_maps, scan_inversions = self._maps(circuit)
|
||||
init = logic.MVArray((len(interface), len(self.patterns)), m=4)
|
||||
# init = PackedVectors(len(self.patterns), len(interface), 2)
|
||||
init = np.full((len(interface), len(self.patterns)), logic.UNASSIGNED)
|
||||
for i, p in enumerate(self.patterns):
|
||||
# init.set_values(i, '0' * len(interface))
|
||||
for si_port in self.si_ports.keys():
|
||||
pattern = logic.mv_xor(p.load[si_port], scan_inversions[si_port])
|
||||
init.data[scan_maps[si_port], i] = pattern.data[:, 0]
|
||||
init.data[pi_map, i] = logic.MVArray(p.launch['_pi']).data[:, 0]
|
||||
launch_bp = logic.BPArray(init)
|
||||
sim4v = LogicSim(circuit, len(init), m=4)
|
||||
sim4v.assign(launch_bp)
|
||||
sim4v.propagate()
|
||||
sim4v.capture(launch_bp)
|
||||
launch = logic.MVArray(launch_bp)
|
||||
pattern = logic.mvarray(p.load[si_port][0])
|
||||
inversions = np.choose((pattern == logic.UNASSIGNED) | (pattern == logic.UNKNOWN),
|
||||
[scan_inversions[si_port], logic.ZERO]).astype(np.uint8)
|
||||
np.bitwise_xor(pattern, inversions, out=pattern)
|
||||
init[scan_maps[si_port], i] = pattern
|
||||
init[pi_map, i] = logic.mvarray(p.launch['_pi'][0] if '_pi' in p.launch else p.capture['_pi'][0])
|
||||
if init_filter: init = init_filter(init)
|
||||
sim8v = LogicSim(circuit, init.shape[-1], m=8)
|
||||
sim8v.s[0] = logic.mv_to_bp(init)
|
||||
sim8v.s_to_c()
|
||||
sim8v.c_prop()
|
||||
sim8v.c_to_s()
|
||||
launch = logic.bp_to_mv(sim8v.s[1])[..., :init.shape[-1]]
|
||||
for i, p in enumerate(self.patterns):
|
||||
# if there was no launch clock, then init = launch
|
||||
if ('P' not in p.launch['_pi']) or ('P' not in p.capture['_pi']):
|
||||
# if there was no launch cycle or launch clock, then init = launch
|
||||
if '_pi' not in p.launch or 'P' not in p.launch['_pi'][0] or 'P' not in p.capture['_pi'][0]:
|
||||
for si_port in self.si_ports.keys():
|
||||
pattern = logic.mv_xor(p.load[si_port], scan_inversions[si_port])
|
||||
launch.data[scan_maps[si_port], i] = pattern.data[:, 0]
|
||||
if '_pi' in p.capture and 'P' in p.capture['_pi']:
|
||||
launch.data[pi_map, i] = logic.MVArray(p.capture['_pi']).data[:, 0]
|
||||
launch.data[po_map, i] = logic.UNASSIGNED
|
||||
pattern = logic.mv_xor(logic.mvarray(p.load[si_port][0]), scan_inversions[si_port])
|
||||
launch[scan_maps[si_port], i] = pattern
|
||||
if '_pi' in p.capture and 'P' in p.capture['_pi'][0]:
|
||||
launch[pi_map, i] = logic.mvarray(p.capture['_pi'][0])
|
||||
launch[po_map, i] = logic.UNASSIGNED
|
||||
if launch_filter: launch = launch_filter(launch)
|
||||
|
||||
return logic.mv_transition(init, launch)
|
||||
|
||||
def responses(self, circuit):
|
||||
"""Assembles and returns a scan test response pattern set for given circuit."""
|
||||
"""Assembles and returns a scan test response pattern set for given circuit.
|
||||
|
||||
:param circuit: The circuit to assemble the patterns for. The patterns will follow the
|
||||
:py:attr:`~kyupy.circuit.Circuit.s_nodes` ordering of the this circuit.
|
||||
:return: A 4-valued multi-valued (mv) logic array (see :py:mod:`~kyupy.logic`).
|
||||
The values for primary outputs and sequential elements are filled, the primary inputs are left unassigned.
|
||||
"""
|
||||
interface, _, po_map, scan_maps, scan_inversions = self._maps(circuit)
|
||||
resp = logic.MVArray((len(interface), len(self.patterns)))
|
||||
# resp = PackedVectors(len(self.patterns), len(interface), 2)
|
||||
resp = np.full((len(interface), len(self.patterns)), logic.UNASSIGNED)
|
||||
for i, p in enumerate(self.patterns):
|
||||
resp.data[po_map, i] = logic.MVArray(p.capture['_po'] if len(p.capture) > 0 else p.launch['_po']).data[:, 0]
|
||||
# if len(p.capture) > 0:
|
||||
# resp.set_values(i, p.capture['_po'], po_map)
|
||||
# else:
|
||||
# resp.set_values(i, p.launch['_po'], po_map)
|
||||
resp[po_map, i] = logic.mvarray(p.capture['_po'][0] if len(p.capture) > 0 else p.launch['_po'][0])
|
||||
for so_port in self.so_ports.keys():
|
||||
pattern = logic.mv_xor(p.unload[so_port], scan_inversions[so_port])
|
||||
resp.data[scan_maps[so_port], i] = pattern.data[:, 0]
|
||||
# resp.set_values(i, p.unload[so_port], scan_maps[so_port], scan_inversions[so_port])
|
||||
pattern = logic.mv_xor(logic.mvarray(p.unload[so_port][0]), scan_inversions[so_port])
|
||||
resp[scan_maps[so_port], i] = pattern
|
||||
return resp
|
||||
|
||||
|
||||
@@ -166,7 +190,7 @@ class StilTransformer(Transformer):
|
||||
def call(args): return Call(args[0], dict(args[1:]))
|
||||
|
||||
@staticmethod
|
||||
def call_parameter(args): return args[0], args[1].value
|
||||
def call_parameter(args): return args[0], (args[1].value.replace('\n', '').replace('N', '-'), args[1].start_pos)
|
||||
|
||||
@staticmethod
|
||||
def signal_group(args): return args[0], args[1:]
|
||||
@@ -197,7 +221,7 @@ class StilTransformer(Transformer):
|
||||
|
||||
|
||||
GRAMMAR = r"""
|
||||
start: "STIL" FLOAT _ignore _block*
|
||||
start: "STIL" FLOAT ( _ignore | ";" ) _block*
|
||||
_block: signal_groups | scan_structures | pattern
|
||||
| "Header" _ignore
|
||||
| "Signals" _ignore
|
||||
@@ -206,6 +230,7 @@ GRAMMAR = r"""
|
||||
| "PatternExec" _ignore
|
||||
| "Procedures" _ignore
|
||||
| "MacroDefs" _ignore
|
||||
| "UserKeywords" /[a-zA-Z]*;/
|
||||
|
||||
signal_groups: "SignalGroups" "{" signal_group* "}"
|
||||
signal_group: quoted "=" "'" quoted ( "+" quoted)* "'" _ignore? ";"?
|
||||
@@ -246,6 +271,6 @@ def parse(text):
|
||||
def load(file):
|
||||
"""Parses the contents of ``file`` and returns a :class:`StilFile` object.
|
||||
|
||||
The given file may be gzip compressed.
|
||||
Files with `.gz`-suffix are decompressed on-the-fly.
|
||||
"""
|
||||
return parse(readtext(file))
|
||||
+402
-290
@@ -1,301 +1,413 @@
|
||||
from .circuit import Node, Line
|
||||
"""KyuPy's Built-In Technology Libraries
|
||||
|
||||
Technology libraries provide cell definitions and their implementation with simulation primitives.
|
||||
A couple of common standard cell libraries are built-in.
|
||||
Others can be easily added by providing a bench-like description of the cells.
|
||||
"""
|
||||
|
||||
def add_and_connect(circuit, name, kind, in1=None, in2=None, out=None):
|
||||
n = Node(circuit, name, kind)
|
||||
if in1 is not None:
|
||||
n.ins[0] = in1
|
||||
in1.reader = n
|
||||
in1.reader_pin = 0
|
||||
if in2 is not None:
|
||||
n.ins[1] = in2
|
||||
in2.reader = n
|
||||
in2.reader_pin = 1
|
||||
if out is not None:
|
||||
n.outs[0] = out
|
||||
out.driver = n
|
||||
out.driver_pin = 0
|
||||
return n
|
||||
import re
|
||||
from itertools import product
|
||||
|
||||
from . import bench
|
||||
|
||||
|
||||
class TechLib:
|
||||
"""Provides some information specific to standard cell libraries necessary
|
||||
for loading gate-level designs. :py:class:`~kyupy.circuit.Node` objects do not
|
||||
have pin names. The methods defined here map pin names to pin directions and defined
|
||||
positions in the ``node.ins`` and ``node.outs`` lists. The default implementation
|
||||
provides mappings for SAED-inspired standard cell libraries.
|
||||
"""Class for standard cell library definitions.
|
||||
|
||||
:py:class:`~kyupy.circuit.Node` objects do not have pin names.
|
||||
This class maps pin names to pin directions and defined positions in the ``node.ins`` and ``node.outs`` lists.
|
||||
Furthermore, it gives access to implementations of complex cells. See also :py:func:`~kyupy.circuit.substitute` and
|
||||
:py:func:`~kyupy.circuit.resolve_tlib_cells`.
|
||||
"""
|
||||
def __init__(self, lib_src):
|
||||
self.cells = dict()
|
||||
"""A dictionary with pin definitions and circuits for each cell kind (type).
|
||||
"""
|
||||
for c_str in re.split(r';\s+', lib_src):
|
||||
c_str = re.sub(r'^\s+', '', c_str)
|
||||
name_len = c_str.find(' ')
|
||||
if name_len <= 0: continue
|
||||
c = bench.parse(c_str[name_len:])
|
||||
c.name = c_str[:name_len]
|
||||
c.eliminate_1to1_forks()
|
||||
i_idx, o_idx = 0, 0
|
||||
pin_dict = dict()
|
||||
for n in c.io_nodes:
|
||||
if len(n.ins) == 0:
|
||||
pin_dict[n.name] = (i_idx, False)
|
||||
i_idx += 1
|
||||
else:
|
||||
pin_dict[n.name] = (o_idx, True)
|
||||
o_idx += 1
|
||||
parts = [s[1:-1].split(',') if s[0] == '{' else [s] for s in re.split(r'({[^}]+})', c.name) if len(s) > 0]
|
||||
for name in [''.join(item) for item in product(*parts)]:
|
||||
self.cells[name] = (c, pin_dict)
|
||||
|
||||
@staticmethod
|
||||
def pin_index(kind, pin):
|
||||
def pin_index(self, kind, pin):
|
||||
"""Returns a pin list position for a given node kind and pin name."""
|
||||
for prefix, pins, index in [('HADD', ('B0', 'SO'), 1),
|
||||
('MUX21', ('S',), 2),
|
||||
('DFF', ('QN',), 1),
|
||||
('SDFF', ('QN',), 1),
|
||||
('SDFF', ('CLK',), 3),
|
||||
('SDFF', ('RSTB',), 4),
|
||||
('SDFF', ('SETB',), 5)]:
|
||||
if kind.startswith(prefix) and pin in pins: return index
|
||||
for index, pins in enumerate([('A1', 'IN1', 'D', 'S', 'INP', 'A', 'Q', 'QN', 'Y', 'Z', 'ZN'),
|
||||
('A2', 'IN2', 'CLK', 'CO', 'SE', 'B'),
|
||||
('A3', 'IN3', 'RSTB', 'CI', 'SI'),
|
||||
('A4', 'IN4', 'SETB'),
|
||||
('A5', 'IN5'),
|
||||
('A6', 'IN6')]):
|
||||
if pin in pins: return index
|
||||
raise ValueError(f'Unknown pin index for {kind}.{pin}')
|
||||
assert kind in self.cells, f'Unknown cell: {kind}'
|
||||
assert pin in self.cells[kind][1], f'Unknown pin: {pin} for cell {kind}'
|
||||
return self.cells[kind][1][pin][0]
|
||||
|
||||
@staticmethod
|
||||
def pin_is_output(kind, pin):
|
||||
def pin_name(self, kind, pos, output=False):
|
||||
"""Returns the pin name for a given node kind, list position, and direction."""
|
||||
assert kind in self.cells, f'Unknown cell: {kind}'
|
||||
for name, (ppos, isout) in self.cells[kind][1].items():
|
||||
if isout == output and ppos == pos:
|
||||
return name
|
||||
return None
|
||||
|
||||
def pin_is_output(self, kind, pin):
|
||||
"""Returns True, if given pin name of a node kind is an output."""
|
||||
if 'MUX' in kind and pin == 'S': return False
|
||||
return pin in ('Q', 'QN', 'Z', 'ZN', 'Y', 'CO', 'S', 'SO', 'C1')
|
||||
assert kind in self.cells, f'Unknown cell: {kind}'
|
||||
assert pin in self.cells[kind][1], f'Unknown pin: {pin} for cell {kind}'
|
||||
return self.cells[kind][1][pin][1]
|
||||
|
||||
@staticmethod
|
||||
def split_complex_gates(circuit):
|
||||
node_list = circuit.nodes
|
||||
for n in node_list:
|
||||
name = n.name
|
||||
ins = n.ins
|
||||
outs = n.outs
|
||||
if n.kind.startswith('AO21X'):
|
||||
n.remove()
|
||||
n_and = add_and_connect(circuit, name+'~and', 'AND2', ins[0], ins[1], None)
|
||||
n_or = add_and_connect(circuit, name+'~or', 'OR2', None, ins[2], outs[0])
|
||||
Line(circuit, n_and, n_or)
|
||||
elif n.kind.startswith('AOI21X'):
|
||||
n.remove()
|
||||
n_and = add_and_connect(circuit, name+'~and', 'AND2', ins[0], ins[1], None)
|
||||
n_nor = add_and_connect(circuit, name+'~nor', 'NOR2', None, ins[2], outs[0])
|
||||
Line(circuit, n_and, n_nor)
|
||||
elif n.kind.startswith('OA21X'):
|
||||
n.remove()
|
||||
n_or = add_and_connect(circuit, name+'~or', 'OR2', ins[0], ins[1], None)
|
||||
n_and = add_and_connect(circuit, name+'~and', 'AND2', None, ins[2], outs[0])
|
||||
Line(circuit, n_or, n_and)
|
||||
elif n.kind.startswith('OAI21X'):
|
||||
n.remove()
|
||||
n_or = add_and_connect(circuit, name+'~or', 'OR2', ins[0], ins[1], None)
|
||||
n_nand = add_and_connect(circuit, name+'~nand', 'NAND2', None, ins[2], outs[0])
|
||||
Line(circuit, n_or, n_nand)
|
||||
elif n.kind.startswith('OA22X'):
|
||||
n.remove()
|
||||
n_or0 = add_and_connect(circuit, name+'~or0', 'OR2', ins[0], ins[1], None)
|
||||
n_or1 = add_and_connect(circuit, name+'~or1', 'OR2', ins[2], ins[3], None)
|
||||
n_and = add_and_connect(circuit, name+'~and', 'AND2', None, None, outs[0])
|
||||
Line(circuit, n_or0, n_and)
|
||||
Line(circuit, n_or1, n_and)
|
||||
elif n.kind.startswith('OAI22X'):
|
||||
n.remove()
|
||||
n_or0 = add_and_connect(circuit, name+'~or0', 'OR2', ins[0], ins[1], None)
|
||||
n_or1 = add_and_connect(circuit, name+'~or1', 'OR2', ins[2], ins[3], None)
|
||||
n_nand = add_and_connect(circuit, name+'~nand', 'NAND2', None, None, outs[0])
|
||||
Line(circuit, n_or0, n_nand)
|
||||
Line(circuit, n_or1, n_nand)
|
||||
elif n.kind.startswith('AO22X'):
|
||||
n.remove()
|
||||
n_and0 = add_and_connect(circuit, name+'~and0', 'AND2', ins[0], ins[1], None)
|
||||
n_and1 = add_and_connect(circuit, name+'~and1', 'AND2', ins[2], ins[3], None)
|
||||
n_or = add_and_connect(circuit, name+'~or', 'OR2', None, None, outs[0])
|
||||
Line(circuit, n_and0, n_or)
|
||||
Line(circuit, n_and1, n_or)
|
||||
elif n.kind.startswith('AOI22X'):
|
||||
n.remove()
|
||||
n_and0 = add_and_connect(circuit, name+'~and0', 'AND2', ins[0], ins[1], None)
|
||||
n_and1 = add_and_connect(circuit, name+'~and1', 'AND2', ins[2], ins[3], None)
|
||||
n_nor = add_and_connect(circuit, name+'~nor', 'NOR2', None, None, outs[0])
|
||||
Line(circuit, n_and0, n_nor)
|
||||
Line(circuit, n_and1, n_nor)
|
||||
elif n.kind.startswith('AO221X'):
|
||||
n.remove()
|
||||
n_and0 = add_and_connect(circuit, name+'~and0', 'AND2', ins[0], ins[1], None)
|
||||
n_and1 = add_and_connect(circuit, name+'~and1', 'AND2', ins[2], ins[3], None)
|
||||
n_or0 = add_and_connect(circuit, name+'~or0', 'OR2', None, None, None)
|
||||
n_or1 = add_and_connect(circuit, name+'~or1', 'OR2', None, ins[4], outs[0])
|
||||
Line(circuit, n_and0, n_or0)
|
||||
Line(circuit, n_and1, n_or0)
|
||||
Line(circuit, n_or0, n_or1)
|
||||
elif n.kind.startswith('AOI221X'):
|
||||
n.remove()
|
||||
n_and0 = add_and_connect(circuit, name+'~and0', 'AND2', ins[0], ins[1], None)
|
||||
n_and1 = add_and_connect(circuit, name+'~and1', 'AND2', ins[2], ins[3], None)
|
||||
n_or = add_and_connect(circuit, name+'~or', 'OR2', None, None, None)
|
||||
n_nor = add_and_connect(circuit, name+'~nor', 'NOR2', None, ins[4], outs[0])
|
||||
Line(circuit, n_and0, n_or)
|
||||
Line(circuit, n_and1, n_or)
|
||||
Line(circuit, n_or, n_nor)
|
||||
elif n.kind.startswith('OA221X'):
|
||||
n.remove()
|
||||
n_or0 = add_and_connect(circuit, name+'~or0', 'OR2', ins[0], ins[1], None)
|
||||
n_or1 = add_and_connect(circuit, name+'~or1', 'OR2', ins[2], ins[3], None)
|
||||
n_and0 = add_and_connect(circuit, name+'~and0', 'AND2', None, None, None)
|
||||
n_and1 = add_and_connect(circuit, name+'~and1', 'AND2', None, ins[4], outs[0])
|
||||
Line(circuit, n_or0, n_and0)
|
||||
Line(circuit, n_or1, n_and0)
|
||||
Line(circuit, n_and0, n_and1)
|
||||
elif n.kind.startswith('OAI221X'):
|
||||
n.remove()
|
||||
n_or0 = add_and_connect(circuit, name+'~or0', 'OR2', ins[0], ins[1], None)
|
||||
n_or1 = add_and_connect(circuit, name+'~or1', 'OR2', ins[2], ins[3], None)
|
||||
n_and0 = add_and_connect(circuit, name+'~and0', 'AND2', None, None, None)
|
||||
n_nand1 = add_and_connect(circuit, name+'~nand1', 'NAND2', None, ins[4], outs[0])
|
||||
Line(circuit, n_or0, n_and0)
|
||||
Line(circuit, n_or1, n_and0)
|
||||
Line(circuit, n_and0, n_nand1)
|
||||
elif n.kind.startswith('AO222X'):
|
||||
n.remove()
|
||||
n_and0 = add_and_connect(circuit, name+'~and0', 'AND2', ins[0], ins[1], None)
|
||||
n_and1 = add_and_connect(circuit, name+'~and1', 'AND2', ins[2], ins[3], None)
|
||||
n_and2 = add_and_connect(circuit, name+'~and2', 'AND2', ins[4], ins[5], None)
|
||||
n_or0 = add_and_connect(circuit, name+'~or0', 'OR2', None, None, None)
|
||||
n_or1 = add_and_connect(circuit, name+'~or1', 'OR2', None, None, outs[0])
|
||||
Line(circuit, n_and0, n_or0)
|
||||
Line(circuit, n_and1, n_or0)
|
||||
Line(circuit, n_and2, n_or1)
|
||||
Line(circuit, n_or0, n_or1)
|
||||
elif n.kind.startswith('AOI222X'):
|
||||
n.remove()
|
||||
n_and0 = add_and_connect(circuit, name+'~and0', 'AND2', ins[0], ins[1], None)
|
||||
n_and1 = add_and_connect(circuit, name+'~and1', 'AND2', ins[2], ins[3], None)
|
||||
n_and2 = add_and_connect(circuit, name+'~and2', 'AND2', ins[4], ins[5], None)
|
||||
n_or0 = add_and_connect(circuit, name+'~or0', 'OR2', None, None, None)
|
||||
n_nor1 = add_and_connect(circuit, name+'~nor1', 'NOR2', None, None, outs[0])
|
||||
Line(circuit, n_and0, n_or0)
|
||||
Line(circuit, n_and1, n_or0)
|
||||
Line(circuit, n_and2, n_nor1)
|
||||
Line(circuit, n_or0, n_nor1)
|
||||
elif n.kind.startswith('OA222X'):
|
||||
n.remove()
|
||||
n_or0 = add_and_connect(circuit, name+'~or0', 'OR2', ins[0], ins[1], None)
|
||||
n_or1 = add_and_connect(circuit, name+'~or1', 'OR2', ins[2], ins[3], None)
|
||||
n_or2 = add_and_connect(circuit, name+'~or2', 'OR2', ins[4], ins[5], None)
|
||||
n_and0 = add_and_connect(circuit, name+'~and0', 'AND2', None, None, None)
|
||||
n_and1 = add_and_connect(circuit, name+'~and1', 'AND2', None, None, outs[0])
|
||||
Line(circuit, n_or0, n_and0)
|
||||
Line(circuit, n_or1, n_and0)
|
||||
Line(circuit, n_or2, n_and1)
|
||||
Line(circuit, n_and0, n_and1)
|
||||
elif n.kind.startswith('OAI222X'):
|
||||
n.remove()
|
||||
n0 = add_and_connect(circuit, name+'~or0', 'OR2', ins[0], ins[1], None)
|
||||
n1 = add_and_connect(circuit, name+'~or1', 'OR2', ins[2], ins[3], None)
|
||||
n2 = add_and_connect(circuit, name+'~or2', 'OR2', ins[4], ins[5], None)
|
||||
n3 = add_and_connect(circuit, name+'~and0', 'AND2', None, None, None)
|
||||
n4 = add_and_connect(circuit, name+'~nand1', 'NAND2', None, None, outs[0])
|
||||
Line(circuit, n0, n3)
|
||||
Line(circuit, n1, n3)
|
||||
Line(circuit, n2, n4)
|
||||
Line(circuit, n3, n4)
|
||||
elif n.kind.startswith('AND3X'):
|
||||
n.remove()
|
||||
n0 = add_and_connect(circuit, name+'~and0', 'AND2', ins[0], ins[1], None)
|
||||
n1 = add_and_connect(circuit, name+'~and1', 'AND2', None, ins[2], outs[0])
|
||||
Line(circuit, n0, n1)
|
||||
elif n.kind.startswith('OR3X'):
|
||||
n.remove()
|
||||
n0 = add_and_connect(circuit, name+'~or0', 'OR2', ins[0], ins[1], None)
|
||||
n1 = add_and_connect(circuit, name+'~or1', 'OR2', None, ins[2], outs[0])
|
||||
Line(circuit, n0, n1)
|
||||
elif n.kind.startswith('XOR3X'):
|
||||
n.remove()
|
||||
n0 = add_and_connect(circuit, name+'~xor0', 'XOR2', ins[0], ins[1], None)
|
||||
n1 = add_and_connect(circuit, name+'~xor1', 'XOR2', None, ins[2], outs[0])
|
||||
Line(circuit, n0, n1)
|
||||
elif n.kind.startswith('NAND3X'):
|
||||
n.remove()
|
||||
n0 = add_and_connect(circuit, name+'~and', 'AND2', ins[0], ins[1], None)
|
||||
n1 = add_and_connect(circuit, name+'~nand', 'NAND2', None, ins[2], outs[0])
|
||||
Line(circuit, n0, n1)
|
||||
elif n.kind.startswith('NOR3X'):
|
||||
n.remove()
|
||||
n0 = add_and_connect(circuit, name+'~or', 'OR2', ins[0], ins[1], None)
|
||||
n1 = add_and_connect(circuit, name+'~nor', 'NOR2', None, ins[2], outs[0])
|
||||
Line(circuit, n0, n1)
|
||||
elif n.kind.startswith('XNOR3X'):
|
||||
n.remove()
|
||||
n0 = add_and_connect(circuit, name+'~xor', 'XOR2', ins[0], ins[1], None)
|
||||
n1 = add_and_connect(circuit, name+'~xnor', 'XNOR2', None, ins[2], outs[0])
|
||||
Line(circuit, n0, n1)
|
||||
elif n.kind.startswith('AND4X'):
|
||||
n.remove()
|
||||
n0 = add_and_connect(circuit, name+'~and0', 'AND2', ins[0], ins[1], None)
|
||||
n1 = add_and_connect(circuit, name+'~and1', 'AND2', ins[2], ins[3], None)
|
||||
n2 = add_and_connect(circuit, name+'~and2', 'AND2', None, None, outs[0])
|
||||
Line(circuit, n0, n2)
|
||||
Line(circuit, n1, n2)
|
||||
elif n.kind.startswith('OR4X'):
|
||||
n.remove()
|
||||
n0 = add_and_connect(circuit, name+'~or0', 'OR2', ins[0], ins[1], None)
|
||||
n1 = add_and_connect(circuit, name+'~or1', 'OR2', ins[2], ins[3], None)
|
||||
n2 = add_and_connect(circuit, name+'~or2', 'OR2', None, None, outs[0])
|
||||
Line(circuit, n0, n2)
|
||||
Line(circuit, n1, n2)
|
||||
elif n.kind.startswith('NAND4X'):
|
||||
n.remove()
|
||||
n0 = add_and_connect(circuit, name+'~and0', 'AND2', ins[0], ins[1], None)
|
||||
n1 = add_and_connect(circuit, name+'~and1', 'AND2', ins[2], ins[3], None)
|
||||
n2 = add_and_connect(circuit, name+'~nand2', 'NAND2', None, None, outs[0])
|
||||
Line(circuit, n0, n2)
|
||||
Line(circuit, n1, n2)
|
||||
elif n.kind.startswith('NOR4X'):
|
||||
n.remove()
|
||||
n0 = add_and_connect(circuit, name+'~or0', 'OR2', ins[0], ins[1], None)
|
||||
n1 = add_and_connect(circuit, name+'~or1', 'OR2', ins[2], ins[3], None)
|
||||
n2 = add_and_connect(circuit, name+'~nor2', 'NOR2', None, None, outs[0])
|
||||
Line(circuit, n0, n2)
|
||||
Line(circuit, n1, n2)
|
||||
elif n.kind.startswith('FADDX'):
|
||||
n.remove()
|
||||
# forks for fan-outs
|
||||
f_a = add_and_connect(circuit, name + '~fork0', '__fork__', ins[0])
|
||||
f_b = add_and_connect(circuit, name + '~fork1', '__fork__', ins[1])
|
||||
f_ci = add_and_connect(circuit, name + '~fork2', '__fork__', ins[2])
|
||||
f_ab = Node(circuit, name + '~fork3')
|
||||
# sum-block
|
||||
n_xor0 = Node(circuit, name + '~xor0', 'XOR2')
|
||||
Line(circuit, f_a, n_xor0)
|
||||
Line(circuit, f_b, n_xor0)
|
||||
Line(circuit, n_xor0, f_ab)
|
||||
if len(outs) > 0 and outs[0] is not None:
|
||||
n_xor1 = add_and_connect(circuit, name + '~xor1', 'XOR2', None, None, outs[0])
|
||||
Line(circuit, f_ab, n_xor1)
|
||||
Line(circuit, f_ci, n_xor1)
|
||||
# carry-block
|
||||
if len(outs) > 1 and outs[1] is not None:
|
||||
n_and0 = Node(circuit, name + '~and0', 'AND2')
|
||||
Line(circuit, f_ab, n_and0)
|
||||
Line(circuit, f_ci, n_and0)
|
||||
n_and1 = Node(circuit, name + '~and1', 'AND2')
|
||||
Line(circuit, f_a, n_and1)
|
||||
Line(circuit, f_b, n_and1)
|
||||
n_or = add_and_connect(circuit, name + '~or0', 'OR2', None, None, outs[1])
|
||||
Line(circuit, n_and0, n_or)
|
||||
Line(circuit, n_and1, n_or)
|
||||
elif n.kind.startswith('HADDX'):
|
||||
n.remove()
|
||||
# forks for fan-outs
|
||||
f_a = add_and_connect(circuit, name + '~fork0', '__fork__', ins[0])
|
||||
f_b = add_and_connect(circuit, name + '~fork1', '__fork__', ins[1])
|
||||
n_xor0 = add_and_connect(circuit, name + '~xor0', 'XOR2', None, None, outs[1])
|
||||
Line(circuit, f_a, n_xor0)
|
||||
Line(circuit, f_b, n_xor0)
|
||||
n_and0 = add_and_connect(circuit, name + '~and0', 'AND2', None, None, outs[0])
|
||||
Line(circuit, f_a, n_and0)
|
||||
Line(circuit, f_b, n_and0)
|
||||
elif n.kind.startswith('MUX21X'):
|
||||
n.remove()
|
||||
f_s = add_and_connect(circuit, name + '~fork0', '__fork__', ins[2])
|
||||
n_not = Node(circuit, name + '~not', 'INV')
|
||||
Line(circuit, f_s, n_not)
|
||||
n_and0 = add_and_connect(circuit, name + '~and0', 'AND2', ins[0])
|
||||
n_and1 = add_and_connect(circuit, name + '~and1', 'AND2', ins[1])
|
||||
n_or0 = add_and_connect(circuit, name + '~or0', 'OR2', None, None, outs[0])
|
||||
Line(circuit, n_not, n_and0)
|
||||
Line(circuit, f_s, n_and1)
|
||||
Line(circuit, n_and0, n_or0)
|
||||
Line(circuit, n_and1, n_or0)
|
||||
elif n.kind.startswith('DFFSSR'):
|
||||
n.kind = 'DFFX1'
|
||||
n_and0 = add_and_connect(circuit, name + '~and0', 'AND2', ins[0], ins[2], None)
|
||||
Line(circuit, n_and0, (n, 0))
|
||||
|
||||
GSC180 = TechLib(r"""
|
||||
BUFX{1,3} input(A) output(Y) Y=BUF1(A) ;
|
||||
CLKBUFX{1,2,3} input(A) output(Y) Y=BUF1(A) ;
|
||||
INVX{1,2,4,8} input(A) output(Y) Y=INV1(A) ;
|
||||
TBUFX{1,2,4,8} input(A,OE) output(Y) Y=AND2(A,OE) ;
|
||||
TINVX1 input(A,OE) output(Y) AB=INV1(A) Y=AND2(AB,OE) ;
|
||||
|
||||
AND2X1 input(A,B) output(Y) Y=AND2(A,B) ;
|
||||
NAND2X{1,2} input(A,B) output(Y) Y=NAND2(A,B) ;
|
||||
NAND3X1 input(A,B,C) output(Y) Y=NAND3(A,B,C) ;
|
||||
NAND4X1 input(A,B,C,D) output(Y) Y=NAND4(A,B,C,D) ;
|
||||
OR2X1 input(A,B) output(Y) Y=OR2(A,B) ;
|
||||
OR4X1 input(A,B,C,D) output(Y) Y=OR4(A,B,C,D) ;
|
||||
NOR2X1 input(A,B) output(Y) Y=NOR2(A,B) ;
|
||||
NOR3X1 input(A,B,C) output(Y) Y=NOR3(A,B,C) ;
|
||||
NOR4X1 input(A,B,C,D) output(Y) Y=NOR4(A,B,C,D) ;
|
||||
XOR2X1 input(A,B) output(Y) Y=XOR2(A,B) ;
|
||||
|
||||
MX2X1 input(A,B,S0) output(Y) Y=MUX21(A,B,S0) ;
|
||||
AOI21X1 input(A0,A1,B0) output(Y) Y=AOI21(A0,A1,B0) ;
|
||||
AOI22X1 input(A0,A1,B0,B1) output(Y) Y=AOI22(A0,A1,B0,B1) ;
|
||||
OAI21X1 input(A0,A1,B0) output(Y) Y=OAI21(A0,A1,B0) ;
|
||||
OAI22X1 input(A0,A1,B0,B1) output(Y) Y=OAI22(A0,A1,B0,B1) ;
|
||||
OAI33X1 input(A0,A1,A2,B0,B1,B2) output(Y) AA=OR2(A0,A1) BB=OR2(B0,B1) Y=OAI22(AA,A2,BB,B2) ;
|
||||
ADDFX1 input(A,B,CI) output(CO,S) AB=XOR2(A,B) CO=XOR2(AB,CI) S=AO22(AB,CI,A,B) ;
|
||||
ADDHX1 input(A,B) output(CO,S) CO=XOR2(A,B) S=AND2(A,B) ;
|
||||
|
||||
DFFX1 input(CK,D) output(Q,QN) Q=DFF(D,CK) QN=INV1(Q) ;
|
||||
DFFSRX1 input(CK,D,RN,SN) output(Q,QN) DR=AND2(D,RN) SET=INV1(SN) DRS=OR2(DR,SET) Q=DFF(DRS,CK) QN=INV1(Q) ;
|
||||
SDFFSRX1 input(CK,D,RN,SE,SI,SN) output(Q,QN) DR=AND2(D,RN) SET=INV1(SN) DRS=OR2(DR,SET) DI=MUX21(DRS,SI,SE) Q=DFF(DI,CK) QN=INV1(Q) ;
|
||||
|
||||
TLATSRX1 input(D,G,RN,SN) output(Q,QN) DR=AND2(D,RN) SET=INV1(SN) DRS=OR2(DR,SET) Q=LATCH(DRS,G) QN=INV1(Q) ;
|
||||
TLATX1 input(C,D) output(Q,QN) Q=LATCH(D,C) QN=INV1(Q) ;
|
||||
""")
|
||||
"""The GSC 180nm generic standard cell library.
|
||||
"""
|
||||
|
||||
|
||||
NANGATE = TechLib(r"""
|
||||
FILLTIE ;
|
||||
FILL_X{1,2,4,8,16} ;
|
||||
ANTENNA input(I) ;
|
||||
|
||||
TIEH output(Z) Z=__const1__() ;
|
||||
TIEL output(ZN) ZN=__const0__() ;
|
||||
|
||||
BUF_X{1,2,4,8,12,16} input(I) output(Z) Z=BUF1(I) ;
|
||||
INV_X{1,2,4,8,12,16} input(I) output(ZN) ZN=INV1(I) ;
|
||||
|
||||
CLKBUF_X{1,2,4,8,12,16} input(I) output(Z) Z=BUF1(I) ;
|
||||
CLKGATETST_X1 input(CLK,E,TE) output(Q) Q=OA21(CLK,E,TE) ;
|
||||
|
||||
AND2_X{1,2} input(A1,A2) output(Z) Z=AND2(A1,A2) ;
|
||||
AND3_X{1,2} input(A1,A2,A3) output(Z) Z=AND3(A1,A2,A3) ;
|
||||
AND4_X{1,2} input(A1,A2,A3,A4) output(Z) Z=AND4(A1,A2,A3,A4) ;
|
||||
NAND2_X{1,2} input(A1,A2) output(ZN) ZN=NAND2(A1,A2) ;
|
||||
NAND3_X{1,2} input(A1,A2,A3) output(ZN) ZN=NAND3(A1,A2,A3) ;
|
||||
NAND4_X{1,2} input(A1,A2,A3,A4) output(ZN) ZN=NAND4(A1,A2,A3,A4) ;
|
||||
OR2_X{1,2} input(A1,A2) output(Z) Z=OR2(A1,A2) ;
|
||||
OR3_X{1,2} input(A1,A2,A3) output(Z) Z=OR3(A1,A2,A3) ;
|
||||
OR4_X{1,2} input(A1,A2,A3,A4) output(Z) Z=OR4(A1,A2,A3,A4) ;
|
||||
NOR2_X{1,2} input(A1,A2) output(ZN) ZN=NOR2(A1,A2) ;
|
||||
NOR3_X{1,2} input(A1,A2,A3) output(ZN) ZN=NOR3(A1,A2,A3) ;
|
||||
NOR4_X{1,2} input(A1,A2,A3,A4) output(ZN) ZN=NOR4(A1,A2,A3,A4) ;
|
||||
XOR2_X1 input(A1,A2) output(Z) Z=XOR2(A1,A2) ;
|
||||
XNOR2_X1 input(A1,A2) output(ZN) ZN=XNOR2(A1,A2) ;
|
||||
|
||||
MUX2_X1 input(I0,I1,S) output(Z) Z=MUX21(I0,I1,S) ;
|
||||
|
||||
HA_X1 input(A,B) output(CO,S) CO=XOR2(A,B) S=AND2(A,B) ;
|
||||
FA_X1 input(A,B,CI) output(CO,S) AB=XOR2(A,B) CO=XOR2(AB,CI) S=AO22(CI,A,B) ;
|
||||
|
||||
AOI21_X{1,2} input(A1,A2,B) output(ZN) ZN=AOI21(A1,A2,B) ;
|
||||
OAI21_X{1,2} input(A1,A2,B) output(ZN) ZN=OAI21(A1,A2,B) ;
|
||||
AOI22_X{1,2} input(A1,A2,B1,B2) output(ZN) ZN=AOI22(A1,A2,B1,B2) ;
|
||||
OAI22_X{1,2} input(A1,A2,B1,B2) output(ZN) ZN=OAI22(A1,A2,B1,B2) ;
|
||||
|
||||
DFFRNQ_X1 input(D,RN,CLK) output(Q) DR=AND2(D,RN) Q=DFF(DR,CLK) ;
|
||||
DFFSNQ_X1 input(D,SN,CLK) output(Q) S=INV1(SN) DS=OR2(D,S) Q=DFF(DS,CLK) ;
|
||||
|
||||
SDFFRNQ_X1 input(D,RN,SE,SI,CLK) output(Q) DR=AND2(D,RN) DI=MUX21(DR,SI,SE) Q=DFF(DI,CLK) ;
|
||||
SDFFSNQ_X1 input(D,SE,SI,SN,CLK) output(Q) S=INV1(SN) DS=OR2(D,S) DI=MUX21(DS,SI,SE) Q=DFF(DI,CLK) ;
|
||||
|
||||
TBUF_X{1,2,4,8,12,16} input(EN,I) output(Z) Z=BUF1(I) ;
|
||||
|
||||
LHQ_X1 input(D,E) output(Q) Q=LATCH(D,E) ;
|
||||
""")
|
||||
"""Nangate 15nm Open Cell Library (NanGate_15nm_OCL_v0.1_2014_06.A).
|
||||
"""
|
||||
|
||||
|
||||
NANGATE45 = TechLib(r"""
|
||||
FILLCELL_X{1,2,4,8,16,32} ;
|
||||
ANTENNA_X1 input(A) ;
|
||||
|
||||
LOGIC0_X1 output(Z) Z=__const0__() ;
|
||||
LOGIC1_X1 output(Z) Z=__const1__() ;
|
||||
|
||||
BUF_X{1,2,4,8,16,32} input(A) output(Z) Z=BUF1(A) ;
|
||||
INV_X{1,2,4,8,16,32} input(A) output(ZN) ZN=INV1(A) ;
|
||||
|
||||
CLKBUF_X{1,2,3} input(A) output(Z) Z=BUF1(A) ;
|
||||
CLKGATETST_X{1,2,4,8} input(CK,E,SE) output(GCK) GCK=OA21(CK,E,SE) ;
|
||||
CLKGATE_X{1,2,4,8} input(CK,E) output(GCK) GCK=AND2(CK,E) ;
|
||||
|
||||
AND2_X{1,2,4} input(A1,A2) output(ZN) ZN=AND2(A1,A2) ;
|
||||
AND3_X{1,2,4} input(A1,A2,A3) output(ZN) ZN=AND3(A1,A2,A3) ;
|
||||
AND4_X{1,2,4} input(A1,A2,A3,A4) output(ZN) ZN=AND4(A1,A2,A3,A4) ;
|
||||
NAND2_X{1,2,4} input(A1,A2) output(ZN) ZN=NAND2(A1,A2) ;
|
||||
NAND3_X{1,2,4} input(A1,A2,A3) output(ZN) ZN=NAND3(A1,A2,A3) ;
|
||||
NAND4_X{1,2,4} input(A1,A2,A3,A4) output(ZN) ZN=NAND4(A1,A2,A3,A4) ;
|
||||
OR2_X{1,2,4} input(A1,A2) output(ZN) ZN=OR2(A1,A2) ;
|
||||
OR3_X{1,2,4} input(A1,A2,A3) output(ZN) ZN=OR3(A1,A2,A3) ;
|
||||
OR4_X{1,2,4} input(A1,A2,A3,A4) output(ZN) ZN=OR4(A1,A2,A3,A4) ;
|
||||
NOR2_X{1,2,4} input(A1,A2) output(ZN) ZN=NOR2(A1,A2) ;
|
||||
NOR3_X{1,2,4} input(A1,A2,A3) output(ZN) ZN=NOR3(A1,A2,A3) ;
|
||||
NOR4_X{1,2,4} input(A1,A2,A3,A4) output(ZN) ZN=NOR4(A1,A2,A3,A4) ;
|
||||
XOR2_X{1,2} input(A,B) output(Z) Z=XOR2(A,B) ;
|
||||
XNOR2_X{1,2} input(A,B) output(ZN) ZN=XNOR2(A,B) ;
|
||||
|
||||
MUX2_X{1,2} input(A,B,S) output(Z) Z=MUX21(A,B,S) ;
|
||||
|
||||
HA_X1 input(A,B) output(CO,S) CO=XOR2(A,B) S=AND2(A,B) ;
|
||||
FA_X1 input(A,B,CI) output(CO,S) AB=XOR2(A,B) CO=XOR2(AB,CI) S=AO22(CI,A,B) ;
|
||||
|
||||
AOI21_X{1,2,4} input(A,B1,B2) output(ZN) ZN=AOI21(B1,B2,A) ;
|
||||
OAI21_X{1,2,4} input(A,B1,B2) output(ZN) ZN=OAI21(B1,B2,A) ;
|
||||
AOI22_X{1,2,4} input(A1,A2,B1,B2) output(ZN) ZN=AOI22(A1,A2,B1,B2) ;
|
||||
OAI22_X{1,2,4} input(A1,A2,B1,B2) output(ZN) ZN=OAI22(A1,A2,B1,B2) ;
|
||||
|
||||
OAI211_X{1,2,4} input(A,B,C1,C2) output(ZN) ZN=OAI211(C1,C2,A,B) ;
|
||||
AOI211_X{1,2,4} input(A,B,C1,C2) output(ZN) ZN=AOI211(C1,C2,A,B) ;
|
||||
|
||||
AOI221_X{1,2,4} input(A,B1,B2,C1,C2) output(ZN) BC=AO22(B1,B2,C1,C2) ZN=NOR2(BC,A) ;
|
||||
OAI221_X{1,2,4} input(A,B1,B2,C1,C2) output(ZN) BC=OA22(B1,B2,C1,C2) ZN=NAND2(BC,A) ;
|
||||
|
||||
AOI222_X{1,2,4} input(A1,A2,B1,B2,C1,C2) output(ZN) BC=AO22(B1,B2,C1,C2) ZN=AOI21(A1,A2,BC) ;
|
||||
OAI222_X{1,2,4} input(A1,A2,B1,B2,C1,C2) output(ZN) BC=OA22(B1,B2,C1,C2) ZN=OAI21(A1,A2,BC) ;
|
||||
|
||||
OAI33_X1 input(A1,A2,A3,B1,B2,B3) output(ZN) AA=OR2(A1,A2) BB=OR2(B1,B2) ZN=OAI22(AA,A3,BB,B3) ;
|
||||
|
||||
DFF_X{1,2} input(D,CK) output(Q,QN) Q=DFF(D,CK) QN=INV1(Q) ;
|
||||
DFFR_X{1,2} input(D,RN,CK) output(Q,QN) DR=AND2(D,RN) Q=DFF(DR,CK) QN=INV1(Q) ;
|
||||
DFFS_X{1,2} input(D,SN,CK) output(Q,QN) S=INV1(SN) DS=OR2(D,S) Q=DFF(DS,CK) QN=INV1(Q) ;
|
||||
DFFRS_X{1,2} input(D,RN,SN,CK) output(Q,QN) S=INV1(SN) DS=OR2(D,S) DRS=AND2(DS,RN) Q=DFF(DRS,CK) QN=INV1(Q) ;
|
||||
|
||||
SDFF_X{1,2} input(D,SE,SI,CK) output(Q,QN) DI=MUX21(D,SI,SE) Q=DFF(DI,CK) QN=INV1(Q) ;
|
||||
SDFFR_X{1,2} input(D,RN,SE,SI,CK) output(Q,QN) DR=AND2(D,RN) DI=MUX21(DR,SI,SE) Q=DFF(DI,CK) QN=INV1(Q) ;
|
||||
SDFFS_X{1,2} input(D,SE,SI,SN,CK) output(Q,QN) S=INV1(SN) DS=OR2(D,S) DI=MUX21(DS,SI,SE) Q=DFF(DI,CK) QN=INV1(Q) ;
|
||||
SDFFRS_X{1,2} input(D,RN,SE,SI,SN,CK) output(Q,QN) S=INV1(SN) DS=OR2(D,S) DRS=AND2(DS,RN) DI=MUX21(DRS,SI,SE) Q=DFF(DI,CK) QN=INV1(Q) ;
|
||||
|
||||
TBUF_X{1,2,4,8,16} input(A,EN) output(Z) Z=BUF1(A) ;
|
||||
|
||||
TINV_X1 input(I,EN) output(ZN) ZN=INV1(I) ;
|
||||
TLAT_X1 input(D,G,OE) output(Q) Q=LATCH(D,G) ;
|
||||
|
||||
DLH_X{1,2} input(D,G) output(Q) Q=LATCH(D,G) ;
|
||||
DLL_X{1,2} input(D,GN) output(Q) G=INV1(GN) Q=LATCH(D,G) ;
|
||||
|
||||
""")
|
||||
"""Nangate 45nm Open Cell Library (NangateOpenCellLibrary_PDKv1_3_v2010_12).
|
||||
This NANGATE-variant that uses 'ZN' as output pin names for AND and OR gates.
|
||||
"""
|
||||
|
||||
|
||||
SAED32 = TechLib(r"""
|
||||
NBUFFX{2,4,8,16,32}$ input(A) output(Y) Y=BUF1(A) ;
|
||||
AOBUFX{1,2,4}$ input(A) output(Y) Y=BUF1(A) ;
|
||||
DELLN{1,2,3}X2$ input(A) output(Y) Y=BUF1(A) ;
|
||||
|
||||
INVX{0,1,2,4,8,16,32}$ input(A) output(Y) Y=INV1(A) ;
|
||||
AOINVX{1,2,4}$ input(A) output(Y) Y=INV1(A) ;
|
||||
IBUFFX{2,4,8,16,32}$ input(A) output(Y) Y=INV1(A) ;
|
||||
|
||||
TIEH$ output(Y) Y=__const1__() ;
|
||||
TIEL$ output(Y) Y=__const0__() ;
|
||||
|
||||
HEAD2X{2,4,8,16,32}$ input(SLEEP) output(SLEEPOUT) SLEEPOUT=BUF1(SLEEP) ;
|
||||
HEADX{2,4,8,16,32}$ input(SLEEP) ;
|
||||
|
||||
FOOT2X{2,4,8,16,32}$ input(SLEEP) output(SLEEPOUT) SLEEPOUT=BUF1(SLEEP) ;
|
||||
FOOTX{2,4,8,16,32}$ input(SLEEP) ;
|
||||
|
||||
ANTENNA$ input(INP) ;
|
||||
CLOAD1$ input(A) ;
|
||||
DCAP$ ;
|
||||
DHFILLH2$ ;
|
||||
DHFILLHL2$ ;
|
||||
DHFILLHLHLS11$ ;
|
||||
SHFILL{1,2,3,64,128}$ ;
|
||||
|
||||
AND2X{1,2,4}$ input(A1,A2) output(Y) Y=AND2(A1,A2) ;
|
||||
AND3X{1,2,4}$ input(A1,A2,A3) output(Y) Y=AND3(A1,A2,A3) ;
|
||||
AND4X{1,2,4}$ input(A1,A2,A3,A4) output(Y) Y=AND4(A1,A2,A3,A4) ;
|
||||
OR2X{1,2,4}$ input(A1,A2) output(Y) Y=OR2(A1,A2) ;
|
||||
OR3X{1,2,4}$ input(A1,A2,A3) output(Y) Y=OR3(A1,A2,A3) ;
|
||||
OR4X{1,2,4}$ input(A1,A2,A3,A4) output(Y) Y=OR4(A1,A2,A3,A4) ;
|
||||
XOR2X{1,2}$ input(A1,A2) output(Y) Y=XOR2(A1,A2) ;
|
||||
XOR3X{1,2}$ input(A1,A2,A3) output(Y) Y=XOR3(A1,A2,A3) ;
|
||||
NAND2X{0,1,2,4}$ input(A1,A2) output(Y) Y=NAND2(A1,A2) ;
|
||||
NAND3X{0,1,2,4}$ input(A1,A2,A3) output(Y) Y=NAND3(A1,A2,A3) ;
|
||||
NAND4X{0,1}$ input(A1,A2,A3,A4) output(Y) Y=NAND4(A1,A2,A3,A4) ;
|
||||
NOR2X{0,1,2,4}$ input(A1,A2) output(Y) Y=NOR2(A1,A2) ;
|
||||
NOR3X{0,1,2,4}$ input(A1,A2,A3) output(Y) Y=NOR3(A1,A2,A3) ;
|
||||
NOR4X{0,1}$ input(A1,A2,A3,A4) output(Y) Y=NOR4(A1,A2,A3,A4) ;
|
||||
XNOR2X{1,2}$ input(A1,A2) output(Y) Y=XNOR2(A1,A2) ;
|
||||
XNOR3X{1,2}$ input(A1,A2,A3) output(Y) Y=XNOR3(A1,A2,A3) ;
|
||||
|
||||
ISOLAND{,AO}X{1,2,4,8}$ input(ISO,D) output(Q) ISOB=NOT1(ISO) Q=AND2(ISOB,D) ;
|
||||
ISOLOR{,AO}X{1,2,4,8}$ input(ISO,D) output(Q) Q=OR2(ISO,D) ;
|
||||
|
||||
AO21X{1,2}$ input(A1,A2,A3) output(Y) Y=AO21(A1,A2,A3) ;
|
||||
OA21X{1,2}$ input(A1,A2,A3) output(Y) Y=OA21(A1,A2,A3) ;
|
||||
AOI21X{1,2}$ input(A1,A2,A3) output(Y) Y=AOI21(A1,A2,A3) ;
|
||||
OAI21X{1,2}$ input(A1,A2,A3) output(Y) Y=OAI21(A1,A2,A3) ;
|
||||
|
||||
AO22X{1,2}$ input(A1,A2,A3,A4) output(Y) Y=AO22(A1,A2,A3,A4) ;
|
||||
OA22X{1,2}$ input(A1,A2,A3,A4) output(Y) Y=OA22(A1,A2,A3,A4) ;
|
||||
AOI22X{1,2}$ input(A1,A2,A3,A4) output(Y) Y=AOI22(A1,A2,A3,A4) ;
|
||||
OAI22X{1,2}$ input(A1,A2,A3,A4) output(Y) Y=OAI22(A1,A2,A3,A4) ;
|
||||
|
||||
MUX21X{1,2}$ input(A1,A2,S0) output(Y) Y=MUX21(A1,A2,S0) ;
|
||||
|
||||
AO221X{1,2}$ input(A1,A2,A3,A4,A5) output(Y) A=AO22(A1,A2,A3,A4) Y=OR2(A5,A) ;
|
||||
OA221X{1,2}$ input(A1,A2,A3,A4,A5) output(Y) A=OA22(A1,A2,A3,A4) Y=AND2(A5,A) ;
|
||||
AOI221X{1,2}$ input(A1,A2,A3,A4,A5) output(Y) A=AO22(A1,A2,A3,A4) Y=NOR2(A5,A) ;
|
||||
OAI221X{1,2}$ input(A1,A2,A3,A4,A5) output(Y) A=OA22(A1,A2,A3,A4) Y=NAND2(A5,A) ;
|
||||
|
||||
AO222X{1,2}$ input(A1,A2,A3,A4,A5,A6) output(Y) A=AO22(A1,A2,A3,A4) Y=AO21(A5,A6,A) ;
|
||||
OA222X{1,2}$ input(A1,A2,A3,A4,A5,A6) output(Y) A=OA22(A1,A2,A3,A4) Y=OA21(A5,A6,A) ;
|
||||
AOI222X{1,2}$ input(A1,A2,A3,A4,A5,A6) output(Y) A=AO22(A1,A2,A3,A4) Y=AOI21(A5,A6,A) ;
|
||||
OAI222X{1,2}$ input(A1,A2,A3,A4,A5,A6) output(Y) A=OA22(A1,A2,A3,A4) Y=OAI21(A5,A6,A) ;
|
||||
|
||||
MUX41X{1,2}$ input(A1,A2,A3,A4,S0,S1) output(Y) A=MUX21(A1,A2,S0) B=MUX21(A3,A4,S0) Y=MUX21(A,B,S1) ;
|
||||
|
||||
DEC24X{1,2}$ input(A0,A1) output(Y0,Y1,Y2,Y3) A0B=INV1(A0) A1B=INV1(A1) Y0=NOR2(A0,A1) Y1=AND(A0,A1B) Y2=AND(A0B,A1) Y3=AND(A0,A1) ;
|
||||
FADDX{1,2}$ input(A,B,CI) output(S,CO) AB=XOR2(A,B) CO=XOR2(AB,CI) S=AO22(AB,CI,A,B) ;
|
||||
HADDX{1,2}$ input(A0,B0) output(SO,C1) C1=XOR2(A0,B0) SO=AND2(A0,B0) ;
|
||||
|
||||
{,AO}DFFARX{1,2}$ input(D,CLK,RSTB) output(Q,QN) DR=AND2(D,RSTB) Q=DFF(DR,CLK) QN=INV1(Q) ;
|
||||
DFFASRX{1,2}$ input(D,CLK,RSTB,SETB) output(Q,QN) DR=AND2(D,RSTB) SET=INV1(SETB) DRS=OR2(DR,SET) Q=DFF(DRS,CLK) QN=INV1(Q) ;
|
||||
DFFASX{1,2}$ input(D,CLK,SETB) output(Q,QN) SET=INV1(SETB) DS=OR2(D,SET) Q=DFF(DS,CLK) QN=INV1(Q) ;
|
||||
DFFSSRX{1,2}$ input(CLK,D,RSTB,SETB) output(Q,QN) DR=AND2(D,RSTB) SET=INV1(SETB) DRS=OR2(DR,SET) Q=DFF(DRS,CLK) QN=INV1(Q) ;
|
||||
DFFX{1,2}$ input(D,CLK) output(Q,QN) Q=DFF(D,CLK) QN=INV1(Q) ;
|
||||
|
||||
SDFFARX{1,2}$ input(D,CLK,RSTB,SE,SI) output(Q,QN) DR=AND2(D,RSTB) DI=MUX21(DR,SI,SE) Q=DFF(DI,CLK) QN=INV1(Q) ;
|
||||
SDFFASRSX{1,2}$ input(D,CLK,RSTB,SETB,SE,SI) output(Q,QN,SO) DR=AND2(D,RSTB) SET=INV1(SETB) DRS=OR2(DR,SET) DI=MUX21(DRS,SI,SE) Q=DFF(DI,CLK) QN=INV1(Q) SO=BUF1(Q) ;
|
||||
SDFFASRX{1,2}$ input(D,CLK,RSTB,SETB,SE,SI) output(Q,QN) DR=AND2(D,RSTB) SET=INV1(SETB) DRS=OR2(DR,SET) DI=MUX21(DRS,SI,SE) Q=DFF(DI,CLK) QN=INV1(Q) ;
|
||||
SDFFASX{1,2}$ input(D,CLK,SETB,SE,SI) output(Q,QN) SET=INV1(SETB) DS=OR2(D,SET) DI=MUX21(DS,SI,SE) Q=DFF(DI,CLK) QN=INV1(Q) ;
|
||||
SDFFSSRX{1,2}$ input(CLK,D,RSTB,SETB,SI,SE) output(Q,QN) DR=AND2(D,RSTB) SET=INV1(SETB) DRS=OR2(DR,SET) DI=MUX21(DRS,SI,SE) Q=DFF(DI,CLK) QN=INV1(Q) ;
|
||||
SDFFX{1,2}$ input(D,CLK,SE,SI) output(Q,QN) DI=MUX21(D,SI,SE) Q=DFF(DI,CLK) QN=INV1(Q) ;
|
||||
|
||||
LATCHX{1,2}$ input(D,CLK) output(Q,QN) Q=LATCH(D,CLK) QN=INV1(Q) ;
|
||||
""".replace('$','_RVT'))
|
||||
"""The SAED 32nm educational technology library.
|
||||
It defines all cells except: negative-edge flip-flops, tri-state, latches, clock gating, level shifters
|
||||
"""
|
||||
|
||||
|
||||
SAED90 = TechLib(r"""
|
||||
NBUFFX{2,4,8,16,32}$ input(INP) output(Z) Z=BUF1(INP) ;
|
||||
AOBUFX{1,2,4}$ input(INP) output(Z) Z=BUF1(INP) ;
|
||||
DELLN{1,2,3}X2$ input(INP) output(Z)Z=BUF1(INP) ;
|
||||
|
||||
INVX{0,1,2,4,8,16,32}$ input(INP) output(ZN) ZN=INV1(INP) ;
|
||||
AOINVX{1,2,4}$ input(INP) output(ZN) ZN=INV1(INP) ;
|
||||
IBUFFX{2,4,8,16,32}$ input(INP) output(ZN) ZN=INV1(INP) ;
|
||||
|
||||
TIEH$ output(Z) Z=__const1__() ;
|
||||
TIEL$ output(ZN) ZN=__const0__() ;
|
||||
|
||||
HEAD2X{2,4,8,16,32}$ input(SLEEP) output(SLEEPOUT) SLEEPOUT=BUF1(SLEEP) ;
|
||||
HEADX{2,4,8,16,32}$ input(SLEEP) ;
|
||||
|
||||
ANTENNA$ input(INP) ;
|
||||
CLOAD1$ input(INP) ;
|
||||
DCAP$ ;
|
||||
DHFILL{HLH,LHL}2 ;
|
||||
DHFILLHLHLS11$ ;
|
||||
SHFILL{1,2,3,64,128}$ ;
|
||||
|
||||
AND2X{1,2,4}$ input(IN1,IN2) output(Q) Q=AND2(IN1,IN2) ;
|
||||
AND3X{1,2,4}$ input(IN1,IN2,IN3) output(Q) Q=AND3(IN1,IN2,IN3) ;
|
||||
AND4X{1,2,4}$ input(IN1,IN2,IN3,IN4) output(Q) Q=AND4(IN1,IN2,IN3,IN4) ;
|
||||
OR2X{1,2,4}$ input(IN1,IN2) output(Q) Q=OR2(IN1,IN2) ;
|
||||
OR3X{1,2,4}$ input(IN1,IN2,IN3) output(Q) Q=OR3(IN1,IN2,IN3) ;
|
||||
OR4X{1,2,4}$ input(IN1,IN2,IN3,IN4) output(Q) Q=OR4(IN1,IN2,IN3,IN4) ;
|
||||
XOR2X{1,2}$ input(IN1,IN2) output(Q) Q=XOR2(IN1,IN2) ;
|
||||
XOR3X{1,2}$ input(IN1,IN2,IN3) output(Q) Q=XOR3(IN1,IN2,IN3) ;
|
||||
NAND2X{0,1,2,4}$ input(IN1,IN2) output(QN) QN=NAND2(IN1,IN2) ;
|
||||
NAND3X{0,1,2,4}$ input(IN1,IN2,IN3) output(QN) QN=NAND3(IN1,IN2,IN3) ;
|
||||
NAND4X{0,1}$ input(IN1,IN2,IN3,IN4) output(QN) QN=NAND4(IN1,IN2,IN3,IN4) ;
|
||||
NOR2X{0,1,2,4}$ input(IN1,IN2) output(QN) QN=NOR2(IN1,IN2) ;
|
||||
NOR3X{0,1,2,4}$ input(IN1,IN2,IN3) output(QN) QN=NOR3(IN1,IN2,IN3) ;
|
||||
NOR4X{0,1}$ input(IN1,IN2,IN3,IN4) output(QN) QN=NOR4(IN1,IN2,IN3,IN4) ;
|
||||
XNOR2X{1,2}$ input(IN1,IN2) output(Q) Q=XNOR2(IN1,IN2) ;
|
||||
XNOR3X{1,2}$ input(IN1,IN2,IN3) output(Q) Q=XNOR3(IN1,IN2,IN3) ;
|
||||
|
||||
ISOLAND{,AO}X{1,2,4,8}$ input(ISO,D) output(Q) ISOB=NOT1(ISO) Q=AND2(ISOB,D) ;
|
||||
ISOLOR{,AO}X{1,2,4,8}$ input(ISO,D) output(Q) Q=OR2(ISO,D) ;
|
||||
|
||||
AO21X{1,2}$ input(IN1,IN2,IN3) output(Q) Q=AO21(IN1,IN2,IN3) ;
|
||||
OA21X{1,2}$ input(IN1,IN2,IN3) output(Q) Q=OA21(IN1,IN2,IN3) ;
|
||||
AOI21X{1,2}$ input(IN1,IN2,IN3) output(QN) QN=AOI21(IN1,IN2,IN3) ;
|
||||
OAI21X{1,2}$ input(IN1,IN2,IN3) output(QN) QN=OAI21(IN1,IN2,IN3) ;
|
||||
|
||||
AO22X{1,2}$ input(IN1,IN2,IN3,IN4) output(Q) Q=AO22(IN1,IN2,IN3,IN4) ;
|
||||
OA22X{1,2}$ input(IN1,IN2,IN3,IN4) output(Q) Q=OA22(IN1,IN2,IN3,IN4) ;
|
||||
AOI22X{1,2}$ input(IN1,IN2,IN3,IN4) output(QN) QN=AOI22(IN1,IN2,IN3,IN4) ;
|
||||
OAI22X{1,2}$ input(IN1,IN2,IN3,IN4) output(QN) QN=OAI22(IN1,IN2,IN3,IN4) ;
|
||||
|
||||
MUX21X{1,2}$ input(IN1,IN2,S) output(Q) Q=MUX21(IN1,IN2,S) ;
|
||||
|
||||
AO221X{1,2}$ input(IN1,IN2,IN3,IN4,IN5) output(Q) A=AO22(IN1,IN2,IN3,IN4) Q=OR2(IN5,A) ;
|
||||
OA221X{1,2}$ input(IN1,IN2,IN3,IN4,IN5) output(Q) A=OA22(IN1,IN2,IN3,IN4) Q=AND2(IN5,A) ;
|
||||
AOI221X{1,2}$ input(IN1,IN2,IN3,IN4,IN5) output(QN) A=AO22(IN1,IN2,IN3,IN4) QN=NOR2(IN5,A) ;
|
||||
OAI221X{1,2}$ input(IN1,IN2,IN3,IN4,IN5) output(QN) A=OA22(IN1,IN2,IN3,IN4) QN=NAND2(IN5,A) ;
|
||||
|
||||
AO222X{1,2}$ input(IN1,IN2,IN3,IN4,IN5,IN6) output(Q) A=AO22(IN1,IN2,IN3,IN4) Q=AO21(IN5,IN6,A) ;
|
||||
OA222X{1,2}$ input(IN1,IN2,IN3,IN4,IN5,IN6) output(Q) A=OA22(IN1,IN2,IN3,IN4) Q=OA21(IN5,IN6,A) ;
|
||||
AOI222X{1,2}$ input(IN1,IN2,IN3,IN4,IN5,IN6) output(QN) A=AO22(IN1,IN2,IN3,IN4) QN=AOI21(IN5,IN6,A) ;
|
||||
OAI222X{1,2}$ input(IN1,IN2,IN3,IN4,IN5,IN6) output(QN) A=OA22(IN1,IN2,IN3,IN4) QN=OAI21(IN5,IN6,A) ;
|
||||
|
||||
MUX41X{1,2}$ input(IN1,IN2,IN3,IN4,S0,S1) output(Q) A=MUX21(IN1,IN2,S0) B=MUX21(IN3,IN4,S0) Q=MUX21(A,B,S1) ;
|
||||
|
||||
DEC24X{1,2}$ input(IN1,IN2) output(Q0,Q1,Q2,Q3) IN1B=INV1(IN1) IN2B=INV1(IN2) Q0=NOR2(IN1,IN2) Q1=AND(IN1,IN2B) Q2=AND(IN1B,IN2) Q3=AND(IN1,IN2) ;
|
||||
FADDX{1,2}$ input(A,B,CI) output(S,CO) AB=XOR2(A,B) CO=XOR2(AB,CI) S=AO22(AB,CI,A,B) ;
|
||||
HADDX{1,2}$ input(A0,B0) output(SO,C1) C1=XOR2(A0,B0) SO=AND2(A0,B0) ;
|
||||
|
||||
{,AO}DFFARX{1,2}$ input(D,CLK,RSTB) output(Q,QN) DR=AND2(D,RSTB) Q=DFF(DR,CLK) QN=INV1(Q) ;
|
||||
DFFASRX{1,2}$ input(D,CLK,RSTB,SETB) output(Q,QN) DR=AND2(D,RSTB) SET=INV1(SETB) DRS=OR2(DR,SET) Q=DFF(DRS,CLK) QN=INV1(Q) ;
|
||||
DFFASX{1,2}$ input(D,CLK,SETB) output(Q,QN) SET=INV1(SETB) DS=OR2(D,SET) Q=DFF(DS,CLK) QN=INV1(Q) ;
|
||||
DFFSSRX{1,2}$ input(CLK,D,RSTB,SETB) output(Q,QN) DR=AND2(D,RSTB) SET=INV1(SETB) DRS=OR2(DR,SET) Q=DFF(DRS,CLK) QN=INV1(Q) ;
|
||||
DFFX{1,2}$ input(D,CLK) output(Q,QN) Q=DFF(D,CLK) QN=INV1(Q) ;
|
||||
|
||||
SDFFARX{1,2}$ input(D,CLK,RSTB,SE,SI) output(Q,QN) DR=AND2(D,RSTB) DI=MUX21(DR,SI,SE) Q=DFF(DI,CLK) QN=INV1(Q) ;
|
||||
SDFFASRSX{1,2}$ input(D,CLK,RSTB,SETB,SE,SI) output(Q,QN,S0) DR=AND2(D,RSTB) SET=INV1(SETB) DRS=OR2(DR,SET) DI=MUX21(DRS,SI,SE) Q=DFF(DI,CLK) QN=INV1(Q) S0=BUF1(Q) ;
|
||||
SDFFASRX{1,2}$ input(D,CLK,RSTB,SETB,SE,SI) output(Q,QN) DR=AND2(D,RSTB) SET=INV1(SETB) DRS=OR2(DR,SET) DI=MUX21(DRS,SI,SE) Q=DFF(DI,CLK) QN=INV1(Q) ;
|
||||
SDFFASX{1,2}$ input(D,CLK,SETB,SE,SI) output(Q,QN) SET=INV1(SETB) DS=OR2(D,SET) DI=MUX21(DS,SI,SE) Q=DFF(DI,CLK) QN=INV1(Q) ;
|
||||
SDFFSSRX{1,2}$ input(CLK,D,RSTB,SETB,SI,SE) output(Q,QN) DR=AND2(D,RSTB) SET=INV1(SETB) DRS=OR2(DR,SET) DI=MUX21(DRS,SI,SE) Q=DFF(DI,CLK) QN=INV1(Q) ;
|
||||
SDFFX{1,2}$ input(D,CLK,SE,SI) output(Q,QN) DI=MUX21(D,SI,SE) Q=DFF(DI,CLK) QN=INV1(Q) ;
|
||||
|
||||
LATCHX{1,2}$ input(D,CLK) output(Q,QN) Q=LATCH(D,CLK) QN=INV1(Q) ;
|
||||
""".replace('$','{,_LVT,_HVT}'))
|
||||
"""The SAED 90nm educational technology library.
|
||||
It defines all cells except: negative-edge flip-flops, tri-state, latches, clock gating, level shifters
|
||||
"""
|
||||
+184
-73
@@ -1,130 +1,230 @@
|
||||
"""A simple and incomplete parser for Verilog files.
|
||||
|
||||
The main purpose of this parser is to load synthesized, non-hierarchical (flat) gate-level netlists.
|
||||
It supports only a very limited subset of Verilog.
|
||||
It supports only a subset of Verilog.
|
||||
"""
|
||||
|
||||
from collections import namedtuple
|
||||
|
||||
from lark import Lark, Transformer
|
||||
from lark import Lark, Transformer, Tree
|
||||
|
||||
from . import readtext
|
||||
from . import log, readtext
|
||||
from .circuit import Circuit, Node, Line
|
||||
from .techlib import TechLib
|
||||
from .techlib import NANGATE
|
||||
|
||||
Instantiation = namedtuple('Instantiation', ['type', 'name', 'pins'])
|
||||
|
||||
|
||||
class SignalDeclaration:
|
||||
|
||||
def __init__(self, kind, tokens):
|
||||
def __init__(self, kind, name, rnge=None):
|
||||
self.left = None
|
||||
self.right = None
|
||||
self.kind = kind
|
||||
if len(tokens.children) == 1:
|
||||
self.basename = tokens.children[0]
|
||||
else:
|
||||
self.basename = tokens.children[2]
|
||||
self.left = int(tokens.children[0].value)
|
||||
self.right = int(tokens.children[1].value)
|
||||
self.basename = name
|
||||
self.rnge = rnge
|
||||
|
||||
@property
|
||||
def names(self):
|
||||
if self.left is None:
|
||||
if self.rnge is None:
|
||||
return [self.basename]
|
||||
if self.left <= self.right:
|
||||
return [f'{self.basename}[{i}]' for i in range(self.left, self.right + 1)]
|
||||
return [f'{self.basename}[{i}]' for i in range(self.left, self.right - 1, -1)]
|
||||
return [f'{self.basename}[{i}]' for i in self.rnge]
|
||||
|
||||
def __repr__(self):
|
||||
return f"{self.kind}:{self.basename}[{self.left}:{self.right}]"
|
||||
return f"{self.kind}:{self.basename}[{self.rnge}]"
|
||||
|
||||
|
||||
class VerilogTransformer(Transformer):
|
||||
def __init__(self, branchforks=False, tlib=TechLib()):
|
||||
def __init__(self, branchforks=False, tlib=NANGATE):
|
||||
super().__init__()
|
||||
self._signal_declarations = {}
|
||||
self.branchforks = branchforks
|
||||
self.tlib = tlib
|
||||
|
||||
@staticmethod
|
||||
def name(args):
|
||||
s = args[0].value
|
||||
if s[0] == '\\':
|
||||
s = s[1:-1]
|
||||
return s
|
||||
return s[1:-1] if s[0] == '\\' else s
|
||||
|
||||
@staticmethod
|
||||
def namedpin(args):
|
||||
return tuple(args) if len(args) > 1 else (args[0], None)
|
||||
|
||||
@staticmethod
|
||||
def instantiation(args):
|
||||
return Instantiation(args[0], args[1],
|
||||
dict((pin.children[0], pin.children[1]) for pin in args[2:]))
|
||||
pinmap = {}
|
||||
for idx, pin in enumerate(args[2:]):
|
||||
p = pin.children[0]
|
||||
if isinstance(p, tuple): # named pin
|
||||
if p[1] is not None:
|
||||
pinmap[p[0]] = p[1]
|
||||
else: # unnamed pin
|
||||
pinmap[idx] = p
|
||||
return Instantiation(args[0], args[1], pinmap)
|
||||
|
||||
def input(self, args):
|
||||
for sd in [SignalDeclaration('input', signal) for signal in args]:
|
||||
self._signal_declarations[sd.basename] = sd
|
||||
def range(self, args):
|
||||
left = int(args[0].value)
|
||||
right = int(args[1].value) if len(args) > 1 else left
|
||||
return range(left, right+1) if left <= right else range(left, right-1, -1)
|
||||
|
||||
def inout(self, args):
|
||||
for sd in [SignalDeclaration('input', signal) for signal in args]: # just treat as input
|
||||
self._signal_declarations[sd.basename] = sd
|
||||
def sigsel(self, args):
|
||||
if len(args) > 1 and isinstance(args[1], range):
|
||||
l = [f'{args[0]}[{i}]' for i in args[1]]
|
||||
return l if len(l) > 1 else l[0]
|
||||
elif "'" in args[0]:
|
||||
width, rest = args[0].split("'")
|
||||
width = int(width)
|
||||
base, const = rest[0], rest[1:].replace('x','0')
|
||||
const = int(const, {'b': 2, 'd':10, 'h':16}[base.lower()])
|
||||
l = []
|
||||
for _ in range(width):
|
||||
l.insert(0, "1'b1" if (const & 1) else "1'b0")
|
||||
const >>= 1
|
||||
return l if len(l) > 1 else l[0]
|
||||
else:
|
||||
return args[0]
|
||||
|
||||
def output(self, args):
|
||||
for sd in [SignalDeclaration('output', signal) for signal in args]:
|
||||
self._signal_declarations[sd.basename] = sd
|
||||
def concat(self, args):
|
||||
sigs = []
|
||||
for a in args:
|
||||
if isinstance(a, list):
|
||||
sigs += a
|
||||
else:
|
||||
sigs.append(a)
|
||||
return sigs
|
||||
|
||||
def wire(self, args):
|
||||
for sd in [SignalDeclaration('wire', signal) for signal in args]:
|
||||
self._signal_declarations[sd.basename] = sd
|
||||
def ternaryif(self, args):
|
||||
sel = args[0]
|
||||
ctrue = args[1]
|
||||
cfalse = args[2]
|
||||
print(f"got ternary if {args[0]} {args[1]}")
|
||||
|
||||
return args[1]
|
||||
|
||||
def declaration(self, kind, args):
|
||||
rnge = None
|
||||
if isinstance(args[0], range):
|
||||
rnge = args[0]
|
||||
args = args[1:]
|
||||
return [SignalDeclaration(kind, signal, rnge) for signal in args]
|
||||
|
||||
def input(self, args): return self.declaration("input", args)
|
||||
def output(self, args): return self.declaration("output", args)
|
||||
def inout(self, args): return self.declaration("input", args) # just treat as input
|
||||
def wire(self, args): return self.declaration("wire", args)
|
||||
|
||||
def module(self, args):
|
||||
c = Circuit(args[0])
|
||||
positions = {}
|
||||
pos = 0
|
||||
const_count = 0
|
||||
sig_decls = {}
|
||||
for decls in args[2:]: # pass 0: collect signal declarations
|
||||
if isinstance(decls, list):
|
||||
if len(decls) > 0 and isinstance(decls[0], SignalDeclaration):
|
||||
for decl in decls:
|
||||
if decl.basename not in sig_decls or sig_decls[decl.basename].kind == 'wire':
|
||||
sig_decls[decl.basename] = decl
|
||||
for intf_sig in args[1].children:
|
||||
for name in self._signal_declarations[intf_sig].names:
|
||||
for name in sig_decls[intf_sig].names:
|
||||
positions[name] = pos
|
||||
pos += 1
|
||||
assignments = []
|
||||
for stmt in args[2:]: # pass 1: instantiate cells and driven signals
|
||||
if isinstance(stmt, Instantiation):
|
||||
if stmt.type not in self.tlib.cells:
|
||||
log.warn(f'Ignoring cell of unknown kind "{stmt.type}"')
|
||||
continue
|
||||
n = Node(c, stmt.name, kind=stmt.type)
|
||||
for p, s in stmt.pins.items():
|
||||
if self.tlib.pin_is_output(n.kind, p):
|
||||
if s in sig_decls:
|
||||
s = sig_decls[s].names
|
||||
if isinstance(s, list) and len(s) == 1:
|
||||
s = s[0]
|
||||
Line(c, (n, self.tlib.pin_index(stmt.type, p)), Node(c, s))
|
||||
elif stmt is not None and stmt.data == 'assign':
|
||||
elif hasattr(stmt, 'data') and stmt.data == 'assign':
|
||||
assignments.append((stmt.children[0], stmt.children[1]))
|
||||
for sd in self._signal_declarations.values():
|
||||
for sd in sig_decls.values():
|
||||
if sd.kind == 'output' or sd.kind == 'input':
|
||||
for name in sd.names:
|
||||
n = Node(c, name, kind=sd.kind)
|
||||
if name in positions:
|
||||
c.interface[positions[name]] = n
|
||||
c.io_nodes[positions[name]] = n
|
||||
if sd.kind == 'input':
|
||||
Line(c, n, Node(c, name))
|
||||
for s1, s2 in assignments: # pass 1.5: process signal assignments
|
||||
if s1 in c.forks:
|
||||
assert s2 not in c.forks, 'assignment between two driven signals'
|
||||
Line(c, c.forks[s1], Node(c, s2))
|
||||
elif s2 in c.forks:
|
||||
assert s1 not in c.forks, 'assignment between two driven signals'
|
||||
Line(c, c.forks[s2], Node(c, s1))
|
||||
deferred_assignments = set()
|
||||
ignored = 0
|
||||
while len(assignments) > 0:
|
||||
more_assignments = []
|
||||
for target, source in assignments: # pass 1.5: process signal assignments
|
||||
target_sigs = []
|
||||
if not isinstance(target, list): target = [target]
|
||||
for s in target:
|
||||
if s in sig_decls:
|
||||
target_sigs += sig_decls[s].names
|
||||
else:
|
||||
target_sigs.append(s)
|
||||
source_sigs = []
|
||||
if not isinstance(source, list): source = [source]
|
||||
for s in source:
|
||||
if s in sig_decls:
|
||||
source_sigs += sig_decls[s].names
|
||||
else:
|
||||
source_sigs.append(s)
|
||||
for t, s in zip(target_sigs, source_sigs):
|
||||
if t in c.forks:
|
||||
assert s not in c.forks, f'assignment between two driven signals: source={s} target={t}'
|
||||
Line(c, c.forks[t], Node(c, s))
|
||||
elif s in c.forks:
|
||||
assert t not in c.forks, 'assignment between two driven signals'
|
||||
Line(c, c.forks[s], Node(c, t))
|
||||
elif s.startswith("1'b"):
|
||||
cnode = Node(c, f'__const{s[3]}_{const_count}__', f'__const{s[3]}__')
|
||||
const_count += 1
|
||||
Line(c, cnode, Node(c, t))
|
||||
else:
|
||||
if (t, s) in deferred_assignments:
|
||||
#log.info(f'ignoring: assign {t} = {s}')
|
||||
ignored += 1
|
||||
else:
|
||||
more_assignments.append((t, s))
|
||||
deferred_assignments.add((t, s))
|
||||
assignments = more_assignments
|
||||
if ignored > 0:
|
||||
log.warn(f'ignored {ignored} assignments')
|
||||
for stmt in args[2:]: # pass 2: connect signals to readers
|
||||
if isinstance(stmt, Instantiation):
|
||||
for p, s in stmt.pins.items():
|
||||
if stmt.name not in c.cells: continue
|
||||
n = c.cells[stmt.name]
|
||||
if self.tlib.pin_is_output(n.kind, p): continue
|
||||
if s.startswith("1'b"):
|
||||
const = f'__const{s[3]}__'
|
||||
if const not in c.cells:
|
||||
Line(c, Node(c, const, const), Node(c, s))
|
||||
cname = f'__const{s[3]}_{const_count}__'
|
||||
cnode = Node(c, cname, f'__const{s[3]}__')
|
||||
const_count += 1
|
||||
s = cname
|
||||
Line(c, cnode, Node(c, s))
|
||||
if s not in c.forks:
|
||||
if f'{s}[0]' in c.forks: # actually a 1-bit bus?
|
||||
s = f'{s}[0]'
|
||||
else:
|
||||
log.warn(f'Signal not driven: {s}')
|
||||
Node(c, s) # generate fork here
|
||||
fork = c.forks[s]
|
||||
if self.branchforks:
|
||||
branchfork = Node(c, fork.name + "~" + n.name + "/" + p)
|
||||
Line(c, fork, branchfork)
|
||||
fork = branchfork
|
||||
Line(c, fork, (n, self.tlib.pin_index(stmt.type, p)))
|
||||
for sd in self._signal_declarations.values():
|
||||
for sd in sig_decls.values():
|
||||
if sd.kind == 'output':
|
||||
for name in sd.names:
|
||||
if name not in c.forks:
|
||||
if f'{name}[0]' in c.forks: # actually a 1-bit bus?
|
||||
name = f'{name}[0]'
|
||||
else:
|
||||
log.warn(f'Output not driven: {name}')
|
||||
continue
|
||||
Line(c, c.forks[name], c.cells[name])
|
||||
return c
|
||||
|
||||
@@ -132,45 +232,56 @@ class VerilogTransformer(Transformer):
|
||||
def start(args): return args[0] if len(args) == 1 else args
|
||||
|
||||
|
||||
GRAMMAR = """
|
||||
GRAMMAR = r"""
|
||||
start: (module)*
|
||||
module: "module" name parameters ";" (_statement)* "endmodule"
|
||||
parameters: "(" [ name ( "," name )* ] ")"
|
||||
parameters: "(" [ _namelist ] ")"
|
||||
_statement: input | output | inout | tri | wire | assign | instantiation
|
||||
input: "input" signal ( "," signal )* ";"
|
||||
output: "output" signal ( "," signal )* ";"
|
||||
inout: "inout" signal ( "," signal )* ";"
|
||||
tri: "tri" name ";"
|
||||
wire: "wire" signal ( "," signal )* ";"
|
||||
assign: "assign" name "=" name ";"
|
||||
input: "input" range? _namelist ";"
|
||||
output: "output" range? _namelist ";"
|
||||
inout: "inout" range? _namelist ";"
|
||||
tri: "tri" range? _namelist ";"
|
||||
wire: "wire" range? _namelist ";"
|
||||
assign: "assign" sigsel "=" sigsel ";"
|
||||
instantiation: name name "(" [ pin ( "," pin )* ] ")" ";"
|
||||
pin: "." name "(" name ")"
|
||||
signal: ( name | "[" /[0-9]+/ ":" /[0-9]+/ "]" name )
|
||||
|
||||
name: ( /[a-z_][a-z0-9_\\[\\]]*/i | /\\\\[^\\t \\r\\n]+[\\t \\r\\n](\\[[0-9]+\\])?/i | /1'b0/i | /1'b1/i )
|
||||
COMMENT: "//" /[^\\n]*/
|
||||
%ignore ( /\\r?\\n/ | COMMENT )+
|
||||
%ignore /[\\t \\f]+/
|
||||
pin: namedpin | sigsel
|
||||
namedpin: "." name "(" sigsel? ")"
|
||||
range: "[" /[0-9]+/ (":" /[0-9]+/)? "]"
|
||||
sigsel: name range? | concat | ternaryif
|
||||
concat: "{" sigsel ( "," sigsel )* "}"
|
||||
ternaryif: sigsel "?" sigsel ":" sigsel
|
||||
_namelist: name ( "," name )*
|
||||
name: ( /[a-z_][a-z0-9_]*/i | /\\[^\t \r\n]+[\t \r\n]/i | /[0-9]+'[bdh][x0-9a-f]+/i )
|
||||
%import common.NEWLINE
|
||||
COMMENT: /\/\*(\*(?!\/)|[^*])*\*\// | /\(\*(\*(?!\))|[^*])*\*\)/ | "//" /(.)*/ NEWLINE
|
||||
%ignore ( /\r?\n/ | COMMENT )+
|
||||
%ignore /[\t \f]+/
|
||||
"""
|
||||
|
||||
|
||||
def parse(text, *, branchforks=False, tlib=TechLib()):
|
||||
def parse(text, tlib=NANGATE, branchforks=False):
|
||||
"""Parses the given ``text`` as Verilog code.
|
||||
|
||||
:param text: A string with Verilog code.
|
||||
:param tlib: A technology library object that defines all known cells.
|
||||
:type tlib: :py:class:`~kyupy.techlib.TechLib`
|
||||
:param branchforks: If set to ``True``, the returned circuit will include additional `forks` on each fanout branch.
|
||||
These forks are needed to correctly annotate interconnect delays
|
||||
(see :py:func:`kyupy.sdf.DelayFile.annotation`).
|
||||
:param tlib: A technology library object that provides pin name mappings.
|
||||
:type tlib: :py:class:`~kyupy.techlib.TechLib`
|
||||
:return: A :class:`~kyupy.circuit.Circuit` object.
|
||||
(see :py:func:`~kyupy.sdf.DelayFile.interconnects()`).
|
||||
:return: A :py:class:`~kyupy.circuit.Circuit` object.
|
||||
"""
|
||||
return Lark(GRAMMAR, parser="lalr", transformer=VerilogTransformer(branchforks, tlib)).parse(text)
|
||||
|
||||
|
||||
def load(file, *args, **kwargs):
|
||||
def load(file, tlib=NANGATE, branchforks=False):
|
||||
"""Parses the contents of ``file`` as Verilog code.
|
||||
|
||||
The given file may be gzip compressed. Takes the same keyword arguments as :py:func:`parse`.
|
||||
:param file: A file name or a file handle. Files with `.gz`-suffix are decompressed on-the-fly.
|
||||
:param tlib: A technology library object that defines all known cells.
|
||||
:type tlib: :py:class:`~kyupy.techlib.TechLib`
|
||||
:param branchforks: If set to ``True``, the returned circuit will include additional `forks` on each fanout branch.
|
||||
These forks are needed to correctly annotate interconnect delays
|
||||
(see :py:func:`~kyupy.sdf.DelayFile.interconnects()`).
|
||||
:return: A :py:class:`~kyupy.circuit.Circuit` object.
|
||||
"""
|
||||
return parse(readtext(file), *args, **kwargs)
|
||||
return parse(readtext(file), tlib, branchforks)
|
||||
+453
-733
File diff suppressed because it is too large.
Load diff
Binary file not shown.
Binary file not shown.
Binary file not shown.
Binary file not shown.
Binary file not shown.
Binary file not shown.
Binary file not shown.
Binary file not shown.
Binary file not shown.
Binary file not shown.
Binary file not shown.
+49
-1
@@ -1,8 +1,56 @@
|
||||
import pytest
|
||||
|
||||
|
||||
@pytest.fixture
|
||||
@pytest.fixture(scope='session')
|
||||
def mydir():
|
||||
import os
|
||||
from pathlib import Path
|
||||
return Path(os.path.realpath(os.path.join(os.getcwd(), os.path.dirname(__file__))))
|
||||
|
||||
@pytest.fixture(scope='session')
|
||||
def b15_2ig_circuit(mydir):
|
||||
from kyupy import verilog
|
||||
from kyupy.techlib import SAED32
|
||||
return verilog.load(mydir / 'b15_2ig.v.gz', branchforks=True, tlib=SAED32)
|
||||
|
||||
@pytest.fixture(scope='session')
|
||||
def b15_2ig_circuit_resolved(b15_2ig_circuit):
|
||||
from kyupy.techlib import SAED32
|
||||
cr = b15_2ig_circuit.copy()
|
||||
cr.resolve_tlib_cells(SAED32)
|
||||
return cr
|
||||
|
||||
@pytest.fixture(scope='session')
|
||||
def b15_4ig_circuit(mydir):
|
||||
from kyupy import verilog
|
||||
from kyupy.techlib import SAED32
|
||||
return verilog.load(mydir / 'b15_4ig.v.gz', branchforks=True, tlib=SAED32)
|
||||
|
||||
@pytest.fixture(scope='session')
|
||||
def b15_4ig_circuit_resolved(b15_4ig_circuit):
|
||||
from kyupy.techlib import SAED32
|
||||
cr = b15_4ig_circuit.copy()
|
||||
cr.resolve_tlib_cells(SAED32)
|
||||
return cr
|
||||
|
||||
@pytest.fixture(scope='session')
|
||||
def b15_2ig_delays(mydir, b15_2ig_circuit):
|
||||
from kyupy import sdf
|
||||
from kyupy.techlib import SAED32
|
||||
return sdf.load(mydir / 'b15_2ig.sdf.gz').iopaths(b15_2ig_circuit, tlib=SAED32)[1:2]
|
||||
|
||||
@pytest.fixture(scope='session')
|
||||
def b15_2ig_sa_nf_test_resp(mydir, b15_2ig_circuit_resolved):
|
||||
from kyupy import stil
|
||||
s = stil.load(mydir / 'b15_2ig.sa_nf.stil.gz')
|
||||
tests = s.tests(b15_2ig_circuit_resolved)[:,1:]
|
||||
resp = s.responses(b15_2ig_circuit_resolved)[:,1:]
|
||||
return (tests, resp)
|
||||
|
||||
@pytest.fixture(scope='session')
|
||||
def b15_4ig_sa_rf_test_resp(mydir, b15_4ig_circuit_resolved):
|
||||
from kyupy import stil
|
||||
s = stil.load(mydir / 'b15_4ig.sa_rf.stil.gz')
|
||||
tests = s.tests(b15_4ig_circuit_resolved)[:,1:]
|
||||
resp = s.responses(b15_4ig_circuit_resolved)[:,1:]
|
||||
return (tests, resp)
|
||||
+33
-6
@@ -7,22 +7,49 @@
|
||||
(TEMPERATURE 25.00:25.00:25.00)
|
||||
(TIMESCALE 1ns)
|
||||
(CELL
|
||||
(CELLTYPE "NAND2X1")
|
||||
(CELLTYPE "NAND2_X1")
|
||||
(INSTANCE nandgate)
|
||||
(DELAY
|
||||
(ABSOLUTE
|
||||
(IOPATH IN1 QN (0.099:0.103:0.103) (0.122:0.127:0.127))
|
||||
(IOPATH IN2 QN (0.083:0.086:0.086) (0.100:0.104:0.104))
|
||||
(IOPATH A1 ZN (0.099:0.103:0.103) (0.122:0.127:0.127))
|
||||
(IOPATH A2 ZN (0.083:0.086:0.086) (0.100:0.104:0.104))
|
||||
)
|
||||
)
|
||||
)
|
||||
(CELL
|
||||
(CELLTYPE "AND2X1")
|
||||
(CELLTYPE "AND2_X1")
|
||||
(INSTANCE andgate)
|
||||
(DELAY
|
||||
(ABSOLUTE
|
||||
(IOPATH IN1 Q (0.367:0.378:0.378) (0.351:0.377:0.377))
|
||||
(IOPATH IN2 Q (0.366:0.375:0.375) (0.359:0.370:0.370))
|
||||
(IOPATH A1 ZN (0.367:0.378:0.378) (0.351:0.377:0.377))
|
||||
(IOPATH A2 ZN (0.366:0.375:0.375) (0.359:0.370:0.370))
|
||||
)
|
||||
)
|
||||
)
|
||||
(CELL
|
||||
(CELLTYPE "OAI21_X1")
|
||||
(INSTANCE oai21gate)
|
||||
(DELAY
|
||||
(ABSOLUTE
|
||||
(IOPATH B1 ZN (0.000:0.025:0.025) (0.000:0.013:0.013))
|
||||
(IOPATH B2 ZN (0.000:0.030:0.030) (0.000:0.016:0.016))
|
||||
( COND (B1 == 1'b0) && (B2 == 1'b1) (IOPATH A ZN (0.000:0.018:0.018)))
|
||||
(COND (B1 == 1'b1) && (B2 == 1'b0) (IOPATH A ZN (0.000:0.018:0.018) (0.000:0.016:0.016)))
|
||||
(COND (B1 == 1'b1) && (B2 == 1'b1) (IOPATH A ZN (0.000:0.019:0.019) (0.000:0.014:0.014)))
|
||||
)
|
||||
)
|
||||
)
|
||||
(CELL
|
||||
(CELLTYPE "MUX2_X1")
|
||||
(INSTANCE mux2gate)
|
||||
(DELAY
|
||||
(ABSOLUTE
|
||||
(COND (B == 1'b0) && (S == 1'b0) (IOPATH A Z (0.000:0.037:0.037) (0.000:0.058:0.058)))
|
||||
(COND (B == 1'b1) && (S == 1'b0) (IOPATH A Z (0.000:0.037:0.037) (0.000:0.058:0.058)))
|
||||
(COND (A == 1'b0) && (S == 1'b1) (IOPATH B Z (0.000:0.035:0.035) (0.000:0.056:0.056)))
|
||||
(COND (A == 1'b1) && (S == 1'b1) (IOPATH B Z (0.000:0.035:0.035) (0.000:0.056:0.056)))
|
||||
(COND (A == 1'b0) && (B == 1'b1) (IOPATH S Z (0.000:0.047:0.047) (0.000:0.073:0.073)))
|
||||
(COND (A == 1'b1) && (B == 1'b0) (IOPATH S Z (0.000:0.072:0.072) (0.000:0.064:0.064)))
|
||||
)
|
||||
)
|
||||
)
|
||||
|
||||
+8
-4
@@ -1,11 +1,15 @@
|
||||
module gates (a, b, o0, o1 );
|
||||
module gates (a, b, c, o0, o1, o2, o3 );
|
||||
input a;
|
||||
input b;
|
||||
input c;
|
||||
output o0;
|
||||
output o1;
|
||||
output o2;
|
||||
output o3;
|
||||
|
||||
AND2X1 andgate (.IN1 ( a ) , .IN2 ( b ) , .Q ( o0 ) ) ;
|
||||
NAND2X1 nandgate (.IN1 ( a ) , .IN2 ( b ) , .QN ( o1 ) ) ;
|
||||
|
||||
AND2_X1 andgate (.A1 ( a ) , .A2 ( b ) , .ZN ( o0 ) ) ;
|
||||
NAND2_X1 nandgate (.A1 ( a ) , .A2 ( b ) , .ZN ( o1 ) ) ;
|
||||
OAI21_X1 oai21gate (.B1(a), .B2(b), .A(c), .ZN(o2) ) ;
|
||||
MUX2_X1 mux2gate (.A(a), .B(b), .S(c), .Z(o3)) ;
|
||||
|
||||
endmodule
|
||||
@@ -0,0 +1,335 @@
|
||||
/* Generated by Yosys 0.9 (git sha1 UNKNOWN, gcc 4.8.5 -fPIC -Os) */
|
||||
|
||||
(* top = 1 *)
|
||||
(* src = "rng_haltonBase2.v:1" *)
|
||||
module rng1(clk, reset, o_output);
|
||||
(* src = "rng_haltonBase2.v:7|rng_haltonBase2.v:19" *)
|
||||
wire [11:0] _00_;
|
||||
wire _01_;
|
||||
wire _02_;
|
||||
wire _03_;
|
||||
wire _04_;
|
||||
wire _05_;
|
||||
wire _06_;
|
||||
wire _07_;
|
||||
wire _08_;
|
||||
wire _09_;
|
||||
wire _10_;
|
||||
wire _11_;
|
||||
wire _12_;
|
||||
wire _13_;
|
||||
wire _14_;
|
||||
wire _15_;
|
||||
wire _16_;
|
||||
wire _17_;
|
||||
wire _18_;
|
||||
wire _19_;
|
||||
wire _20_;
|
||||
wire _21_;
|
||||
wire _22_;
|
||||
wire _23_;
|
||||
wire _24_;
|
||||
wire _25_;
|
||||
wire _26_;
|
||||
wire _27_;
|
||||
wire _28_;
|
||||
wire _29_;
|
||||
wire _30_;
|
||||
wire _31_;
|
||||
wire _32_;
|
||||
wire _33_;
|
||||
wire _34_;
|
||||
(* src = "rng_haltonBase2.v:2" *)
|
||||
input clk;
|
||||
(* src = "rng_haltonBase2.v:7|rng_haltonBase2.v:12" *)
|
||||
wire \halton.clk ;
|
||||
(* init = 12'h000 *)
|
||||
(* src = "rng_haltonBase2.v:7|rng_haltonBase2.v:17" *)
|
||||
wire [11:0] \halton.counter ;
|
||||
(* src = "rng_haltonBase2.v:7|rng_haltonBase2.v:14" *)
|
||||
wire [11:0] \halton.o_output ;
|
||||
(* src = "rng_haltonBase2.v:7|rng_haltonBase2.v:13" *)
|
||||
wire \halton.reset ;
|
||||
(* src = "rng_haltonBase2.v:4" *)
|
||||
output [11:0] o_output;
|
||||
(* src = "rng_haltonBase2.v:3" *)
|
||||
input reset;
|
||||
AND2X1 _35_ (
|
||||
.IN1(\halton.counter [1]),
|
||||
.IN2(\halton.counter [0]),
|
||||
.Q(_01_)
|
||||
);
|
||||
NOR2X0 _36_ (
|
||||
.IN1(\halton.counter [1]),
|
||||
.IN2(\halton.counter [0]),
|
||||
.QN(_02_)
|
||||
);
|
||||
NOR3X0 _37_ (
|
||||
.IN1(reset),
|
||||
.IN2(_01_),
|
||||
.IN3(_02_),
|
||||
.QN(_00_[1])
|
||||
);
|
||||
AND2X1 _38_ (
|
||||
.IN1(\halton.counter [2]),
|
||||
.IN2(_01_),
|
||||
.Q(_03_)
|
||||
);
|
||||
NOR2X0 _39_ (
|
||||
.IN1(\halton.counter [2]),
|
||||
.IN2(_01_),
|
||||
.QN(_04_)
|
||||
);
|
||||
NOR3X0 _40_ (
|
||||
.IN1(reset),
|
||||
.IN2(_03_),
|
||||
.IN3(_04_),
|
||||
.QN(_00_[2])
|
||||
);
|
||||
AND4X1 _41_ (
|
||||
.IN1(\halton.counter [1]),
|
||||
.IN2(\halton.counter [0]),
|
||||
.IN3(\halton.counter [2]),
|
||||
.IN4(\halton.counter [3]),
|
||||
.Q(_05_)
|
||||
);
|
||||
NOR2X0 _42_ (
|
||||
.IN1(\halton.counter [3]),
|
||||
.IN2(_03_),
|
||||
.QN(_06_)
|
||||
);
|
||||
NOR3X0 _43_ (
|
||||
.IN1(reset),
|
||||
.IN2(_05_),
|
||||
.IN3(_06_),
|
||||
.QN(_00_[3])
|
||||
);
|
||||
AND2X1 _44_ (
|
||||
.IN1(\halton.counter [4]),
|
||||
.IN2(_05_),
|
||||
.Q(_07_)
|
||||
);
|
||||
NOR2X0 _45_ (
|
||||
.IN1(\halton.counter [4]),
|
||||
.IN2(_05_),
|
||||
.QN(_08_)
|
||||
);
|
||||
NOR3X0 _46_ (
|
||||
.IN1(reset),
|
||||
.IN2(_07_),
|
||||
.IN3(_08_),
|
||||
.QN(_00_[4])
|
||||
);
|
||||
AND2X1 _47_ (
|
||||
.IN1(\halton.counter [5]),
|
||||
.IN2(_07_),
|
||||
.Q(_09_)
|
||||
);
|
||||
NOR2X0 _48_ (
|
||||
.IN1(\halton.counter [5]),
|
||||
.IN2(_07_),
|
||||
.QN(_10_)
|
||||
);
|
||||
NOR3X0 _49_ (
|
||||
.IN1(reset),
|
||||
.IN2(_09_),
|
||||
.IN3(_10_),
|
||||
.QN(_00_[5])
|
||||
);
|
||||
AND4X1 _50_ (
|
||||
.IN1(\halton.counter [4]),
|
||||
.IN2(\halton.counter [5]),
|
||||
.IN3(\halton.counter [6]),
|
||||
.IN4(_05_),
|
||||
.Q(_11_)
|
||||
);
|
||||
NOR2X0 _51_ (
|
||||
.IN1(\halton.counter [6]),
|
||||
.IN2(_09_),
|
||||
.QN(_12_)
|
||||
);
|
||||
NOR3X0 _52_ (
|
||||
.IN1(reset),
|
||||
.IN2(_11_),
|
||||
.IN3(_12_),
|
||||
.QN(_00_[6])
|
||||
);
|
||||
AND2X1 _53_ (
|
||||
.IN1(\halton.counter [7]),
|
||||
.IN2(_11_),
|
||||
.Q(_13_)
|
||||
);
|
||||
NOR2X0 _54_ (
|
||||
.IN1(\halton.counter [7]),
|
||||
.IN2(_11_),
|
||||
.QN(_14_)
|
||||
);
|
||||
NOR3X0 _55_ (
|
||||
.IN1(reset),
|
||||
.IN2(_13_),
|
||||
.IN3(_14_),
|
||||
.QN(_00_[7])
|
||||
);
|
||||
AND3X1 _56_ (
|
||||
.IN1(\halton.counter [7]),
|
||||
.IN2(\halton.counter [8]),
|
||||
.IN3(_11_),
|
||||
.Q(_15_)
|
||||
);
|
||||
NOR2X0 _57_ (
|
||||
.IN1(\halton.counter [8]),
|
||||
.IN2(_13_),
|
||||
.QN(_16_)
|
||||
);
|
||||
NOR3X0 _58_ (
|
||||
.IN1(reset),
|
||||
.IN2(_15_),
|
||||
.IN3(_16_),
|
||||
.QN(_00_[8])
|
||||
);
|
||||
AND4X1 _59_ (
|
||||
.IN1(\halton.counter [7]),
|
||||
.IN2(\halton.counter [8]),
|
||||
.IN3(\halton.counter [9]),
|
||||
.IN4(_11_),
|
||||
.Q(_17_)
|
||||
);
|
||||
NOR2X0 _60_ (
|
||||
.IN1(\halton.counter [9]),
|
||||
.IN2(_15_),
|
||||
.QN(_18_)
|
||||
);
|
||||
NOR3X0 _61_ (
|
||||
.IN1(reset),
|
||||
.IN2(_17_),
|
||||
.IN3(_18_),
|
||||
.QN(_00_[9])
|
||||
);
|
||||
AND2X1 _62_ (
|
||||
.IN1(\halton.counter [10]),
|
||||
.IN2(_17_),
|
||||
.Q(_19_)
|
||||
);
|
||||
NOR2X0 _63_ (
|
||||
.IN1(\halton.counter [10]),
|
||||
.IN2(_17_),
|
||||
.QN(_20_)
|
||||
);
|
||||
NOR3X0 _64_ (
|
||||
.IN1(reset),
|
||||
.IN2(_19_),
|
||||
.IN3(_20_),
|
||||
.QN(_00_[10])
|
||||
);
|
||||
AND3X1 _65_ (
|
||||
.IN1(\halton.counter [10]),
|
||||
.IN2(\halton.counter [11]),
|
||||
.IN3(_17_),
|
||||
.Q(_21_)
|
||||
);
|
||||
AOI21X1 _66_ (
|
||||
.IN1(\halton.counter [10]),
|
||||
.IN2(_17_),
|
||||
.IN3(\halton.counter [11]),
|
||||
.QN(_22_)
|
||||
);
|
||||
NOR3X0 _67_ (
|
||||
.IN1(reset),
|
||||
.IN2(_21_),
|
||||
.IN3(_22_),
|
||||
.QN(_00_[11])
|
||||
);
|
||||
NOR2X0 _68_ (
|
||||
.IN1(reset),
|
||||
.IN2(\halton.counter [0]),
|
||||
.QN(_00_[0])
|
||||
);
|
||||
(* src = "rng_haltonBase2.v:7|rng_haltonBase2.v:19" *)
|
||||
DFFX1 _69_ (
|
||||
.CLK(clk),
|
||||
.D(_00_[0]),
|
||||
.Q(\halton.counter [0]),
|
||||
.QN(_23_)
|
||||
);
|
||||
(* src = "rng_haltonBase2.v:7|rng_haltonBase2.v:19" *)
|
||||
DFFX1 _70_ (
|
||||
.CLK(clk),
|
||||
.D(_00_[1]),
|
||||
.Q(\halton.counter [1]),
|
||||
.QN(_24_)
|
||||
);
|
||||
(* src = "rng_haltonBase2.v:7|rng_haltonBase2.v:19" *)
|
||||
DFFX1 _71_ (
|
||||
.CLK(clk),
|
||||
.D(_00_[2]),
|
||||
.Q(\halton.counter [2]),
|
||||
.QN(_25_)
|
||||
);
|
||||
(* src = "rng_haltonBase2.v:7|rng_haltonBase2.v:19" *)
|
||||
DFFX1 _72_ (
|
||||
.CLK(clk),
|
||||
.D(_00_[3]),
|
||||
.Q(\halton.counter [3]),
|
||||
.QN(_26_)
|
||||
);
|
||||
(* src = "rng_haltonBase2.v:7|rng_haltonBase2.v:19" *)
|
||||
DFFX1 _73_ (
|
||||
.CLK(clk),
|
||||
.D(_00_[4]),
|
||||
.Q(\halton.counter [4]),
|
||||
.QN(_27_)
|
||||
);
|
||||
(* src = "rng_haltonBase2.v:7|rng_haltonBase2.v:19" *)
|
||||
DFFX1 _74_ (
|
||||
.CLK(clk),
|
||||
.D(_00_[5]),
|
||||
.Q(\halton.counter [5]),
|
||||
.QN(_28_)
|
||||
);
|
||||
(* src = "rng_haltonBase2.v:7|rng_haltonBase2.v:19" *)
|
||||
DFFX1 _75_ (
|
||||
.CLK(clk),
|
||||
.D(_00_[6]),
|
||||
.Q(\halton.counter [6]),
|
||||
.QN(_29_)
|
||||
);
|
||||
(* src = "rng_haltonBase2.v:7|rng_haltonBase2.v:19" *)
|
||||
DFFX1 _76_ (
|
||||
.CLK(clk),
|
||||
.D(_00_[7]),
|
||||
.Q(\halton.counter [7]),
|
||||
.QN(_30_)
|
||||
);
|
||||
(* src = "rng_haltonBase2.v:7|rng_haltonBase2.v:19" *)
|
||||
DFFX1 _77_ (
|
||||
.CLK(clk),
|
||||
.D(_00_[8]),
|
||||
.Q(\halton.counter [8]),
|
||||
.QN(_31_)
|
||||
);
|
||||
(* src = "rng_haltonBase2.v:7|rng_haltonBase2.v:19" *)
|
||||
DFFX1 _78_ (
|
||||
.CLK(clk),
|
||||
.D(_00_[9]),
|
||||
.Q(\halton.counter [9]),
|
||||
.QN(_32_)
|
||||
);
|
||||
(* src = "rng_haltonBase2.v:7|rng_haltonBase2.v:19" *)
|
||||
DFFX1 _79_ (
|
||||
.CLK(clk),
|
||||
.D(_00_[10]),
|
||||
.Q(\halton.counter [10]),
|
||||
.QN(_33_)
|
||||
);
|
||||
(* src = "rng_haltonBase2.v:7|rng_haltonBase2.v:19" *)
|
||||
DFFX1 _80_ (
|
||||
.CLK(clk),
|
||||
.D(_00_[11]),
|
||||
.Q(\halton.counter [11]),
|
||||
.QN(_34_)
|
||||
);
|
||||
assign \halton.clk = clk;
|
||||
assign \halton.o_output = { \halton.counter [0], \halton.counter [1], \halton.counter [2], \halton.counter [3], \halton.counter [4], \halton.counter [5], \halton.counter [6], \halton.counter [7], \halton.counter [8], \halton.counter [9], \halton.counter [10], \halton.counter [11] };
|
||||
assign \halton.reset = reset;
|
||||
assign o_output = { \halton.counter [0], \halton.counter [1], \halton.counter [2], \halton.counter [3], \halton.counter [4], \halton.counter [5], \halton.counter [6], \halton.counter [7], \halton.counter [8], \halton.counter [9], \halton.counter [10], \halton.counter [11] };
|
||||
endmodule
|
||||
+1
-1
@@ -12,4 +12,4 @@ def test_b01(mydir):
|
||||
def test_simple():
|
||||
c = bench.parse('input(a, b) output(z) z=and(a,b)')
|
||||
assert len(c.nodes) == 4
|
||||
assert len(c.interface) == 3
|
||||
assert len(c.io_nodes) == 3
|
||||
+58
-5
@@ -1,5 +1,29 @@
|
||||
from kyupy.circuit import Circuit, Node, Line
|
||||
import pickle
|
||||
|
||||
from kyupy.circuit import GrowingList, Circuit, Node, Line
|
||||
from kyupy import verilog, bench
|
||||
from kyupy.techlib import SAED32
|
||||
|
||||
def test_growing_list():
|
||||
gl = GrowingList()
|
||||
assert gl.free_idx == 0
|
||||
gl[0] = 1
|
||||
assert gl.free_idx == 1
|
||||
gl[2] = 1
|
||||
assert gl.free_idx == 1
|
||||
gl[0] = None
|
||||
assert gl.free_idx == 0
|
||||
gl[0] = 1
|
||||
assert gl.free_idx == 1
|
||||
gl[1] = 1
|
||||
assert gl.free_idx == 3
|
||||
gl.append(1)
|
||||
assert gl.free_idx == 4
|
||||
gl[2] = None
|
||||
assert gl.free_idx == 2
|
||||
gl[2] = 1
|
||||
gl[1] = None
|
||||
assert gl.free_idx == 1
|
||||
|
||||
def test_lines():
|
||||
c = Circuit()
|
||||
@@ -41,7 +65,7 @@ def test_lines():
|
||||
assert c.lines[0].index == 0
|
||||
assert c.lines[1].index == 1
|
||||
|
||||
assert n1.outs[2] is None
|
||||
assert len(n1.outs) == 2
|
||||
assert n2.ins[1] is None
|
||||
assert n2.ins[2] == line2
|
||||
|
||||
@@ -55,9 +79,9 @@ def test_circuit():
|
||||
assert 'in1' in c.cells
|
||||
assert 'and1' not in c.cells
|
||||
|
||||
c.interface[0] = in1
|
||||
c.interface[1] = in2
|
||||
c.interface[2] = out1
|
||||
c.io_nodes[0] = in1
|
||||
c.io_nodes[1] = in2
|
||||
c.io_nodes[2] = out1
|
||||
|
||||
and1 = Node(c, 'and1', kind='and')
|
||||
Line(c, in1, and1)
|
||||
@@ -99,3 +123,32 @@ def test_circuit():
|
||||
|
||||
for n in c.topological_order():
|
||||
repr(n)
|
||||
|
||||
|
||||
def test_pickle(mydir):
|
||||
c = verilog.load(mydir / 'b15_4ig.v.gz', tlib=SAED32)
|
||||
assert c is not None
|
||||
cs = pickle.dumps(c)
|
||||
assert cs is not None
|
||||
c2 = pickle.loads(cs)
|
||||
assert c == c2
|
||||
|
||||
|
||||
def test_substitute():
|
||||
c = bench.parse('input(i1, i2, i3, i4, i5) output(o1) aoi=AOI221(i1, i2, i3, i4, i5) o1=not(aoi)')
|
||||
assert len(c.cells) == 2
|
||||
assert len(c.io_nodes) == 6
|
||||
aoi221_impl = bench.parse('input(in1, in2, in3, in4, in5) output(q) a1=and(in1, in2) a2=and(in3, in4) q=or(a1, a2, in5)')
|
||||
assert len(aoi221_impl.cells) == 3
|
||||
assert len(aoi221_impl.io_nodes) == 6
|
||||
c.substitute(c.cells['aoi'], aoi221_impl)
|
||||
assert len(c.cells) == 4
|
||||
assert len(c.io_nodes) == 6
|
||||
|
||||
|
||||
def test_resolve(mydir):
|
||||
c = verilog.load(mydir / 'b15_4ig.v.gz', tlib=SAED32)
|
||||
s_names = [n.name for n in c.s_nodes]
|
||||
c.resolve_tlib_cells(SAED32)
|
||||
s_names_prim = [n.name for n in c.s_nodes]
|
||||
assert s_names == s_names_prim, 'resolve_tlib_cells does not preserve names or order of s_nodes'
|
||||
+53
-192
@@ -1,214 +1,75 @@
|
||||
import numpy as np
|
||||
import kyupy.logic as lg
|
||||
from kyupy.logic import mvarray, bparray, bp_to_mv, mv_to_bp
|
||||
|
||||
|
||||
def test_mvarray():
|
||||
|
||||
# instantiation with shape
|
||||
|
||||
ary = lg.MVArray(4)
|
||||
assert ary.length == 1
|
||||
assert len(ary) == 1
|
||||
assert ary.width == 4
|
||||
|
||||
ary = lg.MVArray((3, 2))
|
||||
assert ary.length == 2
|
||||
assert len(ary) == 2
|
||||
assert ary.width == 3
|
||||
|
||||
# instantiation with single vector
|
||||
|
||||
ary = lg.MVArray([1, 0, 1])
|
||||
assert ary.length == 1
|
||||
assert ary.width == 3
|
||||
assert str(ary) == "['101']"
|
||||
assert ary[0] == '101'
|
||||
|
||||
ary = lg.MVArray("10X-")
|
||||
assert ary.length == 1
|
||||
assert ary.width == 4
|
||||
assert str(ary) == "['10X-']"
|
||||
assert ary[0] == '10X-'
|
||||
|
||||
ary = lg.MVArray("1")
|
||||
assert ary.length == 1
|
||||
assert ary.width == 1
|
||||
|
||||
ary = lg.MVArray(["1"])
|
||||
assert ary.length == 1
|
||||
assert ary.width == 1
|
||||
|
||||
# instantiation with multiple vectors
|
||||
|
||||
ary = lg.MVArray([[0, 0], [0, 1], [1, 0], [1, 1]])
|
||||
assert ary.length == 4
|
||||
assert ary.width == 2
|
||||
|
||||
ary = lg.MVArray(["000", "001", "110", "---"])
|
||||
assert ary.length == 4
|
||||
assert ary.width == 3
|
||||
assert str(ary) == "['000', '001', '110', '---']"
|
||||
assert ary[2] == '110'
|
||||
|
||||
# casting to 2-valued logic
|
||||
|
||||
ary = lg.MVArray([0, 1, 2, None], m=2)
|
||||
assert ary.data[0] == lg.ZERO
|
||||
assert ary.data[1] == lg.ONE
|
||||
assert ary.data[2] == lg.ZERO
|
||||
assert ary.data[3] == lg.ZERO
|
||||
|
||||
ary = lg.MVArray("0-X1PRFN", m=2)
|
||||
assert ary.data[0] == lg.ZERO
|
||||
assert ary.data[1] == lg.ZERO
|
||||
assert ary.data[2] == lg.ZERO
|
||||
assert ary.data[3] == lg.ONE
|
||||
assert ary.data[4] == lg.ZERO
|
||||
assert ary.data[5] == lg.ONE
|
||||
assert ary.data[6] == lg.ZERO
|
||||
assert ary.data[7] == lg.ONE
|
||||
|
||||
# casting to 4-valued logic
|
||||
|
||||
ary = lg.MVArray([0, 1, 2, None, 'F'], m=4)
|
||||
assert ary.data[0] == lg.ZERO
|
||||
assert ary.data[1] == lg.ONE
|
||||
assert ary.data[2] == lg.UNKNOWN
|
||||
assert ary.data[3] == lg.UNASSIGNED
|
||||
assert ary.data[4] == lg.ZERO
|
||||
|
||||
ary = lg.MVArray("0-X1PRFN", m=4)
|
||||
assert ary.data[0] == lg.ZERO
|
||||
assert ary.data[1] == lg.UNASSIGNED
|
||||
assert ary.data[2] == lg.UNKNOWN
|
||||
assert ary.data[3] == lg.ONE
|
||||
assert ary.data[4] == lg.ZERO
|
||||
assert ary.data[5] == lg.ONE
|
||||
assert ary.data[6] == lg.ZERO
|
||||
assert ary.data[7] == lg.ONE
|
||||
|
||||
# casting to 8-valued logic
|
||||
|
||||
ary = lg.MVArray([0, 1, 2, None, 'F'], m=8)
|
||||
assert ary.data[0] == lg.ZERO
|
||||
assert ary.data[1] == lg.ONE
|
||||
assert ary.data[2] == lg.UNKNOWN
|
||||
assert ary.data[3] == lg.UNASSIGNED
|
||||
assert ary.data[4] == lg.FALL
|
||||
|
||||
ary = lg.MVArray("0-X1PRFN", m=8)
|
||||
assert ary.data[0] == lg.ZERO
|
||||
assert ary.data[1] == lg.UNASSIGNED
|
||||
assert ary.data[2] == lg.UNKNOWN
|
||||
assert ary.data[3] == lg.ONE
|
||||
assert ary.data[4] == lg.PPULSE
|
||||
assert ary.data[5] == lg.RISE
|
||||
assert ary.data[6] == lg.FALL
|
||||
assert ary.data[7] == lg.NPULSE
|
||||
|
||||
# copy constructor and casting
|
||||
|
||||
ary8 = lg.MVArray(ary, m=8)
|
||||
assert ary8.length == 1
|
||||
assert ary8.width == 8
|
||||
assert ary8.data[7] == lg.NPULSE
|
||||
|
||||
ary4 = lg.MVArray(ary, m=4)
|
||||
assert ary4.data[1] == lg.UNASSIGNED
|
||||
assert ary4.data[7] == lg.ONE
|
||||
|
||||
ary2 = lg.MVArray(ary, m=2)
|
||||
assert ary2.data[1] == lg.ZERO
|
||||
assert ary2.data[7] == lg.ONE
|
||||
def assert_equal_shape_and_contents(actual, desired):
|
||||
desired = np.array(desired, dtype=np.uint8)
|
||||
assert actual.shape == desired.shape
|
||||
np.testing.assert_allclose(actual, desired)
|
||||
|
||||
|
||||
def test_mv_operations():
|
||||
x1_2v = lg.MVArray("0011", m=2)
|
||||
x2_2v = lg.MVArray("0101", m=2)
|
||||
x1_4v = lg.MVArray("0000XXXX----1111", m=4)
|
||||
x2_4v = lg.MVArray("0X-10X-10X-10X-1", m=4)
|
||||
x1_8v = lg.MVArray("00000000XXXXXXXX--------11111111PPPPPPPPRRRRRRRRFFFFFFFFNNNNNNNN", m=8)
|
||||
x2_8v = lg.MVArray("0X-1PRFN0X-1PRFN0X-1PRFN0X-1PRFN0X-1PRFN0X-1PRFN0X-1PRFN0X-1PRFN", m=8)
|
||||
def test_mvarray_single_vector():
|
||||
assert_equal_shape_and_contents(mvarray(1, 0, 1), [lg.ONE, lg.ZERO, lg.ONE])
|
||||
assert_equal_shape_and_contents(mvarray([1, 0, 1]), [lg.ONE, lg.ZERO, lg.ONE])
|
||||
assert_equal_shape_and_contents(mvarray('10X-RFPN'), [lg.ONE, lg.ZERO, lg.UNKNOWN, lg.UNASSIGNED, lg.RISE, lg.FALL, lg.PPULSE, lg.NPULSE])
|
||||
assert_equal_shape_and_contents(mvarray(['1']), [lg.ONE])
|
||||
assert_equal_shape_and_contents(mvarray('1'), [lg.ONE])
|
||||
|
||||
assert lg.mv_not(x1_2v)[0] == '1100'
|
||||
assert lg.mv_not(x1_4v)[0] == '1111XXXXXXXX0000'
|
||||
assert lg.mv_not(x1_8v)[0] == '11111111XXXXXXXXXXXXXXXX00000000NNNNNNNNFFFFFFFFRRRRRRRRPPPPPPPP'
|
||||
|
||||
assert lg.mv_or(x1_2v, x2_2v)[0] == '0111'
|
||||
assert lg.mv_or(x1_4v, x2_4v)[0] == '0XX1XXX1XXX11111'
|
||||
assert lg.mv_or(x1_8v, x2_8v)[0] == '0XX1PRFNXXX1XXXXXXX1XXXX11111111PXX1PRFNRXX1RRNNFXX1FNFNNXX1NNNN'
|
||||
def test_mvarray_multi_vector():
|
||||
assert_equal_shape_and_contents(mvarray([0, 0], [0, 1], [1, 0], [1, 1]), [[lg.ZERO, lg.ZERO, lg.ONE, lg.ONE], [lg.ZERO, lg.ONE, lg.ZERO, lg.ONE]])
|
||||
assert_equal_shape_and_contents(mvarray('10X', '--1'), [[lg.ONE, lg.UNASSIGNED], [lg.ZERO, lg.UNASSIGNED], [lg.UNKNOWN, lg.ONE]])
|
||||
|
||||
assert lg.mv_and(x1_2v, x2_2v)[0] == '0001'
|
||||
assert lg.mv_and(x1_4v, x2_4v)[0] == '00000XXX0XXX0XX1'
|
||||
assert lg.mv_and(x1_8v, x2_8v)[0] == '000000000XXXXXXX0XXXXXXX0XX1PRFN0XXPPPPP0XXRPRPR0XXFPPFF0XXNPRFN'
|
||||
|
||||
assert lg.mv_xor(x1_2v, x2_2v)[0] == '0110'
|
||||
assert lg.mv_xor(x1_4v, x2_4v)[0] == '0XX1XXXXXXXX1XX0'
|
||||
assert lg.mv_xor(x1_8v, x2_8v)[0] == '0XX1PRFNXXXXXXXXXXXXXXXX1XX0NFRPPXXNPRFNRXXFRPNFFXXRFNPRNXXPNFRP'
|
||||
def test_mv_ops():
|
||||
x1_8v = mvarray('00000000XXXXXXXX--------11111111PPPPPPPPRRRRRRRRFFFFFFFFNNNNNNNN')
|
||||
x2_8v = mvarray('0X-1PRFN'*8)
|
||||
|
||||
assert_equal_shape_and_contents(lg.mv_not(x1_8v), mvarray('11111111XXXXXXXXXXXXXXXX00000000NNNNNNNNFFFFFFFFRRRRRRRRPPPPPPPP'))
|
||||
assert_equal_shape_and_contents(lg.mv_or(x1_8v, x2_8v), mvarray('0XX1PRFNXXX1XXXXXXX1XXXX11111111PXX1PRFNRXX1RRNNFXX1FNFNNXX1NNNN'))
|
||||
assert_equal_shape_and_contents(lg.mv_and(x1_8v, x2_8v), mvarray('000000000XXXXXXX0XXXXXXX0XX1PRFN0XXPPPPP0XXRPRPR0XXFPPFF0XXNPRFN'))
|
||||
assert_equal_shape_and_contents(lg.mv_xor(x1_8v, x2_8v), mvarray('0XX1PRFNXXXXXXXXXXXXXXXX1XX0NFRPPXXNPRFNRXXFRPNFFXXRFNPRNXXPNFRP'))
|
||||
|
||||
# TODO
|
||||
#assert_equal_shape_and_contents(lg.mv_transition(x1_8v, x2_8v), mvarray('0XXR PRFNXXXXXXXXXXXXXXXX1XX0NFRPPXXNPRFNRXXFRPNFFXXRFNPRNXXPNFRP'))
|
||||
|
||||
x30_8v = mvarray('0000000000000000000000000000000000000000000000000000000000000000')
|
||||
x31_8v = mvarray('1111111111111111111111111111111111111111111111111111111111111111')
|
||||
|
||||
assert_equal_shape_and_contents(lg.mv_latch(x1_8v, x2_8v, x30_8v), mvarray('0XX000000XXXXXXX0XXXXXXX0XX10R110XX000000XXR0R0R0XXF001F0XX10R11'))
|
||||
assert_equal_shape_and_contents(lg.mv_latch(x1_8v, x2_8v, x31_8v), mvarray('1XX01F001XXXXXXX1XXXXXXX1XX111111XX01F001XXR110R1XXF1F1F1XX11111'))
|
||||
|
||||
|
||||
def test_bparray():
|
||||
|
||||
ary = lg.BPArray(4)
|
||||
assert ary.length == 1
|
||||
assert len(ary) == 1
|
||||
assert ary.width == 4
|
||||
bpa = bparray('0X-1PRFN')
|
||||
assert bpa.shape == (8, 3, 1)
|
||||
|
||||
ary = lg.BPArray((3, 2))
|
||||
assert ary.length == 2
|
||||
assert len(ary) == 2
|
||||
assert ary.width == 3
|
||||
bpa = bparray('0X-1PRFN-')
|
||||
assert bpa.shape == (9, 3, 1)
|
||||
|
||||
assert lg.MVArray(lg.BPArray("01", m=2))[0] == '01'
|
||||
assert lg.MVArray(lg.BPArray("0X-1", m=4))[0] == '0X-1'
|
||||
assert lg.MVArray(lg.BPArray("0X-1PRFN", m=8))[0] == '0X-1PRFN'
|
||||
bpa = bparray('000', '001', '010', '011', '100', '101', '110', '111')
|
||||
assert bpa.shape == (3, 3, 1)
|
||||
|
||||
x1_2v = lg.BPArray("0011", m=2)
|
||||
x2_2v = lg.BPArray("0101", m=2)
|
||||
x1_4v = lg.BPArray("0000XXXX----1111", m=4)
|
||||
x2_4v = lg.BPArray("0X-10X-10X-10X-1", m=4)
|
||||
x1_8v = lg.BPArray("00000000XXXXXXXX--------11111111PPPPPPPPRRRRRRRRFFFFFFFFNNNNNNNN", m=8)
|
||||
x2_8v = lg.BPArray("0X-1PRFN0X-1PRFN0X-1PRFN0X-1PRFN0X-1PRFN0X-1PRFN0X-1PRFN0X-1PRFN", m=8)
|
||||
bpa = bparray('000', '001', '010', '011', '100', '101', '110', '111', 'RFX')
|
||||
assert bpa.shape == (3, 3, 2)
|
||||
|
||||
out_2v = lg.BPArray((4, 1), m=2)
|
||||
out_4v = lg.BPArray((16, 1), m=4)
|
||||
out_8v = lg.BPArray((64, 1), m=8)
|
||||
assert_equal_shape_and_contents(bp_to_mv(bparray('0X-1PRFN'))[:,0], mvarray('0X-1PRFN'))
|
||||
assert_equal_shape_and_contents(bparray('0X-1PRFN'), mv_to_bp(mvarray('0X-1PRFN')))
|
||||
|
||||
lg.bp_buf(out_2v.data, x1_2v.data)
|
||||
lg.bp_buf(out_4v.data, x1_4v.data)
|
||||
lg.bp_buf(out_8v.data, x1_8v.data)
|
||||
x1_8v = bparray('00000000XXXXXXXX--------11111111PPPPPPPPRRRRRRRRFFFFFFFFNNNNNNNN')
|
||||
x2_8v = bparray('0X-1PRFN'*8)
|
||||
|
||||
assert lg.MVArray(out_2v)[0] == '0011'
|
||||
assert lg.MVArray(out_4v)[0] == '0000XXXXXXXX1111'
|
||||
assert lg.MVArray(out_8v)[0] == '00000000XXXXXXXXXXXXXXXX11111111PPPPPPPPRRRRRRRRFFFFFFFFNNNNNNNN'
|
||||
out_8v = np.empty((64, 3, 1), dtype=np.uint8)
|
||||
|
||||
lg.bp_not(out_2v.data, x1_2v.data)
|
||||
lg.bp_not(out_4v.data, x1_4v.data)
|
||||
lg.bp_not(out_8v.data, x1_8v.data)
|
||||
assert_equal_shape_and_contents(bp_to_mv(lg.bp8v_buf(out_8v, x1_8v))[:,0], mvarray('00000000XXXXXXXXXXXXXXXX11111111PPPPPPPPRRRRRRRRFFFFFFFFNNNNNNNN'))
|
||||
assert_equal_shape_and_contents(bp_to_mv(lg.bp8v_or(out_8v, x1_8v, x2_8v))[:,0], mvarray('0XX1PRFNXXX1XXXXXXX1XXXX11111111PXX1PRFNRXX1RRNNFXX1FNFNNXX1NNNN'))
|
||||
assert_equal_shape_and_contents(bp_to_mv(lg.bp8v_and(out_8v, x1_8v, x2_8v))[:,0], mvarray('000000000XXXXXXX0XXXXXXX0XX1PRFN0XXPPPPP0XXRPRPR0XXFPPFF0XXNPRFN'))
|
||||
assert_equal_shape_and_contents(bp_to_mv(lg.bp8v_xor(out_8v, x1_8v, x2_8v))[:,0], mvarray('0XX1PRFNXXXXXXXXXXXXXXXX1XX0NFRPPXXNPRFNRXXFRPNFFXXRFNPRNXXPNFRP'))
|
||||
|
||||
assert lg.MVArray(out_2v)[0] == '1100'
|
||||
assert lg.MVArray(out_4v)[0] == '1111XXXXXXXX0000'
|
||||
assert lg.MVArray(out_8v)[0] == '11111111XXXXXXXXXXXXXXXX00000000NNNNNNNNFFFFFFFFRRRRRRRRPPPPPPPP'
|
||||
x30_8v = bparray('0000000000000000000000000000000000000000000000000000000000000000')
|
||||
x31_8v = bparray('1111111111111111111111111111111111111111111111111111111111111111')
|
||||
|
||||
lg.bp_or(out_2v.data, x1_2v.data, x2_2v.data)
|
||||
lg.bp_or(out_4v.data, x1_4v.data, x2_4v.data)
|
||||
lg.bp_or(out_8v.data, x1_8v.data, x2_8v.data)
|
||||
|
||||
assert lg.MVArray(out_2v)[0] == '0111'
|
||||
assert lg.MVArray(out_4v)[0] == '0XX1XXX1XXX11111'
|
||||
assert lg.MVArray(out_8v)[0] == '0XX1PRFNXXX1XXXXXXX1XXXX11111111PXX1PRFNRXX1RRNNFXX1FNFNNXX1NNNN'
|
||||
|
||||
lg.bp_and(out_2v.data, x1_2v.data, x2_2v.data)
|
||||
lg.bp_and(out_4v.data, x1_4v.data, x2_4v.data)
|
||||
lg.bp_and(out_8v.data, x1_8v.data, x2_8v.data)
|
||||
|
||||
assert lg.MVArray(out_2v)[0] == '0001'
|
||||
assert lg.MVArray(out_4v)[0] == '00000XXX0XXX0XX1'
|
||||
assert lg.MVArray(out_8v)[0] == '000000000XXXXXXX0XXXXXXX0XX1PRFN0XXPPPPP0XXRPRPR0XXFPPFF0XXNPRFN'
|
||||
|
||||
lg.bp_xor(out_2v.data, x1_2v.data, x2_2v.data)
|
||||
lg.bp_xor(out_4v.data, x1_4v.data, x2_4v.data)
|
||||
lg.bp_xor(out_8v.data, x1_8v.data, x2_8v.data)
|
||||
|
||||
assert lg.MVArray(out_2v)[0] == '0110'
|
||||
assert lg.MVArray(out_4v)[0] == '0XX1XXXXXXXX1XX0'
|
||||
assert lg.MVArray(out_8v)[0] == '0XX1PRFNXXXXXXXXXXXXXXXX1XX0NFRPPXXNPRFNRXXFRPNFFXXRFNPRNXXPNFRP'
|
||||
assert_equal_shape_and_contents(bp_to_mv(lg.bp8v_latch(out_8v, x1_8v, x2_8v, x30_8v))[:,0], mvarray('0XX000000XXXXXXX0XXXXXXX0XX10R110XX000000XXR0R0R0XXF001F0XX10R11'))
|
||||
assert_equal_shape_and_contents(bp_to_mv(lg.bp8v_latch(out_8v, x1_8v, x2_8v, x31_8v))[:,0], mvarray('1XX01F001XXXXXXX1XXXXXXX1XX111111XX01F001XXR110R1XXF1F1F1XX11111'))
|
||||
+234
-70
@@ -1,96 +1,260 @@
|
||||
from kyupy.logic_sim import LogicSim
|
||||
from kyupy import bench
|
||||
from kyupy.logic import MVArray, BPArray
|
||||
import numpy as np
|
||||
|
||||
from kyupy.logic_sim import LogicSim, LogicSim6V
|
||||
from kyupy import bench, logic, sim
|
||||
from kyupy.logic import mvarray, bparray, bp_to_mv, mv_to_bp
|
||||
|
||||
def assert_equal_shape_and_contents(actual, desired):
|
||||
desired = np.array(desired, dtype=np.uint8)
|
||||
assert actual.shape == desired.shape
|
||||
np.testing.assert_allclose(actual, desired)
|
||||
|
||||
def test_2v():
|
||||
c = bench.parse('input(x, y) output(a, o, n) a=and(x,y) o=or(x,y) n=not(x)')
|
||||
s = LogicSim(c, 4, m=2)
|
||||
assert len(s.interface) == 5
|
||||
mva = MVArray(['00000', '01000', '10000', '11000'], m=2)
|
||||
bpa = BPArray(mva)
|
||||
s.assign(bpa)
|
||||
s.propagate()
|
||||
s.capture(bpa)
|
||||
mva = MVArray(bpa)
|
||||
assert mva[0] == '00001'
|
||||
assert mva[1] == '01011'
|
||||
assert mva[2] == '10010'
|
||||
assert mva[3] == '11110'
|
||||
c = bench.parse(f'''
|
||||
input(i3, i2, i1, i0)
|
||||
output({",".join([f"o{i:02d}" for i in range(33)])})
|
||||
o00=BUF1(i0)
|
||||
o01=INV1(i0)
|
||||
o02=AND2(i0,i1)
|
||||
o03=AND3(i0,i1,i2)
|
||||
o04=AND4(i0,i1,i2,i3)
|
||||
o05=NAND2(i0,i1)
|
||||
o06=NAND3(i0,i1,i2)
|
||||
o07=NAND4(i0,i1,i2,i3)
|
||||
o08=OR2(i0,i1)
|
||||
o09=OR3(i0,i1,i2)
|
||||
o10=OR4(i0,i1,i2,i3)
|
||||
o11=NOR2(i0,i1)
|
||||
o12=NOR3(i0,i1,i2)
|
||||
o13=NOR4(i0,i1,i2,i3)
|
||||
o14=XOR2(i0,i1)
|
||||
o15=XOR3(i0,i1,i2)
|
||||
o16=XOR4(i0,i1,i2,i3)
|
||||
o17=XNOR2(i0,i1)
|
||||
o18=XNOR3(i0,i1,i2)
|
||||
o19=XNOR4(i0,i1,i2,i3)
|
||||
o20=AO21(i0,i1,i2)
|
||||
o21=OA21(i0,i1,i2)
|
||||
o22=AO22(i0,i1,i2,i3)
|
||||
o23=OA22(i0,i1,i2,i3)
|
||||
o24=AOI21(i0,i1,i2)
|
||||
o25=OAI21(i0,i1,i2)
|
||||
o26=AOI22(i0,i1,i2,i3)
|
||||
o27=OAI22(i0,i1,i2,i3)
|
||||
o28=AO211(i0,i1,i2,i3)
|
||||
o29=OA211(i0,i1,i2,i3)
|
||||
o30=AOI211(i0,i1,i2,i3)
|
||||
o31=OAI211(i0,i1,i2,i3)
|
||||
o32=MUX21(i0,i1,i2)
|
||||
''')
|
||||
s = LogicSim(c, 16, m=2)
|
||||
bpa = logic.bparray([f'{i:04b}'+('-'*(s.s_len-4)) for i in range(16)])
|
||||
s.s[0] = bpa
|
||||
s.s_to_c()
|
||||
s.c_prop()
|
||||
s.c_to_s()
|
||||
mva = logic.bp_to_mv(s.s[1])
|
||||
for res, exp in zip(logic.packbits(mva[4:], dtype=np.uint32), [
|
||||
sim.BUF1, sim.INV1,
|
||||
sim.AND2, sim.AND3, sim.AND4,
|
||||
sim.NAND2, sim.NAND3, sim.NAND4,
|
||||
sim.OR2, sim.OR3, sim.OR4,
|
||||
sim.NOR2, sim.NOR3, sim.NOR4,
|
||||
sim.XOR2, sim.XOR3, sim.XOR4,
|
||||
sim.XNOR2, sim.XNOR3, sim.XNOR4,
|
||||
sim.AO21, sim.OA21,
|
||||
sim.AO22, sim.OA22,
|
||||
sim.AOI21, sim.OAI21,
|
||||
sim.AOI22, sim.OAI22,
|
||||
sim.AO211, sim.OA211,
|
||||
sim.AOI211, sim.OAI211,
|
||||
sim.MUX21
|
||||
]):
|
||||
assert res == exp, f'Mismatch for SimPrim {sim.names[exp]} res={bin(res)} exp={bin(exp)}'
|
||||
|
||||
|
||||
def test_4v():
|
||||
c = bench.parse('input(x, y) output(a, o, n) a=and(x,y) o=or(x,y) n=not(x)')
|
||||
s = LogicSim(c, 16, m=4)
|
||||
assert len(s.interface) == 5
|
||||
mva = MVArray(['00000', '01000', '0-000', '0X000',
|
||||
'10000', '11000', '1-000', '1X000',
|
||||
'-0000', '-1000', '--000', '-X000',
|
||||
'X0000', 'X1000', 'X-000', 'XX000'], m=4)
|
||||
bpa = BPArray(mva)
|
||||
s.assign(bpa)
|
||||
s.propagate()
|
||||
s.capture(bpa)
|
||||
mva = MVArray(bpa)
|
||||
assert mva[0] == '00001'
|
||||
assert mva[1] == '01011'
|
||||
assert mva[2] == '0-0X1'
|
||||
assert mva[3] == '0X0X1'
|
||||
assert mva[4] == '10010'
|
||||
assert mva[5] == '11110'
|
||||
assert mva[6] == '1-X10'
|
||||
assert mva[7] == '1XX10'
|
||||
assert mva[8] == '-00XX'
|
||||
assert mva[9] == '-1X1X'
|
||||
assert mva[10] == '--XXX'
|
||||
assert mva[11] == '-XXXX'
|
||||
assert mva[12] == 'X00XX'
|
||||
assert mva[13] == 'X1X1X'
|
||||
assert mva[14] == 'X-XXX'
|
||||
assert mva[15] == 'XXXXX'
|
||||
s = LogicSim(c, 16, m=8) # FIXME: m=4
|
||||
assert s.s_len == 5
|
||||
bpa = bparray(
|
||||
'00---', '01---', '0----', '0X---',
|
||||
'10---', '11---', '1----', '1X---',
|
||||
'-0---', '-1---', '-----', '-X---',
|
||||
'X0---', 'X1---', 'X----', 'XX---')
|
||||
s.s[0] = bpa
|
||||
s.s_to_c()
|
||||
s.c_prop()
|
||||
s.c_to_s()
|
||||
mva = bp_to_mv(s.s[1])
|
||||
assert_equal_shape_and_contents(mva, mvarray(
|
||||
'--001', '--011', '--0X1', '--0X1',
|
||||
'--010', '--110', '--X10', '--X10',
|
||||
'--0XX', '--X1X', '--XXX', '--XXX',
|
||||
'--0XX', '--X1X', '--XXX', '--XXX'))
|
||||
|
||||
|
||||
def test_6v():
|
||||
c = bench.parse('input(x, y) output(a, o, n, xo, no) a=AND2(x,y) o=OR2(x,y) n=INV1(x) xo=XOR2(x,y) no=NOR2(x,y)')
|
||||
s = LogicSim6V(c, 36)
|
||||
assert s.s_len == 7
|
||||
mva = mvarray(
|
||||
'0000101', '0101110', '0R0R1RF', '0F0F1FR', '0P0P1PN', '0N0N1NP',
|
||||
'1001010', '1111000', '1RR10F0', '1FF10R0', '1PP10N0', '1NN10P0',
|
||||
'R00RFRF', 'R1R1FF0', 'RRRRFPF', 'RFPNFNP', 'RPPRFRF', 'RNRNFFP',
|
||||
'F00FRFR', 'F1F1RR0', 'FRPNRNP', 'FFFFRPR', 'FPPFRFR', 'FNFNRRP',
|
||||
'P00PNPN', 'P1P1NN0', 'PRPRNRF', 'PFPFNFR', 'PPPPNPN', 'PNPNNNP',
|
||||
'N00NPNP', 'N1N1PP0', 'NRRNPFP', 'NFFNPRP', 'NPPNPNP', 'NNNNPPP')
|
||||
tests = np.copy(mva)
|
||||
tests[2:] = logic.ZERO
|
||||
s.s[0] = tests
|
||||
s.s_to_c()
|
||||
s.c_prop()
|
||||
s.c_to_s()
|
||||
resp = s.s[1].copy()
|
||||
|
||||
exp_resp = np.copy(mva)
|
||||
exp_resp[:2] = logic.ZERO
|
||||
np.testing.assert_allclose(resp, exp_resp)
|
||||
|
||||
|
||||
def test_8v():
|
||||
c = bench.parse('input(x, y) output(a, o, n, xo) a=and(x,y) o=or(x,y) n=not(x) xo=xor(x,y)')
|
||||
s = LogicSim(c, 64, m=8)
|
||||
assert len(s.interface) == 6
|
||||
mva = MVArray(['000010', '010111', '0-0X1X', '0X0X1X', '0R0R1R', '0F0F1F', '0P0P1P', '0N0N1N',
|
||||
assert s.s_len == 6
|
||||
mva = mvarray(
|
||||
'000010', '010111', '0-0X1X', '0X0X1X', '0R0R1R', '0F0F1F', '0P0P1P', '0N0N1N',
|
||||
'100101', '111100', '1-X10X', '1XX10X', '1RR10F', '1FF10R', '1PP10N', '1NN10P',
|
||||
'-00XXX', '-1X1XX', '--XXXX', '-XXXXX', '-RXXXX', '-FXXXX', '-PXXXX', '-NXXXX',
|
||||
'X00XXX', 'X1X1XX', 'X-XXXX', 'XXXXXX', 'XRXXXX', 'XFXXXX', 'XPXXXX', 'XNXXXX',
|
||||
'R00RFR', 'R1R1FF', 'R-XXFX', 'RXXXFX', 'RRRRFP', 'RFPNFN', 'RPPRFR', 'RNRNFF',
|
||||
'F00FRF', 'F1F1RR', 'F-XXRX', 'FXXXRX', 'FRPNRN', 'FFFFRP', 'FPPFRF', 'FNFNRR',
|
||||
'P00PNP', 'P1P1NN', 'P-XXNX', 'PXXXNX', 'PRPRNR', 'PFPFNF', 'PPPPNP', 'PNPNNN',
|
||||
'N00NPN', 'N1N1PP', 'N-XXPX', 'NXXXPX', 'NRRNPF', 'NFFNPR', 'NPPNPN', 'NNNNPP'], m=8)
|
||||
bpa = BPArray(mva)
|
||||
s.assign(bpa)
|
||||
s.propagate()
|
||||
resp_bp = BPArray(bpa)
|
||||
s.capture(resp_bp)
|
||||
resp = MVArray(resp_bp)
|
||||
'N00NPN', 'N1N1PP', 'N-XXPX', 'NXXXPX', 'NRRNPF', 'NFFNPR', 'NPPNPN', 'NNNNPP')
|
||||
tests = np.copy(mva)
|
||||
tests[2:] = logic.UNASSIGNED
|
||||
bpa = mv_to_bp(tests)
|
||||
s.s[0] = bpa
|
||||
s.s_to_c()
|
||||
s.c_prop()
|
||||
s.c_to_s()
|
||||
resp = bp_to_mv(s.s[1])
|
||||
|
||||
for i in range(64):
|
||||
assert resp[i] == mva[i]
|
||||
exp_resp = np.copy(mva)
|
||||
exp_resp[:2] = logic.UNASSIGNED
|
||||
np.testing.assert_allclose(resp, exp_resp)
|
||||
|
||||
|
||||
def test_loop():
|
||||
c = bench.parse('q=dff(d) d=not(q)')
|
||||
s = LogicSim(c, 4, m=8)
|
||||
assert s.s_len == 1
|
||||
mva = mvarray([['0'], ['1'], ['R'], ['F']])
|
||||
|
||||
# TODO
|
||||
# s.assign(BPArray(mva))
|
||||
# s.propagate()
|
||||
# resp_bp = BPArray((len(s.interface), s.sims))
|
||||
# s.capture(resp_bp)
|
||||
# resp = MVArray(resp_bp)
|
||||
|
||||
# assert resp[0] == '1'
|
||||
# assert resp[1] == '0'
|
||||
# assert resp[2] == 'F'
|
||||
# assert resp[3] == 'R'
|
||||
|
||||
# resp_bp = s.cycle(resp_bp)
|
||||
# resp = MVArray(resp_bp)
|
||||
|
||||
# assert resp[0] == '0'
|
||||
# assert resp[1] == '1'
|
||||
# assert resp[2] == 'R'
|
||||
# assert resp[3] == 'F'
|
||||
|
||||
|
||||
def test_latch():
|
||||
c = bench.parse('input(d, t) output(q) q=latch(d, t)')
|
||||
s = LogicSim(c, 8, m=8)
|
||||
assert s.s_len == 4
|
||||
mva = mvarray('00-0', '00-1', '01-0', '01-1', '10-0', '10-1', '11-0', '11-1')
|
||||
exp = mvarray('0000', '0011', '0100', '0100', '1000', '1011', '1111', '1111')
|
||||
|
||||
# TODO
|
||||
# resp = MVArray(s.cycle(BPArray(mva)))
|
||||
|
||||
# for i in range(len(mva)):
|
||||
# assert resp[i] == exp[i]
|
||||
|
||||
|
||||
def test_b01(mydir):
|
||||
c = bench.load(mydir / 'b01.bench')
|
||||
|
||||
# 2-valued
|
||||
s = LogicSim(c, 8, m=2)
|
||||
assert len(s.interface) == 9
|
||||
mva = MVArray((len(s.interface), 8), m=2)
|
||||
# mva.randomize()
|
||||
bpa = BPArray(mva)
|
||||
s.assign(bpa)
|
||||
s.propagate()
|
||||
s.capture(bpa)
|
||||
|
||||
# 8-valued
|
||||
s = LogicSim(c, 8, m=8)
|
||||
mva = MVArray((len(s.interface), 8), m=8)
|
||||
# mva.randomize()
|
||||
bpa = BPArray(mva)
|
||||
s.assign(bpa)
|
||||
s.propagate()
|
||||
s.capture(bpa)
|
||||
mva = np.zeros((s.s_len, 8), dtype=np.uint8)
|
||||
s.s[0] = mv_to_bp(mva)
|
||||
s.s_to_c()
|
||||
s.c_prop()
|
||||
s.c_to_s()
|
||||
bp_to_mv(s.s[1])
|
||||
|
||||
|
||||
def sim_and_compare(c, test_resp, m=8):
|
||||
tests, resp = test_resp
|
||||
lsim = LogicSim(c, m=m, sims=tests.shape[1])
|
||||
lsim.s[0] = logic.mv_to_bp(tests)
|
||||
lsim.s_to_c()
|
||||
lsim.c_prop()
|
||||
lsim.c_to_s()
|
||||
resp_sim = logic.bp_to_mv(lsim.s[1])[:,:tests.shape[1]]
|
||||
idxs, pats = np.nonzero(((resp == logic.ONE) & (resp_sim != logic.ONE)) | ((resp == logic.ZERO) & (resp_sim != logic.ZERO)))
|
||||
for i, (idx, pat) in enumerate(zip(idxs, pats)):
|
||||
if i >= 10:
|
||||
print(f'...')
|
||||
break
|
||||
print(f'mismatch pattern:{pat} ppio:{idx} exp:{logic.mv_str(resp[idx,pat])} act:{logic.mv_str(resp_sim[idx,pat])}')
|
||||
assert len(idxs) == 0
|
||||
|
||||
def sim_and_compare_6v(c, test_resp):
|
||||
tests, resp = test_resp
|
||||
lsim = LogicSim6V(c, sims=tests.shape[1])
|
||||
lsim.s[0] = tests
|
||||
lsim.s_to_c()
|
||||
lsim.c_prop()
|
||||
lsim.c_to_s()
|
||||
resp_sim = lsim.s[1]
|
||||
idxs, pats = np.nonzero(((resp == logic.ONE) & (resp_sim != logic.ONE)) | ((resp == logic.ZERO) & (resp_sim != logic.ZERO)))
|
||||
for i, (idx, pat) in enumerate(zip(idxs, pats)):
|
||||
if i >= 10:
|
||||
print(f'...')
|
||||
break
|
||||
print(f'mismatch pattern:{pat} ppio:{idx} exp:{logic.mv_str(resp[idx,pat])} act:{logic.mv_str(resp_sim[idx,pat])}')
|
||||
assert len(idxs) == 0
|
||||
|
||||
|
||||
def test_b15_2ig_sa_2v(b15_2ig_circuit_resolved, b15_2ig_sa_nf_test_resp):
|
||||
sim_and_compare(b15_2ig_circuit_resolved, b15_2ig_sa_nf_test_resp, m=2)
|
||||
|
||||
|
||||
def test_b15_2ig_sa_4v(b15_2ig_circuit_resolved, b15_2ig_sa_nf_test_resp):
|
||||
sim_and_compare(b15_2ig_circuit_resolved, b15_2ig_sa_nf_test_resp, m=4)
|
||||
|
||||
|
||||
def test_b15_2ig_sa_6v(b15_2ig_circuit_resolved, b15_2ig_sa_nf_test_resp):
|
||||
sim_and_compare_6v(b15_2ig_circuit_resolved, b15_2ig_sa_nf_test_resp)
|
||||
|
||||
|
||||
def test_b15_2ig_sa_8v(b15_2ig_circuit_resolved, b15_2ig_sa_nf_test_resp):
|
||||
sim_and_compare(b15_2ig_circuit_resolved, b15_2ig_sa_nf_test_resp, m=8)
|
||||
|
||||
|
||||
def test_b15_4ig_sa_2v(b15_4ig_circuit_resolved, b15_4ig_sa_rf_test_resp):
|
||||
sim_and_compare(b15_4ig_circuit_resolved, b15_4ig_sa_rf_test_resp, m=2)
|
||||
|
||||
|
||||
def test_b15_4ig_sa_4v(b15_4ig_circuit_resolved, b15_4ig_sa_rf_test_resp):
|
||||
sim_and_compare(b15_4ig_circuit_resolved, b15_4ig_sa_rf_test_resp, m=4)
|
||||
|
||||
|
||||
def test_b15_4ig_sa_8v(b15_4ig_circuit_resolved, b15_4ig_sa_rf_test_resp):
|
||||
sim_and_compare(b15_4ig_circuit_resolved, b15_4ig_sa_rf_test_resp, m=8)
|
||||
+139
-7
@@ -1,5 +1,8 @@
|
||||
from kyupy import sdf, verilog
|
||||
import numpy as np
|
||||
|
||||
from kyupy import sdf, verilog, bench
|
||||
from kyupy.wave_sim import WaveSim, TMAX, TMIN
|
||||
from kyupy.techlib import SAED32, NANGATE45
|
||||
|
||||
def test_parse():
|
||||
test = '''
|
||||
@@ -69,18 +72,17 @@ def test_parse():
|
||||
'''
|
||||
df = sdf.parse(test)
|
||||
assert df.name == 'test'
|
||||
# print(f'DelayFile(name={df.name}, interconnects={len(df.interconnects)}, iopaths={len(df.iopaths)})')
|
||||
|
||||
|
||||
def test_b14(mydir):
|
||||
df = sdf.load(mydir / 'b14.sdf.gz')
|
||||
assert df.name == 'b14'
|
||||
def test_b15(mydir):
|
||||
df = sdf.load(mydir / 'b15_2ig.sdf.gz')
|
||||
assert df.name == 'b15'
|
||||
|
||||
|
||||
def test_gates(mydir):
|
||||
c = verilog.load(mydir / 'gates.v')
|
||||
c = verilog.load(mydir / 'gates.v', tlib=NANGATE45)
|
||||
df = sdf.load(mydir / 'gates.sdf')
|
||||
lt = df.annotation(c, dataset=1)
|
||||
lt = df.iopaths(c, tlib=NANGATE45)[1]
|
||||
nand_a = c.cells['nandgate'].ins[0]
|
||||
nand_b = c.cells['nandgate'].ins[1]
|
||||
and_a = c.cells['andgate'].ins[0]
|
||||
@@ -97,3 +99,133 @@ def test_gates(mydir):
|
||||
|
||||
assert lt[and_b, 0, 0] == 0.375
|
||||
assert lt[and_b, 0, 1] == 0.370
|
||||
|
||||
|
||||
def test_nand_xor():
|
||||
c = bench.parse("""
|
||||
input(A1,A2)
|
||||
output(lt_1237_U91,lt_1237_U92)
|
||||
lt_1237_U91 = NAND2X0_RVT(A1,A2)
|
||||
lt_1237_U92 = XOR2X1_RVT(A1,A2)
|
||||
""")
|
||||
df = sdf.parse("""
|
||||
(DELAYFILE
|
||||
(CELL
|
||||
(CELLTYPE "NAND2X0_RVT")
|
||||
(INSTANCE lt_1237_U91)
|
||||
(DELAY
|
||||
(ABSOLUTE
|
||||
(IOPATH A1 Y (0.018:0.022:0.021) (0.017:0.019:0.019))
|
||||
(IOPATH A2 Y (0.021:0.024:0.024) (0.018:0.021:0.021))
|
||||
)
|
||||
)
|
||||
)
|
||||
(CELL
|
||||
(CELLTYPE "XOR2X1_RVT")
|
||||
(INSTANCE lt_1237_U92)
|
||||
(DELAY
|
||||
(ABSOLUTE
|
||||
(IOPATH (posedge A1) Y (0.035:0.038:0.038) (0.037:0.062:0.062))
|
||||
(IOPATH (negedge A1) Y (0.035:0.061:0.061) (0.036:0.040:0.040))
|
||||
(IOPATH (posedge A2) Y (0.042:0.043:0.043) (0.051:0.064:0.064))
|
||||
(IOPATH (negedge A2) Y (0.041:0.066:0.066) (0.051:0.053:0.053))
|
||||
)
|
||||
)
|
||||
)
|
||||
)
|
||||
""")
|
||||
d = df.iopaths(c, tlib=SAED32)[1]
|
||||
c.resolve_tlib_cells(SAED32)
|
||||
sim = WaveSim(c, delays=d, sims=16)
|
||||
|
||||
# input A1
|
||||
sim.s[0,0] = [0,1,0,1] * 4 # initial values 0101010101010101
|
||||
sim.s[1,0] = 0.0 # transition time
|
||||
sim.s[2,0] = [0,0,1,1] * 4 # final values 0011001100110011
|
||||
|
||||
# input A2
|
||||
sim.s[0,1] = ([0]*4 + [1]*4)*2 # initial values 0000111100001111
|
||||
sim.s[1,1] = 0.0 # transition time
|
||||
sim.s[2,1] = [0]*8 + [1]*8 # final values 0000000011111111
|
||||
|
||||
# A1: 0FR10FR10FR10FR1
|
||||
# A2: 0000FFFFRRRR1111
|
||||
# nand: 11111RNR1NFF1RF0
|
||||
# xor: 0FR1FPPRRNPF1RF0
|
||||
|
||||
sim.s_to_c()
|
||||
sim.c_prop()
|
||||
sim.c_to_s()
|
||||
|
||||
eat = sim.s[4,2:]
|
||||
lst = sim.s[5,2:]
|
||||
|
||||
# NAND-gate output
|
||||
assert np.allclose(eat[0], [
|
||||
TMAX, TMAX, TMAX, TMAX, TMAX,
|
||||
0.022, # FF -> rising Y: min(0.022, 0.024)
|
||||
TMAX, # RF: pulse filtered
|
||||
0.024, # falling A2 -> rising Y
|
||||
TMAX,
|
||||
TMAX, # FR: pulse filtered
|
||||
0.021, # RR -> falling Y: max(0.019, 0.021)
|
||||
0.021, # rising A2 -> falling Y
|
||||
TMAX,
|
||||
0.022, # falling A1 -> rising Y
|
||||
0.019, # rising A1 -> falling Y
|
||||
TMAX
|
||||
])
|
||||
|
||||
assert np.allclose(lst[0], [
|
||||
TMIN, TMIN, TMIN, TMIN, TMIN,
|
||||
0.022, # FF -> rising Y: min(0.022, 0.024)
|
||||
TMIN, # RF: pulse filtered
|
||||
0.024, # falling A2 -> rising Y
|
||||
TMIN,
|
||||
TMIN, # FR: pulse filtered
|
||||
0.021, # RR -> falling Y: max(0.019, 0.021)
|
||||
0.021, # rising A2 -> falling Y
|
||||
TMIN,
|
||||
0.022, # falling A1 -> rising Y
|
||||
0.019, # rising A1 -> falling Y
|
||||
TMIN
|
||||
])
|
||||
|
||||
#XOR-gate output
|
||||
assert np.allclose(eat[1], [
|
||||
TMAX,
|
||||
0.040, # A1:F -> Y:F
|
||||
0.038, # A1:R -> Y:R
|
||||
TMAX,
|
||||
0.053, # A2:F -> Y:F
|
||||
TMAX, # P filtered
|
||||
TMAX, # P filtered
|
||||
0.066, # A2:F -> Y:R
|
||||
0.043, # A2:R -> Y:R
|
||||
TMAX, # N filtered
|
||||
TMAX, # P filtered
|
||||
0.064, # A2:R -> Y:F
|
||||
TMAX,
|
||||
0.061, # A1:F -> Y:R
|
||||
0.062, # A1:R -> Y:F
|
||||
TMAX,
|
||||
])
|
||||
|
||||
assert np.allclose(lst[1], [
|
||||
TMIN,
|
||||
0.040, # A1:F -> Y:F
|
||||
0.038, # A1:R -> Y:R
|
||||
TMIN,
|
||||
0.053, # A2:F -> Y:F
|
||||
TMIN, # P filtered
|
||||
TMIN, # P filtered
|
||||
0.066, # A2:F -> Y:R
|
||||
0.043, # A2:R -> Y:R
|
||||
TMIN, # N filtered
|
||||
TMIN, # P filtered
|
||||
0.064, # A2:R -> Y:F
|
||||
TMIN,
|
||||
0.061, # A1:F -> Y:R
|
||||
0.062, # A1:R -> Y:F
|
||||
TMIN,
|
||||
])
|
||||
+17
-4
@@ -1,8 +1,21 @@
|
||||
from kyupy import stil
|
||||
from kyupy import stil, verilog
|
||||
from kyupy.techlib import SAED32
|
||||
|
||||
def test_b15(mydir):
|
||||
b15 = verilog.load(mydir / 'b15_2ig.v.gz', tlib=SAED32)
|
||||
|
||||
def test_b14(mydir):
|
||||
s = stil.load(mydir / 'b14.stuck.stil.gz')
|
||||
s = stil.load(mydir / 'b15_2ig.sa_nf.stil.gz')
|
||||
assert len(s.signal_groups) == 10
|
||||
assert len(s.scan_chains) == 1
|
||||
assert len(s.calls) == 2163
|
||||
assert len(s.calls) == 1357
|
||||
tests = s.tests(b15)
|
||||
resp = s.responses(b15)
|
||||
assert len(tests) > 0
|
||||
assert len(resp) > 0
|
||||
|
||||
s2 = stil.load(mydir / 'b15_2ig.tf_nf.stil.gz')
|
||||
tests = s2.tests_loc(b15)
|
||||
resp = s2.responses(b15)
|
||||
assert len(tests) > 0
|
||||
assert len(resp) > 0
|
||||
|
||||
+41
-4
@@ -1,8 +1,45 @@
|
||||
from kyupy import verilog
|
||||
|
||||
from kyupy.techlib import SAED90, SAED32, NANGATE45
|
||||
|
||||
def test_b01(mydir):
|
||||
with open(mydir / 'b01.v', 'r') as f:
|
||||
modules = verilog.parse(f.read())
|
||||
assert modules is not None
|
||||
assert verilog.load(mydir / 'b01.v') is not None
|
||||
c = verilog.parse(f.read(), tlib=SAED90)
|
||||
assert c is not None
|
||||
assert verilog.load(mydir / 'b01.v', tlib=SAED90) is not None
|
||||
|
||||
assert len(c.nodes) == 139
|
||||
assert len(c.lines) == 203
|
||||
stats = c.stats
|
||||
assert stats['input'] == 6
|
||||
assert stats['output'] == 3
|
||||
assert stats['__seq__'] == 5
|
||||
|
||||
|
||||
def test_b15(mydir):
|
||||
c = verilog.load(mydir / 'b15_4ig.v.gz', tlib=SAED32)
|
||||
assert len(c.nodes) == 12067
|
||||
assert len(c.lines) == 20731
|
||||
stats = c.stats
|
||||
assert stats['input'] == 40
|
||||
assert stats['output'] == 71
|
||||
assert stats['__seq__'] == 417
|
||||
|
||||
|
||||
def test_gates(mydir):
|
||||
c = verilog.load(mydir / 'gates.v', tlib=NANGATE45)
|
||||
assert len(c.nodes) == 18
|
||||
assert len(c.lines) == 21
|
||||
stats = c.stats
|
||||
assert stats['input'] == 3
|
||||
assert stats['output'] == 4
|
||||
assert stats['__seq__'] == 0
|
||||
|
||||
|
||||
def test_halton2(mydir):
|
||||
c = verilog.load(mydir / 'rng_haltonBase2.synth_yosys.v', tlib=SAED90)
|
||||
assert len(c.nodes) == 146
|
||||
assert len(c.lines) == 210
|
||||
stats = c.stats
|
||||
assert stats['input'] == 2
|
||||
assert stats['output'] == 12
|
||||
assert stats['__seq__'] == 12
|
||||
+177
-123
@@ -1,148 +1,202 @@
|
||||
import numpy as np
|
||||
|
||||
from kyupy.wave_sim import WaveSim, WaveSimCuda, wave_eval, TMIN, TMAX
|
||||
from kyupy.wave_sim import WaveSim, WaveSimCuda, wave_eval_cpu, TMIN, TMAX
|
||||
from kyupy.logic_sim import LogicSim
|
||||
from kyupy import verilog, sdf, logic
|
||||
from kyupy.logic import MVArray, BPArray
|
||||
from kyupy import logic, bench, sim
|
||||
from kyupy.logic import mvarray
|
||||
|
||||
def test_xnor2_delays():
|
||||
op = (sim.XNOR2, 2, 0, 1, 3, 3, -1, 0, 0)
|
||||
#op = (0b0111, 4, 0, 1)
|
||||
c = np.full((4*16, 1), TMAX, dtype=np.float32) # 4 waveforms of capacity 16
|
||||
c_locs = np.zeros((4,), dtype='int')
|
||||
c_caps = np.zeros((4,), dtype='int')
|
||||
ebuf = np.zeros((4, 1, 2), dtype=np.int32)
|
||||
|
||||
for i in range(4): c_locs[i], c_caps[i] = i*16, 16 # 1:1 mapping
|
||||
delays = np.zeros((1, 4, 2, 2))
|
||||
delays[0, 0, 0, 0] = 0.031 # A rise -> Z rise
|
||||
delays[0, 0, 0, 1] = 0.027 # A rise -> Z fall
|
||||
delays[0, 0, 1, 0] = 0.033 # A fall -> Z rise
|
||||
delays[0, 0, 1, 1] = 0.037 # A fall -> Z fall
|
||||
delays[0, 1, 0, 0] = 0.032 # B rise -> Z rise
|
||||
delays[0, 1, 0, 1] = 0.030 # B rise -> Z fall
|
||||
delays[0, 1, 1, 0] = 0.038 # B fall -> Z rise
|
||||
delays[0, 1, 1, 1] = 0.036 # B fall -> Z fall
|
||||
|
||||
simctl_int = np.asarray([0], dtype=np.int32)
|
||||
|
||||
def wave_assert(inputs, output):
|
||||
for i, a in zip(inputs, c.reshape(-1,16)): a[:len(i)] = i
|
||||
wave_eval_cpu(op, c, c_locs, c_caps, ebuf, 0, delays, simctl_int, 0, 0)
|
||||
for i, v in enumerate(output): np.testing.assert_allclose(c.reshape(-1,16)[2,i], v)
|
||||
|
||||
wave_assert([[TMIN,TMAX],[TMIN,TMAX]], [TMIN,TMAX]) # XNOR(1,1) => 1
|
||||
wave_assert([[TMAX,TMAX],[TMIN,TMAX]], [TMAX]) # XNOR(0,1) => 0
|
||||
# using Afall/Zfall for pulse length, bug: was using Arise/Zfall
|
||||
#wave_assert([[0.07, 0.10, TMAX], [0.0, TMAX]], [TMIN, 0.03, 0.101, 0.137, TMAX])
|
||||
wave_assert([[0.07, 0.10, TMAX], [0.0, TMAX]], [TMIN, 0.03, TMAX])
|
||||
wave_assert([[0.06, 0.10, TMAX], [0.0, TMAX]], [TMIN, 0.03, 0.091, 0.137, TMAX])
|
||||
|
||||
def test_nand_delays():
|
||||
op = (sim.NAND4, 4, 0, 1, 2, 3, -1, 0, 0)
|
||||
#op = (0b0111, 4, 0, 1)
|
||||
c = np.full((5*16, 1), TMAX, dtype=np.float32) # 5 waveforms of capacity 16
|
||||
c_locs = np.zeros((5,), dtype='int')
|
||||
c_caps = np.zeros((5,), dtype='int')
|
||||
ebuf = np.zeros((4, 1, 2), dtype=np.int32)
|
||||
|
||||
for i in range(5): c_locs[i], c_caps[i] = i*16, 16 # 1:1 mapping
|
||||
|
||||
def test_wave_eval():
|
||||
# SDF specifies IOPATH delays with respect to output polarity
|
||||
# SDF pulse rejection value is determined by IOPATH causing last transition and polarity of last transition
|
||||
line_times = np.zeros((3, 2, 2))
|
||||
line_times[0, 0, 0] = 0.1 # A -> Z rise delay
|
||||
line_times[0, 0, 1] = 0.2 # A -> Z fall delay
|
||||
line_times[0, 1, 0] = 0.1 # A -> Z negative pulse limit (terminate in rising Z)
|
||||
line_times[0, 1, 1] = 0.2 # A -> Z positive pulse limit
|
||||
line_times[1, 0, 0] = 0.3 # as above for B -> Z
|
||||
line_times[1, 0, 1] = 0.4
|
||||
line_times[1, 1, 0] = 0.3
|
||||
line_times[1, 1, 1] = 0.4
|
||||
delays = np.zeros((1, 5, 2, 2))
|
||||
delays[0, 0, 0, 0] = 0.1 # A rise -> Z rise
|
||||
delays[0, 0, 0, 1] = 0.2 # A rise -> Z fall
|
||||
delays[0, 0, 1, 0] = 0.1 # A fall -> Z rise
|
||||
delays[0, 0, 1, 1] = 0.2 # A fall -> Z fall
|
||||
delays[0, 1, :, 0] = 0.3 # as above for B -> Z
|
||||
delays[0, 1, :, 1] = 0.4
|
||||
delays[0, 2, :, 0] = 0.5 # as above for C -> Z
|
||||
delays[0, 2, :, 1] = 0.6
|
||||
delays[0, 3, :, 0] = 0.7 # as above for D -> Z
|
||||
delays[0, 3, :, 1] = 0.8
|
||||
|
||||
state = np.zeros((3*16, 1)) + TMAX # 3 waveforms of capacity 16
|
||||
state[::16, 0] = 16 # first entry is capacity
|
||||
a = state[0:16, 0]
|
||||
b = state[16:32, 0]
|
||||
z = state[32:, 0]
|
||||
sat = np.zeros((3, 3), dtype='int')
|
||||
sat[0] = 0, 16, 0
|
||||
sat[1] = 16, 16, 0
|
||||
sat[2] = 32, 16, 0
|
||||
simctl_int = np.asarray([0], dtype=np.int32)
|
||||
|
||||
wave_eval((0b0111, 2, 0, 1), state, sat, 0, line_times)
|
||||
assert z[0] == TMIN
|
||||
def wave_assert(inputs, output):
|
||||
for i, a in zip(inputs, c.reshape(-1,16)): a[:len(i)] = i
|
||||
wave_eval_cpu(op, c, c_locs, c_caps, ebuf, 0, delays, simctl_int, 0, 0)
|
||||
for i, v in enumerate(output): np.testing.assert_allclose(c.reshape(-1,16)[4,i], v)
|
||||
|
||||
a[0] = TMIN
|
||||
wave_eval((0b0111, 2, 0, 1), state, sat, 0, line_times)
|
||||
assert z[0] == TMIN
|
||||
wave_assert([[TMAX,TMAX],[TMAX,TMAX],[TMIN,TMAX],[TMIN,TMAX]], [TMIN,TMAX]) # NAND(0,0,1,1) => 1
|
||||
wave_assert([[TMIN,TMAX],[TMAX,TMAX],[TMIN,TMAX],[TMIN,TMAX]], [TMIN,TMAX]) # NAND(1,0,1,1) => 1
|
||||
wave_assert([[TMIN,TMAX],[TMIN,TMAX],[TMIN,TMAX],[TMIN,TMAX]], [TMAX]) # NAND(1,1,1,1) => 0
|
||||
|
||||
b[0] = TMIN
|
||||
wave_eval((0b0111, 2, 0, 1), state, sat, 0, line_times)
|
||||
assert z[0] == TMAX
|
||||
|
||||
a[0] = 1 # A _/^^^
|
||||
b[0] = 2 # B __/^^
|
||||
wave_eval((0b0111, 2, 0, 1), state, sat, 0, line_times)
|
||||
assert z[0] == TMIN # ^^^\___ B -> Z fall delay
|
||||
assert z[1] == 2.4
|
||||
assert z[2] == TMAX
|
||||
|
||||
a[0] = TMIN # A ^^^^^^
|
||||
b[0] = TMIN # B ^^^\__
|
||||
b[1] = 2
|
||||
wave_eval((0b0111, 2, 0, 1), state, sat, 0, line_times)
|
||||
assert z[0] == 2.3 # ___/^^^ B -> Z rise delay
|
||||
assert z[1] == TMAX
|
||||
|
||||
# pos pulse of 0.35 at B -> 0.45 after delays
|
||||
a[0] = TMIN # A ^^^^^^^^
|
||||
b[0] = TMIN
|
||||
b[1] = 2 # B ^^\__/^^
|
||||
b[2] = 2.35
|
||||
wave_eval((0b0111, 2, 0, 1), state, sat, 0, line_times)
|
||||
assert z[0] == 2.3 # __/^^\__
|
||||
assert z[1] == 2.75
|
||||
assert z[2] == TMAX
|
||||
|
||||
# neg pulse of 0.45 at B -> 0.35 after delays
|
||||
a[0] = TMIN # A ^^^^^^^^
|
||||
b[0] = 2 # B __/^^\__
|
||||
b[1] = 2.45
|
||||
b[2] = TMAX
|
||||
wave_eval((0b0111, 2, 0, 1), state, sat, 0, line_times)
|
||||
assert z[0] == TMIN # ^^\__/^^
|
||||
assert z[1] == 2.4
|
||||
assert z[2] == 2.75
|
||||
assert z[3] == TMAX
|
||||
|
||||
# neg pulse of 0.35 at B -> 0.25 after delays (filtered)
|
||||
a[0] = TMIN # A ^^^^^^^^
|
||||
b[0] = 2 # B __/^^\__
|
||||
b[1] = 2.35
|
||||
b[2] = TMAX
|
||||
wave_eval((0b0111, 2, 0, 1), state, sat, 0, line_times)
|
||||
assert z[0] == TMIN # ^^^^^^
|
||||
assert z[1] == TMAX
|
||||
|
||||
# pos pulse of 0.25 at B -> 0.35 after delays (filtered)
|
||||
a[0] = TMIN # A ^^^^^^^^
|
||||
b[0] = TMIN
|
||||
b[1] = 2 # B ^^\__/^^
|
||||
b[2] = 2.25
|
||||
wave_eval((0b0111, 2, 0, 1), state, sat, 0, line_times)
|
||||
assert z[0] == TMAX # ______
|
||||
# Keep inputs C=1 and D=1.
|
||||
wave_assert([[1,TMAX],[2,TMAX]], [TMIN,2.4,TMAX]) # _/⎺⎺⎺ NAND __/⎺⎺ => ⎺⎺⎺\___ (B->Z fall delay)
|
||||
wave_assert([[TMIN,TMAX],[TMIN,2,TMAX]], [2.3,TMAX]) # ⎺⎺⎺⎺⎺ NAND ⎺⎺\__ => ___/⎺⎺⎺ (B->Z rise delay)
|
||||
wave_assert([[TMIN,TMAX],[TMIN,2,2.35,TMAX]], [2.3,2.75,TMAX]) # ⎺⎺⎺⎺⎺ NAND ⎺\_/⎺ => __/⎺⎺\_ (pos pulse, .35@B -> .45@Z)
|
||||
wave_assert([[TMIN,TMAX],[TMIN,2,2.25,TMAX]], [TMAX]) # ⎺⎺⎺⎺⎺ NAND ⎺\_/⎺ => _______ (pos pulse, .25@B -> .35@Z, filtered)
|
||||
wave_assert([[TMIN,TMAX],[2,2.45,TMAX]], [TMIN,2.4,2.75,TMAX]) # ⎺⎺⎺⎺⎺ NAND _/⎺\_ => ⎺⎺\_/⎺⎺ (neg pulse, .45@B -> .35@Z)
|
||||
wave_assert([[TMIN,TMAX],[2,2.35,TMAX]], [TMIN,TMAX]) # ⎺⎺⎺⎺⎺ NAND _/⎺\_ => ⎺⎺⎺⎺⎺⎺⎺ (neg pulse, .35@B -> .25@Z, filtered)
|
||||
|
||||
|
||||
def compare_to_logic_sim(wsim):
|
||||
tests = MVArray((len(wsim.interface), wsim.sims))
|
||||
def test_tiny_circuit():
|
||||
c = bench.parse('input(x, y) output(a, o, n) a=and(x,y) o=or(x,y) n=not(x)')
|
||||
delays = np.full((1, len(c.lines), 2, 2), 1.0) # unit delay for all lines
|
||||
wsim = WaveSim(c, delays)
|
||||
assert wsim.s.shape[1] == 5
|
||||
|
||||
# values for x
|
||||
wsim.s[:3,0,0] = 0, 10, 0
|
||||
wsim.s[:3,0,1] = 0, 20, 1
|
||||
wsim.s[:3,0,2] = 1, 30, 0
|
||||
wsim.s[:3,0,3] = 1, 40, 1
|
||||
|
||||
# values for y
|
||||
wsim.s[:3,1,0] = 1, 50, 0
|
||||
wsim.s[:3,1,1] = 1, 60, 0
|
||||
wsim.s[:3,1,2] = 1, 70, 0
|
||||
wsim.s[:3,1,3] = 0, 80, 1
|
||||
|
||||
wsim.s_to_c()
|
||||
|
||||
x_c_loc = wsim.c_locs[wsim.ppi_offset+0] # check x waveforms
|
||||
np.testing.assert_allclose(wsim.c[x_c_loc:x_c_loc+3, 0], [TMAX, TMAX, TMAX])
|
||||
np.testing.assert_allclose(wsim.c[x_c_loc:x_c_loc+3, 1], [20, TMAX, TMAX])
|
||||
np.testing.assert_allclose(wsim.c[x_c_loc:x_c_loc+3, 2], [TMIN, 30, TMAX])
|
||||
np.testing.assert_allclose(wsim.c[x_c_loc:x_c_loc+3, 3], [TMIN, TMAX, TMAX])
|
||||
|
||||
y_c_loc = wsim.c_locs[wsim.ppi_offset+1] # check y waveforms
|
||||
np.testing.assert_allclose(wsim.c[y_c_loc:y_c_loc+3, 0], [TMIN, 50, TMAX])
|
||||
np.testing.assert_allclose(wsim.c[y_c_loc:y_c_loc+3, 1], [TMIN, 60, TMAX])
|
||||
np.testing.assert_allclose(wsim.c[y_c_loc:y_c_loc+3, 2], [TMIN, 70, TMAX])
|
||||
np.testing.assert_allclose(wsim.c[y_c_loc:y_c_loc+3, 3], [80, TMAX, TMAX])
|
||||
|
||||
wsim.c_prop()
|
||||
|
||||
a_c_loc = wsim.c_locs[wsim.ppo_offset+2] # check a waveforms
|
||||
np.testing.assert_allclose(wsim.c[a_c_loc:a_c_loc+3, 0], [TMAX, TMAX, TMAX])
|
||||
np.testing.assert_allclose(wsim.c[a_c_loc:a_c_loc+3, 1], [21, 61, TMAX])
|
||||
np.testing.assert_allclose(wsim.c[a_c_loc:a_c_loc+3, 2], [TMIN, 31, TMAX])
|
||||
np.testing.assert_allclose(wsim.c[a_c_loc:a_c_loc+3, 3], [81, TMAX, TMAX])
|
||||
|
||||
o_c_loc = wsim.c_locs[wsim.ppo_offset+3] # check o waveforms
|
||||
np.testing.assert_allclose(wsim.c[o_c_loc:o_c_loc+3, 0], [TMIN, 51, TMAX])
|
||||
np.testing.assert_allclose(wsim.c[o_c_loc:o_c_loc+3, 1], [TMIN, TMAX, TMAX])
|
||||
np.testing.assert_allclose(wsim.c[o_c_loc:o_c_loc+3, 2], [TMIN, 71, TMAX])
|
||||
np.testing.assert_allclose(wsim.c[o_c_loc:o_c_loc+3, 3], [TMIN, TMAX, TMAX])
|
||||
|
||||
n_c_loc = wsim.c_locs[wsim.ppo_offset+4] # check n waveforms
|
||||
np.testing.assert_allclose(wsim.c[n_c_loc:n_c_loc+3, 0], [TMIN, TMAX, TMAX])
|
||||
np.testing.assert_allclose(wsim.c[n_c_loc:n_c_loc+3, 1], [TMIN, 21, TMAX])
|
||||
np.testing.assert_allclose(wsim.c[n_c_loc:n_c_loc+3, 2], [31, TMAX, TMAX])
|
||||
np.testing.assert_allclose(wsim.c[n_c_loc:n_c_loc+3, 3], [TMAX, TMAX, TMAX])
|
||||
|
||||
wsim.c_to_s()
|
||||
|
||||
# check a captures
|
||||
np.testing.assert_allclose(wsim.s[3:7, 2, 0], [0, TMAX, TMIN, 0])
|
||||
np.testing.assert_allclose(wsim.s[3:7, 2, 1], [0, 21, 61, 0])
|
||||
np.testing.assert_allclose(wsim.s[3:7, 2, 2], [1, 31, 31, 0])
|
||||
np.testing.assert_allclose(wsim.s[3:7, 2, 3], [0, 81, 81, 1])
|
||||
|
||||
# check o captures
|
||||
np.testing.assert_allclose(wsim.s[3:7, 3, 0], [1, 51, 51, 0])
|
||||
np.testing.assert_allclose(wsim.s[3:7, 3, 1], [1, TMAX, TMIN, 1])
|
||||
np.testing.assert_allclose(wsim.s[3:7, 3, 2], [1, 71, 71, 0])
|
||||
np.testing.assert_allclose(wsim.s[3:7, 3, 3], [1, TMAX, TMIN, 1])
|
||||
|
||||
# check o captures
|
||||
np.testing.assert_allclose(wsim.s[3:7, 4, 0], [1, TMAX, TMIN, 1])
|
||||
np.testing.assert_allclose(wsim.s[3:7, 4, 1], [1, 21, 21, 0])
|
||||
np.testing.assert_allclose(wsim.s[3:7, 4, 2], [0, 31, 31, 1])
|
||||
np.testing.assert_allclose(wsim.s[3:7, 4, 3], [0, TMAX, TMIN, 0])
|
||||
|
||||
|
||||
def compare_to_logic_sim(wsim: WaveSim):
|
||||
choices = np.asarray([logic.ZERO, logic.ONE, logic.RISE, logic.FALL], dtype=np.uint8)
|
||||
rng = np.random.default_rng(10)
|
||||
tests.data[...] = rng.choice(choices, tests.data.shape)
|
||||
tests_bp = BPArray(tests)
|
||||
wsim.assign(tests_bp)
|
||||
wsim.propagate()
|
||||
cdata = wsim.capture()
|
||||
tests = rng.choice(choices, (wsim.s_len, wsim.sims))
|
||||
|
||||
resp = MVArray(tests)
|
||||
wsim.s[0] = (tests & 2) >> 1
|
||||
wsim.s[3] = (tests & 2) >> 1
|
||||
wsim.s[1] = 0.0
|
||||
wsim.s[2] = tests & 1
|
||||
wsim.s[6] = tests & 1
|
||||
|
||||
for iidx, inode in enumerate(wsim.interface):
|
||||
if len(inode.ins) > 0:
|
||||
for vidx in range(wsim.sims):
|
||||
resp.data[iidx, vidx] = logic.ZERO if cdata[iidx, vidx, 0] < 0.5 else logic.ONE
|
||||
# resp.set_value(vidx, iidx, 0 if cdata[iidx, vidx, 0] < 0.5 else 1)
|
||||
wsim.s_to_c()
|
||||
wsim.c_prop()
|
||||
wsim.c_to_s()
|
||||
|
||||
lsim = LogicSim(wsim.circuit, len(tests_bp))
|
||||
lsim.assign(tests_bp)
|
||||
lsim.propagate()
|
||||
exp_bp = BPArray(tests_bp)
|
||||
lsim.capture(exp_bp)
|
||||
exp = MVArray(exp_bp)
|
||||
resp = np.array(wsim.s[6], dtype=np.uint8) | (np.array(wsim.s[3], dtype=np.uint8)<<1)
|
||||
resp |= ((resp ^ (resp >> 1)) & 1) << 2 # transitions
|
||||
resp[wsim.pi_s_locs] = logic.UNASSIGNED
|
||||
|
||||
for i in range(8):
|
||||
exp_str = exp[i].replace('R', '1').replace('F', '0').replace('P', '0').replace('N', '1')
|
||||
res_str = resp[i].replace('R', '1').replace('F', '0').replace('P', '0').replace('N', '1')
|
||||
assert res_str == exp_str
|
||||
lsim = LogicSim(wsim.circuit, tests.shape[-1])
|
||||
lsim.s[0] = logic.mv_to_bp(tests)
|
||||
lsim.s_to_c()
|
||||
lsim.c_prop()
|
||||
lsim.c_to_s()
|
||||
exp = logic.bp_to_mv(lsim.s[1])[:,:tests.shape[-1]]
|
||||
|
||||
resp[resp == logic.PPULSE] = logic.ZERO
|
||||
resp[resp == logic.NPULSE] = logic.ONE
|
||||
|
||||
exp[exp == logic.PPULSE] = logic.ZERO
|
||||
exp[exp == logic.NPULSE] = logic.ONE
|
||||
|
||||
np.testing.assert_allclose(resp, exp)
|
||||
|
||||
|
||||
def test_b14(mydir):
|
||||
c = verilog.load(mydir / 'b14.v.gz', branchforks=True)
|
||||
df = sdf.load(mydir / 'b14.sdf.gz')
|
||||
lt = df.annotation(c)
|
||||
wsim = WaveSim(c, lt, 8)
|
||||
compare_to_logic_sim(wsim)
|
||||
def test_b15(b15_2ig_circuit_resolved, b15_2ig_delays):
|
||||
compare_to_logic_sim(WaveSim(b15_2ig_circuit_resolved, b15_2ig_delays, 8))
|
||||
|
||||
|
||||
def test_b14_strip_forks(mydir):
|
||||
c = verilog.load(mydir / 'b14.v.gz', branchforks=True)
|
||||
df = sdf.load(mydir / 'b14.sdf.gz')
|
||||
lt = df.annotation(c)
|
||||
wsim = WaveSim(c, lt, 8, strip_forks=True)
|
||||
compare_to_logic_sim(wsim)
|
||||
def test_b15_strip_forks(b15_2ig_circuit_resolved, b15_2ig_delays):
|
||||
compare_to_logic_sim(WaveSim(b15_2ig_circuit_resolved, b15_2ig_delays, 8, strip_forks=True))
|
||||
|
||||
|
||||
def test_b14_cuda(mydir):
|
||||
c = verilog.load(mydir / 'b14.v.gz', branchforks=True)
|
||||
df = sdf.load(mydir / 'b14.sdf.gz')
|
||||
lt = df.annotation(c)
|
||||
wsim = WaveSimCuda(c, lt, 8)
|
||||
compare_to_logic_sim(wsim)
|
||||
def test_b15_cuda(b15_2ig_circuit_resolved, b15_2ig_delays):
|
||||
compare_to_logic_sim(WaveSimCuda(b15_2ig_circuit_resolved, b15_2ig_delays, 8, strip_forks=True))
|
||||
Reference in new issue
Block a user